| /external/mesa3d/src/gallium/drivers/swr/rasterizer/jitter/ |
| H A D | builder_misc.cpp | 369 /// @param vMask - SIMD wide mask that controls whether to access memory load 0
538 /// @param vMask - SIMD wide mask that controls whether to access memory or the src values
540 Value *Builder::GATHERPS(Value* vSrc, Value* pBase, Value* vIndices, Value* vMask, Value* scale) argument
548 vMask = BITCAST(vMask, mSimdFP32Ty);
549 vGather = VGATHERPS(vSrc,pBase,vIndices,vMask,scale);
562 Value *mask = MASK(vMask);
590 /// @param vMask - SIMD wide mask that controls whether to access memory or the src values
592 Value *Builder::GATHERDD(Value* vSrc, Value* pBase, Value* vIndices, Value* vMask, Value* scale) argument
599 vGather = VGATHERDD(vSrc, pBase, vIndices, vMask, scal
642 GATHERPD(Value* vSrc, Value* pBase, Value* vIndices, Value* vMask, Value* scale) argument
1031 Value *vMask; local
1082 Value *vMask = mask; local
1117 Value *vMask; local
1169 Value *vMask = mask; local
1396 SCATTERPS(Value* pDst, Value* vSrc, Value* vOffsets, Value* vMask) argument
[all...] |
| H A D | fetch_jit.cpp | 846 Value *vMask; local
851 vMask = vGatherMask;
853 vGatherResult[0] = GATHERPS(gatherSrc, pStreamBase, vOffsets, vMask, C((char)1));
864 vMask = vGatherMask;
866 vGatherResult[1] = GATHERPS(gatherSrc, pStreamBase, vOffsets, vMask, C((char)1));
893 Value *vMask = vGatherMask; local
896 vVertexElements[currentVertexElement++] = GATHERPS(gatherSrc, pStreamBase, vOffsets, vMask, C((char)1));
1037 Value *vMask; local
1042 vMask = vGatherMask;
1044 vGatherResult[0] = GATHERDD(gatherSrc, pStreamBase, vOffsets, vMask,
1085 Value *vMask = vGatherMask; local
[all...] |
| H A D | blend_jit.cpp | 658 Value* vMask[4]; local
675 vMask[i] = VIMMED1(0xFFFFFFFF);
678 vMask[i] = VIMMED1((1 << info.bpc[i]) - 1);
724 result[i] = AND(result[i], vMask[i]);
|
| H A D | builder_misc.h | 118 void SCATTERPS(Value* pDst, Value* vSrc, Value* vOffsets, Value* vMask);
|
| /external/mesa3d/src/gallium/drivers/swr/rasterizer/core/ |
| H A D | clip.h | 380 const simdscalar vMask = _mm256_set_ps(0, -1, -1, -1, -1, -1, -1, -1); local
404 transposedPrims[0].attrib[VERTEX_POSITION_SLOT][c] = _simd_mask_i32gather_ps(_mm256_undefined_ps(), (const float*)pBase, vOffsets, vMask, 1);
415 transposedPrims[0].attrib[attribSlot][c] = _simd_mask_i32gather_ps(_mm256_undefined_ps(), (const float*)pBase, vOffsets, vMask, 1);
426 transposedPrims[0].attrib[VERTEX_CLIPCULL_DIST_LO_SLOT][c] = _simd_mask_i32gather_ps(_mm256_undefined_ps(), (const float*)pBase, vOffsets, vMask, 1);
436 transposedPrims[0].attrib[VERTEX_CLIPCULL_DIST_HI_SLOT][c] = _simd_mask_i32gather_ps(_mm256_undefined_ps(), (const float*)pBase, vOffsets, vMask, 1);
518 ClipSimd(vMask(primMask), vMask(clipMask), pa, primId, viewportIdx);
558 inline simdscalar GatherComponent(const float* pBuffer, uint32_t attrib, simdscalar vMask, simdscalari vIndices, uint32_t component) argument
562 return _simd_mask_i32gather_ps(vSrc, pBuffer, vOffsets, vMask, 1);
565 inline void ScatterComponent(const float* pBuffer, uint32_t attrib, simdscalar vMask, simdscalar argument
[all...] |
| H A D | depthstencil.h | 228 simdscalar vMask = _simd_and_ps(depthMask, coverageMask); local
229 _simd_maskstore_ps((float*)pDepthBase, _simd_castps_si(vMask), interpZ);
|
| H A D | backend.h | 564 vCoverageMask[sample] = _simd_and_ps(activeLanes, vMask(pCoverageMask[currentSimdIn8x8] & MASK));
585 vCoverageMask[sample] = _simd_and_ps(vCoverageMask[sample], vMask(CalcDepthBoundsAcceptMask(z, minz, maxz)));
616 vCoverageMask[sample] = _simd_and_ps(vCoverageMask[sample], vMask(~clipMask));
|
| H A D | backend.cpp | 534 simdscalar vCoverageMask = vMask(coverageMask);
745 simdscalar vCoverageMask = vMask(coverageMask);
909 activeLanes = vMask(work.anyCoveredSamples & MASK);
1145 simdscalar vCoverageMask = vMask(coverageMask);
|
| H A D | frontend.cpp | 484 return _simd_castps_si(vMask(mask));
|
| /external/mesa3d/src/gallium/drivers/swr/rasterizer/common/ |
| H A D | simdintrin.h | 383 __m256 _simd_mask_i32gather_ps(__m256 vSrc, const float* pBase, __m256i vOffsets, __m256 vMask, const int scale) argument
389 uint32_t mask = _simd_movemask_ps(vMask);
653 simdscalar vMask(int32_t mask) function
|
| /external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/ |
| H A D | StoreTile.h | 606 __m128i vMask = _mm_set1_epi32(0xFFFFFF);
608 vDst0 = _mm_andnot_si128(vMask, vDst0);
609 vDst0 = _mm_or_si128(vDst0, _mm_and_si128(vRow00, vMask));
610 vDst1 = _mm_andnot_si128(vMask, vDst1);
611 vDst1 = _mm_or_si128(vDst1, _mm_and_si128(vRow10, vMask));
|
| /external/valgrind/VEX/priv/ |
| H A D | guest_ppc_toIR.c | 24730 IRTemp vMask = newTemp( Ity_V128 ); local
24748 assign( vMask, binop( Iop_CmpGT8Ux16, mkexpr( vA ), mkexpr( vB ) ) );
24753 mkexpr( vMask ) ) );
24758 unop ( Iop_NotV128, mkexpr( vMask ) ) ) );
24773 assign( vMask, binop( Iop_CmpGT16Ux8, mkexpr( vA ), mkexpr( vB ) ) );
24778 mkexpr( vMask ) ) );
24783 unop ( Iop_NotV128, mkexpr( vMask ) ) ) );
24798 assign( vMask, binop( Iop_CmpGT32Ux4, mkexpr( vA ), mkexpr( vB ) ) );
24803 mkexpr( vMask ) ) );
24808 unop ( Iop_NotV128, mkexpr( vMask ) ) ) );
[all...] |