Searched refs:zs (Results 1 - 25 of 65) sorted by relevance

123

/xsrc/external/mit/MesaLib/dist/src/panfrost/lib/
H A Dpan_cs.h50 const struct pan_image_view *zs, *s; member in struct:pan_fb_zs_attachment::__anoneeb406e80108
110 struct pan_fb_zs_attachment zs; member in struct:pan_fb_info
158 (fb->zs.view.zs || fb->zs.view.s ||
H A Dpan_cs.c160 const struct pan_image_view *s = fb->zs.view.s;
187 const struct pan_image_view *zs = fb->zs.view.zs; local in function:pan_prepare_zs
189 if (!zs)
192 unsigned level = zs->first_level;
194 ext->zs_msaa = mali_sampling_mode(zs);
197 pan_iview_get_surface(zs, 0, 0, 0, &surf);
199 if (drm_is_afbc(zs->image->layout.modifier)) {
201 const struct pan_image_slice_layout *slice = &zs
820 const struct pan_image_view *zs = fb->zs.view.zs; local in function:pan_emit_sfbd
[all...]
H A Dpan_blitter.c191 bool zs = (z || s); local in function:pan_blitter_emit_rsd
244 if (zs) {
264 cfg.properties.allow_forward_pixel_to_kill = !zs;
265 cfg.properties.allow_forward_pixel_to_be_killed = (dev->arch >= 7) || !zs;
274 cfg.properties.force_early_z = !zs;
727 bool zs)
734 if (zs) {
735 if (fb->zs.preload.z)
736 z = fb->zs.view.zs;
725 pan_preload_get_rsd(struct panfrost_device * dev,const struct pan_fb_info * fb,bool zs) argument
802 pan_preload_needed(const struct pan_fb_info * fb,bool zs) argument
914 pan_preload_emit_textures(struct pan_pool * pool,const struct pan_fb_info * fb,bool zs,struct MALI_DRAW * draw) argument
972 pan_preload_emit_dcd(struct pan_pool * pool,struct pan_fb_info * fb,bool zs,mali_ptr coordinates,mali_ptr tsd,mali_ptr rsd,void * out,bool always_write) argument
1093 pan_preload_emit_pre_frame_dcd(struct pan_pool * desc_pool,struct pan_fb_info * fb,bool zs,mali_ptr coords,mali_ptr rsd,mali_ptr tsd) argument
1157 pan_preload_emit_tiler_job(struct pan_pool * desc_pool,struct pan_scoreboard * scoreboard,struct pan_fb_info * fb,bool zs,mali_ptr coords,mali_ptr rsd,mali_ptr tsd) argument
1192 pan_preload_fb_part(struct pan_pool * pool,struct pan_scoreboard * scoreboard,struct pan_fb_info * fb,bool zs,mali_ptr coords,mali_ptr tsd,mali_ptr tiler) argument
[all...]
/xsrc/external/mit/MesaLib.old/dist/src/mesa/swrast/
H A Ds_feedback.c114 const GLfloat zs = 1.0F / ctx->DrawBuffer->_DepthMaxF; local in function:_swrast_select_triangle
116 _mesa_update_hitflag( ctx, v0->attrib[VARYING_SLOT_POS][2] * zs );
117 _mesa_update_hitflag( ctx, v1->attrib[VARYING_SLOT_POS][2] * zs );
118 _mesa_update_hitflag( ctx, v2->attrib[VARYING_SLOT_POS][2] * zs );
126 const GLfloat zs = 1.0F / ctx->DrawBuffer->_DepthMaxF; local in function:_swrast_select_line
127 _mesa_update_hitflag( ctx, v0->attrib[VARYING_SLOT_POS][2] * zs );
128 _mesa_update_hitflag( ctx, v1->attrib[VARYING_SLOT_POS][2] * zs );
135 const GLfloat zs = 1.0F / ctx->DrawBuffer->_DepthMaxF; local in function:_swrast_select_point
136 _mesa_update_hitflag( ctx, v->attrib[VARYING_SLOT_POS][2] * zs );
/xsrc/external/mit/MesaLib/dist/src/mesa/swrast/
H A Ds_feedback.c114 const GLfloat zs = 1.0F / ctx->DrawBuffer->_DepthMaxF; local in function:_swrast_select_triangle
116 _mesa_update_hitflag( ctx, v0->attrib[VARYING_SLOT_POS][2] * zs );
117 _mesa_update_hitflag( ctx, v1->attrib[VARYING_SLOT_POS][2] * zs );
118 _mesa_update_hitflag( ctx, v2->attrib[VARYING_SLOT_POS][2] * zs );
126 const GLfloat zs = 1.0F / ctx->DrawBuffer->_DepthMaxF; local in function:_swrast_select_line
127 _mesa_update_hitflag( ctx, v0->attrib[VARYING_SLOT_POS][2] * zs );
128 _mesa_update_hitflag( ctx, v1->attrib[VARYING_SLOT_POS][2] * zs );
135 const GLfloat zs = 1.0F / ctx->DrawBuffer->_DepthMaxF; local in function:_swrast_select_point
136 _mesa_update_hitflag( ctx, v->attrib[VARYING_SLOT_POS][2] * zs );
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/zink/
H A Dzink_compiler.h104 zink_shader_compile(struct zink_screen *screen, struct zink_shader *zs, nir_shader *nir, const struct zink_shader_key *key);
120 zink_shader_descriptor_is_buffer(struct zink_shader *zs, enum zink_descriptor_type type, unsigned i) argument
122 return zs->bindings[type][i].type == VK_DESCRIPTOR_TYPE_STORAGE_TEXEL_BUFFER ||
123 zs->bindings[type][i].type == VK_DESCRIPTOR_TYPE_UNIFORM_TEXEL_BUFFER;
H A Dzink_program.c87 struct zink_shader *zs, struct zink_gfx_program *prog,
90 gl_shader_stage stage = zs->nir->info.stage;
97 if (ctx && zs->nir->info.num_inlinable_uniforms &&
100 base_size = zs->nir->info.num_inlinable_uniforms;
119 mod = zink_shader_compile(screen, zs, prog->nir[stage], key);
394 struct zink_shader *zs = comp->shader; local in function:zink_program_update_compute_pipeline_state
395 bool use_local_size = !(zs->nir->info.workgroup_size[0] ||
396 zs->nir->info.workgroup_size[1] ||
397 zs->nir->info.workgroup_size[2]);
458 struct zink_shader *zs local in function:zink_program_get_descriptor_usage
86 get_shader_module_for_stage(struct zink_context * ctx,struct zink_screen * screen,struct zink_shader * zs,struct zink_gfx_program * prog,struct zink_gfx_pipeline_state * state) argument
494 struct zink_shader *zs = NULL; local in function:zink_program_descriptor_is_buffer
516 get_num_bindings(struct zink_shader * zs,enum zink_descriptor_type type) argument
842 struct zink_shader *zs = cso; local in function:zink_bind_vs_state
[all...]
H A Dzink_clear.c249 clear->zs.depth = depth;
251 clear->zs.stencil = stencil;
252 clear->zs.bits |= (buffers & PIPE_CLEAR_DEPTHSTENCIL);
336 /* zs bits are both set here if those aspects should be cleared at some point */
340 clear_bits |= zsclear->zs.bits;
345 zsclear ? zsclear->zs.depth : 0,
346 zsclear ? zsclear->zs.stencil : 0);
351 zink_clear(&ctx->base, clear->zs.bits,
354 clear->zs.depth,
355 clear->zs
[all...]
H A Dzink_clear.h45 } zs; member in union:zink_framebuffer_clear_data::__anon7290fca7010a
H A Dzink_compiler.c517 update_so_info(struct zink_shader *zs, const struct pipe_stream_output_info *so_info, argument
531 nir_foreach_shader_out_variable(var, zs->nir)
539 zs->streamout.so_info.stride[output->output_buffer] = so_info->stride[output->output_buffer];
540 if ((zs->nir->info.stage != MESA_SHADER_GEOMETRY || util_bitcount(zs->nir->info.gs.active_stream_mask) == 1) &&
544 var = nir_find_variable_with_location(zs->nir, nir_var_shader_out, slot--);
560 zs->streamout.so_info.output[zs->streamout.so_info.num_outputs] = *output;
562 zs->streamout.so_info_slots[zs
785 zink_shader_compile(struct zink_screen * screen,struct zink_shader * zs,nir_shader * base_nir,const struct zink_shader_key * key) argument
[all...]
/xsrc/external/mit/MesaLib/dist/src/panfrost/vulkan/
H A Dpanvk_cmd_buffer.c240 cmdbuf->state.zs.s_front.compare_mask = compareMask;
243 cmdbuf->state.zs.s_back.compare_mask = compareMask;
257 cmdbuf->state.zs.s_front.write_mask = writeMask;
260 cmdbuf->state.zs.s_back.write_mask = writeMask;
274 cmdbuf->state.zs.s_front.ref = reference;
277 cmdbuf->state.zs.s_back.ref = reference;
389 fbinfo->zs.clear.z = subpass->zs_attachment.clear;
390 fbinfo->zs.clear_value.depth = clears[subpass->zs_attachment.idx].depth;
391 fbinfo->zs.view.zs
[all...]
H A Dpanvk_vX_cs.c686 cfg.stencil_front.mask = state->zs.s_front.compare_mask;
687 cfg.stencil_back.mask = state->zs.s_back.compare_mask;
691 cfg.stencil_mask_misc.stencil_mask_front = state->zs.s_front.write_mask;
692 cfg.stencil_mask_misc.stencil_mask_back = state->zs.s_back.write_mask;
696 cfg.stencil_front.reference_value = state->zs.s_front.ref;
697 cfg.stencil_back.reference_value = state->zs.s_back.ref;
716 (pipeline->zs.z_test && pipeline->zs.z_compare_func != MALI_FUNC_ALWAYS) ||
717 pipeline->zs.s_test;
722 pipeline->zs
[all...]
H A Dpanvk_vX_meta_clear.c164 bool zs = z | s; local in function:panvk_meta_clear_attachments_emit_rsd
187 cfg.properties.allow_forward_pixel_to_be_killed = PAN_ARCH >= 7 || !zs;
188 cfg.properties.allow_forward_pixel_to_kill = !zs;
189 if (zs) {
203 cfg.properties.force_early_z = !zs;
222 if (zs) {
444 shader = meta->clear_attachment.zs.shader;
445 shader_info = &meta->clear_attachment.zs.shader_info;
571 fbinfo->zs.view.zs
[all...]
H A Dpanvk_vX_meta_blit.c74 fbinfo->zs.view.zs = &views[0];
75 fbinfo->zs.preload.z = true;
76 fbinfo->zs.preload.s = util_format_has_stencil(fdesc);
78 fbinfo->zs.view.s = &views[0];
79 fbinfo->zs.preload.s = true;
100 fbinfo->zs.view.s = &views[1];
H A Dpanvk_vX_pipeline.c669 pipeline->zs.z_test = builder->create_info->pDepthStencilState->depthTestEnable;
670 pipeline->zs.z_write = builder->create_info->pDepthStencilState->depthWriteEnable;
671 pipeline->zs.z_compare_func =
673 pipeline->zs.s_test = builder->create_info->pDepthStencilState->stencilTestEnable;
674 pipeline->zs.s_front.fail_op =
676 pipeline->zs.s_front.pass_op =
678 pipeline->zs.s_front.z_fail_op =
680 pipeline->zs.s_front.compare_func =
682 pipeline->zs.s_front.compare_mask =
684 pipeline->zs
[all...]
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/panfrost/
H A Dpan_job.c422 struct pan_image_view *zs,
428 memset(zs, 0, sizeof(*zs));
488 zs->format = surf->format == PIPE_FORMAT_Z32_FLOAT_S8X24_UINT ?
490 zs->dim = MALI_TEXTURE_DIMENSION_2D;
491 zs->last_level = zs->first_level = surf->u.tex.level;
492 zs->first_layer = surf->u.tex.first_layer;
493 zs->last_layer = surf->u.tex.last_layer;
494 zs
419 panfrost_batch_to_fb_info(const struct panfrost_batch * batch,struct pan_fb_info * fb,struct pan_image_view * rts,struct pan_image_view * zs,struct pan_image_view * s,bool reserve) argument
744 struct pan_image_view rts[8], zs, s; local in function:panfrost_batch_submit
[all...]
/xsrc/external/mit/MesaLib/dist/src/gallium/frontends/osmesa/
H A Dosmesa.c108 void *zs; member in struct:osmesa_context
404 if (osmesa->zs) {
406 osmesa->zs, osmesa->zs_stride, true);
730 free(osmesa->zs);
938 if (!c->zs) {
940 c->zs = calloc(c->zs_stride, *height);
941 if (!c->zs)
944 osmesa_read_buffer(c, res, c->zs, c->zs_stride, true);
947 *buffer = c->zs;
/xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/softpipe/
H A Dsp_tex_tile_cache.c208 boolean zs = util_format_is_depth_or_stencil(tc->format); local in function:sp_find_cached_tile_tex
263 if (!zs && util_format_is_pure_uint(tc->format)) {
271 } else if (!zs && util_format_is_pure_sint(tc->format)) {
/xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/v3d/
H A Dv3dx_rcl.c471 cl_emit(&job->rcl, TILE_RENDERING_MODE_CFG_Z_STENCIL, zs) {
472 zs.address = cl_address(rsc->bo, surf->offset);
475 zs.internal_type = surf->internal_type;
476 zs.output_image_format = surf->format;
478 zs.z_stencil_id = 1; /* Separate stencil */
481 zs.padded_height_of_output_image_in_uif_blocks =
485 zs.memory_format = surf->tiling;
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/v3d/
H A Dv3dx_rcl.c219 /* When blitting, no color or zs buffer is loaded; instead the blit
508 cl_emit(&job->rcl, TILE_RENDERING_MODE_CFG_Z_STENCIL, zs) {
509 zs.address = cl_address(rsc->bo, surf->offset);
512 zs.internal_type = surf->internal_type;
513 zs.output_image_format = surf->format;
515 zs.z_stencil_id = 1; /* Separate stencil */
518 zs.padded_height_of_output_image_in_uif_blocks =
522 zs.memory_format = surf->tiling;
/xsrc/external/mit/MesaLib.old/dist/src/mesa/program/
H A Dprog_noise.c333 float zs = z + s; local in function:_mesa_noise3
336 int k = FASTFLOOR(zs);
490 float zs = z + s; local in function:_mesa_noise4
494 int k = FASTFLOOR(zs);
/xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/etnaviv/
H A Detnaviv_state.c467 etna_zsa_state_bind(struct pipe_context *pctx, void *zs) argument
471 ctx->zsa = zs;
476 etna_zsa_state_delete(struct pipe_context *pctx, void *zs) argument
478 FREE(zs);
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/asahi/
H A Dagx_state.h158 struct agx_zsa zs; member in struct:agx_context
/xsrc/external/mit/MesaLib/dist/src/gallium/winsys/radeon/drm/
H A Dradeon_drm_surface.c168 &surf_ws->u.legacy.zs.stencil_level[i],
170 surf_drm->stencil_tiling_index[i] = surf_ws->u.legacy.zs.stencil_tiling_index[i];
210 surf_level_drm_to_winsys(&surf_ws->u.legacy.zs.stencil_level[i],
213 surf_ws->u.legacy.zs.stencil_tiling_index[i] = surf_drm->stencil_tiling_index[i];
/xsrc/external/mit/MesaLib/dist/src/mesa/program/
H A Dprog_noise.c333 float zs = z + s; local in function:_mesa_noise3
336 int k = FASTFLOOR(zs);
490 float zs = z + s; local in function:_mesa_noise4
494 int k = FASTFLOOR(zs);

Completed in 59 milliseconds

123