From 5055c182ebf01ce3020daaf52626b501b29e6267 Mon Sep 17 00:00:00 2001 From: Rajnesh Kanwal Date: Wed, 5 Oct 2022 16:55:20 +0500 Subject: [PATCH] pvr: Sequential dependency should be NONE for 0 constant shared regs. Signed-off-by: Rajnesh Kanwal Reviewed-by: Frank Binns Part-of: --- src/imagination/vulkan/pvr_cmd_buffer.c | 5 ++++- 1 file changed, 4 insertions(+), 1 deletion(-) diff --git a/src/imagination/vulkan/pvr_cmd_buffer.c b/src/imagination/vulkan/pvr_cmd_buffer.c index 878b9c0..763a535 100644 --- a/src/imagination/vulkan/pvr_cmd_buffer.c +++ b/src/imagination/vulkan/pvr_cmd_buffer.c @@ -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); -- 2.7.4