Home
last modified time | relevance | path

Searched refs:prog_data (Results 1 - 25 of 90) sorted by relevance

1234

/third_party/mesa3d/src/intel/compiler/
H A Dtest_simd_selection.cpp47 prog_data = rzalloc(mem_ctx, struct brw_cs_prog_data);
56 return brw_simd_should_compile(mem_ctx, simd, devinfo, prog_data, in should_compile()
62 struct brw_cs_prog_data *prog_data; member in SIMDSelectionTest
70 prog_data->base.stage = MESA_SHADER_COMPUTE; in SIMDSelectionCS()
71 prog_data->local_size[0] = 32; in SIMDSelectionCS()
72 prog_data->local_size[1] = 1; in SIMDSelectionCS()
73 prog_data->local_size[2] = 1; in SIMDSelectionCS()
82 brw_simd_mark_compiled(SIMD8, prog_data, not_spilled); in TEST_F()
84 brw_simd_mark_compiled(SIMD16, prog_data, not_spilled); in TEST_F()
87 ASSERT_EQ(brw_simd_select(prog_data), SIMD1 in TEST_F()
[all...]
H A Dbrw_simd_selection.c53 struct brw_cs_prog_data *prog_data, in brw_simd_should_compile()
58 assert(!test_bit(prog_data->prog_mask, simd)); in brw_simd_should_compile()
66 const bool workgroup_size_variable = prog_data->local_size[0] == 0; in brw_simd_should_compile()
69 if (test_bit(prog_data->prog_spilled, simd)) { in brw_simd_should_compile()
75 const unsigned workgroup_size = prog_data->local_size[0] * in brw_simd_should_compile()
76 prog_data->local_size[1] * in brw_simd_should_compile()
77 prog_data->local_size[2]; in brw_simd_should_compile()
88 if (simd > 0 && test_bit(prog_data->prog_mask, simd - 1) && in brw_simd_should_compile()
108 if (!INTEL_DEBUG(DEBUG_DO32) && prog_data->prog_mask) { in brw_simd_should_compile()
133 brw_simd_mark_compiled(unsigned simd, struct brw_cs_prog_data *prog_data, boo argument
50 brw_simd_should_compile(void *mem_ctx, unsigned simd, const struct intel_device_info *devinfo, struct brw_cs_prog_data *prog_data, unsigned required, const char **error) brw_simd_should_compile() argument
147 brw_simd_select(const struct brw_cs_prog_data *prog_data) brw_simd_select() argument
164 brw_simd_select_for_workgroup_size(const struct intel_device_info *devinfo, const struct brw_cs_prog_data *prog_data, const unsigned *sizes) brw_simd_select_for_workgroup_size() argument
[all...]
H A Dbrw_interpolation_map.c39 gfx4_frag_prog_set_interp_modes(struct brw_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 brw_wm_prog_data *prog_data) in brw_setup_vue_interpolation()
64 memset(prog_data->interp_mode, 0, sizeof(prog_data in brw_setup_vue_interpolation()
60 brw_setup_vue_interpolation(const struct brw_vue_map *vue_map, nir_shader *nir, struct brw_wm_prog_data *prog_data) brw_setup_vue_interpolation() argument
[all...]
H A Dbrw_compiler.h819 brw_stage_prog_data_add_params(struct brw_stage_prog_data *prog_data, in brw_stage_prog_data_add_params() argument
822 unsigned old_nr_params = prog_data->nr_params; in brw_stage_prog_data_add_params()
823 prog_data->nr_params += nr_new_params; in brw_stage_prog_data_add_params()
824 prog_data->param = reralloc(ralloc_parent(prog_data->param), in brw_stage_prog_data_add_params()
825 prog_data->param, uint32_t, in brw_stage_prog_data_add_params()
826 prog_data->nr_params); in brw_stage_prog_data_add_params()
827 return prog_data->param + old_nr_params; in brw_stage_prog_data_add_params()
994 _brw_wm_prog_data_prog_offset(const struct brw_wm_prog_data *prog_data, in _brw_wm_prog_data_prog_offset() argument
999 case 16: return prog_data in _brw_wm_prog_data_prog_offset()
1010 _brw_wm_prog_data_dispatch_grf_start_reg(const struct brw_wm_prog_data *prog_data, unsigned simd_width) _brw_wm_prog_data_dispatch_grf_start_reg() argument
1026 _brw_wm_prog_data_reg_blocks(const struct brw_wm_prog_data *prog_data, unsigned simd_width) _brw_wm_prog_data_reg_blocks() argument
1084 brw_cs_prog_data_prog_offset(const struct brw_cs_prog_data *prog_data, unsigned dispatch_width) brw_cs_prog_data_prog_offset() argument
1583 struct brw_vs_prog_data *prog_data; global() member
1616 struct brw_tcs_prog_data *prog_data; global() member
1644 struct brw_tes_prog_data *prog_data; global() member
1673 struct brw_gs_prog_data *prog_data; global() member
1728 struct brw_task_prog_data *prog_data; global() member
1745 struct brw_mesh_prog_data *prog_data; global() member
1768 struct brw_wm_prog_data *prog_data; global() member
1805 struct brw_cs_prog_data *prog_data; global() member
1836 struct brw_bs_prog_data *prog_data; global() member
1963 brw_stage_has_packed_dispatch(ASSERTED const struct intel_device_info *devinfo, gl_shader_stage stage, const struct brw_stage_prog_data *prog_data) brw_stage_has_packed_dispatch() argument
[all...]
H A Dbrw_vec4_gs_visitor.cpp43 struct brw_gs_prog_data *prog_data, in vec4_gs_visitor()
49 &prog_data->base, shader, mem_ctx, in vec4_gs_visitor()
52 gs_prog_data(prog_data) in vec4_gs_visitor()
99 unsigned input_array_stride = prog_data->urb_read_length * 2; in setup_varying_inputs()
134 prog_data->dispatch_mode == DISPATCH_MODE_4X2_DUAL_OBJECT ? 1 : 2; in setup_payload()
293 * c->prog_data.control_data_header_size_bits is large enough to make it in emit_control_data_bits()
590 struct brw_gs_prog_data *prog_data = params->prog_data; in brw_compile_gs() local
599 prog_data->base.base.stage = MESA_SHADER_GEOMETRY; in brw_compile_gs()
600 prog_data in brw_compile_gs()
40 vec4_gs_visitor(const struct brw_compiler *compiler, void *log_data, struct brw_gs_compile *c, struct brw_gs_prog_data *prog_data, const nir_shader *shader, void *mem_ctx, bool no_spills, bool debug_enabled) vec4_gs_visitor() argument
[all...]
H A Dintel_clc.c199 for (unsigned i = 0; i < kernel->prog_data.base.num_relocs; i++) { in print_kernel()
200 const struct brw_shader_reloc *reloc = &kernel->prog_data.base.relocs[i]; in print_kernel()
206 _mesa_sha1_update(&sha1_ctx, kernel->prog_data.base.relocs, in print_kernel()
207 kernel->prog_data.base.num_relocs * in print_kernel()
208 sizeof(kernel->prog_data.base.relocs[0])); in print_kernel()
211 struct brw_cs_prog_data cs_prog_data = kernel->prog_data; in print_kernel()
230 kernel->prog_data.base.program_size); in print_kernel()
238 kernel->prog_data.base.program_size); in print_kernel()
241 fprintf(fp, " .prog_data = {\n"); in print_kernel()
242 print_cs_prog_data_fields(fp, prefix, " ", &kernel->prog_data); in print_kernel()
[all...]
H A Dbrw_mesh.cpp203 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 in brw_compile_task()
692 struct brw_mesh_prog_data *prog_data = params->prog_data; brw_compile_mesh() local
[all...]
H A Dbrw_vec4_tcs.cpp40 struct brw_tcs_prog_data *prog_data, in vec4_tcs_visitor()
44 : vec4_visitor(compiler, log_data, &key->base.tex, &prog_data->base, in vec4_tcs_visitor()
108 (struct brw_tcs_prog_data *) prog_data; in emit_thread_end()
361 struct brw_tcs_prog_data *prog_data = params->prog_data; in brw_compile_tcs() local
362 struct brw_vue_prog_data *vue_prog_data = &prog_data->base; in brw_compile_tcs()
369 prog_data->base.base.ray_queries = nir->info.ray_queries; in brw_compile_tcs()
370 prog_data->base.base.total_scratch = 0; in brw_compile_tcs()
395 prog_data->patch_count_threshold = brw::get_patch_count_threshold(key->input_vertices); in brw_compile_tcs()
407 prog_data in brw_compile_tcs()
37 vec4_tcs_visitor(const struct brw_compiler *compiler, void *log_data, const struct brw_tcs_prog_key *key, struct brw_tcs_prog_data *prog_data, const nir_shader *nir, void *mem_ctx, bool debug_enabled) vec4_tcs_visitor() argument
[all...]
H A Dbrw_shader.cpp1330 struct brw_tes_prog_data *prog_data = params->prog_data; in brw_compile_tes() local
1336 prog_data->base.base.stage = MESA_SHADER_TESS_EVAL; in brw_compile_tes()
1337 prog_data->base.base.ray_queries = nir->info.ray_queries; in brw_compile_tes()
1348 brw_compute_vue_map(devinfo, &prog_data->base.vue_map, in brw_compile_tes()
1352 unsigned output_size_bytes = prog_data->base.vue_map.num_slots * 4 * 4; in brw_compile_tes()
1360 prog_data->base.clip_distance_mask = in brw_compile_tes()
1362 prog_data->base.cull_distance_mask = in brw_compile_tes()
1366 prog_data->include_primitive_id = in brw_compile_tes()
1370 prog_data in brw_compile_tes()
[all...]
H A Dbrw_fs_visitor.cpp92 struct brw_wm_prog_data *wm_prog_data = brw_wm_prog_data(this->prog_data); in emit_dummy_fs()
124 const struct brw_wm_prog_data *prog_data = brw_wm_prog_data(this->prog_data); in interp_reg() local
126 assert(prog_data->urb_setup[location] >= 0); in interp_reg()
127 unsigned nr = prog_data->urb_setup[location]; in interp_reg()
130 assert(nr >= prog_data->num_per_primitive_inputs); in interp_reg()
131 nr -= prog_data->num_per_primitive_inputs; in interp_reg()
133 const unsigned per_vertex_start = prog_data->num_per_primitive_inputs; in interp_reg()
149 const struct brw_wm_prog_data *prog_data = brw_wm_prog_data(this->prog_data); in per_primitive_reg() local
622 struct brw_wm_prog_data *prog_data = brw_wm_prog_data(this->prog_data); emit_single_fb_write() local
666 struct brw_wm_prog_data *prog_data = brw_wm_prog_data(this->prog_data); emit_fb_writes() local
1133 fs_visitor(const struct brw_compiler *compiler, void *log_data, void *mem_ctx, const brw_base_prog_key *key, struct brw_stage_prog_data *prog_data, const nir_shader *shader, unsigned dispatch_width, bool debug_enabled) fs_visitor() argument
1151 fs_visitor(const struct brw_compiler *compiler, void *log_data, void *mem_ctx, struct brw_gs_compile *c, struct brw_gs_prog_data *prog_data, const nir_shader *shader, bool debug_enabled) fs_visitor() argument
[all...]
H A Dbrw_private.h39 struct brw_cs_prog_data *prog_data,
44 struct brw_cs_prog_data *prog_data,
47 int brw_simd_select(const struct brw_cs_prog_data *prog_data);
50 const struct brw_cs_prog_data *prog_data,
H A Dbrw_fs.cpp1276 struct brw_wm_prog_data *wm_prog_data = brw_wm_prog_data(this->prog_data);
1427 struct brw_wm_prog_data *wm_prog_data = brw_wm_prog_data(this->prog_data);
1523 struct brw_gs_prog_data *gs_prog_data = brw_gs_prog_data(prog_data);
1577 prog_data->curb_read_length = uniform_push_length + ubo_push_length;
1582 if (is_compute && brw_cs_prog_data(prog_data)->uses_inline_data) {
1723 assert(i < prog_data->curb_read_length);
1736 this->first_non_payload_grf = payload.num_regs + prog_data->curb_read_length;
1766 struct brw_wm_prog_data *prog_data,
1770 memset(prog_data->urb_setup, -1,
1771 sizeof(prog_data
[all...]
H A Dtest_vec4_dead_code_eliminate.cpp39 struct brw_vue_prog_data *prog_data; member in dead_code_eliminate_vec4_test
49 struct brw_vue_prog_data *prog_data) in dead_code_eliminate_vec4_visitor()
50 : vec4_visitor(compiler, NULL, NULL, prog_data, shader, mem_ctx, in dead_code_eliminate_vec4_visitor()
53 prog_data->dispatch_mode = DISPATCH_MODE_4X2_DUAL_OBJECT; in dead_code_eliminate_vec4_visitor()
96 prog_data = ralloc(ctx, struct brw_vue_prog_data); in SetUp()
100 v = new dead_code_eliminate_vec4_visitor(compiler, ctx, shader, prog_data); in SetUp()
46 dead_code_eliminate_vec4_visitor(struct brw_compiler *compiler, void *mem_ctx, nir_shader *shader, struct brw_vue_prog_data *prog_data) dead_code_eliminate_vec4_visitor() argument
H A Dbrw_vec4.cpp785 assert(prog_data->total_grf || in opt_set_dependency_control()
1541 push_length = DIV_ROUND_UP(prog_data->base.nr_params, 8); in setup_push_ranges()
1546 struct brw_ubo_range *range = &prog_data->base.ubo_ranges[i]; in setup_push_ranges()
1563 push_length = DIV_ROUND_UP(prog_data->base.nr_params, 8); in setup_uniforms()
1582 prog_data->base.dispatch_grf_start_reg = reg; in setup_uniforms()
1583 prog_data->base.curb_read_length = push_length; in setup_uniforms()
1734 prog_data->base.dispatch_grf_start_reg + in convert_to_hw_regs()
1740 prog_data->base.dispatch_grf_start_reg + in convert_to_hw_regs()
1963 get_lowered_simd_width(devinfo, prog_data->dispatch_mode, stage, inst); in lower_simd_width()
2021 prog_data in lower_simd_width()
2540 struct brw_vs_prog_data *prog_data = params->prog_data; brw_compile_vs() local
[all...]
/third_party/mesa3d/src/gallium/drivers/iris/
H A Diris_disk_cache.c89 const struct brw_stage_prog_data *prog_data = shader->prog_data; in iris_disk_cache_store() local
114 blob_write_bytes(&blob, shader->prog_data, brw_prog_data_size(stage)); in iris_disk_cache_store()
115 blob_write_bytes(&blob, shader->map, shader->prog_data->program_size); in iris_disk_cache_store()
120 blob_write_bytes(&blob, prog_data->relocs, in iris_disk_cache_store()
121 prog_data->num_relocs * sizeof(struct brw_shader_reloc)); in iris_disk_cache_store()
122 blob_write_bytes(&blob, prog_data->param, in iris_disk_cache_store()
123 prog_data->nr_params * sizeof(uint32_t)); in iris_disk_cache_store()
179 struct brw_stage_prog_data *prog_data = ralloc_size(NULL, prog_data_size); in iris_disk_cache_retrieve() local
188 blob_copy_bytes(&blob, prog_data, prog_data_siz in iris_disk_cache_retrieve()
[all...]
/third_party/mesa3d/src/gallium/drivers/crocus/
H A Dcrocus_disk_cache.c90 const struct brw_stage_prog_data *prog_data = shader->prog_data; in crocus_disk_cache_store() local
113 blob_write_bytes(&blob, shader->prog_data, brw_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 brw_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 in crocus_disk_cache_retrieve()
[all...]
H A Dgen4_blorp_exec.h71 const struct brw_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 brw_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 in blorp_emit_wm_state()
[all...]
H A Dcrocus_program_cache.c190 struct brw_stage_prog_data *prog_data, in crocus_upload_shader()
218 shader->prog_data = prog_data; in crocus_upload_shader()
226 ralloc_steal(shader, shader->prog_data); in crocus_upload_shader()
228 ralloc_steal(shader->prog_data, prog_data->param); in crocus_upload_shader()
252 *((void **)prog_data_out) = shader->prog_data; in crocus_blorp_lookup_shader()
268 struct brw_stage_prog_data *prog_data = ralloc_size(NULL, prog_data_size); in crocus_blorp_upload_shader() local
269 memcpy(prog_data, prog_data_templ, prog_data_size); in crocus_blorp_upload_shader()
275 ice, CROCUS_CACHE_BLORP, key_size, key, kernel, kernel_size, prog_data, in crocus_blorp_upload_shader()
187 crocus_upload_shader(struct crocus_context *ice, enum crocus_program_cache_id cache_id, uint32_t key_size, const void *key, const void *assembly, uint32_t asm_size, struct brw_stage_prog_data *prog_data, uint32_t prog_data_size, uint32_t *streamout, enum brw_param_builtin *system_values, unsigned num_system_values, unsigned num_cbufs, const struct crocus_binding_table *bt) crocus_upload_shader() argument
[all...]
/third_party/mesa3d/src/broadcom/compiler/
H A Dvir.c666 struct v3d_prog_data *prog_data) in v3d_set_prog_data_uniforms()
669 struct v3d_uniform_list *ulist = &prog_data->uniforms; in v3d_set_prog_data_uniforms()
672 ulist->data = ralloc_array(prog_data, uint32_t, count); in v3d_set_prog_data_uniforms()
675 ulist->contents = ralloc_array(prog_data, enum quniform_contents, count); in v3d_set_prog_data_uniforms()
682 struct v3d_vs_prog_data *prog_data) in v3d_vs_set_prog_data()
688 for (int i = 0; i < ARRAY_SIZE(prog_data->vattr_sizes); i++) { in v3d_vs_set_prog_data()
689 prog_data->vattr_sizes[i] = c->vattr_sizes[i]; in v3d_vs_set_prog_data()
690 prog_data->vpm_input_size += c->vattr_sizes[i]; in v3d_vs_set_prog_data()
693 memset(prog_data->driver_location_map, -1, in v3d_vs_set_prog_data()
694 sizeof(prog_data in v3d_vs_set_prog_data()
665 v3d_set_prog_data_uniforms(struct v3d_compile *c, struct v3d_prog_data *prog_data) v3d_set_prog_data_uniforms() argument
681 v3d_vs_set_prog_data(struct v3d_compile *c, struct v3d_vs_prog_data *prog_data) v3d_vs_set_prog_data() argument
754 v3d_gs_set_prog_data(struct v3d_compile *c, struct v3d_gs_prog_data *prog_data) v3d_gs_set_prog_data() argument
798 v3d_set_fs_prog_data_inputs(struct v3d_compile *c, struct v3d_fs_prog_data *prog_data) v3d_set_fs_prog_data_inputs() argument
820 v3d_fs_set_prog_data(struct v3d_compile *c, struct v3d_fs_prog_data *prog_data) v3d_fs_set_prog_data() argument
837 v3d_cs_set_prog_data(struct v3d_compile *c, struct v3d_compute_prog_data *prog_data) v3d_cs_set_prog_data() argument
850 v3d_set_prog_data(struct v3d_compile *c, struct v3d_prog_data *prog_data) v3d_set_prog_data() argument
1902 struct v3d_prog_data *prog_data; v3d_compile() local
[all...]
/third_party/mesa3d/src/gallium/drivers/v3d/
H A Dv3d_disk_cache.c143 const void *prog_data = blob_read_bytes(&blob, prog_data_size); in v3d_disk_cache_retrieve() local
167 shader->prog_data.base = rzalloc_size(shader, prog_data_size); in v3d_disk_cache_retrieve()
168 memcpy(shader->prog_data.base, prog_data, prog_data_size); in v3d_disk_cache_retrieve()
170 shader->prog_data.base->uniforms.count = ulist_count; in v3d_disk_cache_retrieve()
172 shader->prog_data.base->uniforms.contents = in v3d_disk_cache_retrieve()
173 ralloc_array(shader->prog_data.base, enum quniform_contents, ulist_count); in v3d_disk_cache_retrieve()
174 memcpy(shader->prog_data.base->uniforms.contents, ulist_contents, ulist_contents_size); in v3d_disk_cache_retrieve()
176 shader->prog_data.base->uniforms.data = in v3d_disk_cache_retrieve()
177 ralloc_array(shader->prog_data in v3d_disk_cache_retrieve()
[all...]
H A Dv3dx_draw.c377 gs_bin->prog_data.gs->base.threads == 4; in v3d_emit_gs_state_record()
379 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()
516 job->tmu_dirty_rcl |= v3d->prog.cs->prog_data.vs->base.tmu_dirty_rcl; in v3d_emit_gl_shader_state()
517 job->tmu_dirty_rcl |= v3d->prog.vs->prog_data.vs->base.tmu_dirty_rcl; in v3d_emit_gl_shader_state()
520 v3d->prog.gs_bin->prog_data.gs->base.tmu_dirty_rcl; in v3d_emit_gl_shader_state()
524 v3d->prog.gs->prog_data.gs->base.tmu_dirty_rcl; in v3d_emit_gl_shader_state()
526 job->tmu_dirty_rcl |= v3d->prog.fs->prog_data.fs->base.tmu_dirty_rcl; in v3d_emit_gl_shader_state()
565 v3d->prog.cs->prog_data in v3d_emit_gl_shader_state()
[all...]
H A Dv3d_program.c400 &shader->prog_data.base, s, in v3d_get_compiled_shader()
404 ralloc_steal(shader, shader->prog_data.base); in v3d_get_compiled_shader()
427 if (shader->prog_data.base->spill_size > in v3d_get_compiled_shader()
435 shader->prog_data.base->spill_size); in v3d_get_compiled_shader()
441 shader->prog_data.base->spill_size; in v3d_get_compiled_shader()
634 if (v3d->prog.fs->prog_data.fs->flat_shade_flags != in v3d_update_compiled_fs()
635 old_fs->prog_data.fs->flat_shade_flags) { in v3d_update_compiled_fs()
639 if (v3d->prog.fs->prog_data.fs->noperspective_flags != in v3d_update_compiled_fs()
640 old_fs->prog_data.fs->noperspective_flags) { in v3d_update_compiled_fs()
644 if (v3d->prog.fs->prog_data in v3d_update_compiled_fs()
[all...]
/third_party/mesa3d/src/intel/vulkan/
H A Danv_nir_compute_push_layout.c35 struct brw_stage_prog_data *prog_data, in anv_nir_compute_push_layout()
128 prog_data->nr_params = nir->num_uniforms / 4; in anv_nir_compute_push_layout()
129 prog_data->param = rzalloc_array(mem_ctx, uint32_t, prog_data->nr_params); in anv_nir_compute_push_layout()
188 brw_nir_analyze_ubo_ranges(compiler, nir, NULL, prog_data->ubo_ranges); in anv_nir_compute_push_layout()
200 if (total_push_regs + prog_data->ubo_ranges[i].length > max_push_regs) in anv_nir_compute_push_layout()
201 prog_data->ubo_ranges[i].length = max_push_regs - total_push_regs; in anv_nir_compute_push_layout()
202 total_push_regs += prog_data->ubo_ranges[i].length; in anv_nir_compute_push_layout()
215 prog_data->push_reg_mask_param = in anv_nir_compute_push_layout()
222 struct brw_ubo_range *ubo_range = &prog_data in anv_nir_compute_push_layout()
32 anv_nir_compute_push_layout(nir_shader *nir, const struct anv_physical_device *pdevice, bool robust_buffer_access, struct brw_stage_prog_data *prog_data, struct anv_pipeline_bind_map *map, void *mem_ctx) anv_nir_compute_push_layout() argument
272 anv_nir_validate_push_layout(struct brw_stage_prog_data *prog_data, struct anv_pipeline_bind_map *map) anv_nir_validate_push_layout() argument
[all...]
H A Danv_pipeline_cache.c81 VK_MULTIALLOC_DECL_SIZE(&ma, struct brw_stage_prog_data, prog_data, in anv_shader_bin_create()
149 memcpy(prog_data, prog_data_in, prog_data_size); in anv_shader_bin_create()
152 prog_data->relocs = prog_data_relocs; in anv_shader_bin_create()
154 prog_data->nr_params * sizeof(*prog_data_param)); in anv_shader_bin_create()
155 prog_data->param = prog_data_param; in anv_shader_bin_create()
156 shader->prog_data = prog_data; in anv_shader_bin_create()
196 blob_write_bytes(blob, shader->prog_data, shader->prog_data_size); in anv_shader_bin_serialize()
197 blob_write_bytes(blob, shader->prog_data->relocs, in anv_shader_bin_serialize()
198 shader->prog_data in anv_shader_bin_serialize()
252 union brw_any_prog_data prog_data; anv_shader_bin_deserialize() local
322 anv_device_upload_kernel(struct anv_device *device, struct vk_pipeline_cache *cache, gl_shader_stage stage, const void *key_data, uint32_t key_size, const void *kernel_data, uint32_t kernel_size, const struct brw_stage_prog_data *prog_data, uint32_t prog_data_size, const struct brw_compile_stats *stats, uint32_t num_stats, const nir_xfb_info *xfb_info, const struct anv_pipeline_bind_map *bind_map) anv_device_upload_kernel() argument
[all...]
/third_party/mesa3d/src/intel/blorp/
H A Dblorp_genX_exec.h724 const struct brw_wm_prog_data *prog_data = params->wm_prog_data; in blorp_emit_sf_config() local
759 if (prog_data) { in blorp_emit_sf_config()
760 sbe.NumberofSFOutputAttributes = prog_data->num_varying_inputs; in blorp_emit_sf_config()
761 sbe.VertexURBEntryReadLength = brw_blorp_get_urb_length(prog_data); in blorp_emit_sf_config()
762 sbe.ConstantInterpolationEnable = prog_data->flat_inputs; in blorp_emit_sf_config()
792 if (prog_data) { in blorp_emit_sf_config()
793 sbe.NumberofSFOutputAttributes = prog_data->num_varying_inputs; in blorp_emit_sf_config()
794 sbe.VertexURBEntryReadLength = brw_blorp_get_urb_length(prog_data); in blorp_emit_sf_config()
795 sbe.ConstantInterpolationEnable = prog_data->flat_inputs; in blorp_emit_sf_config()
812 if (prog_data) { in blorp_emit_sf_config()
829 const struct brw_wm_prog_data *prog_data = params->wm_prog_data; blorp_emit_ps_config() local
2139 const struct brw_stage_prog_data *prog_data = &cs_prog_data->base; blorp_exec_compute() local
[all...]

Completed in 24 milliseconds

1234