pvr: Sequential dependency should be NONE for 0 constant shared regs.

Signed-off-by: Rajnesh Kanwal <rajnesh.kanwal@imgtec.com>
Reviewed-by: Frank Binns <frank.binns@imgtec.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/19371>
This commit is contained in:
Rajnesh Kanwal 2022-10-05 16:55:20 +05:00 committed by Marge Bot
parent 279c7c6d5a
commit 5055c182eb

View file

@ -3100,7 +3100,7 @@ static void pvr_compute_update_kernel(
.pds_data_offset = pipeline->state.primary_program.data_offset,
.pds_code_offset = pipeline->state.primary_program.code_offset,
.sd_type = PVRX(CDMCTRL_SD_TYPE_USC),
.sd_type = PVRX(CDMCTRL_SD_TYPE_NONE),
.usc_unified_size =
DIV_ROUND_UP(pipeline->state.shader.input_register_count << 2U,
@ -3135,6 +3135,9 @@ static void pvr_compute_update_kernel(
coeff_regs += pipeline->state.shader.const_shared_reg_count;
if (pipeline->state.shader.const_shared_reg_count > 0)
info.sd_type = PVRX(CDMCTRL_SD_TYPE_USC);
work_size =
pvr_compute_flat_pad_workgroup_size(pdevice, work_size, coeff_regs);