Home
last modified time | relevance | path

Searched refs:_simd_set1_epi32 (Results 1 – 12 of 12) sorted by relevance

/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/
Dclip.h75 clipCodes = _simd_and_ps(vRes, _simd_castsi_ps(_simd_set1_epi32(FRUSTUM_LEFT))); in ComputeClipCodes()
79 …clipCodes = _simd_or_ps(clipCodes, _simd_and_ps(vRes, _simd_castsi_ps(_simd_set1_epi32(FRUSTUM_TOP… in ComputeClipCodes()
83 …clipCodes = _simd_or_ps(clipCodes, _simd_and_ps(vRes, _simd_castsi_ps(_simd_set1_epi32(FRUSTUM_RIG… in ComputeClipCodes()
87 …clipCodes = _simd_or_ps(clipCodes, _simd_and_ps(vRes, _simd_castsi_ps(_simd_set1_epi32(FRUSTUM_BOT… in ComputeClipCodes()
101 …clipCodes = _simd_or_ps(clipCodes, _simd_and_ps(vRes, _simd_castsi_ps(_simd_set1_epi32(FRUSTUM_NEA… in ComputeClipCodes()
105 …clipCodes = _simd_or_ps(clipCodes, _simd_and_ps(vRes, _simd_castsi_ps(_simd_set1_epi32(FRUSTUM_FAR… in ComputeClipCodes()
110 clipCodes = _simd_or_ps(clipCodes, _simd_and_ps(vRes, _simd_castsi_ps(_simd_set1_epi32(NEGW)))); in ComputeClipCodes()
115 …clipCodes = _simd_or_ps(clipCodes, _simd_and_ps(vRes, _simd_castsi_ps(_simd_set1_epi32(GUARDBAND_L… in ComputeClipCodes()
120 …clipCodes = _simd_or_ps(clipCodes, _simd_and_ps(vRes, _simd_castsi_ps(_simd_set1_epi32(GUARDBAND_T… in ComputeClipCodes()
125 …clipCodes = _simd_or_ps(clipCodes, _simd_and_ps(vRes, _simd_castsi_ps(_simd_set1_epi32(GUARDBAND_R… in ComputeClipCodes()
[all …]
Dbinner.cpp135 bbox.xmin = _simd_sub_epi32(vMinX, _simd_set1_epi32(CT::BoundingBoxOffsetT::value)); in calcBoundingBoxIntVertical()
136 bbox.xmax = _simd_add_epi32(vMaxX, _simd_set1_epi32(CT::BoundingBoxOffsetT::value)); in calcBoundingBoxIntVertical()
137 bbox.ymin = _simd_sub_epi32(vMinY, _simd_set1_epi32(CT::BoundingBoxOffsetT::value)); in calcBoundingBoxIntVertical()
138 bbox.ymax = _simd_add_epi32(vMaxY, _simd_set1_epi32(CT::BoundingBoxOffsetT::value)); in calcBoundingBoxIntVertical()
670 simdscalari xmin = _simd_add_epi32(bbox.xmin, _simd_set1_epi32(127)); in BinTriangles()
671 xmin = _simd_and_si(xmin, _simd_set1_epi32(~255)); in BinTriangles()
672 simdscalari xmax = _simd_add_epi32(bbox.xmax, _simd_set1_epi32(128)); in BinTriangles()
673 xmax = _simd_and_si(xmax, _simd_set1_epi32(~255)); in BinTriangles()
677 simdscalari ymin = _simd_add_epi32(bbox.ymin, _simd_set1_epi32(127)); in BinTriangles()
678 ymin = _simd_and_si(ymin, _simd_set1_epi32(~255)); in BinTriangles()
[all …]
Ddepthstencil.h49 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()
189 …WithMask = _simd_castsi_ps(_simd_and_si(_simd_castps_si(sbuf.v[0]), _simd_set1_epi32(stencilTestMa… in DepthStencilTest()
261 simdscalar stencilRefps = _simd_castsi_ps(_simd_set1_epi32(stencilRefValue)); in DepthStencilWrite()
274 simdscalari vWriteMask = _simd_set1_epi32(stencilWriteMask); in DepthStencilWrite()
Dmultisample.h125 INLINE static simdscalari FullSampleMask(){return _simd_set1_epi32(0x1);};
174 INLINE static simdscalari FullSampleMask(){return _simd_set1_epi32(0x1);};
237 static const simdscalari mask =_simd_set1_epi32(0x3);
290 static const simdscalari mask =_simd_set1_epi32(0x3);
358 static const simdscalari mask = _simd_set1_epi32(0xF);
411 static const simdscalari mask = _simd_set1_epi32(0xF);
483 static const simdscalari mask = _simd_set1_epi32(0xFF);
536 static const simdscalari mask = _simd_set1_epi32(0xFF);
616 static const simdscalari mask = _simd_set1_epi32(0xFFFF);
669 static const simdscalari mask = _simd_set1_epi32(0xFFFF);
Dformat_conversion.h104 vCompi = _simd_max_epu32(vCompi, _simd_set1_epi32(iMin)); in Clamp()
105 vCompi = _simd_min_epu32(vCompi, _simd_set1_epi32(iMax)); in Clamp()
113 vCompi = _simd_max_epi32(vCompi, _simd_set1_epi32(iMin)); in Clamp()
114 vCompi = _simd_min_epi32(vCompi, _simd_set1_epi32(iMax)); in Clamp()
Dformat_types.h957 const simdscalari vSignMask = _simd_set1_epi32(0x80000000);
958 const simdscalari vExpMask = _simd_set1_epi32(FLOAT_EXP_MASK);
959 const simdscalari vManMask = _simd_set1_epi32(FLOAT_MANTISSA_MASK);
960 …const simdscalari vExpMin = _simd_set1_epi32(FLOAT_EXP_MASK & uint32_t(FLOAT_EXP_MIN << FLOA…
961 …const simdscalari vExpMinFtz = _simd_set1_epi32(FLOAT_EXP_MASK & uint32_t(FLOAT_EXP_MIN_FTZ << …
962 …const simdscalari vExpMax = _simd_set1_epi32(FLOAT_EXP_MASK & uint32_t(FLOAT_EXP_MAX << FLOA…
973 …simdscalari vHalfExp = _simd_add_epi32(_simd_sub_epi32(vExp, vExpMin), _simd_set1_epi32(1U << F…
976 …simdscalari vDst = _simd_and_si(_simd_srli_epi32(vHalfExp, 13), _simd_set1_epi32(HALF_EXP_M…
982 vDst = _simd_or_si(vDst, _simd_and_si(vInfMask, _simd_set1_epi32(HALF_EXP_MASK)));
987 _simd_and_si(vClampMask, _simd_set1_epi32(0x7BFF)));
Dfrontend.cpp822 vPrimId = _simd_set1_epi32(pPrimitiveId[inputPrim]); in GeometryShaderStage()
833 … simdscalari vNumViewports = _simd_set1_epi32(KNOB_NUM_VIEWPORTS_SCISSORS); in GeometryShaderStage()
841 vViewPortIdx = _simd_set1_epi32(0); in GeometryShaderStage()
1094 _simd_set1_epi32(dsContext.PrimitiveID)); in TessellationStages()
1116 … GenMask(tessPa.NumPrims()), _simd_set1_epi32(dsContext.PrimitiveID), _simd_set1_epi32(0)); in TessellationStages()
1274 vIndex = _simd_add_epi32(_simd_set1_epi32(work.startVertexID), vScale); in ProcessDraw()
1371 … GenMask(pa.NumPrims()), pa.GetPrimID(work.startPrimID), _simd_set1_epi32(0)); in ProcessDraw()
1386 vIndex = _simd_add_epi32(vIndex, _simd_set1_epi32(KNOB_SIMD_WIDTH)); in ProcessDraw()
Dpa.h234 … _simd_set1_epi32(startID + this->primIDIncr * (this->numPrimsComplete / KNOB_SIMD_WIDTH))); in GetPrimID()
444 return _simd_add_epi32(_simd_set1_epi32(startID), this->vPrimId); in GetPrimID()
531 this->vPrimId = _simd_add_epi32(vPrimId, _simd_set1_epi32(KNOB_SIMD_WIDTH)); in Advance()
553 … this->vOffsets[v] = _simd_mullo_epi32(vVertexBatch, _simd_set1_epi32(sizeof(simdvertex))); in ComputeOffsets()
557 simdscalari vVertexIndex = _simd_and_si(vIndices, _simd_set1_epi32(simdMask)); in ComputeOffsets()
558 … _simd_add_epi32(this->vOffsets[v], _simd_mullo_epi32(vVertexIndex, _simd_set1_epi32(sizeof(float)… in ComputeOffsets()
585 offsets = _simd_add_epi32(offsets, _simd_set1_epi32(slot * sizeof(simdvector))); in Assemble()
1135 return _simd_add_epi32(_simd_set1_epi32(startID), m_vPrimId); in GetPrimID()
Dbackend.h299 vec = _simd_blendv_epi32(_simd_setzero_si(), _simd_set1_epi32(1), vec);
373 const __m256i vSampleMask = _simd_and_si(_simd_set1_epi32(sampleMask), vFullyCoveredMask);
Dbackend.cpp929 …const simdscalar vSampleMask = _simd_castsi_ps(_simd_cmpgt_epi32(_simd_set1_epi32(state.blendState… in BackendPixelRate()
/external/mesa3d/src/gallium/drivers/swr/rasterizer/common/
Dsimdintrin.h609 #define _simd_set1_epi32 _mm256_set1_epi32 macro
1156 return _simd_castsi_ps(_simd_and_si(ai, _simd_set1_epi32(0x7fffffff))); in _simd_abs_ps()
Dsimd16intrin.h311 return _simd_set1_epi32(0); in _simd16_extract_si()
639 const simdscalari mask = _simd_set1_epi32(7); in SIMD16_EMU_AVX512_2()