AlexIndustrial/mesa
1
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
209,460 Commits 1 Branch 0 Tags
77f2b9bcc3011ec1101ac3e4d85e2af8f0d7c637
Commit Graph

209460 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Eric Engestrom 77f2b9bcc3 iris/ci: drop already included skip list 
It matches `$DRIVER_NAME-skips.txt`.

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:07 +00:00
Eric Engestrom e43ab3fab7 anv/ci: drop already included skip list 
It matches `$GPU_VERSION-skips.txt`.

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:07 +00:00
Eric Engestrom eee467f78a broadcom/ci: drop redundant HWCI_TEST_SCRIPT already set by .broadcom-test 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:06 +00:00
Eric Engestrom fb32b79550 broadcom/ci: drop redundant script: already set by .broadcom-test 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:05 +00:00
Eric Engestrom a4dc14dedc turnip/ci: drop redundant GPU_VERSION 
It's already set by `.a750-mupuf`.

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:05 +00:00
Eric Engestrom d40438031c radv/ci: deduplicate GPU_VERSION in ci-tron jobs 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:04 +00:00
Eric Engestrom 84ca8c54f7 radv/ci: deduplicate DEQP_SUITE: radv-valve in ci-tron jobs 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:03 +00:00
Eric Engestrom a484a2d868 ci-tron: set SCRIPTS_DIR where its path is defined 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:02 +00:00
Eric Engestrom b53723d2a4 ci-tron: cleanup redundancy in artifacts exclude variable 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:02 +00:00
Eric Engestrom 3752723a78 ci-tron: drop unnecessary HWCI_TEST_SCRIPT: deqp-runner.sh re-defines 
This is already the default for ci-tron jobs.

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:01 +00:00
Eric Engestrom e95e8fca2b ci-tron: set pipefail to show the correct error message when failing to download the install tarball 
This requires `bash` as posix `sh` doesn't have that option.

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:01 +00:00
Karol Herbst c2c0e13b78 nak: optimize load_subgroup_id 
If a dimension in workgroup_size is 1 we can simply emit a 0 instead of
loading a system value. Helps a couple of compute shaders.

Totals:
CodeSize: 934788544 -> 934788048 (-0.00%)
Static cycle count: 222856984 -> 222856908 (-0.00%)

Totals from 8 (0.01% of 87622) affected shaders:
CodeSize: 34992 -> 34496 (-1.42%)
Static cycle count: 8593 -> 8517 (-0.88%)

Reviewed-by: Faith Ekstrand <faith.ekstrand@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36428>
 2025-07-30 23:03:19 +00:00
Alejandro Piñeiro fa8731b859 broadcom/compiler: update compact arrays comment 
PIPE_CAP_NIR_COMPACT_ARRAYS is gone since commit
2e5d49b3dd

v3d properly uses the compact_arrays option from
nir_shader_compiler_options since commit
d694c1b094

Reviewed-by: Juan A. Suarez <jasuarez@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36446>
 2025-07-30 22:45:33 +00:00
Alyssa Rosenzweig 4f1bafa6d5 nir: drop load_sample_id_no_per_sample 
unused now.

Signed-off-by: Alyssa Rosenzweig <alyssa@rosenzweig.io>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36429>
 2025-07-30 22:13:23 +00:00
Alyssa Rosenzweig 04be5a8910 nir/lower_system_values: simplify load_helper_invocation lowering 
The two backends (ir3, dxil) using the lowering have
info->fs.uses_sample_shading matching set when sample shading is used -- the VK
drivers pass the rasterization state flag into the compiler, while
freedreno and d3d12 have caps->force_persample_interp so the frontend
creates a shader variant with info->fs.uses_sample_shading set.

This means that we can drop the sample-id SHL/AND in the pixel-rate
shading case, which in turn means that drivers don't need to have a
load_sample_id() that doesn't trigger sample-rate shading (which Adreno
doesn't have).

Signed-off-by: Alyssa Rosenzweig <alyssa@rosenzweig.io>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36429>
 2025-07-30 22:13:23 +00:00
