| /external/mesa3d/src/gallium/drivers/swr/rasterizer/jitter/functionpasses/ |
| D | lower_x86.cpp | 531 auto vSrc = pCallInst->getArgOperand(0); in VGATHER_EMU() local
539 VectorType* pVectorType = cast<VectorType>(vSrc->getType()); in VGATHER_EMU()
543 uint32_t numElem = vSrc->getType()->getVectorNumElements(); in VGATHER_EMU()
544 auto srcTy = vSrc->getType()->getVectorElementType(); in VGATHER_EMU()
554 auto pTmp = B->ALLOCA(vSrc->getType()); in VGATHER_EMU()
555 B->STORE(vSrc, pTmp); in VGATHER_EMU()
557 v32Gather = UndefValue::get(vSrc->getType()); in VGATHER_EMU()
606 auto v32Mask = B->BITCAST(pThis->VectorMask(vi1Mask), vSrc->getType()); in VGATHER_EMU()
607 v32Gather = B->CALL(pX86IntrinFunc, {vSrc, pBase, vi32Indices, v32Mask, i8Scale}); in VGATHER_EMU()
613 if (cast<VectorType>(vSrc->getType())->getElementType() == B->mDoubleTy) in VGATHER_EMU()
[all …]
|
| /external/mesa3d/src/gallium/drivers/swr/rasterizer/jitter/ |
| D | builder_mem.cpp | 184 Value* Builder::GATHERPS(Value* vSrc, in GATHERPS() argument
193 return VGATHERPS(vSrc, pBase, vIndices, vMask, C(scale)); in GATHERPS()
204 Value* Builder::GATHERDD(Value* vSrc, in GATHERDD() argument
213 return VGATHERDD(vSrc, pBase, vIndices, vMask, C(scale)); in GATHERDD()
225 Builder::GATHERPD(Value* vSrc, Value* pBase, Value* vIndices, Value* vMask, uint8_t scale) in GATHERPD() argument
227 return VGATHERPD(vSrc, pBase, vIndices, vMask, C(scale)); in GATHERPD()
652 Value* pDst, Value* vSrc, Value* vOffsets, Value* vMask, MEM_CLIENT usage) in SCATTERPS() argument
656 SWR_ASSERT(cast<VectorType>(vSrc->getType())->getElementType()->isFloatTy()); in SCATTERPS()
658 SWR_ASSERT(vSrc->getType()->getVectorElementType()->isFloatTy()); in SCATTERPS()
660 VSCATTERPS(pDst, vMask, vOffsets, vSrc, C(1)); in SCATTERPS()
|
| D | builder_gfx_mem.cpp | 68 Value* BuilderGfxMem::GATHERPS(Value* vSrc, in GATHERPS() argument
81 Value* vGather = Builder::GATHERPS(vSrc, pBase, vIndices, vMask, scale); in GATHERPS()
93 Value* BuilderGfxMem::GATHERDD(Value* vSrc, in GATHERDD() argument
107 Value* vGather = Builder::GATHERDD(vSrc, pBase, vIndices, vMask, scale); in GATHERDD()
112 Value* pDst, Value* vSrc, Value* vOffsets, Value* vMask, MEM_CLIENT usage) in SCATTERPS() argument
121 Builder::SCATTERPS(pDst, BITCAST(vSrc, mSimdFP32Ty), vOffsets, vMask, usage); in SCATTERPS()
|
| D | builder_gfx_mem.h | 98 Value* vSrc,
|
| D | builder_mem.h | 154 Value* vSrc,
|
| /external/mesa3d/src/gallium/drivers/swr/rasterizer/jitter/shader_lib/ |
| D | Scatter.cpp | 34 extern "C" void ScatterPS_256(uint8_t* pBase, SIMD256::Integer vIndices, SIMD256::Float vSrc, uint8… in ScatterPS_256() argument
39 SIMD256::store_ps(src, vSrc); in ScatterPS_256()
|
| /external/mesa3d/src/gallium/drivers/swr/rasterizer/core/ |
| D | fifo.hpp | 104 __m256 vSrc = _mm256_load_ps(pSrc + i * KNOB_SIMD_WIDTH); in enqueue_try_nosync() local
105 _mm256_stream_ps(pDst + i * KNOB_SIMD_WIDTH, vSrc); in enqueue_try_nosync()
|
| D | clip.h | 867 Float<SIMD_T> vSrc = SIMD_T::setzero_ps();
869 return SIMD_T::mask_i32gather_ps(vSrc, pBuffer, vOffsets, vMask);
877 Float<SIMD_T> const& vSrc)
882 const float* pSrc = reinterpret_cast<const float*>(&vSrc);
|