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

radv: remove unused radv_device parameter to few functions

Browse source 
Signed-off-by: Samuel Pitoiset <samuel.pitoiset@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/40375>
This commit is contained in:
Samuel Pitoiset 2026-03-12 12:45:18 +01:00 • committed by Marge Bot
parent 8d1e148c37
commit 744cedf3a1
3 changed files with 9 additions and 9 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

2
src/amd/vulkan/radv_cmd_buffer.c
View file

@ -12862,7 +12862,7 @@ radv_bind_graphics_shaders(struct radv_cmd_buffer *cmd_buffer)
struct radv_shader *gs = cmd_buffer->state.shaders[MESA_SHADER_GEOMETRY];
if (cmd_buffer->state.shaders[MESA_SHADER_GEOMETRY]->info.is_ngg) {
gfx10_ngg_set_esgs_ring_itemsize(device, &es->info, &gs->info, &gs->info.ngg_info);
gfx10_ngg_set_esgs_ring_itemsize(&es->info, &gs->info, &gs->info.ngg_info);
gfx10_get_ngg_info(device, &es->info, &gs->info, &gs->info.ngg_info);
radv_precompute_registers_hw_ngg(device, gs);
} else {

12
src/amd/vulkan/radv_shader_info.c
View file

@ -1250,8 +1250,8 @@ radv_get_pre_rast_input_topology(const struct radv_shader_info *es_info, const s
}
static unsigned
gfx10_get_ngg_vert_prim_lds_size(const struct radv_device *device, const struct radv_shader_info *es_info,
const struct radv_shader_info *gs_info, const struct gfx10_ngg_info *ngg_info)
gfx10_get_ngg_vert_prim_lds_size(const struct radv_shader_info *es_info, const struct radv_shader_info *gs_info,
const struct gfx10_ngg_info *ngg_info)
{
if (gs_info) {
const unsigned esgs_ring_lds_bytes = ngg_info->esgs_ring_size;
@ -1291,7 +1291,7 @@ gfx10_get_ngg_info(const struct radv_device *device, struct radv_shader_info *es
out->prim_amp_factor = gs_info ? gs_info->gs.vertices_out : 1;
const struct radv_shader_info *rinfo = gs_info ? gs_info : es_info;
out->lds_size = rinfo->ngg_lds_scratch_size + gfx10_get_ngg_vert_prim_lds_size(device, es_info, gs_info, out);
out->lds_size = rinfo->ngg_lds_scratch_size + gfx10_get_ngg_vert_prim_lds_size(es_info, gs_info, out);
unsigned workgroup_size = ac_compute_ngg_workgroup_size(info.hw_max_esverts, info.max_gsprims * gs_num_invocations,
info.max_out_verts, out->prim_amp_factor);
@ -1302,8 +1302,8 @@ gfx10_get_ngg_info(const struct radv_device *device, struct radv_shader_info *es
}
void
gfx10_ngg_set_esgs_ring_itemsize(const struct radv_device *device, struct radv_shader_info *es_info,
struct radv_shader_info *gs_info, struct gfx10_ngg_info *out)
gfx10_ngg_set_esgs_ring_itemsize(struct radv_shader_info *es_info, struct radv_shader_info *gs_info,
struct gfx10_ngg_info *out)
{
if (gs_info) {
out->vgt_esgs_ring_itemsize = es_info->esgs_itemsize / 4;
@ -1405,7 +1405,7 @@ radv_link_shaders_info(struct radv_device *device, struct radv_shader_stage *sta
radv_determine_ngg_settings(device, ngg_stage, fs_stage, gfx_state);
if (es_stage) {
gfx10_ngg_set_esgs_ring_itemsize(device, &es_stage->info, gs_stage ? &gs_stage->info : NULL,
gfx10_ngg_set_esgs_ring_itemsize(&es_stage->info, gs_stage ? &gs_stage->info : NULL,
&prerast_stage->info.ngg_info);
assert(es_stage->info.workgroup_size == 256);
}

4
src/amd/vulkan/radv_shader_info.h
View file

@ -341,8 +341,8 @@ void radv_get_legacy_gs_info(const struct radv_device *device, struct radv_shade
void gfx10_get_ngg_info(const struct radv_device *device, struct radv_shader_info *es_info,
struct radv_shader_info *gs_info, struct gfx10_ngg_info *out);
void gfx10_ngg_set_esgs_ring_itemsize(const struct radv_device *device, struct radv_shader_info *es_info,
struct radv_shader_info *gs_info, struct gfx10_ngg_info *out);
void gfx10_ngg_set_esgs_ring_itemsize(struct radv_shader_info *es_info, struct radv_shader_info *gs_info,
struct gfx10_ngg_info *out);
void radv_nir_shader_info_link(struct radv_device *device, const struct radv_graphics_state_key *gfx_state,
struct radv_shader_stage *stages);