Home
last modified time | relevance | path

Searched refs:prog_data (Results 1 – 25 of 160) sorted by relevance

1234567

/aosp_15_r20/external/mesa3d/src/intel/compiler/
H A Dtest_simd_selection.cpp47 , prog_data(rzalloc(mem_ctx, struct brw_cs_prog_data)) in SIMDSelectionTest()
50 .prog_data = prog_data, in SIMDSelectionTest()
62 struct brw_cs_prog_data *prog_data; member in SIMDSelectionTest
69 prog_data->base.stage = MESA_SHADER_COMPUTE; in SIMDSelectionCS()
70 prog_data->local_size[0] = 32; in SIMDSelectionCS()
71 prog_data->local_size[1] = 1; in SIMDSelectionCS()
72 prog_data->local_size[2] = 1; in SIMDSelectionCS()
91 prog_data->local_size[0] = devinfo->max_cs_workgroup_threads; in TEST_F()
92 prog_data->local_size[1] = 32; in TEST_F()
93 prog_data->local_size[2] = 1; in TEST_F()
[all …]
H A Dbrw_compile_fs.cpp28 struct brw_wm_prog_data *prog_data = brw_wm_prog_data(s.prog_data); in brw_emit_single_fb_write() local
42 (prog_data->uses_omask ? s.sample_mask : brw_reg()), in brw_emit_single_fb_write()
49 if (prog_data->uses_kill) { in brw_emit_single_fb_write()
106 struct brw_wm_prog_data *prog_data = brw_wm_prog_data(s.prog_data); in brw_emit_fb_writes() local
130 prog_data->dual_src_blend = (s.dual_src_output.file != BAD_FILE && in brw_emit_fb_writes()
132 assert(!prog_data->dual_src_blend || key->nr_color_regions == 1); in brw_emit_fb_writes()
141 prog_data->dual_src_blend) { in brw_emit_fb_writes()
177 struct brw_wm_prog_data *wm_prog_data = brw_wm_prog_data(s.prog_data); in brw_emit_interpolation_setup()
652 struct brw_wm_prog_data *prog_data, in calculate_urb_setup() argument
656 memset(prog_data->urb_setup, -1, sizeof(prog_data->urb_setup)); in calculate_urb_setup()
[all …]
H A Dbrw_compiler.h574 brw_stage_prog_data_add_params(struct brw_stage_prog_data *prog_data, in brw_stage_prog_data_add_params() argument
577 unsigned old_nr_params = prog_data->nr_params; in brw_stage_prog_data_add_params()
578 prog_data->nr_params += nr_new_params; in brw_stage_prog_data_add_params()
579 prog_data->param = reralloc(ralloc_parent(prog_data->param), in brw_stage_prog_data_add_params()
580 prog_data->param, uint32_t, in brw_stage_prog_data_add_params()
581 prog_data->nr_params); in brw_stage_prog_data_add_params()
582 return prog_data->param + old_nr_params; in brw_stage_prog_data_add_params()
586 brw_stage_prog_data_add_printf(struct brw_stage_prog_data *prog_data,
819 _brw_wm_prog_data_prog_offset(const struct brw_wm_prog_data *prog_data, in _brw_wm_prog_data_prog_offset() argument
824 case 16: return prog_data->prog_offset_16; in _brw_wm_prog_data_prog_offset()
[all …]
H A Dbrw_compile_vs.cpp17 struct brw_vs_prog_data *vs_prog_data = brw_vs_prog_data(s.prog_data); in brw_assign_vs_urb_setup()
68 struct brw_vs_prog_data *prog_data = params->prog_data; in brw_compile_vs() local
73 prog_data->base.base.stage = MESA_SHADER_VERTEX; in brw_compile_vs()
74 prog_data->base.base.ray_queries = nir->info.ray_queries; in brw_compile_vs()
75 prog_data->base.base.total_scratch = 0; in brw_compile_vs()
80 prog_data->inputs_read = nir->info.inputs_read; in brw_compile_vs()
81 prog_data->double_inputs_read = nir->info.vs.double_inputs; in brw_compile_vs()
88 prog_data->base.clip_distance_mask = in brw_compile_vs()
90 prog_data->base.cull_distance_mask = in brw_compile_vs()
94 unsigned nr_attribute_slots = util_bitcount64(prog_data->inputs_read); in brw_compile_vs()
[all …]
H A Dbrw_compile_gs.cpp38 struct brw_gs_prog_data *gs_prog_data = brw_gs_prog_data(s.prog_data); in brw_emit_gs_thread_end()
76 struct brw_vue_prog_data *vue_prog_data = brw_vue_prog_data(s.prog_data); in brw_assign_gs_urb_setup()
141 struct brw_gs_prog_data *prog_data = params->prog_data; in brw_compile_gs() local
149 prog_data->base.base.stage = MESA_SHADER_GEOMETRY; in brw_compile_gs()
150 prog_data->base.base.ray_queries = nir->info.ray_queries; in brw_compile_gs()
151 prog_data->base.base.total_scratch = 0; in brw_compile_gs()
173 prog_data->base.clip_distance_mask = in brw_compile_gs()
175 prog_data->base.cull_distance_mask = in brw_compile_gs()
179 prog_data->include_primitive_id = in brw_compile_gs()
182 prog_data->invocations = nir->info.gs.invocations; in brw_compile_gs()
[all …]
H A Dbrw_compile_tes.cpp19 struct brw_vue_prog_data *vue_prog_data = brw_vue_prog_data(s.prog_data); in brw_assign_tes_urb_setup()
67 struct brw_tes_prog_data *prog_data = params->prog_data; in brw_compile_tes() local
71 prog_data->base.base.stage = MESA_SHADER_TESS_EVAL; in brw_compile_tes()
72 prog_data->base.base.ray_queries = nir->info.ray_queries; in brw_compile_tes()
84 brw_compute_vue_map(devinfo, &prog_data->base.vue_map, in brw_compile_tes()
88 unsigned output_size_bytes = prog_data->base.vue_map.num_slots * 4 * 4; in brw_compile_tes()
97 prog_data->base.clip_distance_mask = in brw_compile_tes()
99 prog_data->base.cull_distance_mask = in brw_compile_tes()
103 prog_data->include_primitive_id = in brw_compile_tes()
107 prog_data->base.urb_entry_size = ALIGN(output_size_bytes, 64) / 64; in brw_compile_tes()
[all …]
H A Dbrw_compile_cs.cpp33 const struct brw_stage_prog_data *prog_data = &cs_prog_data->base; in cs_fill_push_const_info() local
34 int subgroup_id_index = brw_get_subgroup_id_param_index(devinfo, prog_data); in cs_fill_push_const_info()
38 subgroup_id_index == (int)prog_data->nr_params - 1); in cs_fill_push_const_info()
44 per_thread_dwords = prog_data->nr_params - cross_thread_dwords; in cs_fill_push_const_info()
48 cross_thread_dwords = prog_data->nr_params; in cs_fill_push_const_info()
59 prog_data->nr_params); in cs_fill_push_const_info()
70 if (s.devinfo->platform == INTEL_PLATFORM_HSW && s.prog_data->total_shared > 0) { in run_cs()
105 struct brw_cs_prog_data *prog_data = params->prog_data; in brw_compile_cs() local
111 prog_data->base.stage = MESA_SHADER_COMPUTE; in brw_compile_cs()
112 prog_data->base.total_shared = nir->info.shared_size; in brw_compile_cs()
[all …]
H A Dbrw_fs_thread_payload.cpp45 struct brw_vue_prog_data *vue_prog_data = brw_vue_prog_data(v.prog_data); in tcs_thread_payload()
46 struct brw_tcs_prog_data *tcs_prog_data = brw_tcs_prog_data(v.prog_data); in tcs_thread_payload()
105 struct brw_vue_prog_data *vue_prog_data = brw_vue_prog_data(v.prog_data); in gs_thread_payload()
106 struct brw_gs_prog_data *gs_prog_data = brw_gs_prog_data(v.prog_data); in gs_thread_payload()
163 struct brw_wm_prog_data *prog_data = brw_wm_prog_data(v.prog_data); in setup_fs_payload_gfx20() local
182 if (prog_data->barycentric_interp_modes & (1 << i)) { in setup_fs_payload_gfx20()
189 if (prog_data->uses_src_depth) { in setup_fs_payload_gfx20()
195 if (prog_data->uses_src_w) { in setup_fs_payload_gfx20()
203 if (prog_data->uses_sample_mask) { in setup_fs_payload_gfx20()
213 if (prog_data->uses_pos_offset && j == 0) { in setup_fs_payload_gfx20()
[all …]
H A Dbrw_simd_selection.cpp62 if (std::holds_alternative<struct brw_cs_prog_data *>(state.prog_data)) in get_cs_prog_data()
63 return std::get<struct brw_cs_prog_data *>(state.prog_data); in get_cs_prog_data()
71 if (std::holds_alternative<struct brw_cs_prog_data *>(state.prog_data)) in get_prog_data()
72 return &std::get<struct brw_cs_prog_data *>(state.prog_data)->base; in get_prog_data()
73 else if (std::holds_alternative<struct brw_bs_prog_data *>(state.prog_data)) in get_prog_data()
74 return &std::get<struct brw_bs_prog_data *>(state.prog_data)->base; in get_prog_data()
88 const auto prog_data = get_prog_data(state); in brw_simd_should_compile() local
156 switch (prog_data->stage) { in brw_simd_should_compile()
232 const struct brw_cs_prog_data *prog_data, in brw_simd_select_for_workgroup_size() argument
235 if (!sizes || (prog_data->local_size[0] == sizes[0] && in brw_simd_select_for_workgroup_size()
[all …]
H A Dbrw_compiler.c310 const struct brw_stage_prog_data *prog_data, in brw_write_shader_relocs() argument
314 for (unsigned i = 0; i < prog_data->num_relocs; i++) { in brw_write_shader_relocs()
315 assert(prog_data->relocs[i].offset % 8 == 0); in brw_write_shader_relocs()
316 void *dst = program + prog_data->relocs[i].offset; in brw_write_shader_relocs()
318 if (prog_data->relocs[i].id == values[j].id) { in brw_write_shader_relocs()
319 uint32_t value = values[j].value + prog_data->relocs[i].delta; in brw_write_shader_relocs()
320 switch (prog_data->relocs[i].type) { in brw_write_shader_relocs()
337 brw_stage_prog_data_add_printf(struct brw_stage_prog_data *prog_data, in brw_stage_prog_data_add_printf() argument
341 prog_data->printf_info_count++; in brw_stage_prog_data_add_printf()
342 prog_data->printf_info = reralloc(mem_ctx, prog_data->printf_info, in brw_stage_prog_data_add_printf()
[all …]
H A Dbrw_compile_bs.cpp65 struct brw_bs_prog_data *prog_data, in compile_single_bs() argument
73 prog_data->base.stage = shader->info.stage; in compile_single_bs()
74 prog_data->max_stack_size = MAX2(prog_data->max_stack_size, in compile_single_bs()
84 .prog_data = prog_data, in compile_single_bs()
105 &prog_data->base, shader, in compile_single_bs()
155 struct brw_bs_prog_data *prog_data = params->prog_data; in brw_compile_bs() local
160 prog_data->base.stage = shader->info.stage; in brw_compile_bs()
161 prog_data->base.ray_queries = shader->info.ray_queries; in brw_compile_bs()
162 prog_data->base.total_scratch = 0; in brw_compile_bs()
164 prog_data->max_stack_size = 0; in brw_compile_bs()
[all …]
/aosp_15_r20/external/mesa3d/src/intel/compiler/elk/
H A Delk_test_simd_selection.cpp47 , prog_data(rzalloc(mem_ctx, struct elk_cs_prog_data)) in SIMDSelectionTest()
50 .prog_data = prog_data, in SIMDSelectionTest()
62 struct elk_cs_prog_data *prog_data; member in SIMDSelectionTest
69 prog_data->base.stage = MESA_SHADER_COMPUTE; in SIMDSelectionCS()
70 prog_data->local_size[0] = 32; in SIMDSelectionCS()
71 prog_data->local_size[1] = 1; in SIMDSelectionCS()
72 prog_data->local_size[2] = 1; in SIMDSelectionCS()
91 prog_data->local_size[0] = devinfo->max_cs_workgroup_threads; in TEST_F()
92 prog_data->local_size[1] = 32; in TEST_F()
93 prog_data->local_size[2] = 1; in TEST_F()
[all …]
H A Delk_compiler.h761 elk_stage_prog_data_add_params(struct elk_stage_prog_data *prog_data, in elk_stage_prog_data_add_params() argument
764 unsigned old_nr_params = prog_data->nr_params; in elk_stage_prog_data_add_params()
765 prog_data->nr_params += nr_new_params; in elk_stage_prog_data_add_params()
766 prog_data->param = reralloc(ralloc_parent(prog_data->param), in elk_stage_prog_data_add_params()
767 prog_data->param, uint32_t, in elk_stage_prog_data_add_params()
768 prog_data->nr_params); in elk_stage_prog_data_add_params()
769 return prog_data->param + old_nr_params; in elk_stage_prog_data_add_params()
956 _elk_wm_prog_data_prog_offset(const struct elk_wm_prog_data *prog_data, in _elk_wm_prog_data_prog_offset() argument
961 case 16: return prog_data->prog_offset_16; in _elk_wm_prog_data_prog_offset()
962 case 32: return prog_data->prog_offset_32; in _elk_wm_prog_data_prog_offset()
[all …]
H A Delk_vec4_gs_visitor.cpp45 struct elk_gs_prog_data *prog_data, in vec4_gs_visitor() argument
50 &prog_data->base, shader, in vec4_gs_visitor()
53 gs_prog_data(prog_data) in vec4_gs_visitor()
100 unsigned input_array_stride = prog_data->urb_read_length * 2; in setup_varying_inputs()
135 prog_data->dispatch_mode == INTEL_DISPATCH_MODE_4X2_DUAL_OBJECT ? 1 : 2; in setup_payload()
590 struct elk_gs_prog_data *prog_data = params->prog_data; in elk_compile_gs() local
599 prog_data->base.base.stage = MESA_SHADER_GEOMETRY; in elk_compile_gs()
600 prog_data->base.base.total_scratch = 0; in elk_compile_gs()
621 prog_data->base.clip_distance_mask = in elk_compile_gs()
623 prog_data->base.cull_distance_mask = in elk_compile_gs()
[all …]
H A Delk_simd_selection.cpp54 if (std::holds_alternative<struct elk_cs_prog_data *>(state.prog_data)) in get_cs_prog_data()
55 return std::get<struct elk_cs_prog_data *>(state.prog_data); in get_cs_prog_data()
63 if (std::holds_alternative<struct elk_cs_prog_data *>(state.prog_data)) in get_prog_data()
64 return &std::get<struct elk_cs_prog_data *>(state.prog_data)->base; in get_prog_data()
78 const auto prog_data = get_prog_data(state); in elk_simd_should_compile() local
130 switch (prog_data->stage) { in elk_simd_should_compile()
192 const struct elk_cs_prog_data *prog_data, in elk_simd_select_for_workgroup_size() argument
195 if (!sizes || (prog_data->local_size[0] == sizes[0] && in elk_simd_select_for_workgroup_size()
196 prog_data->local_size[1] == sizes[1] && in elk_simd_select_for_workgroup_size()
197 prog_data->local_size[2] == sizes[2])) { in elk_simd_select_for_workgroup_size()
[all …]
H A Delk_interpolation_map.c39 gfx4_frag_prog_set_interp_modes(struct elk_wm_prog_data *prog_data, in gfx4_frag_prog_set_interp_modes() argument
46 if (slot != -1 && prog_data->interp_mode[slot] == INTERP_MODE_NONE) { in gfx4_frag_prog_set_interp_modes()
47 prog_data->interp_mode[slot] = interp; in gfx4_frag_prog_set_interp_modes()
49 if (prog_data->interp_mode[slot] == INTERP_MODE_FLAT) { in gfx4_frag_prog_set_interp_modes()
50 prog_data->contains_flat_varying = true; in gfx4_frag_prog_set_interp_modes()
51 } else if (prog_data->interp_mode[slot] == INTERP_MODE_NOPERSPECTIVE) { in gfx4_frag_prog_set_interp_modes()
52 prog_data->contains_noperspective_varying = true; in gfx4_frag_prog_set_interp_modes()
61 struct elk_wm_prog_data *prog_data) in elk_setup_vue_interpolation() argument
64 memset(prog_data->interp_mode, 0, sizeof(prog_data->interp_mode)); in elk_setup_vue_interpolation()
74 prog_data->interp_mode[pos_slot] = INTERP_MODE_NOPERSPECTIVE; in elk_setup_vue_interpolation()
[all …]
H A Delk_fs_visitor.cpp54 const struct elk_wm_prog_data *prog_data = elk_wm_prog_data(this->prog_data); in interp_reg() local
56 assert(prog_data->urb_setup[location] >= 0); in interp_reg()
57 unsigned nr = prog_data->urb_setup[location]; in interp_reg()
58 channel += prog_data->urb_setup_channel[location]; in interp_reg()
61 assert(nr >= prog_data->num_per_primitive_inputs); in interp_reg()
62 nr -= prog_data->num_per_primitive_inputs; in interp_reg()
64 const unsigned per_vertex_start = prog_data->num_per_primitive_inputs; in interp_reg()
80 const struct elk_wm_prog_data *prog_data = elk_wm_prog_data(this->prog_data); in per_primitive_reg() local
82 comp += prog_data->urb_setup_channel[location]; in per_primitive_reg()
84 assert(prog_data->urb_setup[location] >= 0); in per_primitive_reg()
[all …]
/aosp_15_r20/external/mesa3d/src/intel/vulkan/
H A DgenX_simple_shader.c43 const struct brw_wm_prog_data *prog_data = in genX() local
44 brw_wm_prog_data_const(state->kernel->prog_data); in genX()
169 sbe.NumberofSFOutputAttributes = prog_data->num_varying_inputs; in genX()
170 sbe.VertexURBEntryReadLength = MAX2((prog_data->num_varying_inputs + 1) / 2, 1); in genX()
171 sbe.ConstantInterpolationEnable = prog_data->flat_inputs; in genX()
181 intel_set_ps_dispatch_state(&ps, device->info, prog_data, in genX()
185 ps.VectorMaskEnable = prog_data->uses_vmask; in genX()
189 ps.PushConstantEnable = prog_data->base.nr_params > 0 || in genX()
190 prog_data->base.ubo_ranges[0].length; in genX()
194 brw_wm_prog_data_dispatch_grf_start_reg(prog_data, ps, 0); in genX()
[all …]
H A Danv_pipeline_cache.c204 brw_stage_prog_data_printf_num_args(const struct brw_stage_prog_data *prog_data) in brw_stage_prog_data_printf_num_args() argument
207 for (unsigned i = 0; i < prog_data->printf_info_count; i++) in brw_stage_prog_data_printf_num_args()
208 count += prog_data->printf_info[i].num_args; in brw_stage_prog_data_printf_num_args()
213 brw_stage_prog_data_printf_string_size(const struct brw_stage_prog_data *prog_data) in brw_stage_prog_data_printf_string_size() argument
216 for (unsigned i = 0; i < prog_data->printf_info_count; i++) in brw_stage_prog_data_printf_string_size()
217 size += prog_data->printf_info[i].string_size; in brw_stage_prog_data_printf_string_size()
225 const struct brw_stage_prog_data *prog_data) in copy_uprintf() argument
227 for (unsigned i = 0; i < prog_data->printf_info_count; i++) { in copy_uprintf()
228 out_infos[i] = prog_data->printf_info[i]; in copy_uprintf()
231 prog_data->printf_info[i].arg_sizes, in copy_uprintf()
[all …]
H A DgenX_cmd_compute.c131 const struct brw_cs_prog_data *prog_data = get_cs_prog_data(pipeline); in genX() local
132 genX(cmd_buffer_ensure_cfe_state)(cmd_buffer, prog_data->base.total_scratch); in genX()
271 const struct brw_cs_prog_data *prog_data, in GENX()
285 .SharedLocalMemorySize = intel_compute_slm_encode_size(GFX_VER, prog_data->base.total_shared), in GENX()
288 prog_data->base.total_shared, in GENX()
291 .NumberOfBarriers = prog_data->uses_barrier, in GENX()
298 const struct brw_cs_prog_data *prog_data, in emit_indirect_compute_walker() argument
308 brw_cs_get_dispatch_info(devinfo, prog_data, NULL); in emit_indirect_compute_walker()
316 .GenerateLocalID = prog_data->generate_local_id != 0, in emit_indirect_compute_walker()
317 .EmitLocal = prog_data->generate_local_id, in emit_indirect_compute_walker()
[all …]
/aosp_15_r20/external/mesa3d/src/broadcom/compiler/
H A Dvir.c784 struct v3d_prog_data *prog_data) in v3d_set_prog_data_uniforms() argument
787 struct v3d_uniform_list *ulist = &prog_data->uniforms; in v3d_set_prog_data_uniforms()
790 ulist->data = ralloc_array(prog_data, uint32_t, count); in v3d_set_prog_data_uniforms()
793 ulist->contents = ralloc_array(prog_data, enum quniform_contents, count); in v3d_set_prog_data_uniforms()
800 struct v3d_vs_prog_data *prog_data) in v3d_vs_set_prog_data() argument
806 for (int i = 0; i < ARRAY_SIZE(prog_data->vattr_sizes); i++) { in v3d_vs_set_prog_data()
807 prog_data->vattr_sizes[i] = c->vattr_sizes[i]; in v3d_vs_set_prog_data()
808 prog_data->vpm_input_size += c->vattr_sizes[i]; in v3d_vs_set_prog_data()
811 memset(prog_data->driver_location_map, -1, in v3d_vs_set_prog_data()
812 sizeof(prog_data->driver_location_map)); in v3d_vs_set_prog_data()
[all …]
/aosp_15_r20/external/mesa3d/src/gallium/drivers/v3d/
H A Dv3dx_draw.c375 gs_bin->prog_data.gs->base.threads == 4; in v3d_emit_gs_state_record()
377 gs_bin->prog_data.gs->base.single_seg; in v3d_emit_gs_state_record()
387 gs->prog_data.gs->base.threads == 4; in v3d_emit_gs_state_record()
389 gs->prog_data.gs->base.single_seg; in v3d_emit_gs_state_record()
508 v3d->prog.fs->prog_data.fs->writes_z; in emit_shader_state_record()
510 v3d->prog.fs->prog_data.fs->disable_ez; in emit_shader_state_record()
512 v3d->prog.fs->prog_data.fs->uses_center_w; in emit_shader_state_record()
514 (v3d->prog.gs && v3d->prog.gs->prog_data.gs->uses_pid) || in emit_shader_state_record()
515 v3d->prog.fs->prog_data.fs->uses_pid; in emit_shader_state_record()
517 !v3d->prog.gs && v3d->prog.fs->prog_data.fs->uses_pid; in emit_shader_state_record()
[all …]
/aosp_15_r20/external/coreboot/tests/lib/
H A Dcbmem_stage_cache-test.c73 struct prog prog_data = {0}; in test_stage_cache_add() local
77 prog_data = (struct prog)PROG_INIT(PROG_ROMSTAGE, "test_prog"); in test_stage_cache_add()
78 prog_set_area(&prog_data, data, data_sz); in test_stage_cache_add()
79 prog_set_entry(&prog_data, prog_entry_mock, &arg); in test_stage_cache_add()
81 stage_cache_add(id, &prog_data); in test_stage_cache_add()
85 assert_int_equal(meta->load_addr, (uintptr_t)prog_start(&prog_data)); in test_stage_cache_add()
86 assert_int_equal(meta->entry_addr, (uintptr_t)prog_entry(&prog_data)); in test_stage_cache_add()
87 assert_int_equal(meta->arg, (uintptr_t)prog_entry_arg(&prog_data)); in test_stage_cache_add()
150 struct prog prog_data = {0}; in test_stage_cache_load_stage() local
157 prog_data = (struct prog)PROG_INIT(PROG_RAMSTAGE, "test_prog"); in test_stage_cache_load_stage()
[all …]
/aosp_15_r20/external/mesa3d/src/gallium/drivers/crocus/
H A Dcrocus_disk_cache.c90 const struct elk_stage_prog_data *prog_data = shader->prog_data; in crocus_disk_cache_store() local
113 blob_write_bytes(&blob, shader->prog_data, elk_prog_data_size(stage)); in crocus_disk_cache_store()
114 blob_write_bytes(&blob, map + shader->offset, shader->prog_data->program_size); in crocus_disk_cache_store()
118 blob_write_bytes(&blob, prog_data->param, in crocus_disk_cache_store()
119 prog_data->nr_params * sizeof(uint32_t)); in crocus_disk_cache_store()
165 struct elk_stage_prog_data *prog_data = ralloc_size(NULL, prog_data_size); in crocus_disk_cache_retrieve() local
173 blob_copy_bytes(&blob, prog_data, prog_data_size); in crocus_disk_cache_retrieve()
174 assembly = blob_read_bytes(&blob, prog_data->program_size); in crocus_disk_cache_retrieve()
183 prog_data->param = NULL; in crocus_disk_cache_retrieve()
184 if (prog_data->nr_params) { in crocus_disk_cache_retrieve()
[all …]
H A Dgen4_blorp_exec.h71 const struct elk_sf_prog_data *prog_data = params->sf_prog_data; in blorp_emit_sf_state() local
81 sf.GRFRegisterCount = DIV_ROUND_UP(prog_data->total_grf, 16) - 1; in blorp_emit_sf_state()
82 sf.VertexURBEntryReadLength = prog_data->urb_read_length; in blorp_emit_sf_state()
105 const struct elk_wm_prog_data *prog_data = params->wm_prog_data; in blorp_emit_wm_state() local
117 if (prog_data) { in blorp_emit_wm_state()
119 prog_data->base.dispatch_grf_start_reg; in blorp_emit_wm_state()
120 wm.SetupURBEntryReadLength = prog_data->num_varying_inputs * 2; in blorp_emit_wm_state()
124 wm.PixelShaderKillsPixel = prog_data->uses_kill; in blorp_emit_wm_state()
128 wm._8PixelDispatchEnable = prog_data->dispatch_8; in blorp_emit_wm_state()
129 wm._16PixelDispatchEnable = prog_data->dispatch_16; in blorp_emit_wm_state()
[all …]

1234567