Emma Anholt ceaa8de981 tu: Implement sampleShadingEnable by flagging uses_sample_shading. 
This will unblock getting correct helper invocation lowering without
forcing sample shading, by correctly setting NIR's uses_sample_shading
whenever it should be active.

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36429>
 2025-07-30 22:13:23 +00:00
Emma Anholt cfeedd2025 freedreno: Drop min_samples handling code. 
The frontend already does it for us based on
!caps->force_persample_interp, and the caller in util_blitter also handles
things through per-sample interpolation.

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36429>
 2025-07-30 22:13:23 +00:00
Emma Anholt c1392168e5 tu: Rename per_samp to sample_shading to match ir3. 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36429>
 2025-07-30 22:13:23 +00:00
Emma Anholt 6e0e6b0caf ir3: Rename per_samp to sample_shading. 
per_samp ("do sample shading") was confusing compared to has_per_samp
("shader key has some flags per texture sampler to inspect").

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36429>
 2025-07-30 22:13:23 +00:00
Eric Engestrom 5f3050e967 docs: add sha sum for 25.1.7 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36477>
 2025-07-30 20:43:32 +00:00
Eric Engestrom 8a1de6a5b4 docs: add release notes for 25.1.7 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36477>
 2025-07-30 20:43:32 +00:00
Eric Engestrom ae2daad127 docs: update calendar for 25.1.7 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36477>
 2025-07-30 20:43:31 +00:00
Eric Engestrom 803ef8b783 docs: update calendar for 25.2.0-rc3 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36476>
 2025-07-30 20:38:49 +00:00
Mike Blumenkrantz dedfb5ef78 zink: trigger multi-context buffer invalidate on internal buffer invalidate 
this is the same as zink_context_replace_buffer_storage()

cc: mesa-stable

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36473>
 2025-07-30 20:20:15 +00:00
Mike Blumenkrantz f1ba8f44d9 zink: fix tc buffer replacement rebind condition 
this check is to detect multi-context rebinds, not to determine whether
all rebinds on the same context were successful

cc: mesa-stable

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36473>
 2025-07-30 20:20:15 +00:00
Mike Blumenkrantz b4280887ed zink: check for multi-context image/buffer rebinds during dispatch 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36473>
 2025-07-30 20:20:14 +00:00
Mike Blumenkrantz 1c5e5aa4eb zink: also add access stage sync when rebinding buffers 
cc: mesa-stable

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36473>
 2025-07-30 20:20:14 +00:00
Jason Macnak 72d07c16a3 gfxstream: Add gfxstream TLS connection manager reset 
... which is still needed to keep the end2end tests happy
when one thread creates and destroys instances multiple times
(which happens in the MultiThreadedShutdown test).

Test: GfxstreamEnd2EndTests
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36471>
 2025-07-30 19:41:14 +00:00
Thomas H.P. Andersen b08a23550f zink: do not overwrite existing error for miptail on uncommit 
a7f86e38ca added the call to
sparse_backing_free. It reuses the ok variable and overwrites the
existing value

Fixes: a7f86e38ca
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36467>
 2025-07-30 19:19:05 +00:00
Caio Oliveira f2a49081de brw: Use ralloc helpers for string handling in brw_eu_validate 
Acked-by: Matt Turner <mattst88@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36339>
 2025-07-30 17:59:26 +00:00
Eric R. Smith 904a4ab364 panvk: use minimum attachment size for frame buffer size 
We were using the maximum of all attachment sizes as the bounding box
for the frame buffer. But in fact we want the minimum, as we do not
want to draw outside of any attachment boundaries.

Reviewed-by: Lars-Ivar Hesselberg Simonsen <lars-ivar.simonsen@arm.com>
Reviewed-by: Mary Guillemard <mary.guillemard@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36360>
 2025-07-30 17:00:13 +00:00
Job Noorman 326baef472 ir3/a750: don't allocate const space for primitive_param/map 
These are lowered to UBOs on a750.

