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
209475 commits 66 branches 933 tags 964 MiB
Commit graph

209475 commits

This branch
This branch
All branches
Author SHA1 Message Date
Lionel Landwerlin
9efb3ee511 anv: fix wsi image aliasing 
The private BO can get removed due to WSI aliasing and that breaks the
submission code (expecting one).

Delay the registration on the device to when the image actually gets
bound and there is a private BO.

Fixes: b21e62b71a ("anv: avoid leaking private binding for aliased wsi image")
Reviewed-by: Yiwei Zhang <zzyiwei@chromium.org>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36474>
 2025-07-31 07:48:23 +00:00
Job Noorman
19d2f5e086 freedreno/a7xx: disable consts_ubo upload
Some checks are pending
macOS-CI / macOS-CI (dri) (push) Waiting to run
Details
macOS-CI / macOS-CI (xlib) (push) Waiting to run
Details 
consts_ubo is treated as any UBO on a7xx and loaded to the const file
via the preamble.

Signed-off-by: Job Noorman <jnoorman@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36470>
 2025-07-31 06:03:41 +00:00
Job Noorman
0abaae5a39 tu: remove consts_ubo upload code 
consts_ubo is now treated as any UBO and loaded to the const file via
the preamble.

Signed-off-by: Job Noorman <jnoorman@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36470>
 2025-07-31 06:03:41 +00:00
Job Noorman
bd58347769 ir3: treat consts_ubo as normal UBO 
Lowering UBO ranges to the const file happens via the preamble on
turnip (all gens) and freedreno (a7xx+). The only exception is the
consts_ubo, which is uploaded to the const file via CP.

Make this more consistent, and remove some special-casing code, by
treating consts_ubo as any other UBO.

Signed-off-by: Job Noorman <jnoorman@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36470>
 2025-07-31 06:03:41 +00:00
Guilherme Gallo
5ad4e6d3d1 ci/panfrost: Disable DUTs under maintenance
Some checks are pending
macOS-CI / macOS-CI (dri) (push) Waiting to run
Details
macOS-CI / macOS-CI (xlib) (push) Waiting to run
Details 
Collabora's farm 2025-07-31 maintenance will make the following DUTs
offline for a few hours:
  - rk3288-veyron-jaq
  - sun50i-h6-pine-h64

So let's disable them before it blocks the pipelines.

----

Planned downtime for those DUTs in the farm:

Start: 2025-07-31 08:00 BST
End: 2025-07-31 10:00 BST

Signed-off-by: Guilherme Gallo <guilherme.gallo@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36480>
 2025-07-30 22:19:52 -03:00
Eric Engestrom
fdcad6e547 meson: include VkLayer_MESA_anti_lag in the devenv
Some checks are pending
macOS-CI / macOS-CI (dri) (push) Waiting to run
Details
macOS-CI / macOS-CI (xlib) (push) Waiting to run
Details 
See https://github.com/KhronosGroup/Vulkan-Loader/blob/main/docs/LoaderLayerInterface.md#linux-layer-discovery

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36346>
 2025-07-30 23:53:51 +00:00
Eric Engestrom
55d5c3dd8f meson: include VkLayer_MESA_vram_report_limit in the devenv 
See https://github.com/KhronosGroup/Vulkan-Loader/blob/main/docs/LoaderLayerInterface.md#linux-layer-discovery

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36346>
 2025-07-30 23:53:51 +00:00
Eric Engestrom
56c910aafc meson: include VkLayer_MESA_screenshot in the devenv 
See https://github.com/KhronosGroup/Vulkan-Loader/blob/main/docs/LoaderLayerInterface.md#linux-layer-discovery

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36346>
 2025-07-30 23:53:51 +00:00
Eric Engestrom
45789ac396 meson: fix VkLayer_MESA_device_select in the devenv 
It's an implicit layer, not an explicit one like the others in that MR,
which I missed in the previous commit.

Fixes: 294d8ce80a ("meson: include VkLayer_MESA_device_select in the devenv")
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36346>
 2025-07-30 23:53:51 +00:00
Eric Engestrom
dd15dbae4b ci/prepare-artifacts: turn file copies into a loop 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:11 +00:00
Eric Engestrom
e7102511b0 ci/prepare-artifacts: drop redundant copy 
`fossilize-runner.sh` is already matched by `*-runner.sh`.

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:11 +00:00
Eric Engestrom
bf87c6522b ci/prepare-artifacts: move git version dump out of static file copy block 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:10 +00:00
Eric Engestrom
cd89b49f6a ci/deqp-runner: fix path to install folder 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:10 +00:00
Eric Engestrom
6d5f17371c llvmpipe/ci: set DRIVER_NAME to not have to manually add llvmpipe-skips.txt in asan job variant 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:09 +00:00
Eric Engestrom
4b4e1a81b9 nouveau/ci: drop already included *-skips.tx 
`all-skips.txt` is always included, and `nouveau-gm20b-skips.txt`
matches `$GPU_VERSION-skips.txt`.

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36354>
 2025-07-30 23:18:08 +00:00
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
Some checks are pending
macOS-CI / macOS-CI (dri) (push) Waiting to run
Details
macOS-CI / macOS-CI (xlib) (push) Waiting to run
Details 
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
Some checks are pending
macOS-CI / macOS-CI (dri) (push) Waiting to run
Details
macOS-CI / macOS-CI (xlib) (push) Waiting to run
Details 
... 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
Some checks are pending
macOS-CI / macOS-CI (dri) (push) Waiting to run
Details
macOS-CI / macOS-CI (xlib) (push) Waiting to run
Details 
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