OpenGrok
Home
Sort by relevance
Sort by last modified time
Full Search
Definition
Symbol
File Path
History
|
|
Help
Searched
refs:KNOB_SIMD_WIDTH
(Results
1 - 17
of
17
) sorted by null
/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/
knobs.h
54
#define
KNOB_SIMD_WIDTH
8
59
#define
KNOB_SIMD_WIDTH
8
66
#define
KNOB_SIMD_WIDTH
16
71
#define
KNOB_SIMD_WIDTH
8
142
#if
KNOB_SIMD_WIDTH
==8 && KNOB_TILE_X_DIM < 4
152
#if
KNOB_SIMD_WIDTH
== 8
fifo.hpp
58
T* pNewBlock = (T*)arena.AllocAligned(sizeof(T)*mBlockSize,
KNOB_SIMD_WIDTH
*4);
112
__m256 vSrc = _simd_load_ps(pSrc + i*
KNOB_SIMD_WIDTH
);
113
_simd_stream_ps(pDst + i*
KNOB_SIMD_WIDTH
, vSrc);
116
const uint32_t numSimdLines = sizeof(T) / (
KNOB_SIMD_WIDTH
*4);
117
static_assert(numSimdLines *
KNOB_SIMD_WIDTH
* 4 == sizeof(T),
131
T* newBlock = (T*)arena.AllocAligned(sizeof(T)*mBlockSize,
KNOB_SIMD_WIDTH
*4);
pa.h
177
const uint32_t numSimdVerts = this->streamSizeInVerts /
KNOB_SIMD_WIDTH
;
202
(
KNOB_SIMD_WIDTH
- (this->numPrimsComplete + this->nextNumPrimsIncrement - this->numPrims)) :
KNOB_SIMD_WIDTH
;
234
_simd_set1_epi32(startID + this->primIDIncr * (this->numPrimsComplete /
KNOB_SIMD_WIDTH
)));
341
OSALIGNSIMD(uint32_t) indices[MAX_NUM_VERTS_PER_PRIM][
KNOB_SIMD_WIDTH
]; // current index buffer for gather
415
uint32_t vertexIndex = this->headVertex /
KNOB_SIMD_WIDTH
;
416
this->headVertex = (this->headVertex +
KNOB_SIMD_WIDTH
) % this->numVerts;
423
uint32_t vertexIndex = this->headVertex /
KNOB_SIMD_WIDTH
;
437
this->headVertex +=
KNOB_SIMD_WIDTH
;
467
return ((this->headVertex +
KNOB_SIMD_WIDTH
) % this->numVerts) == this->tailVertex
[
all
...]
frontend.cpp
482
uint32_t numActive = (numItemsRemaining >=
KNOB_SIMD_WIDTH
) ?
KNOB_SIMD_WIDTH
: numItemsRemaining;
590
return (remainder >=
KNOB_SIMD_WIDTH
) ?
KNOB_SIMD_WIDTH
: remainder;
695
const uint32_t numSimdBatches = (state.gsState.maxNumVerts +
KNOB_SIMD_WIDTH
- 1) /
KNOB_SIMD_WIDTH
;
697
const uint32_t instanceStride = inputPrimStride *
KNOB_SIMD_WIDTH
;
704
cutInstanceStride = cutPrimStride *
KNOB_SIMD_WIDTH
;
709
cutInstanceStride = cutPrimStride *
KNOB_SIMD_WIDTH
;
876
const uint32_t numSimdBatches = (state.gsState.maxNumVerts +
KNOB_SIMD_WIDTH
- 1) / KNOB_SIMD_WIDTH
[
all
...]
binner.cpp
522
int cullZeroAreaMask = maskLo | (maskHi << (
KNOB_SIMD_WIDTH
/ 2));
547
frontWindingTris = maskLo | (maskHi << (
KNOB_SIMD_WIDTH
/ 2));
626
SWR_ASSERT(
KNOB_SIMD_WIDTH
== 8, "Need to update degenerate mask code for avx512");
701
GatherScissors<
KNOB_SIMD_WIDTH
>::Gather(&state.scissorsInFixedPoint[0], pViewportIndex,
747
OSALIGNSIMD(uint32_t) aMTLeft[
KNOB_SIMD_WIDTH
], aMTRight[
KNOB_SIMD_WIDTH
], aMTTop[
KNOB_SIMD_WIDTH
], aMTBottom[
KNOB_SIMD_WIDTH
];
762
OSALIGNSIMD(uint32_t) aRTAI[
KNOB_SIMD_WIDTH
];
[
all
...]
tilemgr.cpp
103
hotTile.pBuffer = (uint8_t*)AllocHotTileMem(size,
KNOB_SIMD_WIDTH
* 4, numaNode);
127
hotTile.pBuffer = (uint8_t*)AllocHotTileMem(size,
KNOB_SIMD_WIDTH
* 4, numaNode);
197
hotTile.pBuffer = (uint8_t*)AlignedMalloc(size,
KNOB_SIMD_WIDTH
* 4);
312
pfBuf +=
KNOB_SIMD_WIDTH
;
314
pfBuf +=
KNOB_SIMD_WIDTH
;
316
pfBuf +=
KNOB_SIMD_WIDTH
;
318
pfBuf +=
KNOB_SIMD_WIDTH
;
340
pfBuf +=
KNOB_SIMD_WIDTH
;
format_types.h
81
#if
KNOB_SIMD_WIDTH
== 8
93
#if
KNOB_SIMD_WIDTH
== 8
102
#if
KNOB_SIMD_WIDTH
== 8
122
#if
KNOB_SIMD_WIDTH
== 8
195
#if
KNOB_SIMD_WIDTH
== 8
207
#if
KNOB_SIMD_WIDTH
== 8
216
#if
KNOB_SIMD_WIDTH
== 8
237
#if
KNOB_SIMD_WIDTH
== 8
310
#if
KNOB_SIMD_WIDTH
== 8
321
#if
KNOB_SIMD_WIDTH
==
[
all
...]
pa_avx.cpp
35
#if (
KNOB_SIMD_WIDTH
== 8)
76
// We have an input of
KNOB_SIMD_WIDTH
* TotalControlPoints and we output
77
//
KNOB_SIMD_WIDTH
* 1 patch. This function is called once per attribute.
87
uint32_t input_vec = input_cp /
KNOB_SIMD_WIDTH
;
88
uint32_t input_lane = input_cp %
KNOB_SIMD_WIDTH
;
113
// We have an input of
KNOB_SIMD_WIDTH
* TotalControlPoints and we output
114
//
KNOB_SIMD_WIDTH
* 1 patch. This function is called once per attribute.
124
float vec[
KNOB_SIMD_WIDTH
];
125
for (uint32_t lane = 0; lane <
KNOB_SIMD_WIDTH
; ++lane)
128
uint32_t input_vec = input_cp /
KNOB_SIMD_WIDTH
;
[
all
...]
backend.cpp
105
pTileBuffer += (
KNOB_SIMD_WIDTH
* FormatTraits<format>::GetBPC(comp) / 8);
421
#if
KNOB_SIMD_WIDTH
== 8
624
pColorBuffer[rt] += (2 *
KNOB_SIMD_WIDTH
* FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp) / 8;
630
pColorBuffer[rt] += (
KNOB_SIMD_WIDTH
* FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp) / 8;
633
pDepthBuffer += (
KNOB_SIMD_WIDTH
* FormatTraits<KNOB_DEPTH_HOT_TILE_FORMAT>::bpp) / 8;
634
pStencilBuffer += (
KNOB_SIMD_WIDTH
* FormatTraits<KNOB_STENCIL_HOT_TILE_FORMAT>::bpp) / 8;
[
all
...]
backend.h
57
#if
KNOB_SIMD_WIDTH
== 8
140
INLINE generateInputCoverage(const uint64_t *const coverageMask, uint32_t (&inputMask)[
KNOB_SIMD_WIDTH
], const uint32_t sampleMask)
143
assert(
KNOB_SIMD_WIDTH
== 8);
263
for(int32_t i =
KNOB_SIMD_WIDTH
- 1; i >= 0; i--)
281
uint32_t inputMask[
KNOB_SIMD_WIDTH
];
294
assert(
KNOB_SIMD_WIDTH
== 8);
303
INLINE generateInputCoverage(const uint64_t *const coverageMask, uint32_t (&inputMask)[
KNOB_SIMD_WIDTH
], const uint32_t sampleMask)
307
for(int i = 0; i <
KNOB_SIMD_WIDTH
; i++)
329
uint32_t inputMask[
KNOB_SIMD_WIDTH
];
335
unsigned long sampleNum[
KNOB_SIMD_WIDTH
];
[
all
...]
utils.h
143
#if
KNOB_SIMD_WIDTH
== 8
148
#if
KNOB_SIMD_WIDTH
== 8
269
memcpy(pDst, pSrc, (bpp *
KNOB_SIMD_WIDTH
) / 8);
293
#if
KNOB_SIMD_WIDTH
== 8
370
#if
KNOB_SIMD_WIDTH
== 8
411
#if
KNOB_SIMD_WIDTH
== 8
463
#if
KNOB_SIMD_WIDTH
== 8
514
#if
KNOB_SIMD_WIDTH
== 8
568
#if
KNOB_SIMD_WIDTH
== 8
638
#if
KNOB_SIMD_WIDTH
==
[
all
...]
format_conversion.h
70
pSrc += (FormatTraits<SrcFormat>::GetBPC(comp) *
KNOB_SIMD_WIDTH
) / 8;
192
pDst += (FormatTraits<DstFormat>::GetBPC(comp) *
KNOB_SIMD_WIDTH
) / 8;
api.cpp
72
void* pContextMem = AlignedMalloc(sizeof(SWR_CONTEXT),
KNOB_SIMD_WIDTH
* 4);
132
pContext->ppScratch[i] = (uint8_t*)AlignedMalloc(32 * sizeof(KILOBYTE),
KNOB_SIMD_WIDTH
* 4);
[
all
...]
/external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/
StoreTile.h
519
for (uint32_t t = 0; t <
KNOB_SIMD_WIDTH
; ++t)
[
all
...]
TilingFunctions.h
47
float color[FormatTraits<HotTileFormat>::numComps][
KNOB_SIMD_WIDTH
];
103
uint8_t color[FormatTraits<R8_UINT>::numComps][
KNOB_SIMD_WIDTH
];
/external/mesa3d/src/gallium/drivers/swr/rasterizer/common/
simdintrin.h
35
#if
KNOB_SIMD_WIDTH
== 8
56
#if
KNOB_SIMD_WIDTH
== 8
372
for (uint32_t i = 0; i <
KNOB_SIMD_WIDTH
; ++i)
665
OSALIGNSIMD(float) rArray[
KNOB_SIMD_WIDTH
], sArray[
KNOB_SIMD_WIDTH
];
[
all
...]
/external/mesa3d/src/gallium/drivers/swr/
swr_screen.cpp
[
all
...]
Completed in 521 milliseconds