Lines Matching defs:zs
93 struct zink_shader *zs, struct zink_gfx_program *prog,
96 gl_shader_stage stage = zs->nir->info.stage;
103 if (pstage == PIPE_SHADER_TESS_CTRL && !zs->is_generated) {
107 if (ctx && zs->nir->info.num_inlinable_uniforms &&
109 if (zs->can_inline && (screen->is_cpu || prog->inlined_variant_count[pstage] < ZINK_MAX_INLINED_VARIANTS))
110 inline_size = zs->nir->info.num_inlinable_uniforms;
132 if (pstage == PIPE_SHADER_TESS_CTRL && zs->is_generated && zs->spirv) {
134 mod = zink_shader_tcs_compile(screen, zs, patch_vertices);
136 mod = zink_shader_compile(screen, zs, prog->nir[stage], key);
159 if (pstage == PIPE_SHADER_TESS_CTRL && zs->is_generated)
292 struct zink_shader *zs = comp->shader;
298 if (ctx && zs->nir->info.num_inlinable_uniforms &&
301 inline_size = zs->nir->info.num_inlinable_uniforms;
326 mod = zink_shader_compile(screen, zs, comp->shader->nir, key);
514 struct zink_shader *zs = comp->shader;
515 bool use_local_size = !(zs->nir->info.workgroup_size[0] ||
516 zs->nir->info.workgroup_size[1] ||
517 zs->nir->info.workgroup_size[2]);
584 struct zink_shader *zs = NULL;
591 zs = ctx->gfx_stages[stage];
594 zs = ctx->compute_stage;
600 if (!zs)
604 return zs->ubos_used;
606 return zs->ssbos_used;
608 return BITSET_TEST_RANGE(zs->nir->info.textures_used, 0, PIPE_MAX_SAMPLERS - 1);
610 return BITSET_TEST_RANGE(zs->nir->info.images_used, 0, PIPE_MAX_SAMPLERS - 1);
620 struct zink_shader *zs = NULL;
627 zs = ctx->gfx_stages[stage];
630 zs = ctx->compute_stage;
636 if (!zs)
638 return zink_shader_descriptor_is_buffer(zs, type, i);
642 get_num_bindings(struct zink_shader *zs, enum zink_descriptor_type type)
647 return zs->num_bindings[type];
652 for (int i = 0; i < zs->num_bindings[type]; i++)
653 num_bindings += zs->bindings[type][i].size;
1035 struct zink_shader *zs = cso;
1036 ctx->shader_reads_drawid = BITSET_TEST(zs->nir->info.system_values_read, SYSTEM_VALUE_DRAW_ID);
1037 ctx->shader_reads_basevertex = BITSET_TEST(zs->nir->info.system_values_read, SYSTEM_VALUE_BASE_VERTEX);