/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/ |
D | format_utils.h | 206 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 …]
|
D | frontend.h | 91 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 …]
|
D | multisample.h | 65 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 …]
|
D | clip.cpp | 184 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 …]
|
D | format_types.h | 124 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 …]
|
D | state.h | 252 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 …]
|
D | backend_impl.h | 195 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 …]
|
D | depthstencil.h | 38 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()
|
D | frontend.cpp | 487 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 …]
|
D | binner.h | 141 simdscalari& scisXmin, in GatherScissors() 142 simdscalari& scisYmin, in GatherScissors() 143 simdscalari& scisXmax, in GatherScissors() 144 simdscalari& scisYmax) in GatherScissors()
|
D | utils.h | 41 simdscalari ymin; 42 simdscalari ymax; 43 simdscalari xmin; 44 simdscalari xmax;
|
D | clip.h | 1301 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 …]
|
D | context.h | 231 simdscalari const& primID, 232 simdscalari const& viewportIdx, 233 simdscalari const& rtIdx);
|
D | binner.cpp | 1219 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()
|
D | pa_avx.cpp | 754 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()
|
D | pa.h | 67 typedef simdscalari SIMDSCALARI;
|
/external/mesa3d/src/gallium/drivers/swr/rasterizer/common/ |
D | simdintrin.h | 268 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()
|
D | intrin.h | 56 typedef simd8scalari simdscalari; typedef
|
/external/mesa3d/src/gallium/drivers/swr/rasterizer/memory/ |
D | StoreTile.h | 490 …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 …]
|