/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/ |
knobs.h | 57 #define KNOB_SIMD_WIDTH 8 62 #define KNOB_SIMD_WIDTH 8 67 #define KNOB_SIMD_WIDTH 8 134 #if KNOB_SIMD_WIDTH==8 && KNOB_TILE_X_DIM < 4 144 #if KNOB_SIMD_WIDTH == 8
|
fifo.hpp | 58 T* pNewBlock = (T*)arena.AllocAligned(sizeof(T)*mBlockSize, KNOB_SIMD_WIDTH*4); 112 __m256 vSrc = _mm256_load_ps(pSrc + i*KNOB_SIMD_WIDTH); 113 _mm256_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);
|
frontend.cpp | 483 uint32_t numActive = (numItemsRemaining >= KNOB_SIMD_WIDTH) ? KNOB_SIMD_WIDTH : numItemsRemaining; 671 return (remainder >= KNOB_SIMD_WIDTH) ? KNOB_SIMD_WIDTH : remainder; 723 uint8_t* pGsOut[KNOB_SIMD_WIDTH]; 812 for (uint32_t i = 0; i < KNOB_SIMD_WIDTH; ++i) 859 for (uint32_t i = 0; i < KNOB_SIMD_WIDTH; ++i) [all...] |
format_types.h | 82 #if KNOB_SIMD_WIDTH == 8 94 #if KNOB_SIMD_WIDTH == 8 103 #if KNOB_SIMD_WIDTH == 8 123 #if KNOB_SIMD_WIDTH == 8 197 #if KNOB_SIMD_WIDTH == 8 209 #if KNOB_SIMD_WIDTH == 8 218 #if KNOB_SIMD_WIDTH == 8 239 #if KNOB_SIMD_WIDTH == 8 313 #if KNOB_SIMD_WIDTH == 8 324 #if KNOB_SIMD_WIDTH == [all...] |
backend_impl.h | 45 #if KNOB_SIMD_WIDTH == 8 152 INLINE generateInputCoverage(const uint64_t *const coverageMask, uint32_t (&inputMask)[KNOB_SIMD_WIDTH], const uint32_t sampleMask) 155 assert(KNOB_SIMD_WIDTH == 8); 276 for(int32_t i = KNOB_SIMD_WIDTH - 1; i >= 0; i--) 294 uint32_t inputMask[KNOB_SIMD_WIDTH]; 307 assert(KNOB_SIMD_WIDTH == 8); 316 INLINE generateInputCoverage(const uint64_t *const coverageMask, uint32_t (&inputMask)[KNOB_SIMD_WIDTH], const uint32_t sampleMask) 320 for(int i = 0; i < KNOB_SIMD_WIDTH; i++) 343 uint32_t inputMask[KNOB_SIMD_WIDTH]; 349 unsigned long sampleNum[KNOB_SIMD_WIDTH]; [all...] |
tilemgr.cpp | 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_utils.h | 83 #if KNOB_SIMD_WIDTH == 8 204 memcpy(pDst, pSrc, (bpp * KNOB_SIMD_WIDTH) / 8); 228 #if KNOB_SIMD_WIDTH == 8 305 #if KNOB_SIMD_WIDTH == 8 346 #if KNOB_SIMD_WIDTH == 8 398 #if KNOB_SIMD_WIDTH == 8 449 #if KNOB_SIMD_WIDTH == 8 503 #if KNOB_SIMD_WIDTH == 8 573 #if KNOB_SIMD_WIDTH == 8 642 #if KNOB_SIMD_WIDTH == [all...] |
backend_sample.cpp | 235 psContext.pColorBuffer[rt] += (2 * KNOB_SIMD_WIDTH * FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp) / 8; 244 psContext.pColorBuffer[rt] += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp) / 8; 247 pDepthBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_DEPTH_HOT_TILE_FORMAT>::bpp) / 8; 248 pStencilBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_STENCIL_HOT_TILE_FORMAT>::bpp) / 8;
|
backend_singlesample.cpp | 217 psContext.pColorBuffer[rt] += (2 * KNOB_SIMD_WIDTH * FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp) / 8; 226 psContext.pColorBuffer[rt] += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp) / 8; 229 pDepthBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_DEPTH_HOT_TILE_FORMAT>::bpp) / 8; 230 pStencilBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_STENCIL_HOT_TILE_FORMAT>::bpp) / 8;
|
format_conversion.h | 70 pSrc += (FormatTraits<SrcFormat>::GetBPC(comp) * KNOB_SIMD_WIDTH) / 8; 194 pDst += (FormatTraits<DstFormat>::GetBPC(comp) * KNOB_SIMD_WIDTH) / 8;
|
backend.cpp | 301 pDepthBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_DEPTH_HOT_TILE_FORMAT>::bpp) / 8; 302 pStencilBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_STENCIL_HOT_TILE_FORMAT>::bpp) / 8;
|
pa_avx.cpp | 35 #if (KNOB_SIMD_WIDTH == 8) 358 // We have an input of KNOB_SIMD_WIDTH * TotalControlPoints and we output 359 // KNOB_SIMD_WIDTH * 1 patch. This function is called once per attribute. 367 primIndex += KNOB_SIMD_WIDTH; 381 uint32_t input_vec = input_cp / KNOB_SIMD_WIDTH; 382 uint32_t input_lane = input_cp % KNOB_SIMD_WIDTH; 412 // We have an input of KNOB_SIMD_WIDTH * TotalControlPoints and we output 413 // KNOB_SIMD_WIDTH * 1 patch. This function is called once per attribute. 423 lane_offset = KNOB_SIMD_WIDTH; 432 float vec[KNOB_SIMD_WIDTH]; [all...] |
backend_clear.cpp | 47 pTileBuffer += (KNOB_SIMD_WIDTH * FormatTraits<format>::GetBPC(comp) / 8);
|
pa.h | 56 SIMD_WIDTH = KNOB_SIMD_WIDTH, 57 SIMD_WIDTH_DIV2 = KNOB_SIMD_WIDTH / 2, [all...] |
api.cpp | 71 void* pContextMem = AlignedMalloc(sizeof(SWR_CONTEXT), KNOB_SIMD_WIDTH * 4); 158 pContext->ppScratch[i] = (uint8_t*)AlignedMalloc(32 * sizeof(KILOBYTE), KNOB_SIMD_WIDTH * 4); [all...] |
binner.cpp | [all...] |
state.h | 314 uint8_t* pStreams[KNOB_SIMD_WIDTH]; // OUT: output stream (contains vertices for all output streams) [all...] |
/external/mesa3d/src/gallium/drivers/swr/rasterizer/common/ |
intrin.h | 50 #if KNOB_SIMD_WIDTH == 8
|
simdintrin.h | 30 #if KNOB_SIMD_WIDTH == 8 195 OSALIGNSIMD(float) rArray[KNOB_SIMD_WIDTH], sArray[KNOB_SIMD_WIDTH];
|
/external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/ |
StoreTile.h | 521 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/ |
swr_screen.cpp | [all...] |
swr_shader.cpp | 658 MEMSET(pStream, C((char)0), VERTEX_COUNT_SIZE + CONTROL_HEADER_SIZE, sizeof(float) * KNOB_SIMD_WIDTH); [all...] |