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

gallium: remove pipe_compute_caps::images_supported

Browse source 
Acked-by: Mike Blumenkrantz <michael.blumenkrantz@gmail.com>
Reviewed-by: Marek Olšák <marek.olsak@amd.com>
Reviewed-by: Alyssa Rosenzweig <alyssa@rosenzweig.io>
Reviewed-by: Mary Guillemard <mary.guillemard@collabora.com>
Reviewed-by: Jose Maria Casanova Crespo <jmcasanova@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/34623>
This commit is contained in:
Karol Herbst 2025-04-20 17:15:14 +02:00
parent 9d73da9155
commit 44051e6fbd
11 changed files with 0 additions and 16 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

2
docs/gallium/screen.rst
View file

@ -778,8 +778,6 @@ pipe_screen::get_compute_param.
inside a block. Non 0 indicates support for OpenCL subgroups including
implementing ``get_compute_state_subgroup_size`` if multiple subgroup sizes
are supported.
* ``pipe_compute_caps.images_supported``: Whether images are supported
non-zero means yes, zero means no
* ``pipe_compute_caps.subgroup_sizes``: Ored power of two sizes of a basic execution
unit in threads. Also known as wavefront size, warp size or SIMD width.
E.g. ``64 | 32``.

2
src/gallium/drivers/asahi/agx_pipe.c
View file

@ -1951,8 +1951,6 @@ agx_init_compute_caps(struct pipe_screen *pscreen)
caps->max_compute_units = agx_get_num_cores(dev);
caps->images_supported = true;
caps->subgroup_sizes = 32;
caps->max_variable_threads_per_block = 1024; // TODO

2
src/gallium/drivers/crocus/crocus_screen.c
View file

@ -222,8 +222,6 @@ crocus_init_compute_caps(struct crocus_screen *screen)
/* MaxComputeSharedMemorySize */
caps->max_local_size = 64 * 1024;
caps->images_supported = true;
caps->subgroup_sizes = ELK_SUBGROUP_SIZE;
caps->max_variable_threads_per_block = max_invocations;

2
src/gallium/drivers/freedreno/freedreno_screen.c
View file

@ -344,8 +344,6 @@ fd_init_compute_caps(struct fd_screen *screen)
caps->max_compute_units = 9999; // TODO
caps->images_supported = true;
caps->subgroup_sizes = 32; // TODO
caps->max_variable_threads_per_block = compiler->max_variable_workgroup_size;

2
src/gallium/drivers/iris/iris_screen.c
View file

@ -269,8 +269,6 @@ iris_init_compute_caps(struct iris_screen *screen)
/* MaxComputeSharedMemorySize */
caps->max_local_size = 64 * 1024;
caps->images_supported = true;
caps->subgroup_sizes = 32 | 16 | 8;
caps->max_subgroups = devinfo->max_cs_workgroup_threads;

1
src/gallium/drivers/llvmpipe/lp_screen.c
View file

@ -182,7 +182,6 @@ llvmpipe_init_compute_caps(struct pipe_screen *screen)
caps->max_mem_alloc_size = 1 << 31;
caps->max_private_size = 1 << 31;
caps->max_input_size = 1576;
caps->images_supported = !!LP_MAX_TGSI_SHADER_IMAGES;
caps->subgroup_sizes = lp_native_vector_width / 32;
caps->max_subgroups = 1024 / (lp_native_vector_width / 32);
caps->max_compute_units = 8;

1
src/gallium/drivers/nouveau/nvc0/nvc0_screen.c
View file

@ -179,7 +179,6 @@ nvc0_init_compute_caps(struct nvc0_screen *screen)
caps->max_private_size = 512 << 10; /* l[] */
caps->max_input_size = 4096; /* c[], arbitrary limit */
caps->subgroup_sizes = 32;
caps->images_supported = !!NVC0_MAX_IMAGES;
caps->max_compute_units = screen->mp_count_compute;
caps->max_clock_frequency = 512; /* FIXME: arbitrary limit */
caps->address_bits = 64;

1
src/gallium/drivers/panfrost/pan_screen.c
View file

@ -459,7 +459,6 @@ panfrost_init_compute_caps(struct panfrost_screen *screen)
caps->max_input_size = 4096;
caps->max_clock_frequency = 800; /* MHz -- TODO */
caps->max_compute_units = dev->core_count;
caps->images_supported = true;
caps->subgroup_sizes = pan_subgroup_size(dev->arch);
caps->max_variable_threads_per_block = 1024; // TODO
}

1
src/gallium/drivers/v3d/v3d_screen.c
View file

@ -227,7 +227,6 @@ v3d_init_compute_caps(struct v3d_screen *screen)
caps->max_mem_alloc_size = MIN2(V3D_MAX_BUFFER_RANGE, si.totalram);
caps->max_compute_units = 1;
caps->images_supported = true;
caps->subgroup_sizes = 16;
}

1
src/gallium/drivers/zink/zink_screen.c
View file

@ -669,7 +669,6 @@ zink_init_compute_caps(struct zink_screen *screen)
caps->max_local_size =
screen->info.props.limits.maxComputeSharedMemorySize;
caps->images_supported = true;
caps->subgroup_sizes = screen->info.props11.subgroupSize;
caps->max_mem_alloc_size = screen->clamp_video_mem;
caps->max_global_size = screen->total_video_mem;

1
src/gallium/include/pipe/p_defines.h
View file

@ -806,7 +806,6 @@ struct pipe_compute_caps {
unsigned max_variable_threads_per_block;
uint64_t max_mem_alloc_size;
uint64_t max_global_size;
bool images_supported;
};
struct pipe_caps {