| /third_party/mesa3d/src/intel/compiler/ |
| D | test_simd_selection.cpp | 47 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), SIMD16); in TEST_F()
[all …]
|
| D | brw_simd_selection.c | 53 struct brw_cs_prog_data *prog_data, in brw_simd_should_compile() argument
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, bool spilled) in brw_simd_mark_compiled() argument
[all …]
|
| D | brw_compiler.h | 819 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->prog_offset_16; in _brw_wm_prog_data_prog_offset()
1000 case 32: return prog_data->prog_offset_32; in _brw_wm_prog_data_prog_offset()
[all …]
|
| D | brw_vec4_gs_visitor.cpp | 43 struct brw_gs_prog_data *prog_data, in vec4_gs_visitor() argument
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()
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->base.base.ray_queries = nir->info.ray_queries; in brw_compile_gs()
601 prog_data->base.base.total_scratch = 0; in brw_compile_gs()
622 prog_data->base.clip_distance_mask = in brw_compile_gs()
[all …]
|
| D | brw_interpolation_map.c | 39 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() argument
64 memset(prog_data->interp_mode, 0, sizeof(prog_data->interp_mode)); in brw_setup_vue_interpolation()
74 prog_data->interp_mode[pos_slot] = INTERP_MODE_NOPERSPECTIVE; in brw_setup_vue_interpolation()
[all …]
|
| D | brw_mesh.cpp | 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()
[all …]
|
| D | intel_clc.c | 199 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()
242 print_cs_prog_data_fields(fp, prefix, " ", &kernel->prog_data); in print_kernel()
539 fprintf(stdout, " uses_barrier : %u\n", kernel.prog_data.uses_barrier); in main()
[all …]
|
| D | brw_fs.cpp | 1276 struct brw_wm_prog_data *wm_prog_data = brw_wm_prog_data(this->prog_data); in emit_samplepos_setup()
1427 struct brw_wm_prog_data *wm_prog_data = brw_wm_prog_data(this->prog_data); in emit_samplemaskin_setup()
1523 struct brw_gs_prog_data *gs_prog_data = brw_gs_prog_data(prog_data); in emit_gs_thread_end()
1577 prog_data->curb_read_length = uniform_push_length + ubo_push_length; in assign_curb_setup()
1582 if (is_compute && brw_cs_prog_data(prog_data)->uses_inline_data) { in assign_curb_setup()
1723 assert(i < prog_data->curb_read_length); in assign_curb_setup()
1736 this->first_non_payload_grf = payload.num_regs + prog_data->curb_read_length; in assign_curb_setup()
1766 struct brw_wm_prog_data *prog_data, in calculate_urb_setup() argument
1770 memset(prog_data->urb_setup, -1, in calculate_urb_setup()
1771 sizeof(prog_data->urb_setup[0]) * VARYING_SLOT_MAX); in calculate_urb_setup()
[all …]
|
| D | brw_vec4_tcs.cpp | 40 struct brw_tcs_prog_data *prog_data, in vec4_tcs_visitor() argument
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->instances = nir->info.tess.tcs_vertices_out; in brw_compile_tcs()
408 prog_data->include_primitive_id = has_primitive_id; in brw_compile_tcs()
[all …]
|
| D | brw_fs_visitor.cpp | 92 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
151 assert(prog_data->urb_setup[location] >= 0); in per_primitive_reg()
153 const unsigned regnr = prog_data->urb_setup[location]; in per_primitive_reg()
[all …]
|
| D | brw_shader.cpp | 1330 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->base.urb_entry_size = ALIGN(output_size_bytes, 64) / 64; in brw_compile_tes()
1372 prog_data->base.urb_read_length = 0; in brw_compile_tes()
[all …]
|
| D | brw_private.h | 39 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,
|
| D | test_vec4_dead_code_eliminate.cpp | 39 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() argument
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()
|
| /third_party/mesa3d/src/gallium/drivers/iris/ |
| D | iris_disk_cache.c | 89 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_size); in iris_disk_cache_retrieve()
189 assembly = blob_read_bytes(&blob, prog_data->program_size); in iris_disk_cache_retrieve()
[all …]
|
| D | iris_program_cache.c | 162 u_upload_alloc(uploader, 0, shader->prog_data->program_size, 64, in iris_upload_shader()
165 memcpy(shader->map, assembly, shader->prog_data->program_size); in iris_upload_shader()
170 shader->prog_data->const_data_offset; in iris_upload_shader()
183 shader->prog_data, reloc_values, in iris_upload_shader()
214 *((void **) prog_data_out) = shader->prog_data; in iris_blorp_lookup_shader()
234 void *prog_data = ralloc_size(NULL, prog_data_size); in iris_blorp_upload_shader() local
235 memcpy(prog_data, prog_data_templ, prog_data_size); in iris_blorp_upload_shader()
244 iris_finalize_program(shader, prog_data, NULL, NULL, 0, 0, 0, &bt); in iris_blorp_upload_shader()
253 *((void **) prog_data_out) = shader->prog_data; in iris_blorp_upload_shader()
|
| /third_party/mesa3d/src/gallium/drivers/crocus/ |
| D | gen4_blorp_exec.h | 71 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->dispatch_16; in blorp_emit_wm_state()
[all …]
|
| D | crocus_disk_cache.c | 90 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->param = NULL; in crocus_disk_cache_retrieve()
184 if (prog_data->nr_params) { in crocus_disk_cache_retrieve()
[all …]
|
| D | crocus_program_cache.c | 190 struct brw_stage_prog_data *prog_data, in crocus_upload_shader() argument
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()
279 *((void **)prog_data_out) = shader->prog_data; in crocus_blorp_upload_shader()
344 shader->prog_data->program_size, NULL, stderr); in crocus_print_program_cache()
|
| /third_party/mesa3d/src/broadcom/compiler/ |
| D | vir.c | 666 struct v3d_prog_data *prog_data) in v3d_set_prog_data_uniforms() argument
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() argument
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->driver_location_map)); in v3d_vs_set_prog_data()
[all …]
|
| /third_party/mesa3d/src/gallium/drivers/v3d/ |
| D | v3d_disk_cache.c | 143 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.base, uint32_t, ulist_count); in v3d_disk_cache_retrieve()
178 memcpy(shader->prog_data.base->uniforms.data, ulist_data, ulist_data_size); in v3d_disk_cache_retrieve()
[all …]
|
| D | v3dx_draw.c | 377 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.vs, in v3d_emit_gl_shader_state()
[all …]
|
| D | v3d_program.c | 400 &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.fs->centroid_flags != in v3d_update_compiled_fs()
[all …]
|
| /third_party/mesa3d/src/intel/vulkan/ |
| D | anv_nir_compute_push_layout.c | 35 struct brw_stage_prog_data *prog_data, in anv_nir_compute_push_layout() argument
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->ubo_ranges[i]; in anv_nir_compute_push_layout()
244 prog_data->zero_push_reg |= BITFIELD64_RANGE(range_start_reg, in anv_nir_compute_push_layout()
[all …]
|
| D | anv_pipeline_cache.c | 81 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->num_relocs * in anv_shader_bin_serialize()
199 sizeof(shader->prog_data->relocs[0])); in anv_shader_bin_serialize()
[all …]
|
| /third_party/mesa3d/src/intel/blorp/ |
| D | blorp_genX_exec.h | 724 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()
[all …]
|