Totals from 6243 (3.79% of 164705) affected shaders:
CodeSize: 7820588 -> 7819720 (-0.01%); split: -0.01%, +0.00%
Preamble Instrs: 799947 -> 799511 (-0.05%); split: -0.06%, +0.00%
Constlen: 400268 -> 375072 (-6.29%)

Signed-off-by: Job Noorman <jnoorman@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36460>
 2025-07-30 16:05:15 +00:00
Job Noorman f95a62897c tu: add constlen shader stat 
Signed-off-by: Job Noorman <jnoorman@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36460>
 2025-07-30 16:05:15 +00:00
Caio Oliveira dde6fa5728 spirv: Implement SPV_KHR_untyped_pointers 
The untyped pointer types only have a storage class associated, and the
operations using them would carry the necessary "data type" information.

Untyped pointers themselves are identified by "vtn_type::pointed" being
NULL.  For the NIR lowering the operations will have explicit casts
before them when applicable and the nir_derefs representing untyped
pointers will use the "void" glsl_type.

Reviewed-by: Faith Ekstrand <faith.ekstrand@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36427>
 2025-07-30 15:35:33 +00:00
Caio Oliveira 8eaf1dced0 spirv: Load block descriptors as soon as we hit them 
With changes suggested by Faith.

Reviewed-by: Faith Ekstrand <faith.ekstrand@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36427>
 2025-07-30 15:35:33 +00:00
Faith Ekstrand d1be63c355 spirv: Assert that vtn_pointer_to_deref() doesn't return NULL 
There are a few things that could cause us to return NULL here and we
should just fail to parse the SPIR-V if that ever happens instead of
crashing when someone tries to access it.

Reviewed-by: Caio Oliveira <caio.oliveira@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36427>
 2025-07-30 15:35:32 +00:00
Faith Ekstrand 8a993cf900 spirv: Simplify pointer_to/from_ssa a bit 
This adds a vtn_pointer_ssa_is_desc_index() helper and makes both
to/from_ssa work in terms of it, ensuring we never screw up the
condition and turn a deref into a block index or vice versa.

Reviewed-by: Caio Oliveira <caio.oliveira@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36427>
 2025-07-30 15:35:31 +00:00
Faith Ekstrand df8ee49bc6 spirv: Drop block_index/offset pointers 
These haven't existed in a while but the vtn_pointer fields stayed
around.  Drop offset since no one uses it and rename block_index to
desc_idx with a better comment.

Reviewed-by: Caio Oliveira <caio.oliveira@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36427>
 2025-07-30 15:35:31 +00:00
Faith Ekstrand 46d02bd244 spirv: Assert !ptr_as_array for blocks and acceleration structures 
As of ea9deafff4 ("spirv: Add more restrictions around Blocks"), this
case can't happen.

Reviewed-by: Caio Oliveira <caio.oliveira@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36427>
 2025-07-30 15:35:30 +00:00
Corentin Noël a11f2f80b6 virgl: Stop using deprecated util_framebuffer_init 
Introduce a new virgl_framebuffer_state to be able to store surface handles
directly.

Signed-off-by: Corentin Noël <corentin.noel@collabora.com>
Reviewed-by: Gert Wollny <gert.wollny@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/35681>
 2025-07-30 10:17:21 +00:00
Juan A. Suarez Romero 6596cf08e4 v3d: implement robust buffer access 
This is the last piece to expose KHR_robustness. The main bulk of the
job is done already in the broadcom compiler through lowerings, so we
only need to set the proper key in order to enable the robustness.

Signed-off-by: Juan A. Suarez Romero <jasuarez@igalia.com>
Reviewed-by: Jose Maria Casanova Crespo <jmcasanova@igalia.com>
Reviewed-by: Iago Toral Quiroga <itoral@igalia.com>
Reviewed-by: Maíra Canal <mcanal@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/35965>
 2025-07-30 11:28:19 +02:00
Juan A. Suarez Romero 7c5ef9de02 v3d: handle QUNIFORM_GET_UBO_SIZE 
This uniform will be used when creating context with robust buffer
access.

