HomeSort by relevance Sort by last modified time
    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