Home
last modified time | relevance | path

Searched refs:KNOB_SIMD_WIDTH (Results 1 – 23 of 23) sorted by relevance

/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/
Dfifo.hpp58 T* pNewBlock = (T*)arena.AllocAligned(sizeof(T)*mBlockSize, KNOB_SIMD_WIDTH*4); in clear()
112 __m256 vSrc = _mm256_load_ps(pSrc + i*KNOB_SIMD_WIDTH); in enqueue_try_nosync()
113 _mm256_stream_ps(pDst + i*KNOB_SIMD_WIDTH, vSrc); in enqueue_try_nosync()
116 const uint32_t numSimdLines = sizeof(T) / (KNOB_SIMD_WIDTH*4); in enqueue_try_nosync()
117 static_assert(numSimdLines * KNOB_SIMD_WIDTH * 4 == sizeof(T), in enqueue_try_nosync()
131 T* newBlock = (T*)arena.AllocAligned(sizeof(T)*mBlockSize, KNOB_SIMD_WIDTH*4); in enqueue_try_nosync()
Dknobs.h57 #define KNOB_SIMD_WIDTH 8 macro
62 #define KNOB_SIMD_WIDTH 8 macro
67 #define KNOB_SIMD_WIDTH 8 macro
134 #if KNOB_SIMD_WIDTH==8 && KNOB_TILE_X_DIM < 4
144 #if KNOB_SIMD_WIDTH == 8
Dfrontend.cpp483 … uint32_t numActive = (numItemsRemaining >= KNOB_SIMD_WIDTH) ? KNOB_SIMD_WIDTH : numItemsRemaining; in GenerateMask()
671 return (remainder >= KNOB_SIMD_WIDTH) ? KNOB_SIMD_WIDTH : remainder; in GetNumInvocations()
723 uint8_t* pGsOut[KNOB_SIMD_WIDTH];
812 for (uint32_t i = 0; i < KNOB_SIMD_WIDTH; ++i) in GeometryShaderStage()
859 for (uint32_t i = 0; i < KNOB_SIMD_WIDTH; ++i) in GeometryShaderStage()
930 …TransposeSOAtoAOS<SIMD256, KNOB_SIMD_WIDTH>((uint8_t*)pGsBuffers->pGsTransposed, pVertexBaseAOS, v… in GeometryShaderStage()
1101 for (uint32_t i = 0; i < KNOB_SIMD_WIDTH; ++i) in AllocateGsBuffers()
1128 ScalarPatch patchData[KNOB_SIMD_WIDTH];
1245 memset(hsContext.pCPout, 0x90, sizeof(ScalarPatch) * KNOB_SIMD_WIDTH); in TessellationStages()
1280 …t requiredDSVectorInvocations = AlignUp(tsData.NumDomainPoints, KNOB_SIMD_WIDTH) / KNOB_SIMD_WIDTH; in TessellationStages()
[all …]
Dformat_types.h82 #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 == 8
[all …]
Dbackend_impl.h45 #if KNOB_SIMD_WIDTH == 8
152 …utCoverage(const uint64_t *const coverageMask, uint32_t (&inputMask)[KNOB_SIMD_WIDTH], const uint3… in generateInputCoverage()
155 assert(KNOB_SIMD_WIDTH == 8); in generateInputCoverage()
276 for(int32_t i = KNOB_SIMD_WIDTH - 1; i >= 0; i--) in generateInputCoverage()
294 uint32_t inputMask[KNOB_SIMD_WIDTH]; in generateInputCoverage()
307 assert(KNOB_SIMD_WIDTH == 8);
316 …utCoverage(const uint64_t *const coverageMask, uint32_t (&inputMask)[KNOB_SIMD_WIDTH], const uint3…
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 …]
Dformat_utils.h83 #if KNOB_SIMD_WIDTH == 8
204 memcpy(pDst, pSrc, (bpp * KNOB_SIMD_WIDTH) / 8); in Transpose()
228 #if KNOB_SIMD_WIDTH == 8 in Transpose()
305 #if KNOB_SIMD_WIDTH == 8 in Transpose()
346 #if KNOB_SIMD_WIDTH == 8 in Transpose()
398 #if KNOB_SIMD_WIDTH == 8 in Transpose()
449 #if KNOB_SIMD_WIDTH == 8 in Transpose()
503 #if KNOB_SIMD_WIDTH == 8 in Transpose()
573 #if KNOB_SIMD_WIDTH == 8 in Transpose()
642 #if KNOB_SIMD_WIDTH == 8 in Transpose()
Dtilemgr.cpp312 pfBuf += KNOB_SIMD_WIDTH; in ClearColorHotTile()
314 pfBuf += KNOB_SIMD_WIDTH; in ClearColorHotTile()
316 pfBuf += KNOB_SIMD_WIDTH; in ClearColorHotTile()
318 pfBuf += KNOB_SIMD_WIDTH; in ClearColorHotTile()
340 pfBuf += KNOB_SIMD_WIDTH; in ClearDepthHotTile()
Dbackend_singlesample.cpp217 …psContext.pColorBuffer[rt] += (2 * KNOB_SIMD_WIDTH * FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp… in BackendSingleSample()
226 …psContext.pColorBuffer[rt] += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp) / … in BackendSingleSample()
229 pDepthBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_DEPTH_HOT_TILE_FORMAT>::bpp) / 8; in BackendSingleSample()
230 … pStencilBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_STENCIL_HOT_TILE_FORMAT>::bpp) / 8; in BackendSingleSample()
Dbackend_sample.cpp235 …psContext.pColorBuffer[rt] += (2 * KNOB_SIMD_WIDTH * FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp… in BackendSampleRate()
244 …psContext.pColorBuffer[rt] += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp) / … in BackendSampleRate()
247 pDepthBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_DEPTH_HOT_TILE_FORMAT>::bpp) / 8; in BackendSampleRate()
248 … pStencilBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_STENCIL_HOT_TILE_FORMAT>::bpp) / 8; in BackendSampleRate()
Dpa_avx.cpp35 #if (KNOB_SIMD_WIDTH == 8)
367 primIndex += KNOB_SIMD_WIDTH; in PaPatchListSingle()
381 uint32_t input_vec = input_cp / KNOB_SIMD_WIDTH; in PaPatchListSingle()
382 uint32_t input_lane = input_cp % KNOB_SIMD_WIDTH; in PaPatchListSingle()
423 lane_offset = KNOB_SIMD_WIDTH; in PaPatchListTerm()
432 float vec[KNOB_SIMD_WIDTH]; in PaPatchListTerm()
433 for (uint32_t lane = 0; lane < KNOB_SIMD_WIDTH; ++lane) in PaPatchListTerm()
443 uint32_t input_vec = input_cp / KNOB_SIMD_WIDTH; in PaPatchListTerm()
444 uint32_t input_lane = input_cp % KNOB_SIMD_WIDTH; in PaPatchListTerm()
800 primIndex += KNOB_SIMD_WIDTH; in PaTriListSingle0()
[all …]
Dformat_conversion.h70 pSrc += (FormatTraits<SrcFormat>::GetBPC(comp) * KNOB_SIMD_WIDTH) / 8; in LoadSOA()
194 pDst += (FormatTraits<DstFormat>::GetBPC(comp) * KNOB_SIMD_WIDTH) / 8; in StoreSOA()
Dbackend.cpp301 pDepthBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_DEPTH_HOT_TILE_FORMAT>::bpp) / 8; in BackendNullPS()
302 … pStencilBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_STENCIL_HOT_TILE_FORMAT>::bpp) / 8; in BackendNullPS()
Dbackend_clear.cpp47 pTileBuffer += (KNOB_SIMD_WIDTH * FormatTraits<format>::GetBPC(comp) / 8); in ClearRasterTile()
Dapi.cpp71 void* pContextMem = AlignedMalloc(sizeof(SWR_CONTEXT), KNOB_SIMD_WIDTH * 4); in SwrCreateContext()
158 … pContext->ppScratch[i] = (uint8_t*)AlignedMalloc(32 * sizeof(KILOBYTE), KNOB_SIMD_WIDTH * 4); in SwrCreateContext()
1625 …vateState = pState->pArena->AllocAligned(pContext->privateStateSize, KNOB_SIMD_WIDTH*sizeof(float)… in SwrGetPrivateContextState()
Dbinner.cpp807 SWR_ASSERT(KNOB_SIMD_WIDTH == 8, "Need to update degenerate mask code for avx512"); in BinTrianglesImpl()
1131 …BinTrianglesImpl<SIMD256, KNOB_SIMD_WIDTH, CT>(pDC, pa, workerId, tri, triMask, primID, viewportId… in BinTriangles()
1554 BinPointsImpl<SIMD256, KNOB_SIMD_WIDTH>( in BinPoints()
1877 …BinLinesImpl<SIMD256, KNOB_SIMD_WIDTH>(pDC, pa, workerId, prim, primMask, primID, viewportIdx, rtI… in BinLines()
Dpa.h56 SIMD_WIDTH = KNOB_SIMD_WIDTH,
57 SIMD_WIDTH_DIV2 = KNOB_SIMD_WIDTH / 2,
Dstate.h314 …uint8_t* pStreams[KNOB_SIMD_WIDTH]; // OUT: output stream (contains vertices for all output stream…
/external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/
DStoreTile.h521 for (uint32_t t = 0; t < KNOB_SIMD_WIDTH; ++t)
1277 ppRows[0] += KNOB_SIMD_WIDTH * DST_BYTES_PER_PIXEL / 2;
1278 ppRows[1] += KNOB_SIMD_WIDTH * DST_BYTES_PER_PIXEL / 2;
1279 pSrc += SRC_BYTES_PER_PIXEL * KNOB_SIMD_WIDTH;
1364 ppRows[0] += KNOB_SIMD_WIDTH * DST_BYTES_PER_PIXEL / 2;
1365 ppRows[1] += KNOB_SIMD_WIDTH * DST_BYTES_PER_PIXEL / 2;
1366 pSrc += SRC_BYTES_PER_PIXEL * KNOB_SIMD_WIDTH;
1451 ppRows[0] += KNOB_SIMD_WIDTH * DST_BYTES_PER_PIXEL / 2;
1452 ppRows[1] += KNOB_SIMD_WIDTH * DST_BYTES_PER_PIXEL / 2;
1453 pSrc += SRC_BYTES_PER_PIXEL * KNOB_SIMD_WIDTH;
[all …]
DTilingFunctions.h47 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/
Dsimdintrin.h30 #if KNOB_SIMD_WIDTH == 8
195 OSALIGNSIMD(float) rArray[KNOB_SIMD_WIDTH], sArray[KNOB_SIMD_WIDTH]; in _simd_mov()
Dintrin.h50 #if KNOB_SIMD_WIDTH == 8
/external/mesa3d/src/gallium/drivers/swr/
Dswr_screen.cpp1163 screen->hJitMgr = JitCreateContext(KNOB_SIMD_WIDTH, "", "swr"); in swr_create_screen_internal()
Dswr_shader.cpp658 …SET(pStream, C((char)0), VERTEX_COUNT_SIZE + CONTROL_HEADER_SIZE, sizeof(float) * KNOB_SIMD_WIDTH); in CompileGS()