HomeSort by: relevance | last modified time | path
    Searched defs:zs (Results 1 - 25 of 29) sorted by relevancy

1 2

  /xsrc/external/mit/MesaLib/dist/src/gallium/drivers/zink/
zink_clear.h 45 } zs; member in union:zink_framebuffer_clear_data::__anon2058
zink_program.c 87 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
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 = NULL local
494 struct zink_shader *zs = NULL; local
842 struct zink_shader *zs = cso; local
    [all...]
zink_descriptors.c 1538 calc_descriptor_state_hash_ssbo(struct zink_context *ctx, struct zink_shader *zs, enum pipe_shader_type shader, int i, int idx, uint32_t hash)
1552 calc_descriptor_state_hash_sampler(struct zink_context *ctx, struct zink_shader *zs, enum pipe_shader_type shader, int i, int idx, uint32_t hash)
1554 for (unsigned k = 0; k < zs->bindings[ZINK_DESCRIPTOR_TYPE_SAMPLER_VIEW][i].size; k++) {
1556 bool is_buffer = zink_shader_descriptor_is_buffer(zs, ZINK_DESCRIPTOR_TYPE_SAMPLER_VIEW, i);
1572 calc_descriptor_state_hash_image(struct zink_context *ctx, struct zink_shader *zs, enum pipe_shader_type shader, int i, int idx, uint32_t hash)
1574 for (unsigned k = 0; k < zs->bindings[ZINK_DESCRIPTOR_TYPE_IMAGE][i].size; k++) {
1575 bool is_buffer = zink_shader_descriptor_is_buffer(zs, ZINK_DESCRIPTOR_TYPE_IMAGE, i);
1586 struct zink_shader *zs = shader == PIPE_SHADER_COMPUTE ? ctx->compute_stage : ctx->gfx_stages[shader]; local
1589 for (int i = 0; i < zs->num_bindings[type]; i++) {
1591 if (zs->bindings[type][i].type == VK_DESCRIPTOR_TYPE_UNIFORM_BUFFER_DYNAMIC
    [all...]
  /xsrc/external/mit/MesaLib/dist/src/mesa/swrast/
s_feedback.c 114 const GLfloat zs = 1.0F / ctx->DrawBuffer->_DepthMaxF; local
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
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
136 _mesa_update_hitflag( ctx, v->attrib[VARYING_SLOT_POS][2] * zs );
  /xsrc/external/mit/MesaLib.old/dist/src/mesa/swrast/
s_feedback.c 114 const GLfloat zs = 1.0F / ctx->DrawBuffer->_DepthMaxF; local
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
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
136 _mesa_update_hitflag( ctx, v->attrib[VARYING_SLOT_POS][2] * zs );
  /xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/softpipe/
sp_tex_tile_cache.c 208 boolean zs = util_format_is_depth_or_stencil(tc->format); local
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/dist/src/panfrost/lib/
pan_cs.c 160 const struct pan_image_view *s = fb->zs.view.s;
187 const struct pan_image_view *zs = fb->zs.view.zs; local
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->image->layout.slices[level]
820 const struct pan_image_view *zs = fb->zs.view.zs; local
    [all...]
pan_cs.h 50 const struct pan_image_view *zs, *s; member in struct:pan_fb_zs_attachment::__anon2784
110 struct pan_fb_zs_attachment zs; member in struct:pan_fb_info
158 (fb->zs.view.zs || fb->zs.view.s ||
pan_blitter.c 191 bool zs = (z || s); local
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;
    [all...]
  /xsrc/external/mit/MesaLib/dist/src/gallium/drivers/panfrost/
pan_job.c 422 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->image = &z_rsrc->image
744 struct pan_image_view rts[8], zs, s; local
    [all...]
  /xsrc/external/mit/MesaLib/dist/src/panfrost/vulkan/
panvk_vX_meta_clear.c 164 bool zs = z | s; local
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 = &view
    [all...]
  /xsrc/external/mit/MesaLib/dist/src/gallium/drivers/asahi/
agx_state.h 158 struct agx_zsa zs; member in struct:agx_context
  /xsrc/external/mit/MesaLib/dist/src/gallium/drivers/nouveau/nvc0/
nvc0_state_validate.c 735 bool zs = nvc0->zsa && local
737 rasterizer_discard = !zs &&
  /xsrc/external/mit/MesaLib/dist/src/gallium/frontends/osmesa/
osmesa.c 108 void *zs; member in struct:osmesa_context
410 if (osmesa->zs) {
412 osmesa->zs, osmesa->zs_stride, true);
736 free(osmesa->zs);
944 if (!c->zs) {
946 c->zs = calloc(c->zs_stride, *height);
947 if (!c->zs)
950 osmesa_read_buffer(c, res, c->zs, c->zs_stride, true);
953 *buffer = c->zs;
  /xsrc/external/mit/MesaLib/dist/src/mesa/program/
prog_noise.c 333 float zs = z + s; local
336 int k = FASTFLOOR(zs);
490 float zs = z + s; local
494 int k = FASTFLOOR(zs);
  /xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/nouveau/nvc0/
nvc0_state_validate.c 726 bool zs = nvc0->zsa && local
728 rasterizer_discard = !zs &&
  /xsrc/external/mit/MesaLib.old/dist/src/mesa/program/
prog_noise.c 333 float zs = z + s; local
336 int k = FASTFLOOR(zs);
490 float zs = z + s; local
494 int k = FASTFLOOR(zs);
  /xsrc/external/mit/MesaLib/dist/src/mesa/math/
m_matrix.c 688 GLfloat xx, yy, zz, xy, yz, zx, xs, ys, zs, one_c, s, c; local
823 zs = z * s;
828 M(0,1) = (one_c * xy) - zs;
832 M(1,0) = (one_c * xy) + zs;
  /xsrc/external/mit/MesaLib.old/dist/src/mesa/math/
m_matrix.c 799 GLfloat xx, yy, zz, xy, yz, zx, xs, ys, zs, one_c, s, c; local
934 zs = z * s;
939 M(0,1) = (one_c * xy) - zs;
943 M(1,0) = (one_c * xy) + zs;
  /xsrc/external/mit/MesaLib/dist/src/amd/common/
ac_surface.h 146 } zs; member in union:legacy_surf_layout::__anon450
303 } zs; member in union:gfx9_surf_layout::__anon457
  /xsrc/external/mit/MesaLib/dist/src/gallium/drivers/radeonsi/
si_descriptors.c 305 va += tex->surface.u.gfx9.zs.stencil_offset;
347 state[3] |= S_00A00C_SW_MODE(tex->surface.u.gfx9.zs.stencil_swizzle_mode);
379 state[3] |= S_008F1C_SW_MODE(tex->surface.u.gfx9.zs.stencil_swizzle_mode);
380 state[4] |= S_008F20_PITCH(tex->surface.u.gfx9.zs.stencil_epitch);
2792 struct si_texture* zs = (struct si_texture *)sctx->framebuffer.state.zsbuf->texture; local
2793 if (zs &&
2794 (zs->buffer.flags & RADEON_FLAG_ENCRYPTED)) {
si_state.h 111 bool zs : 1; member in struct:si_dsa_order_invariance
  /xsrc/external/mit/MesaLib/dist/src/gallium/frontends/nine/
device9.c 1302 unsigned type, /* 0 = RT, 1 = ZS, 2 = plain */
1681 boolean zs; local
1702 zs = util_format_is_depth_or_stencil(dst_res->format);
1703 user_assert(!zs || !This->in_scene, D3DERR_INVALIDCALL);
1704 user_assert(!zs || !pSourceRect ||
1709 user_assert(!zs || !pDestRect ||
1714 user_assert(!zs ||
1717 user_assert(zs || !util_format_is_depth_or_stencil(src_res->format),
1719 user_assert(!zs || dst->desc.Format == src->desc.Format,
1791 blit.mask = zs ? PIPE_MASK_ZS : PIPE_MASK_RGBA
    [all...]
  /xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/radeonsi/
si_state.h 99 bool zs:1; member in struct:si_dsa_order_invariance
  /xsrc/external/mit/MesaLib.old/dist/src/gallium/state_trackers/nine/
device9.c 1195 unsigned type, /* 0 = RT, 1 = ZS, 2 = plain */
1573 boolean zs; local
1590 zs = util_format_is_depth_or_stencil(dst_res->format);
1591 user_assert(!zs || !This->in_scene, D3DERR_INVALIDCALL);
1592 user_assert(!zs || !pSourceRect ||
1597 user_assert(!zs || !pDestRect ||
1602 user_assert(!zs ||
1605 user_assert(zs || !util_format_is_depth_or_stencil(src_res->format),
1607 user_assert(!zs || dst->desc.Format == src->desc.Format,
1679 blit.mask = zs ? PIPE_MASK_ZS : PIPE_MASK_RGBA
    [all...]

Completed in 43 milliseconds

1 2