Home
last modified time | relevance | path

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

/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/
Dformat_utils.h185 …simdscalari &vMask0, const simdscalari &vMask1, const simdscalari &vMask2, const simdscalari &vMas… in vTranspose8x8()
226 simdscalari src = _simd_load_si((const simdscalari*)pSrc); in Transpose()
241 simdscalari dst01 = _simd_shuffle_epi8(src, in Transpose()
243 simdscalari dst23 = _mm256_permute2x128_si256(src, src, 0x01); in Transpose()
246 simdscalari dst = _simd_or_si(dst01, dst23); in Transpose()
247 _simd_store_si((simdscalari*)pDst, dst); in Transpose()
306 simdscalari src = _simd_load_si((const simdscalari*)pSrc); in Transpose()
323 simdscalari cvt0 = _simd_cvtepu8_epi16(src0); in Transpose_16()
324 simdscalari cvt1 = _simd_cvtepu8_epi16(src1); in Transpose_16()
326 simdscalari shl1 = _simd_slli_epi32(cvt1, 8); in Transpose_16()
[all …]
Dfrontend.h81 void triangleSetupABIntVertical(const simdscalari vX[3], const simdscalari vY[3], simdscalari (&vA)… in triangleSetupABIntVertical()
148 void calcDeterminantIntVertical(const simdscalari vA[3], const simdscalari vB[3], simdscalari *pvDe… in calcDeterminantIntVertical()
153 simdscalari vA1Lo = _simd_unpacklo_epi32(vA[1], vA[1]); // 0 0 1 1 4 4 5 5 in calcDeterminantIntVertical()
154 simdscalari vA1Hi = _simd_unpackhi_epi32(vA[1], vA[1]); // 2 2 3 3 6 6 7 7 in calcDeterminantIntVertical()
156 simdscalari vB2Lo = _simd_unpacklo_epi32(vB[2], vB[2]); in calcDeterminantIntVertical()
157 simdscalari vB2Hi = _simd_unpackhi_epi32(vB[2], vB[2]); in calcDeterminantIntVertical()
159 simdscalari vA1B2Lo = _simd_mul_epi32(vA1Lo, vB2Lo); // 0 1 4 5 in calcDeterminantIntVertical()
160 simdscalari vA1B2Hi = _simd_mul_epi32(vA1Hi, vB2Hi); // 2 3 6 7 in calcDeterminantIntVertical()
163 simdscalari vA2Lo = _simd_unpacklo_epi32(vA[2], vA[2]); in calcDeterminantIntVertical()
164 simdscalari vA2Hi = _simd_unpackhi_epi32(vA[2], vA[2]); in calcDeterminantIntVertical()
[all …]
Dmultisample.h58 INLINE static simdscalari FullSampleMask() = delete;
68 INLINE static simdscalari FullSampleMask(){return _simd_set1_epi32(0x1);};
84 INLINE static simdscalari FullSampleMask(){return _simd_set1_epi32(0x1);};
100 INLINE static simdscalari FullSampleMask()
102 static const simdscalari mask =_simd_set1_epi32(0x3);
120 INLINE static simdscalari FullSampleMask()
122 static const simdscalari mask =_simd_set1_epi32(0x3);
139 INLINE static simdscalari FullSampleMask()
141 static const simdscalari mask = _simd_set1_epi32(0xF);
159 INLINE static simdscalari FullSampleMask()
[all …]
Dformat_types.h124 simdscalari src = _simd_castps_si(in);
165 …simdscalari inlo = _simd_castps_si(_simd16_extract_ps(in, 0)); // r0 r1 r2 r3 r4 r5 r6 r7…
166 … simdscalari inhi = _simd_castps_si(_simd16_extract_ps(in, 1)); // r8 r9 rA rB rC rD rE rF
168 …simdscalari permlo = _simd_permute2f128_si(inlo, inhi, 0x20); // r0 r1 r2 r3 r8 r9 rA rB…
169 …simdscalari permhi = _simd_permute2f128_si(inlo, inhi, 0x31); // r4 r5 r6 r7 rC rD rE rF…
171 …simdscalari pack = _simd_packus_epi32(permlo, permhi); // r0 r1 r2 r3 r4 r5 r6 r7…
173 const simdscalari zero = _simd_setzero_si();
240 simdscalari src = _simd_castps_si(in);
281 …simdscalari inlo = _simd_castps_si(_simd16_extract_ps(in, 0)); // r0 r1 r2 r3 r4 r5 r6 r7…
282 … simdscalari inhi = _simd_castps_si(_simd16_extract_ps(in, 1)); // r8 r9 rA rB rC rD rE rF
[all …]
Dclip.cpp164 … simdscalari const &primId, simdscalari const &viewportIdx, simdscalari const &rtIdx) in ClipTriangles()
174 simdscalari const &primId, simdscalari const &viewportIdx, simdscalari const &rtIdx) in ClipLines()
184 simdscalari const &primId, simdscalari const &viewportIdx, simdscalari const &rtIdx) in ClipPoints()
Dstate.h226 simdscalari VertexID; // IN: Vertex ID
227 simdscalari mask; // IN: Active mask for shader
280 simdscalari PrimitiveID; // IN: (SIMD) primitive ID generated from the draw call
281 simdscalari mask; // IN: Active mask for shader
299 simdscalari mask; // IN: Active mask for shader
311 simdscalari PrimitiveID; // IN: input primitive ID generated from the draw call
313 simdscalari mask; // IN: Active mask for shader
336 simdscalari activeMask; // OUT: mask for kill
338 simdscalari oMask; // OUT: mask for output coverage
590 simdscalari VertexID; // OUT: vector of vertex IDs
[all …]
Dbackend_impl.h157 simdscalari mask[2]; in generateInputCoverage()
158 simdscalari sampleCoverage[2]; in generateInputCoverage()
188 simdscalari src = _simd_set1_epi32(0); in generateInputCoverage()
189 simdscalari index0 = _simd_set_epi32(7, 6, 5, 4, 3, 2, 1, 0), index1; in generateInputCoverage()
226 simdscalari packedCoverage0 = _simd_shuffle_epi8(sampleCoverage[0], mask[0]); in generateInputCoverage()
228 simdscalari packedCoverage1; in generateInputCoverage()
237 simdscalari hiToLow = _mm256_permute2f128_si256(packedCoverage0, packedCoverage0, 0x83); in generateInputCoverage()
241 simdscalari packedSampleCoverage; in generateInputCoverage()
256 simdscalari permMask = _simd_set_epi32(0x7, 0x7, 0x7, 0x7, 0x7, 0x7, 0x4, 0x0); in generateInputCoverage()
260 simdscalari packedSampleCoverage; in generateInputCoverage()
[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()
Dbinner.h136 simdscalari &scisXmin, simdscalari &scisYmin, simdscalari &scisXmax, simdscalari &scisYmax) in GatherScissors()
Dutils.h40 simdscalari ymin;
41 simdscalari ymax;
42 simdscalari xmin;
43 simdscalari xmax;
Dfrontend.cpp481 static INLINE simdscalari GenerateMask(uint32_t numItemsRemaining) in GenerateMask()
800 simdscalari const &primID) in GeometryShaderStage()
1032 simdscalari vPrimId = _simd_set1_epi32(pPrimitiveId[inputPrim]); in GeometryShaderStage()
1035 simdscalari vViewportIdx = SIMD16::setzero_si(); in GeometryShaderStage()
1036 simdscalari vRtIdx = SIMD16::setzero_si(); in GeometryShaderStage()
1171 simdscalari const &primID) in TessellationStages()
1356 const simdscalari primID_lo = _simd16_extract_si(primID, 0); in TessellationStages()
1357 const simdscalari primID_hi = _simd16_extract_si(primID, 1); in TessellationStages()
1440 simdscalari vViewportIdx = SIMD16::setzero_si(); in TessellationStages()
1441 simdscalari vRtIdx = SIMD16::setzero_si(); in TessellationStages()
[all …]
Dcontext.h217 …uint32_t primMask, simdscalari const &primID, simdscalari const &viewportIdx, simdscalari const &r…
Dclip.h1144 …, simdvector prims[], uint32_t primMask, simdscalari const &primId, simdscalari const &viewportIdx…
1145 …, simdvector prims[], uint32_t primMask, simdscalari const &primId, simdscalari const &viewportIdx…
1146 …, simdvector prims[], uint32_t primMask, simdscalari const &primId, simdscalari const &viewportIdx…
Dtilemgr.cpp351 simdscalari valS = _simd_set1_epi8(clearVal); in ClearStencilHotTile()
353 simdscalari* pBuf = (simdscalari*)pHotTile->pBuffer; in ClearStencilHotTile()
Dformat_conversion.h104 simdscalari vCompi = _simd_castps_si(vComp); in Clamp()
113 simdscalari vCompi = _simd_castps_si(vComp); in Clamp()
Dbinner.cpp1127 simdscalari const &primID, in BinTriangles()
1128 simdscalari const &viewportIdx, in BinTriangles()
1129 simdscalari const &rtIdx) in BinTriangles()
1550 simdscalari const &primID, in BinPoints()
1551 simdscalari const &viewportIdx, in BinPoints()
1552 simdscalari const &rtIdx) in BinPoints()
1873 simdscalari const &primID, in BinLines()
1874 simdscalari const &viewportIdx, in BinLines()
1875 simdscalari const &rtIdx) in BinLines()
Dpa_avx.cpp678 const simdscalari perm0 = _simd_set_epi32(5, 2, 7, 4, 1, 6, 3, 0); in PaTriList2()
679 const simdscalari perm1 = _simd_set_epi32(6, 3, 0, 5, 2, 7, 4, 1); in PaTriList2()
680 const simdscalari perm2 = _simd_set_epi32(7, 4, 1, 6, 3, 0, 5, 2); in PaTriList2()
2882 simdscalari id8 = _simd_set_epi32(7, 6, 5, 4, 3, 2, 1, 0); in PA_STATE_OPT()
2883 simdscalari id4 = _simd_set_epi32(3, 3, 2, 2, 1, 1, 0, 0); in PA_STATE_OPT()
Dpa.h67 typedef simdscalari SIMDSCALARI;
/external/mesa3d/src/gallium/drivers/swr/rasterizer/common/
Dintrin.h53 typedef simd8scalari simdscalari; typedef
Dsimdintrin.h326 simdscalari ai = _simd_castps_si(a); in _simd_abs_ps()
/external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/
DStoreTile.h513 simdscalari packed = _simd_castps_si(dst.x);
568 …simdscalari destlo = _simd_loadu2_si(reinterpret_cast<simd4scalari *>(ppDsts[1]), reinterpret_cast…
569 …simdscalari desthi = _simd_loadu2_si(reinterpret_cast<simd4scalari *>(ppDsts[3]), reinterpret_cast…
732 simdscalari src0 = _simd_cvtps_epi32(vComp0); // padded byte rrrrrrrr
733 simdscalari src1 = _simd_cvtps_epi32(vComp1); // padded byte gggggggg
734 simdscalari src2 = _simd_cvtps_epi32(vComp2); // padded byte bbbbbbbb
735 simdscalari src3 = _simd_cvtps_epi32(vComp3); // padded byte aaaaaaaa
771 simdscalari final = _mm256_castsi128_si256(vRow00);
784 simdscalari final = _mm256_or_si256(src0, src2);
891 simdscalari src0 = _simd_cvtps_epi32(vComp0); // padded byte rrrrrrrr
[all …]