Home
last modified time | relevance | path

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

/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/
Dutils.h80 simdscalari ymin;
81 simdscalari ymax;
82 simdscalari xmin;
83 simdscalari xmax;
291 simdscalari src = _simd_load_si((const simdscalari*)pSrc); in Transpose()
306 simdscalari dst01 = _mm256_shuffle_epi8(src, in Transpose()
308 simdscalari dst23 = _mm256_permute2x128_si256(src, src, 0x01); in Transpose()
311 simdscalari dst = _mm256_or_si256(dst01, dst23); in Transpose()
312 _simd_store_si((simdscalari*)pDst, dst); in Transpose()
371 simdscalari src = _simd_load_si((const simdscalari*)pSrc); in Transpose()
[all …]
Dbinner.cpp38 …mdvector prims[3], simdscalar vRecipW[2], uint32_t primMask, simdscalari primID, simdscalari viewp…
53 INLINE simdscalari fpToFixedPointVertical(const simdscalar vIn) in fpToFixedPointVertical()
65 INLINE static void FPToFixedPoint(const simdvector * const tri, simdscalari(&vXi)[3], simdscalari(&… in FPToFixedPoint()
84 …id calcBoundingBoxIntVertical(const simdvector * const tri, simdscalari(&vX)[3], simdscalari(&vY)[… in calcBoundingBoxIntVertical()
86 simdscalari vMinX = vX[0]; in calcBoundingBoxIntVertical()
90 simdscalari vMaxX = vX[0]; in calcBoundingBoxIntVertical()
94 simdscalari vMinY = vY[0]; in calcBoundingBoxIntVertical()
98 simdscalari vMaxY = vY[0]; in calcBoundingBoxIntVertical()
112 …Vertical<FEConservativeRastT>(const simdvector * const tri, simdscalari(&vX)[3], simdscalari(&vY)[… in calcBoundingBoxIntVertical()
117 simdscalari vMinX = vX[0]; in calcBoundingBoxIntVertical()
[all …]
Dfrontend.h95 void triangleSetupABIntVertical(const simdscalari vX[3], const simdscalari vY[3], simdscalari (&vA)… in triangleSetupABIntVertical()
145 void calcDeterminantIntVertical(const simdscalari vA[3], const simdscalari vB[3], simdscalari *pvDe… in calcDeterminantIntVertical()
149 simdscalari vA1Lo = _simd_unpacklo_epi32(vA[1], vA[1]); // 0 0 1 1 4 4 5 5 in calcDeterminantIntVertical()
150 simdscalari vA1Hi = _simd_unpackhi_epi32(vA[1], vA[1]); // 2 2 3 3 6 6 7 7 in calcDeterminantIntVertical()
152 simdscalari vB2Lo = _simd_unpacklo_epi32(vB[2], vB[2]); in calcDeterminantIntVertical()
153 simdscalari vB2Hi = _simd_unpackhi_epi32(vB[2], vB[2]); in calcDeterminantIntVertical()
155 simdscalari vA1B2Lo = _simd_mul_epi32(vA1Lo, vB2Lo); // 0 1 4 5 in calcDeterminantIntVertical()
156 simdscalari vA1B2Hi = _simd_mul_epi32(vA1Hi, vB2Hi); // 2 3 6 7 in calcDeterminantIntVertical()
159 simdscalari vA2Lo = _simd_unpacklo_epi32(vA[2], vA[2]); in calcDeterminantIntVertical()
160 simdscalari vA2Hi = _simd_unpackhi_epi32(vA[2], vA[2]); in calcDeterminantIntVertical()
[all …]
Dclip.h66 …nst API_STATE& state, const simdvector& vertex, simdscalar& clipCodes, simdscalari viewportIndexes) in ComputeClipCodes()
143 void ComputeClipCodes(simdvector vertex[], simdscalari viewportIndexes) in ComputeClipCodes()
266 …imMask, const simdscalar& vClipMask, PA_STATE& pa, const simdscalari& vPrimId, const simdscalari& … in ClipSimd()
339 … simdscalari vNumClippedVerts = ClipPrims((float*)&vertices[0], vPrimMask, vClipMask, numAttribs); in ClipSimd()
368 const simdscalari vOffsets = _mm256_set_epi32( in ClipSimd()
463 …uteStage(PA_STATE& pa, simdvector prim[], uint32_t primMask, simdscalari primId, simdscalari viewp… in ExecuteStage()
537 inline simdscalari ComputeOffsets(uint32_t attrib, simdscalari vIndices, uint32_t component) in ComputeOffsets()
546 simdscalari vOffsets = _simd_mullo_epi32(vIndices, _simd_set1_epi32(simdVertexStride)); in ComputeOffsets()
558 …therComponent(const float* pBuffer, uint32_t attrib, simdscalar vMask, simdscalari vIndices, uint3… in GatherComponent()
560 simdscalari vOffsets = ComputeOffsets(attrib, vIndices, component); in GatherComponent()
[all …]
Dmultisample.h72 INLINE static simdscalari FullSampleMask() = delete;
125 INLINE static simdscalari FullSampleMask(){return _simd_set1_epi32(0x1);};
174 INLINE static simdscalari FullSampleMask(){return _simd_set1_epi32(0x1);};
235 INLINE static simdscalari FullSampleMask()
237 static const simdscalari mask =_simd_set1_epi32(0x3);
288 INLINE static simdscalari FullSampleMask()
290 static const simdscalari mask =_simd_set1_epi32(0x3);
356 INLINE static simdscalari FullSampleMask()
358 static const simdscalari mask = _simd_set1_epi32(0xF);
409 INLINE static simdscalari FullSampleMask()
[all …]
Dformat_types.h123 simdscalari src = _simd_castps_si(in);
163 …simdscalari inlo = _simd_castps_si(_simd16_extract_ps(in, 0)); // r0 r1 r2 r3 r4 r5 r6 r7…
164 … simdscalari inhi = _simd_castps_si(_simd16_extract_ps(in, 1)); // r8 r9 rA rB rC rD rE rF
166 …simdscalari permlo = _simd_permute2f128_si(inlo, inhi, 0x20); // r0 r1 r2 r3 r8 r9 rA rB…
167 …simdscalari permhi = _simd_permute2f128_si(inlo, inhi, 0x31); // r4 r5 r6 r7 rC rD rE rF…
169 …simdscalari pack = _simd_packus_epi32(permlo, permhi); // r0 r1 r2 r3 r4 r5 r6 r7…
171 const simdscalari zero = _simd_setzero_si();
238 simdscalari src = _simd_castps_si(in);
278 …simdscalari inlo = _simd_castps_si(_simd16_extract_ps(in, 0)); // r0 r1 r2 r3 r4 r5 r6 r7…
279 … simdscalari inhi = _simd_castps_si(_simd16_extract_ps(in, 1)); // r8 r9 rA rB rC rD rE rF
[all …]
Dstate.h205 simdscalari VertexID; // IN: Vertex ID
206 simdscalari mask; // IN: Active mask for shader
252 simdscalari PrimitiveID; // IN: (SIMD) primitive ID generated from the draw call
253 simdscalari mask; // IN: Active mask for shader
270 simdscalari mask; // IN: Active mask for shader
281 simdscalari PrimitiveID; // IN: input primitive ID generated from the draw call
283 simdscalari mask; // IN: Active mask for shader
286 simdscalari vertexCount; // OUT: num vertices emitted per SIMD lane
308 simdscalari activeMask; // OUT: mask for kill
310 simdscalari oMask; // OUT: mask for output coverage
[all …]
Dclip.cpp182 …a, uint32_t workerId, simdvector prims[], uint32_t primMask, simdscalari primId, simdscalari viewp… in ClipTriangles()
191 …a, uint32_t workerId, simdvector prims[], uint32_t primMask, simdscalari primId, simdscalari viewp… in ClipLines()
199 …a, uint32_t workerId, simdvector prims[], uint32_t primMask, simdscalari primId, simdscalari viewp… in ClipPoints()
Dpa.h58 virtual simdscalari GetPrimID(uint32_t startID) = 0;
93 simdscalari primID;
231 simdscalari GetPrimID(uint32_t startID) in GetPrimID()
342 …simdscalari vOffsets[MAX_NUM_VERTS_PER_PRIM]; // byte offsets for currently assembling s…
348 simdscalari vPrimId; // vector of prim ID
442 simdscalari GetPrimID(uint32_t startID) in GetPrimID()
548 simdscalari vIndices = *(simdscalari*)&this->indices[v][0]; in ComputeOffsets()
552 simdscalari vVertexBatch = _simd_srai_epi32(vIndices, simdShift); in ComputeOffsets()
557 simdscalari vVertexIndex = _simd_and_si(vIndices, _simd_set1_epi32(simdMask)); in ComputeOffsets()
582 simdscalari offsets = this->vOffsets[v]; in Assemble()
[all …]
Ddepthstencil.h35 simdscalari stencil = _simd_castps_si(stencilps); in StencilOp()
49 simdscalari stencilincr = _simd_adds_epu8(stencil, _simd_set1_epi32(1)); in StencilOp()
55 simdscalari stencildecr = _simd_subs_epu8(stencil, _simd_set1_epi32(1)); in StencilOp()
61 simdscalari stencilincr = _simd_add_epi8(stencil, _simd_set1_epi32(1)); in StencilOp()
67 simdscalari stencildecr = _simd_add_epi8(stencil, _simd_set1_epi32((-1) & 0xff)); in StencilOp()
274 simdscalari vWriteMask = _simd_set1_epi32(stencilWriteMask); in DepthStencilWrite()
Dfrontend.cpp480 static INLINE simdscalari GenerateMask(uint32_t numItemsRemaining) in GenerateMask()
656 simdscalari primID) in GeometryShaderStage()
812 simdscalari vPrimId; in GeometryShaderStage()
826 simdscalari vViewPortIdx; in GeometryShaderStage()
833 … simdscalari vNumViewports = _simd_set1_epi32(KNOB_NUM_VIEWPORTS_SCISSORS); in GeometryShaderStage()
834 … simdscalari vClearMask = _simd_cmplt_epi32(_simd_castps_si(vpiAttrib[0].x), vNumViewports); in GeometryShaderStage()
950 simdscalari primID) in TessellationStages()
1265 simdscalari vIndex; in ProcessDraw()
Dtilemgr.cpp351 simdscalari valS = _simd_set1_epi8(clearVal); in ClearStencilHotTile()
353 simdscalari* pBuf = (simdscalari*)pHotTile->pBuffer; in ClearStencilHotTile()
Dformat_conversion.h103 simdscalari vCompi = _simd_castps_si(vComp); in Clamp()
112 simdscalari vCompi = _simd_castps_si(vComp); in Clamp()
Dcontext.h218 uint32_t primMask, simdscalari primID, simdscalari viewportIdx);
Dpa_avx.cpp246 const simdscalari perm0 = _simd_set_epi32(5, 2, 7, 4, 1, 6, 3, 0); in PaTriList2()
247 const simdscalari perm1 = _simd_set_epi32(6, 3, 0, 5, 2, 7, 4, 1); in PaTriList2()
248 const simdscalari perm2 = _simd_set_epi32(7, 4, 1, 6, 3, 0, 5, 2); in PaTriList2()
1144 simdscalari id8 = _mm256_set_epi32(7, 6, 5, 4, 3, 2, 1, 0); in PA_STATE_OPT()
1145 simdscalari id4 = _mm256_set_epi32(3, 3, 2, 2, 1, 1, 0, 0); in PA_STATE_OPT()
Dbackend.h723 (simdscalari*)&coverageMask);
727 simdscalari outputMask = _simd_castps_si(_simd_and_ps(coverageMask, depthPassMask));
800 reinterpret_cast<simdscalari *>(&coverageMask));
804 simdscalari outputMask = _simd_castps_si(_simd_and_ps(coverageMask, depthPassMask));
/external/mesa3d/src/gallium/drivers/swr/rasterizer/common/
Dsimdintrin.h37 typedef __m256i simdscalari; typedef
624 simdscalari _simd_loadu2_si(const __m128i *hiaddr, const __m128i *loaddr) in _simd_loadu2_si()
633 void _simd_storeu2_si(__m128i *hiaddr, __m128i *loaddr, simdscalari a) in _simd_storeu2_si()
640 simdscalari _simd_blendv_epi32(simdscalari a, simdscalari b, simdscalar mask) in _simd_blendv_epi32()
646 simdscalari _simd_blendv_epi32(simdscalari a, simdscalari b, simdscalari mask) in _simd_blendv_epi32()
1155 simdscalari ai = _simd_castps_si(a); in _simd_abs_ps()
Dsimd16intrin.h302 INLINE simdscalari _simd16_extract_si(simd16scalari a, int imm8) in _simd16_extract_si()
328 INLINE simd16scalari _simd16_insert_si(simd16scalari a, simdscalari b, int imm8) in _simd16_insert_si()
639 const simdscalari mask = _simd_set1_epi32(7); in SIMD16_EMU_AVX512_2()
742 INLINE simd16scalari _simd16_cvtepu8_epi16(simdscalari a) in _simd16_cvtepu8_epi16()
762 INLINE simd16scalari _simd16_cvtepu16_epi32(simdscalari a) in _simd16_cvtepu16_epi32()
/external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/
DStoreTile.h511 simdscalari packed = _simd_castps_si(dst.x);
566 …simdscalari destlo = _simd_loadu2_si(reinterpret_cast<__m128i *>(ppDsts[1]), reinterpret_cast<__m1…
567 …simdscalari desthi = _simd_loadu2_si(reinterpret_cast<__m128i *>(ppDsts[3]), reinterpret_cast<__m1…