fdo-mirrors/mesa
1
0
Fork 0
mirror of https://gitlab.freedesktop.org/mesa/mesa.git synced 2026-01-06 02:20:11 +01:00
Code Issues Projects Releases Packages Wiki Activity Actions 1

pvr: Use the correct size for the unified store allocation

Browse source 
Signed-off-by: Karmjit Mahil <Karmjit.Mahil@imgtec.com>
Reviewed-by: Frank Binns <frank.binns@imgtec.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/24209>
This commit is contained in:
Karmjit Mahil 2023-07-14 13:36:46 +01:00 • committed by Marge Bot
parent 0137de917b
commit 0ba29bf641
3 changed files with 3 additions and 1 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

2
src/imagination/vulkan/pvr_cmd_buffer.c
View file

@ -4425,7 +4425,7 @@ void pvr_compute_update_kernel_private(
.sd_type = PVRX(CDMCTRL_SD_TYPE_NONE),
.usc_unified_size =
DIV_ROUND_UP(pipeline->coeff_regs_count << 2U,
DIV_ROUND_UP(pipeline->unified_store_regs_count << 2U,
PVRX(CDMCTRL_KERNEL0_USC_UNIFIED_SIZE_UNIT_SIZE)),
/* clang-format off */

1
src/imagination/vulkan/pvr_private.h
View file

@ -1001,6 +1001,7 @@ struct pvr_private_compute_pipeline {
uint32_t pds_data_size_dw;
uint32_t pds_temps_used;
uint32_t coeff_regs_count;
uint32_t unified_store_regs_count;
VkExtent3D workgroup_size;
/* Used by pvr_compute_update_shared_private(). */

1
src/imagination/vulkan/pvr_query_compute.c
View file

@ -553,6 +553,7 @@ VkResult pvr_add_query_program(struct pvr_cmd_buffer *cmd_buffer,
pipeline.pds_temps_used = query_prog->primary_num_temps;
pipeline.coeff_regs_count = shader_factory_info->coeff_regs;
pipeline.unified_store_regs_count = shader_factory_info->input_regs;
pipeline.const_shared_regs_count = shader_factory_info->const_shared_regs;
const_buffer = vk_alloc(&cmd_buffer->vk.pool->alloc,