diff options
| author | Simon Perretta <simon.perretta@imgtec.com> | 2023-10-05 20:55:15 +0100 |
|---|---|---|
| committer | Frank Binns <frank.binns@imgtec.com> | 2023-10-31 15:33:01 +0000 |
| commit | fcc21bea41d6561ffa1b7bafa326d69c4fd1dd1b (patch) | |
| tree | cc9d8fe95cc9af4c8c40690d9fb0664181fba9ea | |
| parent | f102f454192f7839fa247583621dd8fcd657f2bc (diff) | |
pvr: pass uses_barrier flag, disable allocation starvation
Signed-off-by: Simon Perretta <simon.perretta@imgtec.com>
| -rw-r--r-- | src/imagination/vulkan/pvr_cmd_buffer.c | 6 |
1 files changed, 3 insertions, 3 deletions
diff --git a/src/imagination/vulkan/pvr_cmd_buffer.c b/src/imagination/vulkan/pvr_cmd_buffer.c index 8439e737a2a..c4beeadc22a 100644 --- a/src/imagination/vulkan/pvr_cmd_buffer.c +++ b/src/imagination/vulkan/pvr_cmd_buffer.c @@ -4395,7 +4395,7 @@ void pvr_compute_update_kernel_private( pipeline->workgroup_size.depth; uint32_t coeff_regs; - if (work_size > ROGUE_MAX_INSTANCES_PER_TASK) { + if (work_size > ROGUE_MAX_INSTANCES_PER_TASK && false) { /* Enforce a single workgroup per cluster through allocation starvation. */ coeff_regs = dev_runtime_info->cdm_max_local_mem_size_regs; @@ -4477,7 +4477,7 @@ static void pvr_compute_update_kernel( uint32_t work_size = shader_state->work_size; uint32_t coeff_regs; - if (work_size > ROGUE_MAX_INSTANCES_PER_TASK) { + if (work_size > ROGUE_MAX_INSTANCES_PER_TASK && false) { /* Enforce a single workgroup per cluster through allocation starvation. */ coeff_regs = dev_runtime_info->cdm_max_local_mem_size_regs; @@ -4504,7 +4504,7 @@ static void pvr_compute_update_kernel( info.local_size[2] = 1U; info.max_instances = - pvr_compute_flat_slot_size(pdevice, coeff_regs, false, work_size); + pvr_compute_flat_slot_size(pdevice, coeff_regs, shader_state->uses_barrier, work_size); pvr_compute_generate_control_stream(csb, sub_cmd, &info); } |