Lines Matching defs:nir
96 gl_shader_stage stage = zs->nir->info.stage;
107 if (ctx && zs->nir->info.num_inlinable_uniforms &&
110 inline_size = zs->nir->info.num_inlinable_uniforms;
136 mod = zink_shader_compile(screen, zs, prog->nir[stage], key);
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);
374 if (((struct zink_compute_program*)pg)->shader->nir->info.stage == MESA_SHADER_KERNEL) {
413 nir_shader *producer = shaders[i]->nir;
418 if (!prog->nir[producer->info.stage])
419 prog->nir[producer->info.stage] = nir_shader_clone(prog, producer);
420 if (!prog->nir[j])
421 prog->nir[j] = nir_shader_clone(prog, consumer->nir);
422 zink_compiler_assign_io(prog->nir[producer->info.stage], prog->nir[j]);
472 i == (prog->last_vertex_stage->nir->info.stage == MESA_SHADER_TESS_EVAL ? 4 : 3))
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]);
557 comp->module->shader = zink_shader_compile(screen, shader, shader->nir, NULL);
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);
700 ralloc_free(prog->nir[i]);
933 if (shader && shader->nir->info.num_inlinable_uniforms)
987 enum pipe_shader_type old = ctx->last_vertex_stage ? pipe_shader_type_from_mesa(ctx->last_vertex_stage->nir->info.stage) : PIPE_SHADER_TYPES;
994 enum pipe_shader_type current = ctx->last_vertex_stage ? pipe_shader_type_from_mesa(ctx->last_vertex_stage->nir->info.stage) : PIPE_SHADER_VERTEX;
1008 if (ctx->last_vertex_stage->nir->info.outputs_written & (VARYING_BIT_VIEWPORT | VARYING_BIT_VIEWPORT_MASK))
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);
1053 nir_shader *nir = ctx->gfx_stages[PIPE_SHADER_FRAGMENT]->nir;
1054 if (nir->info.outputs_written & (1 << FRAG_RESULT_SAMPLE_MASK)) {
1070 nir_shader *nir = ctx->gfx_stages[PIPE_SHADER_FRAGMENT]->nir;
1071 if (nir->info.outputs_written & (1 << FRAG_RESULT_SAMPLE_MASK)) {
1088 nir_shader *nir = ctx->gfx_stages[PIPE_SHADER_FRAGMENT]->nir;
1089 if (nir->info.fs.uses_fbfetch_output) {
1090 nir_foreach_shader_out_variable(var, ctx->gfx_stages[PIPE_SHADER_FRAGMENT]->nir) {
1107 bool had_points = ctx->gfx_stages[PIPE_SHADER_GEOMETRY] ? ctx->gfx_stages[PIPE_SHADER_GEOMETRY]->nir->info.gs.output_primitive == SHADER_PRIM_POINTS : false;
1111 if (!had_points && ctx->last_vertex_stage->nir->info.gs.output_primitive == SHADER_PRIM_POINTS)
1148 struct nir_shader *nir;
1150 nir = zink_tgsi_to_nir(pctx->screen, shader->prog);
1152 nir = (struct nir_shader *)shader->prog;
1154 return zink_shader_create(zink_screen(pctx->screen), nir, NULL);
1173 nir_shader *nir;
1175 nir = zink_tgsi_to_nir(pctx->screen, shader->tokens);
1177 nir = (struct nir_shader *)shader->ir.nir;
1179 return zink_shader_create(zink_screen(pctx->screen), nir, &shader->stream_output);