Home
last modified time | relevance | path

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

/third_party/mesa3d/src/gallium/drivers/swr/rasterizer/core/
Dformat_utils.h206 const simdscalari& vMask0, in vTranspose8x8()
207 const simdscalari& vMask1, in vTranspose8x8()
208 const simdscalari& vMask2, in vTranspose8x8()
209 const simdscalari& vMask3, in vTranspose8x8()
210 const simdscalari& vMask4, in vTranspose8x8()
211 const simdscalari& vMask5, in vTranspose8x8()
212 const simdscalari& vMask6, in vTranspose8x8()
213 const simdscalari& vMask7) in vTranspose8x8()
259 simdscalari src = _simd_load_si((const simdscalari*)pSrc); in Transpose()
275 simdscalari dst01 = _simd_shuffle_epi8(src, in Transpose()
[all …]
Dfrontend.h91 void triangleSetupABIntVertical(const simdscalari vX[3], in triangleSetupABIntVertical()
92 const simdscalari vY[3], in triangleSetupABIntVertical()
93 simdscalari (&vA)[3], in triangleSetupABIntVertical()
94 simdscalari (&vB)[3]) in triangleSetupABIntVertical()
164 void calcDeterminantIntVertical(const simdscalari vA[3], in calcDeterminantIntVertical()
165 const simdscalari vB[3], in calcDeterminantIntVertical()
166 simdscalari* pvDet) in calcDeterminantIntVertical()
171 simdscalari vA1Lo = _simd_unpacklo_epi32(vA[1], vA[1]); // 0 0 1 1 4 4 5 5 in calcDeterminantIntVertical()
172 simdscalari vA1Hi = _simd_unpackhi_epi32(vA[1], vA[1]); // 2 2 3 3 6 6 7 7 in calcDeterminantIntVertical()
174 simdscalari vB2Lo = _simd_unpacklo_epi32(vB[2], vB[2]); in calcDeterminantIntVertical()
[all …]
Dmultisample.h65 INLINE static simdscalari FullSampleMask() = delete;
75 INLINE static simdscalari FullSampleMask() { return _simd_set1_epi32(0x1); };
91 INLINE static simdscalari FullSampleMask() { return _simd_set1_epi32(0x1); };
115 INLINE static simdscalari FullSampleMask()
117 static const simdscalari mask = _simd_set1_epi32(0x3);
135 INLINE static simdscalari FullSampleMask()
137 static const simdscalari mask = _simd_set1_epi32(0x3);
162 INLINE static simdscalari FullSampleMask()
164 static const simdscalari mask = _simd_set1_epi32(0xF);
182 INLINE static simdscalari FullSampleMask()
[all …]
Dclip.cpp184 simdscalari const& primId, in ClipRectangles()
185 simdscalari const& viewportIdx, in ClipRectangles()
186 simdscalari const& rtIdx) in ClipRectangles()
199 simdscalari const& primId, in ClipTriangles()
200 simdscalari const& viewportIdx, in ClipTriangles()
201 simdscalari const& rtIdx) in ClipTriangles()
214 simdscalari const& primId, in ClipLines()
215 simdscalari const& viewportIdx, in ClipLines()
216 simdscalari const& rtIdx) in ClipLines()
229 simdscalari const& primId, in ClipPoints()
[all …]
Dformat_types.h124 simdscalari src = _simd_castps_si(in);
168 … simdscalari inlo = _simd_castps_si(_simd16_extract_ps(in, 0)); // r0 r1 r2 r3 r4 r5 r6 r7 (32b)
169 simdscalari inhi = _simd_castps_si(_simd16_extract_ps(in, 1)); // r8 r9 rA rB rC rD rE rF
171 … simdscalari permlo = _simd_permute2f128_si(inlo, inhi, 0x20); // r0 r1 r2 r3 r8 r9 rA rB (32b)
172 … simdscalari permhi = _simd_permute2f128_si(inlo, inhi, 0x31); // r4 r5 r6 r7 rC rD rE rF (32b)
174 …simdscalari pack = _simd_packus_epi32(permlo, permhi); // r0 r1 r2 r3 r4 r5 r6 r7 r8 r9 r…
176 const simdscalari zero = _simd_setzero_si();
245 simdscalari src = _simd_castps_si(in);
289 … simdscalari inlo = _simd_castps_si(_simd16_extract_ps(in, 0)); // r0 r1 r2 r3 r4 r5 r6 r7 (32b)
290 simdscalari inhi = _simd_castps_si(_simd16_extract_ps(in, 1)); // r8 r9 rA rB rC rD rE rF
[all …]
Dstate.h252 simdscalari VertexID; // IN: Vertex ID
253 simdscalari mask; // IN: Active mask for shader
310 …simdscalari PrimitiveID; // IN: (SIMD) primitive ID generated from the draw …
311 simdscalari mask; // IN: Active mask for shader
330 simdscalari mask; // IN: Active mask for shader
343 simdscalari PrimitiveID; // IN: input primitive ID generated from the draw call
345 simdscalari mask; // IN: Active mask for shader
369 simdscalari activeMask; // OUT: mask for kill
371 simdscalari oMask; // OUT: mask for output coverage
591 simdscalari VertexID; // OUT: vector of vertex IDs
[all …]
Dbackend_impl.h195 simdscalari mask[2]; in generateInputCoverage()
196 simdscalari sampleCoverage[2]; in generateInputCoverage()
228 simdscalari src = _simd_set1_epi32(0); in generateInputCoverage()
229 simdscalari index0 = _simd_set_epi32(7, 6, 5, 4, 3, 2, 1, 0), index1; in generateInputCoverage()
306 simdscalari packedCoverage0 = _simd_shuffle_epi8(sampleCoverage[0], mask[0]); in generateInputCoverage()
308 simdscalari packedCoverage1; in generateInputCoverage()
318 simdscalari hiToLow = _mm256_permute2f128_si256(packedCoverage0, packedCoverage0, 0x83); in generateInputCoverage()
324 simdscalari packedSampleCoverage; in generateInputCoverage()
343 simdscalari permMask = _simd_set_epi32(0x7, 0x7, 0x7, 0x7, 0x7, 0x7, 0x4, 0x0); in generateInputCoverage()
347 simdscalari packedSampleCoverage; in generateInputCoverage()
[all …]
Ddepthstencil.h38 simdscalari stencil = _simd_castps_si(stencilps); in StencilOp()
52 simdscalari stencilincr = _simd_adds_epu8(stencil, _simd_set1_epi32(1)); in StencilOp()
58 simdscalari stencildecr = _simd_subs_epu8(stencil, _simd_set1_epi32(1)); in StencilOp()
64 simdscalari stencilincr = _simd_add_epi8(stencil, _simd_set1_epi32(1)); in StencilOp()
70 simdscalari stencildecr = _simd_add_epi8(stencil, _simd_set1_epi32((-1) & 0xff)); in StencilOp()
326 simdscalari vWriteMask = _simd_set1_epi32(stencilWriteMask); in DepthStencilWrite()
Dfrontend.cpp487 static INLINE simdscalari GenerateMask(uint32_t numItemsRemaining) in GenerateMask()
829 simdscalari const& primID) in GeometryShaderStage()
1112 simdscalari vPrimId = _simd_set1_epi32(pPrimitiveId[inputPrim]); in GeometryShaderStage()
1115 simdscalari vViewportIdx = SIMD::setzero_si(); in GeometryShaderStage()
1116 simdscalari vRtIdx = SIMD::setzero_si(); in GeometryShaderStage()
1133 simdscalari vNumViewports = in GeometryShaderStage()
1135 simdscalari vClearMask = in GeometryShaderStage()
1265 simdscalari const& primID) in TessellationStages()
1496 const simdscalari primID_lo = _simd16_extract_si(primID, 0); in TessellationStages()
1497 const simdscalari primID_hi = _simd16_extract_si(primID, 1); in TessellationStages()
[all …]
Dbinner.h141 simdscalari& scisXmin, in GatherScissors()
142 simdscalari& scisYmin, in GatherScissors()
143 simdscalari& scisXmax, in GatherScissors()
144 simdscalari& scisYmax) in GatherScissors()
Dutils.h41 simdscalari ymin;
42 simdscalari ymax;
43 simdscalari xmin;
44 simdscalari xmax;
Dclip.h1301 simdscalari const& primId,
1302 simdscalari const& viewportIdx,
1303 simdscalari const& rtIdx);
1309 simdscalari const& primId,
1310 simdscalari const& viewportIdx,
1311 simdscalari const& rtIdx);
1317 simdscalari const& primId,
1318 simdscalari const& viewportIdx,
1319 simdscalari const& rtIdx);
1325 simdscalari const& primId,
[all …]
Dcontext.h231 simdscalari const& primID,
232 simdscalari const& viewportIdx,
233 simdscalari const& rtIdx);
Dbinner.cpp1219 simdscalari const& primID, in BinTriangles()
1220 simdscalari const& viewportIdx, in BinTriangles()
1221 simdscalari const& rtIdx) in BinTriangles()
1646 simdscalari const& primID, in BinPoints()
1647 simdscalari const& viewportIdx, in BinPoints()
1648 simdscalari const& rtIdx) in BinPoints()
1954 simdscalari const& primID, in BinLines()
1955 simdscalari const& viewportIdx, in BinLines()
1956 simdscalari const& rtIdx) in BinLines()
Dpa_avx.cpp754 const simdscalari perm0 = _simd_set_epi32(5, 2, 7, 4, 1, 6, 3, 0); in PaTriList2()
755 const simdscalari perm1 = _simd_set_epi32(6, 3, 0, 5, 2, 7, 4, 1); in PaTriList2()
756 const simdscalari perm2 = _simd_set_epi32(7, 4, 1, 6, 3, 0, 5, 2); in PaTriList2()
3054 simdscalari id8 = _simd_set_epi32(7, 6, 5, 4, 3, 2, 1, 0); in PA_STATE_OPT()
3055 simdscalari id4 = _simd_set_epi32(3, 3, 2, 2, 1, 1, 0, 0); in PA_STATE_OPT()
Dpa.h67 typedef simdscalari SIMDSCALARI;
/third_party/mesa3d/src/gallium/drivers/swr/rasterizer/common/
Dsimdintrin.h268 static SIMDINLINE simdscalari InterpolateComponentFlatInt(const uint32_t* pInterpBuffer) in InterpolateComponentFlatInt()
272 simdscalari vA = _simd_set1_epi32(interpA); in InterpolateComponentFlatInt()
316 simdscalari ai = _simd_castps_si(a); in _simd_abs_ps()
Dintrin.h56 typedef simd8scalari simdscalari; typedef
/third_party/mesa3d/src/gallium/drivers/swr/rasterizer/memory/
DStoreTile.h490 …simdscalari destlo = _simd_loadu2_si(reinterpret_cast<simd4scalari *>(ppDsts[1]), reinterpret_cast…
491 …simdscalari desthi = _simd_loadu2_si(reinterpret_cast<simd4scalari *>(ppDsts[3]), reinterpret_cast…
616 simdscalari src0 = _simd_cvtps_epi32(vComp0); // padded byte rrrrrrrr
617 simdscalari src1 = _simd_cvtps_epi32(vComp1); // padded byte gggggggg
618 simdscalari src2 = _simd_cvtps_epi32(vComp2); // padded byte bbbbbbbb
619 simdscalari src3 = _simd_cvtps_epi32(vComp3); // padded byte aaaaaaaa
655 simdscalari final = _mm256_castsi128_si256(vRow00);
668 simdscalari final = _mm256_or_si256(src0, src2);
773 simdscalari src0 = _simd_cvtps_epi32(vComp0); // padded byte rrrrrrrr
774 simdscalari src1 = _simd_cvtps_epi32(vComp1); // padded byte gggggggg
[all …]