203    struct brw_task_prog_data *prog_data = params->prog_data;  in brw_compile_task()  local
206    prog_data->base.base.stage = MESA_SHADER_TASK;  in brw_compile_task()
207    prog_data->base.base.total_shared = nir->info.shared_size;  in brw_compile_task()
208    prog_data->base.base.total_scratch = 0;  in brw_compile_task()
210    prog_data->base.local_size[0] = nir->info.workgroup_size[0];  in brw_compile_task()
211    prog_data->base.local_size[1] = nir->info.workgroup_size[1];  in brw_compile_task()
212    prog_data->base.local_size[2] = nir->info.workgroup_size[2];  in brw_compile_task()
214    prog_data->uses_drawid =  in brw_compile_task()
217    brw_nir_lower_tue_outputs(nir, &prog_data->map);  in brw_compile_task()
226       if (!brw_simd_should_compile(mem_ctx, simd, compiler->devinfo, &prog_data->base,  in brw_compile_task()
244                                &prog_data->base.base, shader, dispatch_width,  in brw_compile_task()
247       if (prog_data->base.prog_mask) {  in brw_compile_task()
248          unsigned first = ffs(prog_data->base.prog_mask) - 1;  in brw_compile_task()
252       const bool allow_spilling = !prog_data->base.prog_mask;  in brw_compile_task()
255          brw_simd_mark_compiled(simd, &prog_data->base, v[simd]->spilled_any_registers);  in brw_compile_task()
260    int selected_simd = brw_simd_select(&prog_data->base);  in brw_compile_task()
268    prog_data->base.prog_mask = 1 << selected_simd;  in brw_compile_task()
272       brw_print_tue_map(stderr, &prog_data->map);  in brw_compile_task()
276                   &prog_data->base.base, false, MESA_SHADER_TASK);  in brw_compile_task()
692    struct brw_mesh_prog_data *prog_data = params->prog_data;  in brw_compile_mesh()  local
695    prog_data->base.base.stage = MESA_SHADER_MESH;  in brw_compile_mesh()
696    prog_data->base.base.total_shared = nir->info.shared_size;  in brw_compile_mesh()
697    prog_data->base.base.total_scratch = 0;  in brw_compile_mesh()
699    prog_data->base.local_size[0] = nir->info.workgroup_size[0];  in brw_compile_mesh()
700    prog_data->base.local_size[1] = nir->info.workgroup_size[1];  in brw_compile_mesh()
701    prog_data->base.local_size[2] = nir->info.workgroup_size[2];  in brw_compile_mesh()
703    prog_data->clip_distance_mask = (1 << nir->info.clip_distance_array_size) - 1;  in brw_compile_mesh()
704    prog_data->cull_distance_mask =  in brw_compile_mesh()
707    prog_data->primitive_type = nir->info.mesh.primitive_type;  in brw_compile_mesh()
710    prog_data->index_format = BRW_INDEX_FORMAT_U32;  in brw_compile_mesh()
712    prog_data->uses_drawid =  in brw_compile_mesh()
717    brw_compute_mue_map(nir, &prog_data->map);  in brw_compile_mesh()
718    brw_nir_lower_mue_outputs(nir, &prog_data->map);  in brw_compile_mesh()
727       if (!brw_simd_should_compile(mem_ctx, simd, compiler->devinfo, &prog_data->base,  in brw_compile_mesh()
739       if (prog_data->map.per_primitive_header_size_dw > 0)  in brw_compile_mesh()
740          NIR_PASS_V(shader, brw_nir_initialize_mue, &prog_data->map, dispatch_width);  in brw_compile_mesh()
744       NIR_PASS(_, shader, brw_nir_adjust_offset_for_arrayed_indices, &prog_data->map);  in brw_compile_mesh()
757                                &prog_data->base.base, shader, dispatch_width,  in brw_compile_mesh()
760       if (prog_data->base.prog_mask) {  in brw_compile_mesh()
761          unsigned first = ffs(prog_data->base.prog_mask) - 1;  in brw_compile_mesh()
765       const bool allow_spilling = !prog_data->base.prog_mask;  in brw_compile_mesh()
768          brw_simd_mark_compiled(simd, &prog_data->base, v[simd]->spilled_any_registers);  in brw_compile_mesh()
773    int selected_simd = brw_simd_select(&prog_data->base);  in brw_compile_mesh()
781    prog_data->base.prog_mask = 1 << selected_simd;  in brw_compile_mesh()
789       brw_print_mue_map(stderr, &prog_data->map);  in brw_compile_mesh()
793                   &prog_data->base.base, false, MESA_SHADER_MESH);  in brw_compile_mesh()