OpenGrok
Home
Sort by relevance
Sort by last modified time
Full Search
Definition
Symbol
File Path
History
|
|
Help
Searched
refs:coverageMask
(Results
1 - 10
of
10
) sorted by null
/external/mesa3d/src/gallium/drivers/swr/rasterizer/archrast/
archrast.cpp
85
mDSSingleSample.earlyZTestFailCount += _mm_popcnt_u32((!event.data.depthPassMask) & event.data.
coverageMask
);
89
mDSSingleSample.earlyStencilTestFailCount += _mm_popcnt_u32((!event.data.stencilPassMask) & event.data.
coverageMask
);
97
mDSSampleRate.earlyZTestFailCount += _mm_popcnt_u32((!event.data.depthPassMask) & event.data.
coverageMask
);
101
mDSSampleRate.earlyStencilTestFailCount += _mm_popcnt_u32((!event.data.stencilPassMask) & event.data.
coverageMask
);
109
mDSNullPS.earlyZTestFailCount += _mm_popcnt_u32((!event.data.depthPassMask) & event.data.
coverageMask
);
113
mDSNullPS.earlyStencilTestFailCount += _mm_popcnt_u32((!event.data.stencilPassMask) & event.data.
coverageMask
);
121
mDSSingleSample.lateZTestFailCount += _mm_popcnt_u32((!event.data.depthPassMask) & event.data.
coverageMask
);
125
mDSSingleSample.lateStencilTestFailCount += _mm_popcnt_u32((!event.data.stencilPassMask) & event.data.
coverageMask
);
133
mDSSampleRate.lateZTestFailCount += _mm_popcnt_u32((!event.data.depthPassMask) & event.data.
coverageMask
);
137
mDSSampleRate.lateStencilTestFailCount += _mm_popcnt_u32((!event.data.stencilPassMask) & event.data.
coverageMask
);
[
all
...]
/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/
backend_sample.cpp
81
const uint64_t* pCoverageMask = (T::InputCoverage == SWR_INPUT_COVERAGE_INNER_CONSERVATIVE) ? &work.innerCoverageMask : &work.
coverageMask
[0];
90
CalcCentroid<T, false>(&psContext, samplePos, coeffs, work.
coverageMask
, state.blendState.sampleMask);
96
simdmask
coverageMask
= work.
coverageMask
[sample] & MASK;
98
if (
coverageMask
)
113
coverageMask
&= CalcDepthBoundsAcceptMask(z, minz, maxz);
133
coverageMask
&= ~ComputeUserClipMask(state.backendState.clipDistanceMask, work.pUserClipBuffer, psContext.vI.sample, psContext.vJ.sample);
136
simdscalar vCoverageMask = _simd_vmask_ps(
coverageMask
);
157
work.
coverageMask
[sample] >>= (SIMD_TILE_Y_DIM * SIMD_TILE_X_DIM);
189
work.
coverageMask
[sample] >>= (SIMD_TILE_Y_DIM * SIMD_TILE_X_DIM)
[
all
...]
backend_impl.h
152
INLINE generateInputCoverage(const uint64_t *const
coverageMask
, uint32_t (&inputMask)[KNOB_SIMD_WIDTH], const uint32_t sampleMask)
163
uint32_t centerCoverage = ((uint32_t)(*
coverageMask
) & MASK);
215
sampleCoverage[0] = _mm256_castps_si256(_simd_mask_i32gather_ps(_mm256_castsi256_ps(src), (const float*)
coverageMask
, index0, _mm256_castsi256_ps(mask[0]), 8));
219
sampleCoverage[1] = _mm256_castps_si256(_simd_mask_i32gather_ps(_mm256_castsi256_ps(src), (const float*)
coverageMask
, index1, _mm256_castsi256_ps(mask[1]), 8));
292
INLINE generateInputCoverage(const uint64_t *const
coverageMask
, simdscalar &inputCoverage, const uint32_t sampleMask)
295
generateInputCoverage<T, T::InputCoverage>(
coverageMask
, inputMask, sampleMask);
304
INLINE generateInputCoverage(const uint64_t *const
coverageMask
, simdscalar &inputCoverage, const uint32_t sampleMask)
308
simdscalari vec = _simd_set1_epi32(
coverageMask
[0]);
316
INLINE generateInputCoverage(const uint64_t *const
coverageMask
, uint32_t (&inputMask)[KNOB_SIMD_WIDTH], const uint32_t sampleMask)
318
uint32_t simdCoverage = (
coverageMask
[0] & MASK)
[
all
...]
backend_singlesample.cpp
79
simdmask
coverageMask
= work.
coverageMask
[0] & MASK;
81
if (
coverageMask
)
92
coverageMask
&= CalcDepthBoundsAcceptMask(z, minz, maxz);
97
const uint64_t* pCoverageMask = (T::InputCoverage == SWR_INPUT_COVERAGE_INNER_CONSERVATIVE) ? &work.innerCoverageMask : &work.
coverageMask
[0];
106
CalcCentroid<T, true>(&psContext, samplePos, coeffs, work.
coverageMask
, state.blendState.sampleMask);
117
coverageMask
&= ~ComputeUserClipMask(state.backendState.clipDistanceMask, work.pUserClipBuffer, psContext.vI.center, psContext.vJ.center);
120
simdscalar vCoverageMask = _simd_vmask_ps(
coverageMask
);
203
work.
coverageMask
[0] >>= (SIMD_TILE_Y_DIM * SIMD_TILE_X_DIM);
depthstencil.h
120
bool frontFacing, uint32_t viewportIndex, simdscalar const &iZ, uint8_t* pDepthBase, simdscalar const &
coverageMask
,
210
depthWriteMask = _simd_and_ps(depthWriteMask,
coverageMask
);
218
bool frontFacing, simdscalar const &iZ, uint8_t* pDepthBase, const simdscalar& depthMask, const simdscalar&
coverageMask
,
228
simdscalar vMask = _simd_and_ps(depthMask,
coverageMask
);
263
simdscalar stencilFailMask = _simd_andnot_ps(stencilMask,
coverageMask
);
279
stencilResult.v[0] = _simd_blendv_ps(origStencil, stencilps,
coverageMask
);
backend.cpp
240
simdmask
coverageMask
= work.
coverageMask
[sample] & MASK;
242
if (
coverageMask
)
257
coverageMask
&= CalcDepthBoundsAcceptMask(z, minz, maxz);
277
coverageMask
&= ~ComputeUserClipMask(state.backendState.clipDistanceMask, work.pUserClipBuffer, psContext.vI.sample, psContext.vJ.sample);
280
simdscalar vCoverageMask = _simd_vmask_ps(
coverageMask
);
298
work.
coverageMask
[sample] >>= (SIMD_TILE_Y_DIM * SIMD_TILE_X_DIM);
rasterizer.cpp
291
// compute coverage mask from x,y packed into the
coverageMask
flag
293
uint32_t tX = workDesc.triFlags.
coverageMask
& 0x7;
294
uint32_t tY = (workDesc.triFlags.
coverageMask
>> 4) & 0x7;
296
triDesc.
coverageMask
[0] = 1ULL << coverageMap[tY][tX];
rasterizer_impl.h
96
uint64_t
coverageMask
= 0;
137
coverageMask
|= (mask << bit);
239
coverageMask
|= (mask << bit);
256
return
coverageMask
;
[
all
...]
context.h
62
uint32_t
coverageMask
: (SIMD_TILE_X_DIM * SIMD_TILE_Y_DIM);
86
uint64_t
coverageMask
[SWR_MAX_NUM_MULTISAMPLES];
binner.cpp
[
all
...]
Completed in 243 milliseconds