Home
last modified time | relevance | path

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

/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/
Dfifo.hpp57 T* pNewBlock = (T*)arena.AllocAligned(sizeof(T) * mBlockSize, KNOB_SIMD_WIDTH * 4); in clear()
104 __m256 vSrc = _mm256_load_ps(pSrc + i * KNOB_SIMD_WIDTH); in enqueue_try_nosync()
105 _mm256_stream_ps(pDst + i * KNOB_SIMD_WIDTH, vSrc); in enqueue_try_nosync()
108 const uint32_t numSimdLines = sizeof(T) / (KNOB_SIMD_WIDTH * 4); in enqueue_try_nosync()
109 static_assert(numSimdLines * KNOB_SIMD_WIDTH * 4 == sizeof(T), in enqueue_try_nosync()
123 T* newBlock = (T*)arena.AllocAligned(sizeof(T) * mBlockSize, KNOB_SIMD_WIDTH * 4); in enqueue_try_nosync()
Dknobs.h66 #define KNOB_SIMD_WIDTH 8 macro
123 #if KNOB_SIMD_WIDTH == 8 && KNOB_TILE_X_DIM < 4
133 #if KNOB_SIMD_WIDTH == 8
Dfrontend.cpp490 (numItemsRemaining >= KNOB_SIMD_WIDTH) ? KNOB_SIMD_WIDTH : numItemsRemaining; in GenerateMask()
686 return (remainder >= KNOB_SIMD_WIDTH) ? KNOB_SIMD_WIDTH : remainder; in GetNumInvocations()
740 uint8_t* pGsOut[KNOB_SIMD_WIDTH];
841 for (uint32_t i = 0; i < KNOB_SIMD_WIDTH; ++i) in GeometryShaderStage()
881 for (uint32_t i = 0; i < KNOB_SIMD_WIDTH; ++i) in GeometryShaderStage()
976 TransposeSOAtoAOS<SIMD256, KNOB_SIMD_WIDTH>((uint8_t*)pGsBuffers->pGsTransposed, in GeometryShaderStage()
1195 for (uint32_t i = 0; i < KNOB_SIMD_WIDTH; ++i) in AllocateGsBuffers()
1359 uint32_t requiredAllocSize = KNOB_SIMD_WIDTH * tsState.hsAllocationSize; in TessellationStages()
1373 memset(hsContext.pCPout, 0x90, sizeof(ScalarPatch) * KNOB_SIMD_WIDTH); in TessellationStages()
1414 AlignUp(tsData.NumDomainPoints, KNOB_SIMD_WIDTH) / KNOB_SIMD_WIDTH; in TessellationStages()
[all …]
Dformat_types.h81 #if KNOB_SIMD_WIDTH == 8
93 #if KNOB_SIMD_WIDTH == 8
102 #if KNOB_SIMD_WIDTH == 8
123 #if KNOB_SIMD_WIDTH == 8
201 #if KNOB_SIMD_WIDTH == 8
213 #if KNOB_SIMD_WIDTH == 8
222 #if KNOB_SIMD_WIDTH == 8
244 #if KNOB_SIMD_WIDTH == 8
322 #if KNOB_SIMD_WIDTH == 8
333 #if KNOB_SIMD_WIDTH == 8
[all …]
Dbackend_impl.h52 #if KNOB_SIMD_WIDTH == 8
189 uint32_t (&inputMask)[KNOB_SIMD_WIDTH], in generateInputCoverage()
193 assert(KNOB_SIMD_WIDTH == 8); in generateInputCoverage()
363 for (int32_t i = KNOB_SIMD_WIDTH - 1; i >= 0; i--) in generateInputCoverage()
384 uint32_t inputMask[KNOB_SIMD_WIDTH]; in generateInputCoverage()
405 assert(KNOB_SIMD_WIDTH == 8);
415 uint32_t (&inputMask)[KNOB_SIMD_WIDTH],
420 for (int i = 0; i < KNOB_SIMD_WIDTH; i++)
450 uint32_t inputMask[KNOB_SIMD_WIDTH];
456 unsigned long sampleNum[KNOB_SIMD_WIDTH];
[all …]
Dformat_utils.h83 #if KNOB_SIMD_WIDTH == 8
239 memcpy(pDst, pSrc, (bpp * KNOB_SIMD_WIDTH) / 8); in Transpose()
261 #if KNOB_SIMD_WIDTH == 8 in Transpose()
356 #if KNOB_SIMD_WIDTH == 8 in Transpose()
403 #if KNOB_SIMD_WIDTH == 8 in Transpose()
461 #if KNOB_SIMD_WIDTH == 8 in Transpose()
518 #if KNOB_SIMD_WIDTH == 8 in Transpose()
578 #if KNOB_SIMD_WIDTH == 8 in Transpose()
654 #if KNOB_SIMD_WIDTH == 8 in Transpose()
729 #if KNOB_SIMD_WIDTH == 8 in Transpose()
Dbackend_singlesample.cpp294 (2 * KNOB_SIMD_WIDTH * FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp) / 8; in BackendSingleSample()
298 pDepthBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_DEPTH_HOT_TILE_FORMAT>::bpp) / 8; in BackendSingleSample()
300 (KNOB_SIMD_WIDTH * FormatTraits<KNOB_STENCIL_HOT_TILE_FORMAT>::bpp) / 8; in BackendSingleSample()
Dpa_avx.cpp35 #if (KNOB_SIMD_WIDTH == 8)
439 primIndex += KNOB_SIMD_WIDTH; in PaPatchListSingle()
453 uint32_t input_vec = input_cp / KNOB_SIMD_WIDTH; in PaPatchListSingle()
454 uint32_t input_lane = input_cp % KNOB_SIMD_WIDTH; in PaPatchListSingle()
495 lane_offset = KNOB_SIMD_WIDTH; in PaPatchListTerm()
504 float vec[KNOB_SIMD_WIDTH]; in PaPatchListTerm()
505 for (uint32_t lane = 0; lane < KNOB_SIMD_WIDTH; ++lane) in PaPatchListTerm()
516 uint32_t input_vec = input_cp / KNOB_SIMD_WIDTH; in PaPatchListTerm()
517 uint32_t input_lane = input_cp % KNOB_SIMD_WIDTH; in PaPatchListTerm()
917 primIndex += KNOB_SIMD_WIDTH; in PaTriListSingle0()
[all …]
Dbackend_sample.cpp311 (2 * KNOB_SIMD_WIDTH * FormatTraits<KNOB_COLOR_HOT_TILE_FORMAT>::bpp) / 8; in BackendSampleRate()
315 pDepthBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_DEPTH_HOT_TILE_FORMAT>::bpp) / 8; in BackendSampleRate()
317 (KNOB_SIMD_WIDTH * FormatTraits<KNOB_STENCIL_HOT_TILE_FORMAT>::bpp) / 8; in BackendSampleRate()
Dbackend.cpp381 pDepthBuffer += (KNOB_SIMD_WIDTH * FormatTraits<KNOB_DEPTH_HOT_TILE_FORMAT>::bpp) / 8; in BackendNullPS()
383 (KNOB_SIMD_WIDTH * FormatTraits<KNOB_STENCIL_HOT_TILE_FORMAT>::bpp) / 8; in BackendNullPS()
Dapi.cpp68 void* pContextMem = AlignedMalloc(sizeof(SWR_CONTEXT), KNOB_SIMD_WIDTH * 4); in SwrCreateContext()
194 (uint8_t*)AlignedMalloc(KNOB_WORKER_SCRATCH_SPACE_SIZE, KNOB_SIMD_WIDTH * 4); in SwrCreateContext()
1676 KNOB_SIMD_WIDTH * sizeof(float)); in SwrGetPrivateContextState()
Dbinner.cpp856 SWR_ASSERT(KNOB_SIMD_WIDTH == 8, "Need to update degenerate mask code for avx512"); in BinTrianglesImpl()
1223 BinTrianglesImpl<SIMD256, KNOB_SIMD_WIDTH, CT>( in BinTriangles()
1650 BinPointsImpl<SIMD256, KNOB_SIMD_WIDTH>( in BinPoints()
1958 BinLinesImpl<SIMD256, KNOB_SIMD_WIDTH>( in BinLines()
Dstate.h346 …uint8_t* pStreams[KNOB_SIMD_WIDTH]; // OUT: output stream (contains vertices for all output str…
Dpa.h56 SIMD_WIDTH = KNOB_SIMD_WIDTH,
57 SIMD_WIDTH_DIV2 = KNOB_SIMD_WIDTH / 2,
/external/mesa3d/src/gallium/drivers/swr/rasterizer/common/
Dintrin.h53 #if KNOB_SIMD_WIDTH == 8
Dsimdintrin.h30 #if KNOB_SIMD_WIDTH == 8
/external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/
DTilingFunctions.h48 float color[FormatTraits<HotTileFormat>::numComps][KNOB_SIMD_WIDTH];
104 uint8_t color[FormatTraits<R8_UINT>::numComps][KNOB_SIMD_WIDTH];
/external/mesa3d/src/gallium/drivers/swr/
Dswr_screen.cpp1136 screen->hJitMgr = JitCreateContext(KNOB_SIMD_WIDTH, "", "swr"); in swr_create_screen_internal()
Dswr_shader.cpp1623 … C((char)0), VERTEX_COUNT_SIZE + CONTROL_HEADER_SIZE, MaybeAlign(sizeof(float) * KNOB_SIMD_WIDTH)); in CompileGS()
1625 …SET(pStream, C((char)0), VERTEX_COUNT_SIZE + CONTROL_HEADER_SIZE, sizeof(float) * KNOB_SIMD_WIDTH); in CompileGS()