Home
last modified time | relevance | path

Searched refs:coverageMask (Results 1 – 11 of 11) sorted by relevance

/external/mesa3d/src/gallium/drivers/swr/rasterizer/archrast/
Darchrast.cpp85 …ample.earlyZTestFailCount += _mm_popcnt_u32((!event.data.depthPassMask) & event.data.coverageMask); in Handle()
89 …rlyStencilTestFailCount += _mm_popcnt_u32((!event.data.stencilPassMask) & event.data.coverageMask); in Handle()
97 …eRate.earlyZTestFailCount += _mm_popcnt_u32((!event.data.depthPassMask) & event.data.coverageMask); in Handle()
101 …rlyStencilTestFailCount += _mm_popcnt_u32((!event.data.stencilPassMask) & event.data.coverageMask); in Handle()
109 …ullPS.earlyZTestFailCount += _mm_popcnt_u32((!event.data.depthPassMask) & event.data.coverageMask); in Handle()
113 …rlyStencilTestFailCount += _mm_popcnt_u32((!event.data.stencilPassMask) & event.data.coverageMask); in Handle()
121 …Sample.lateZTestFailCount += _mm_popcnt_u32((!event.data.depthPassMask) & event.data.coverageMask); in Handle()
125 …ateStencilTestFailCount += _mm_popcnt_u32((!event.data.stencilPassMask) & event.data.coverageMask); in Handle()
133 …leRate.lateZTestFailCount += _mm_popcnt_u32((!event.data.depthPassMask) & event.data.coverageMask); in Handle()
137 …ateStencilTestFailCount += _mm_popcnt_u32((!event.data.stencilPassMask) & event.data.coverageMask); in Handle()
[all …]
Devents.proto214 uint64_t coverageMask;
221 uint64_t coverageMask;
228 uint64_t coverageMask;
235 uint64_t coverageMask;
242 uint64_t coverageMask;
249 uint64_t coverageMask;
/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/
Dbackend_sample.cpp81 …verage == SWR_INPUT_COVERAGE_INNER_CONSERVATIVE) ? &work.innerCoverageMask : &work.coverageMask[0]; in BackendSampleRate()
90 …CalcCentroid<T, false>(&psContext, samplePos, coeffs, work.coverageMask, state.blendState.sampleMa… in BackendSampleRate()
96 simdmask coverageMask = work.coverageMask[sample] & MASK; in BackendSampleRate() local
98 if (coverageMask) in BackendSampleRate()
113 coverageMask &= CalcDepthBoundsAcceptMask(z, minz, maxz); in BackendSampleRate()
133 …coverageMask &= ~ComputeUserClipMask(state.backendState.clipDistanceMask, work.pUserClipBuffer, ps… in BackendSampleRate()
136 simdscalar vCoverageMask = _simd_vmask_ps(coverageMask); in BackendSampleRate()
157 work.coverageMask[sample] >>= (SIMD_TILE_Y_DIM * SIMD_TILE_X_DIM); in BackendSampleRate()
189 work.coverageMask[sample] >>= (SIMD_TILE_Y_DIM * SIMD_TILE_X_DIM); in BackendSampleRate()
214 work.coverageMask[sample] >>= (SIMD_TILE_Y_DIM * SIMD_TILE_X_DIM); in BackendSampleRate()
Dbackend_impl.h152 …INLINE generateInputCoverage(const uint64_t *const coverageMask, uint32_t (&inputMask)[KNOB_SIMD_W… in generateInputCoverage()
163 uint32_t centerCoverage = ((uint32_t)(*coverageMask) & MASK); in generateInputCoverage()
215 …si256(_simd_mask_i32gather_ps(_mm256_castsi256_ps(src), (const float*)coverageMask, index0, _mm256… in generateInputCoverage()
219 …si256(_simd_mask_i32gather_ps(_mm256_castsi256_ps(src), (const float*)coverageMask, index1, _mm256… in generateInputCoverage()
292 …INLINE generateInputCoverage(const uint64_t *const coverageMask, simdscalar &inputCoverage, const … in generateInputCoverage()
295 generateInputCoverage<T, T::InputCoverage>(coverageMask, inputMask, sampleMask); in generateInputCoverage()
304 …INLINE generateInputCoverage(const uint64_t *const coverageMask, simdscalar &inputCoverage, const …
308 simdscalari vec = _simd_set1_epi32(coverageMask[0]);
316 …INLINE generateInputCoverage(const uint64_t *const coverageMask, uint32_t (&inputMask)[KNOB_SIMD_W…
318 uint32_t simdCoverage = (coverageMask[0] & MASK);
[all …]
Dbackend_singlesample.cpp79 simdmask coverageMask = work.coverageMask[0] & MASK; in BackendSingleSample() local
81 if (coverageMask) in BackendSingleSample()
92 coverageMask &= CalcDepthBoundsAcceptMask(z, minz, maxz); in BackendSingleSample()
97 …verage == SWR_INPUT_COVERAGE_INNER_CONSERVATIVE) ? &work.innerCoverageMask : &work.coverageMask[0]; in BackendSingleSample()
106 …CalcCentroid<T, true>(&psContext, samplePos, coeffs, work.coverageMask, state.blendState.sampleMas… in BackendSingleSample()
117 …coverageMask &= ~ComputeUserClipMask(state.backendState.clipDistanceMask, work.pUserClipBuffer, ps… in BackendSingleSample()
120 simdscalar vCoverageMask = _simd_vmask_ps(coverageMask); in BackendSingleSample()
203 work.coverageMask[0] >>= (SIMD_TILE_Y_DIM * SIMD_TILE_X_DIM); in BackendSingleSample()
Ddepthstencil.h120 … uint32_t viewportIndex, simdscalar const &iZ, uint8_t* pDepthBase, simdscalar const &coverageMask, in DepthStencilTest() argument
210 depthWriteMask = _simd_and_ps(depthWriteMask, coverageMask); in DepthStencilTest()
218 …scalar const &iZ, uint8_t* pDepthBase, const simdscalar& depthMask, const simdscalar& coverageMask, in DepthStencilWrite() argument
228 simdscalar vMask = _simd_and_ps(depthMask, coverageMask); in DepthStencilWrite()
263 simdscalar stencilFailMask = _simd_andnot_ps(stencilMask, coverageMask); in DepthStencilWrite()
279 stencilResult.v[0] = _simd_blendv_ps(origStencil, stencilps, coverageMask); in DepthStencilWrite()
Dbackend.cpp240 simdmask coverageMask = work.coverageMask[sample] & MASK; in BackendNullPS() local
242 if (coverageMask) in BackendNullPS()
257 coverageMask &= CalcDepthBoundsAcceptMask(z, minz, maxz); in BackendNullPS()
277 …coverageMask &= ~ComputeUserClipMask(state.backendState.clipDistanceMask, work.pUserClipBuffer, ps… in BackendNullPS()
280 simdscalar vCoverageMask = _simd_vmask_ps(coverageMask); in BackendNullPS()
298 work.coverageMask[sample] >>= (SIMD_TILE_Y_DIM * SIMD_TILE_X_DIM); in BackendNullPS()
Drasterizer_impl.h96 uint64_t coverageMask = 0; in rasterizePartialTile() local
137 coverageMask |= (mask << bit); in rasterizePartialTile()
239 coverageMask |= (mask << bit); in rasterizePartialTile()
256 return coverageMask; in rasterizePartialTile()
1179 triDesc.coverageMask[sampleNum] = 0xffffffffffffffffULL;
1192 triDesc.anyCoveredSamples = triDesc.coverageMask[sampleNum];
1237 …triDesc.coverageMask[sampleNum] = rasterizePartialTile<RT::NumEdgesT::value, typename RT::ValidEdg…
1240 triDesc.anyCoveredSamples |= triDesc.coverageMask[sampleNum];
1251 triDesc.coverageMask[sampleNum] = 0;
1260 gToss = triDesc.coverageMask[0];
[all …]
Drasterizer.cpp293 uint32_t tX = workDesc.triFlags.coverageMask & 0x7; in RasterizeSimplePoint()
294 uint32_t tY = (workDesc.triFlags.coverageMask >> 4) & 0x7; in RasterizeSimplePoint()
296 triDesc.coverageMask[0] = 1ULL << coverageMap[tY][tX]; in RasterizeSimplePoint()
Dcontext.h62 uint32_t coverageMask : (SIMD_TILE_X_DIM * SIMD_TILE_Y_DIM);
86 uint64_t coverageMask[SWR_MAX_NUM_MULTISAMPLES]; member
Dbinner.cpp1311 work.desc.tri.triFlags.coverageMask = tX | (tY << 4); in BinPostSetupPointsImpl()