| /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...] |
