Lines Matching refs:nir
96 nir_shader *nir,
163 NIR_PASS_V(nir, nir_lower_blend, &options);
172 NIR_PASS_V(nir, nir_shader_instructions_pass,
250 nir_shader *nir;
256 NULL, &nir);
262 NIR_PASS_V(nir, nir_lower_io_to_temporaries,
263 nir_shader_get_entrypoint(nir), true, true);
276 NIR_PASS_V(nir, nir_lower_indirect_derefs,
280 NIR_PASS_V(nir, nir_opt_copy_prop_vars);
281 NIR_PASS_V(nir, nir_opt_combine_stores, nir_var_all);
282 NIR_PASS_V(nir, nir_opt_trivial_continues);
314 NIR_PASS_V(nir, nir_lower_tex, &lower_tex_options);
316 NIR_PASS_V(nir, panvk_per_arch(nir_lower_descriptors),
319 NIR_PASS_V(nir, nir_lower_explicit_io, nir_var_mem_ubo,
321 NIR_PASS_V(nir, nir_lower_explicit_io, nir_var_mem_ssbo,
323 NIR_PASS_V(nir, nir_lower_explicit_io,
328 if (!nir->info.shared_memory_explicit_layout) {
329 NIR_PASS_V(nir, nir_lower_vars_to_explicit_types,
334 NIR_PASS_V(nir, nir_lower_explicit_io,
339 NIR_PASS_V(nir, nir_shader_instructions_pass,
345 NIR_PASS_V(nir, nir_lower_system_values);
346 NIR_PASS_V(nir, nir_lower_compute_system_values, NULL);
348 NIR_PASS_V(nir, nir_split_var_copies);
349 NIR_PASS_V(nir, nir_lower_var_copies);
356 NIR_PASS_V(nir, nir_lower_io_arrays_to_elements_no_indirects, true);
357 panvk_lower_blend(pdev, nir, &inputs, blend_state, static_blend_constants);
360 nir_assign_io_var_locations(nir, nir_var_shader_in, &nir->num_inputs, stage);
361 nir_assign_io_var_locations(nir, nir_var_shader_out, &nir->num_outputs, stage);
366 NIR_PASS_V(nir, nir_lower_global_vars_to_local);
368 nir_shader_gather_info(nir, nir_shader_get_entrypoint(nir));
370 fprintf(stderr, "translated nir:\n");
371 nir_print_shader(nir, stderr);
374 GENX(pan_shader_compile)(nir, &inputs, &shader->binary, &shader->info);
389 shader->local_size.x = nir->info.workgroup_size[0];
390 shader->local_size.y = nir->info.workgroup_size[1];
391 shader->local_size.z = nir->info.workgroup_size[2];
393 ralloc_free(nir);