Signed-off-by: Juan A. Suarez Romero <jasuarez@igalia.com>
Reviewed-by: Jose Maria Casanova Crespo <jmcasanova@igalia.com>
Reviewed-by: Iago Toral Quiroga <itoral@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/35965>
 2025-07-30 11:26:20 +02:00
Juan A. Suarez Romero 2d47bec557 v3d: implement get device reset status 
This implements supports for GPU reset notifications, which is part of
the KHR_robustness extension.

It requires support from kernel in order to expose it.

Signed-off-by: Juan A. Suarez Romero <jasuarez@igalia.com>
Reviewed-by: Jose Maria Casanova Crespo <jmcasanova@igalia.com>
Reviewed-by: Iago Toral Quiroga <itoral@igalia.com>
Reviewed-by: Maíra Canal <mcanal@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/35965>
 2025-07-30 11:26:20 +02:00
Juan A. Suarez Romero 99c5915b56 broadcom/simulator: add support for GPU reset counters 
As this is a simulator, it will always report no reset.

Signed-off-by: Juan A. Suarez Romero <jasuarez@igalia.com>
Reviewed-by: Jose Maria Casanova Crespo <jmcasanova@igalia.com>
Reviewed-by: Iago Toral Quiroga <itoral@igalia.com>
Reviewed-by: Maíra Canal <mcanal@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/35965>
 2025-07-30 11:26:20 +02:00
Juan A. Suarez Romero 40a937407a broadcom: check for GPU reset counters support 
This checks if kernel supports GPU reset counters, which are actually
two counters: one for resets caused by current context, and another one
for resets caused in general.

Signed-off-by: Juan A. Suarez Romero <jasuarez@igalia.com>
Reviewed-by: Jose Maria Casanova Crespo <jmcasanova@igalia.com>
Reviewed-by: Iago Toral Quiroga <itoral@igalia.com>
Reviewed-by: Maíra Canal <mcanal@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/35965>
 2025-07-30 11:26:20 +02:00
Juan A. Suarez Romero d94114c1d2 drm-uapi: update v3d_drm.h for reset counters 
Taken from commits 5774b3cf and 769c153c of drm-misc-next kernel tree.

Signed-off-by: Juan A. Suarez Romero <jasuarez@igalia.com>
Reviewed-by: Maíra Canal <mcanal@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/35965>
 2025-07-30 11:26:20 +02:00
Juan A. Suarez Romero 2188994c81 broadcom: remove obvious comment 
It is obvious that we check the return value to see if kernel supports
the feature, so no need to add a comment.

Signed-off-by: Juan A. Suarez Romero <jasuarez@igalia.com>
Reviewed-by: Iago Toral Quiroga <itoral@igalia.com>
Reviewed-by: Maíra Canal <mcanal@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/35965>
 2025-07-30 11:26:19 +02:00
David Rosca f4436d606e radeonsi: Add missing DEBUG_NAMED_VALUE_END to radeonsi_shader_debug_options 
AddressSanitizer: global-buffer-overflow ../src/util/u_debug.c:331 in debug_parse_flags_option

Fixes: 5c92fe45a1 ("radeonsi: support more than 64 options for AMD_DEBUG")
Reviewed-by: Qiang Yu <yuq825@gmail.com>
Reviewed-by: Marek Olšák <marek.olsak@amd.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36434>
 2025-07-30 08:33:10 +00:00
Lionel Landwerlin 60932e8fae brw: always ensure coarse pixel is disabled on Gfx9 
No HW support there.

Signed-off-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Reviewed-by: Ivan Briano <ivan.briano@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36457>
 2025-07-30 07:57:19 +00:00
Lionel Landwerlin aa6810b706 brw: consider LOAD_PAYLOAD fully defined 
It's mostly used for SEND messages and fully defines the register data
(that's its purpose after all).

Signed-off-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Reviewed-by: Ivan Briano <ivan.briano@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36457>
 2025-07-30 07:57:19 +00:00