-
4f5c1c6c
by Dylan Baker at 2025-11-07T08:14:36-08:00
.pick_status.json: Update to 04a0d512fa68a48bc2a2632a0a4ff2c3ac10c6ca
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
e9f677df
by Sagar Ghuge at 2025-11-07T08:14:38-08:00
anv: Use correct engine class for companion RCS
Fixes: 6f138fe7235 ("anv: avoid null pointer access in utrace copies on CCS")
Signed-off-by: Sagar Ghuge <sagar.ghuge@intel.com>
Reviewed-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
(cherry picked from commit 43d98a3f1a4ec7d199b933de9e9c3675efc87710)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
8eec2395
by Samuel Pitoiset at 2025-11-07T08:14:40-08:00
aco: fix reserving VGPRs for 64-bit attributes in VS prologs
Otherwise the fetch index would be overwritten if the attribute format
is 64-bit and more than 2 components are loaded.
Cc: mesa-stable
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14242
Signed-off-by: Samuel Pitoiset <samuel.pitoiset@gmail.com>
(cherry picked from commit ba5bf81aa29e7bb1f688ff8f0aa016ecaa9c1b1d)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
e817b525
by Samuel Pitoiset at 2025-11-07T08:14:41-08:00
radv,aco: wait for all VMEM loads when the prolog loads large 64-bit attributes
Not the most optimal solution but 64-bit vertex attributes are rarely
used. Could still revisit if we find a real use case that matters.
This fixes recent VKCTS coverage:
dEQP-VK.pipeline.fast_linked_library.vertex_input.component_mismatch.r64g64b64.*_to_dvec2
dEQP-VK.pipeline.shader_object_.*.vertex_input.component_mismatch.r64g64b64.*_to_dvec2
Cc: mesa-stable
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14243
Signed-off-by: Samuel Pitoiset <samuel.pitoiset@gmail.com>
(cherry picked from commit a0d607bfdb10761e7c1c9889a8ddb49fb1a0e1e6)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
3d9d9ca0
by Yiwei Zhang at 2025-11-07T08:14:41-08:00
llvmpipe: zero is also a valid fd
Fixes: a062544d3d0 ("llvmpipe: Use an anonymous file for memory allocations")
Reviewed-by: Christian Gmeiner <cgmeiner@igalia.com>
(cherry picked from commit 3a655c212b1b39e02cb85a11738c3c60131e3927)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
36aff345
by Yiwei Zhang at 2025-11-07T08:14:42-08:00
llvmpipe: fix udmabuf mmap error check
Upon failing to mmap, MAP_FAILED (void *)-1 is returned instead of NULL.
Fixes: d74ea2c117f ("llvmpipe: Implement dmabuf handling")
Reviewed-by: Christian Gmeiner <cgmeiner@igalia.com>
(cherry picked from commit 3e07f57d4ad7dcc85690de9f595a94ef9ad3fae1)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
eface4be
by Yiwei Zhang at 2025-11-07T08:14:42-08:00
llvmpipe: add a missing alloc error handling in fd import
Fixes: d74ea2c117f ("llvmpipe: Implement dmabuf handling")
Suggested-by: Christian Gmeiner <cgmeiner@igalia.com>
(cherry picked from commit 66414c6b70cfb2c1b815342af958a578e7f17ac7)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
e96e71fb
by Yiwei Zhang at 2025-11-07T08:14:43-08:00
llvmpipe: misc fixes for sparse binding
This change:
1. Move size validation within sparse binding, but not escape to
non-sparse code path.
2. Error out if sparse is requested on unsupported platforms.
Fixes: d747c4a8746 ("lavapipe: Implement sparse buffers and images")
Reviewed-by: Christian Gmeiner <cgmeiner@igalia.com>
(cherry picked from commit e0acc5c2b47630efd55f0f427cc515125c24af25)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
7fb0030c
by David Rosca at 2025-11-07T08:14:44-08:00
radeonsi/vcn: Fix AV1 bidir compound encode with order_hint disabled
Cc: mesa-stable
Reviewed-by: Benjamin Cheng <benjamin.cheng@amd.com>
(cherry picked from commit 1a8a8db8c50692e345bc05572e409c10e8d44027)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
3a633555
by David Rosca at 2025-11-07T08:14:44-08:00
radv/video: Don't require encode FW version >= interface version
Otherwise this breaks backwards compatibility when bumping interface
version for new features.
Cc: mesa-stable
Reviewed-by: Benjamin Cheng <benjamin.cheng@amd.com>
(cherry picked from commit 96db490318f0852aaf01b1f23a4a82a8574f4126)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
3f169d14
by David Rosca at 2025-11-07T08:14:45-08:00
radv/video: Fix AV1 bidir compound encode with order_hint disabled
Cc: mesa-stable
Reviewed-by: Benjamin Cheng <benjamin.cheng@amd.com>
(cherry picked from commit bcb6e6b6e6441f799099be43f579f23a164e2a08)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
4b46e872
by Georg Lehmann at 2025-11-07T08:14:45-08:00
aco/gfx10_3: work around NSA hazard
4+ dword NSA can hang if exec becomes non-zero again directly before
the instruction.
Foz-DB Navi21:
Totals from 608 (0.74% of 82161) affected shaders:
Instrs: 945138 -> 946431 (+0.14%)
CodeSize: 5171580 -> 5176864 (+0.10%)
Latency: 13356895 -> 13357113 (+0.00%)
InvThroughput: 3043234 -> 3043236 (+0.00%); split: -0.00%, +0.00%
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/9852
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/13981
Cc: mesa-stable
Reviewed-by: Timur Kristóf <timur.kristof@gmail.com>
Reviewed-by: Daniel Schürmann <daniel@schuermann.dev>
(cherry picked from commit b2172467d1aa1997a18a711fdf0bbc9d95b5aaac)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
269a6fe0
by Ian Romanick at 2025-11-07T08:14:46-08:00
brw: Correctly generate conditional modifier for BFN
Fixes: 4193895145b ("brw/cmod: Enable limited cmod propagation for BFN")
Reviewed-by: Caio Oliveira <caio.oliveira@intel.com>
(cherry picked from commit 34fe598b39c56b061619097c6e0eef2dffcc0dfb)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
ec8518d1
by Lionel Landwerlin at 2025-11-07T08:14:46-08:00
brw: avoid invalid URB messages
Some new CTS tests have geometry shader looking like this :
void main()
{
gl_Position = gl_in[0].gl_Position;
EmitVertex();
EndPrimitive();
// <-- some storage buffer write
}
The generate shader has :
- a message to write the position
- a message to write to the storage buffer
- a final message to end the thread
This generates an empty EOT URB messages which is apparently not legal
(simulation complains, HW hangs) :
send(8) nullUD g126UD nullUD 0x04088007 0x00000000
urb MsgDesc: offset 0 SIMD8 write masked mlen 2 ex_mlen 0 rlen 0 { align1 1Q A@1 EOT };
Instead emit a write with actual data and the mask set at 0 to discard
the effect :
mov(8) g127<1>UD 0x00000000UD { align1 WE_all 1Q };
mov(8) g125<1>UD 0x00000000UD { align1 1Q };
send(8) nullUD g126UD g125UD 0x04088007 0x00000040
urb MsgDesc: offset 0 SIMD8 write masked mlen 2 ex_mlen 1 rlen 0 { align1 1Q A@1 EOT };
Signed-off-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Cc: mesa-stable
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
(cherry picked from commit ff57c316964a73a7f763e2ff3ddfda99542813e1)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
c167b0a8
by Yiwei Zhang at 2025-11-07T08:14:47-08:00
glcpp/meson: fix libglcpp generated header dependency
Explicitly declare glcpp-parse.h as a file dependency to ensure
glcpp_parse custom target completes before compiling glcpp-lex.c.
Cc: mesa-stable
(cherry picked from commit 53482178efdb81071e55fd44a338f3f6139633bd)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
96d95998
by Emma Anholt at 2025-11-07T08:14:47-08:00
v3dv: Fix assertion failure for not-found primary_fd during enumeration.
Found when I had v3dv built in my aarch64 turnip setup.
Fixes: 451a0bd49002 ("v3dv: use v3d primary node for VK_EXT_physical_device_drm")
(cherry picked from commit bb532a7a39c92bc10fb098d37ab577070f0e1652)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
478d9217
by Lionel Landwerlin at 2025-11-07T08:14:48-08:00
anv: avoid invalid timestamp generation due to skipped commands
We skip the stall emission for STATE_BASE_ADDRESS since this one can
be skipped on Gfx12.5+ and instead add a new sba tracepoint that has
valid timestamps.
Signed-off-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Fixes: 0147908a89 ("anv: predicate emission of STATE_BASE_ADDRESS")
Reviewed-by: Casey Bowman <casey.g.bowman@intel.com>
(cherry picked from commit cff047280a94a380aba2385329eecbcc55426a71)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
38e258d5
by Timothy Arceri at 2025-11-07T08:14:48-08:00
mesa: skip redundant uniform update optimisation if unsafe
If multiple contexts are updating uniform values we can't assume
a uniform update can skip flushing.
Fixes: b32e20e6301f ("mesa: skip redundant uniform updates for glUniformHandle")
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14129
Reviewed-by: Marek Olšák <marek.olsak@amd.com>
(cherry picked from commit 34db720660af39d5a91f75da8376e5677bcfe352)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
dafde343
by Benjamin Cheng at 2025-11-07T08:14:49-08:00
vulkan/video: NULL check codec-specific chain
It seems applications are allowed to do no-op updates by not passing any
codec-specific extension structures.
Cc: mesa-stable
Reviewed-by: David Rosca <david.rosca@amd.com>
(cherry picked from commit 4d22427079ed7b358baa7ac36cc2fb8bb01c070f)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
e21d4172
by David Rosca at 2025-11-07T08:14:50-08:00
vulkan/video: Avoid NULL pointers in session parameters
Always copy parameters that are not guarded by a flag, zero init
the structs if not provided by application.
Fixes vk_layer_validation_tests PositiveVideoEncode*.GetEncodedSessionParams
Cc: mesa-stable
Reviewed-by: Benjamin Cheng <benjamin.cheng@amd.com>
(cherry picked from commit 6a1c6ab95b1b1d559ad5b64932ddce156c90caf5)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
11a4adec
by David Rosca at 2025-11-07T08:14:50-08:00
radv/video: Correctly handle no feedback query for encode
Fixes vk_layer_validation_tests PositiveVideoEncodeAV1.*
Cc: mesa-stable
Reviewed-by: Benjamin Cheng <benjamin.cheng@amd.com>
(cherry picked from commit 23a3587aa62b60f65de9205dd96f877adb4a728f)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
7aa2c707
by David Rosca at 2025-11-07T08:14:51-08:00
radv/video: Add NULL checks for picture parameters
Fixes vk_layer_validation_tests PositiveVideoDecode.* and
PositiveVideoDecode*.InlineSessionParams
Cc: mesa-stable
Reviewed-by: Benjamin Cheng <benjamin.cheng@amd.com>
(cherry picked from commit bd151bf8b227b934be717b4f887d5c6473048782)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
b17381dc
by Daniel Schürmann at 2025-11-07T08:14:52-08:00
radv/null_device: set more options which affect compilation
Cc: mesa-stable
(cherry picked from commit 23ef756496340ccbe4b777ca5279c7fca44cb724)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
8a813632
by Lionel Landwerlin at 2025-11-07T08:14:52-08:00
vulkan/runtime: simplify robustness state hashing
We're doing the same in vk_pipeline_precomp_shader_create().
Also fixes valgrind warning due to uninitialized fields
Signed-off-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Cc: mesa-stable
Reviewed-by: Faith Ekstrand <faith.ekstrand@collabora.com>
(cherry picked from commit fc6d17a2900ec8bed96748cbe6da9188f94b44b4)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
9e809986
by Yiwei Zhang at 2025-11-07T08:14:53-08:00
panvk: fix mem alloc size for VkBuffer backed by imported blob AHB
For AHB VkBuffer import, the allocationSize comes from the raw external
AHB props query and it can be larger than the underlying buffer memory
requirement. So we must respect the allocationSize for the actual mem
import to support mapping the whole AHB size, and the dedicated buffer
info has to be stripped to obey the spec.
Test: CtsNativeHardwareTestCases no longer crashes on debug build panvk
Fixes: 66bbd9eec83 ("panvk: implement AHB image deferred init and memory alloc")
Tested-by: Valentine Burley <valentine.burley@collabora.com>
Reviewed-by: Lars-Ivar Hesselberg Simonsen <lars-ivar.simonsen@arm.com>
Reviewed-by: Christoph Pillmayer <christoph.pillmayer@arm.com>
(cherry picked from commit 4ec2a921d3437cfd6dc01c63b3cac180e308188e)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
f3268818
by Danylo Piliaiev at 2025-11-07T08:14:53-08:00
tu: Use cmd->rp_trace u_trace for draw calls
Fixes: 707c97f6340 ("tu: Add tracepoints around draws, with shader sha1s.")
Signed-off-by: Danylo Piliaiev <dpiliaiev@igalia.com>
(cherry picked from commit c04e3755889fd02d5788d694d77aaf94d86a62b9)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
c4e0f4d9
by Mario Kleiner at 2025-11-07T08:14:54-08:00
wsi/display: Accept 0 nits for HDR light level properties for "undefined"
CTA-861-G section 6.9.1 Static Metadata Type 1 declares that zero values
for different groups of HDR Metadata properties are allowed, including
zero nits values for max display mastering luminance, max content light
level, max frame-average light level and min display mastering luminance.
A zero value is meant to be treated by the video sink as "undefined" /
"unknown", and handled accordingly. This is common for dynamically
generated visual content.
Therefore don't assert on some minimum nits level > 0, but only check for
a non-negative level.
Fixes: b4176393a0aa ("wsi/display: Implement VK_EXT_hdr_metadata on KHR_display swapchain")
Signed-off-by: Mario Kleiner <mario.kleiner.de@gmail.com>
Reviewed-by: Autumn Ashton <misyl@froggi.es>
(cherry picked from commit 19dc09aded4953aeacc2b15233643a0e4881314e)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
b777384e
by Mario Kleiner at 2025-11-07T08:14:54-08:00
wsi/display: Initially set default HDR metadata from EDID for HDR modes
For a selected non-default imageColorSpace during swapchain creation,
make sure that proper HDR setup also works even if a client app does not
explicitly call vkSetHdrMetadataEXT() in time.
Assign the EDID provided metadata here, so the 1st atomic commit will
set Colorspace and HDR metadata properties on the connector, to make sure
HDR or other wide color gamut modes get enabled.
Without this, the chain->color_outcome_serial would stay at zero and
the properties would not ever get assigned during drm_atomic_commit(),
leaving HDR disabled on the display sink.
Fixes: 13137393f67b ("wsi/display: Expose HDR10 colorspace based on EDID")
Signed-off-by: Mario Kleiner <mario.kleiner.de@gmail.com>
Reviewed-by: Autumn Ashton <misyl@froggi.es>
(cherry picked from commit 19b2e3b81b6326836f333846263ce22f5059db58)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
70e3af18
by Mario Kleiner at 2025-11-07T08:14:55-08:00
wsi/display: Allow atomic modeset for change of Colorspace or HDR poperties
At least some drivers need a full modeset to change the Colorspace
property or to en-/disable HDR mode. E.g., at least amdgpu-kms as
tested under Linux 6.8 on Polaris needs it. Otherwise the atomic
commit for disabling HDR in _wsi_display_cleanup_state() will fail,
and the connector stays stuck in HDR mode after vkDestroySwapchainKHR().
Fixes: 1ed78dd7ec4a ("wsi/display: Clean up DRM hdr/color state on swapchain destruction")
Signed-off-by: Mario Kleiner <mario.kleiner.de@gmail.com>
Reviewed-by: Autumn Ashton <misyl@froggi.es>
(cherry picked from commit ba82d36dce27f420c0784afbf4e05cd0cb0d18f5)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
d3d820d6
by Christian Gmeiner at 2025-11-07T08:14:55-08:00
anv: Fix needs_temp_copy() incorrectly matching depth/stencil formats
The needs_temp_copy() function was incorrectly identifying some
depth/stencil formats as needing RGB<->RGBA conversion.
VK_FORMAT_D32_SFLOAT_S8_UINT maps to PIPE_FORMAT_Z32_FLOAT_S8X24_UINT,
which has 3 channels (F32 depth, UP8 stencil, X24 padding). The
component count check (== 3) was matching this as an RGB color format,
causing depth/stencil images to incorrectly use the RGB conversion path.
Add an explicit vk_format_is_depth_or_stencil() check before the
component count test to ensure depth/stencil formats always use the
direct copy path.
Fixes: f97b51186f ("anv: intermediate RGB <-> RGBX copy for HIC")
Signed-off-by: Christian Gmeiner <cgmeiner@igalia.com>
Reviewed-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
(cherry picked from commit 0be53b2ed87e4c5c776ff290984186c729c16216)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
d48e4a3f
by Dylan Baker at 2025-11-13T08:10:00-08:00
.pick_status.json: Update to 294e72e2b517bc744f909fbce9e154efa698dd10
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
1460a031
by Lars-Ivar Hesselberg Simonsen at 2025-11-13T08:10:09-08:00
panvk: Fix IUB decode
The base address used for bounds checking the entry was wrong. Directly
pass the end_of_entry address instead.
Fixes: db4bcd48d7a ("panvk: Fix IUB decode")
Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
(cherry picked from commit 89293120f0601e96c9e6c044305413e7d3c6d33e)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
02ba16ec
by Benjamin Cheng at 2025-11-13T08:10:14-08:00
radv/video: Fix dummy DPB addresses
This fixes the VVL PositiveVideoDecodeAV1.* tests, which trigger error
concealment. These DPB addresses would not be normally used, but get
used by the error concealment path.
Fixes: d103b76ad68 ("radv/video: add VK_KHR_video_decode_av1 support.")
Reviewed-by: David Rosca <david.rosca@amd.com>
(cherry picked from commit 82d944b38849ba556e21b1af0ae399211b2d8f58)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
594ae17e
by Sagar Ghuge at 2025-11-13T08:10:15-08:00
anv: Drop unwanted untyped flush for AS query
CmdWriteAccelerationStructuresPropertiesKHR writes the data with MI
commands, we no longer dispatch shaders to write the properties.
As a result, we don't need to flush untyped cache.
Fixes: f0e18c475b ("intel: remove GRL/intel-clc")
Signed-off-by: Sagar Ghuge <sagar.ghuge@intel.com>
Reviewed-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Reviewed-by: Tapani Pälli <tapani.palli@intel.com>
(cherry picked from commit 14194e59a42e8899dd945ecf3a17a6fd995a6d85)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
f299249d
by Faith Ekstrand at 2025-11-13T08:10:17-08:00
drm-uapi: Import the new NVIDIA modifiers
Imported from kernel commit eef295a850820 of drm-misc-fixes
Backport-to: 25.2
Reviewed-by: James Jones <jajones@nvidia.com>
(cherry picked from commit 3247452b2c092fe1954a7ef8a33bacc91981f42d)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
e3349383
by Faith Ekstrand at 2025-11-13T08:10:18-08:00
nil: Add support for Blackwell 8 and 16-bit modifiers
Backport-to: 25.2
Reviewed-by: James Jones <jajones@nvidia.com>
(cherry picked from commit f1cb63a21d4b1a8f6903ecec2ebee4c02c129c68)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
263e1823
by Karol Herbst at 2025-11-13T08:10:19-08:00
st/interop: fix fence leak
Cc: mesa-stable
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14050
Fixes: 1396dc1c387 ("mesa/st, dri2, wgl, glx: Modify flush_objects interop func to export a fence_fd")
Tested-by: Dmitry Baryshkov <dmitry.baryshkov@oss.qualcomm.com>
(cherry picked from commit 87550fc6571968c61afbb23f0bc0b079b6cd8527)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
0ef221f4
by Dave Airlie at 2025-11-13T08:10:20-08:00
c11/threads: fix build on c23
C23/glibc is now including once_init in stdlib.h
https://patchwork.sourceware.org/project/glibc/patch/78061085-f04a-0c45-107b-5a8a15521083@redhat.com/#213088
Just fix up our use of it.
Cc: mesa-stable
Reviewed-by: Yonggang Luo <luoyonggang@gmail.com>
(cherry picked from commit 179e744f7577d98df7c79d7324c22acfb32a0154)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
14097ed7
by Lionel Landwerlin at 2025-11-13T08:10:21-08:00
anv/blorp/iris: rework Wa_14025112257
Drivers already have to track this workaround, so remove the logic
from Blorp and let the driver manage this.
Also in Anv don't accumulate this workaround, emit it directly in
place right after COMPUTE_WALKER. Accumulating can be problematic when
you want to dispatch concurrent compute shaders that do not need any
cache flush interaction (typical example with the internal
simple_shader framework).
Signed-off-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Fixes: 3e0ad0176b ("anv: Emit state cache invalidation after every compute dispatch")
Reviewed-by: Alyssa Rosenzweig <alyssa.rosenzweig@intel.com>
Reviewed-by: Sagar Ghuge <sagar.ghuge@intel.com>
(cherry picked from commit c478b6355afd653db8a211aa533fffd628cb780d)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
b6ae45d3
by Eric Engestrom at 2025-11-13T08:10:22-08:00
ci: track src/c11/ changes
It's used by mesa_util, so let's just consider changes to it can affect
any job.
Fixes: b2ddec4e98fea9b824e7 ("c11: Implement c11/time.h with c11/impl/time.c")
Reviewed-by: Yonggang Luo <luoyonggang@gmail.com>
(cherry picked from commit 2ec3e536fdaa8641088ba4d3a268dc50287ee388)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
5c3427b1
by Eric Engestrom at 2025-11-13T08:10:23-08:00
ci: track src/android_stub/ changes
Fixes: 932f51d593418c95bf8f ("ci: Include enough Android headers to let us compile test EGL")
Suggested-by: Yonggang Luo <luoyonggang@gmail.com>
(cherry picked from commit f689322d27b3bffcad1ad5c387d5a959007fde2a)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
2cd6bc19
by Karol Herbst at 2025-11-13T08:10:23-08:00
rusticl/queue: fix error code for invalid queue properties part 1
Cc: mesa-stable
(cherry picked from commit e83400cab283094c02172a0bb96a3ec8bf9dfeeb)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
efd2f1d6
by Karol Herbst at 2025-11-13T08:10:24-08:00
rusticl/queue: fix error code for invalid queue properties part 2
Fixes: 2c202eb7870 ("rusticl: verify validity of property names and values")
(cherry picked from commit e98abe35c020b2e42e557d690df1a2c25bd1b7b0)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
3bb77d69
by Karol Herbst at 2025-11-13T08:10:25-08:00
rusticl/queue: fix error code for invalid sampler kernel arg
Fixes: 5795ee0e083 ("rusticl: translate spirv to nir and first steps to kernel arg handling")
(cherry picked from commit c0f0baeaca1c9a84f9631fc67f33c0a6e295b841)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
e42294ba
by Karol Herbst at 2025-11-13T08:10:26-08:00
rusticl/kernel: take no kernel_info reference inside the launch closure
Otherwise patterns like this wouldn't work:
clCreateKernel(prog)
clEnqueueNDRangeKernel
clReleaseKernel
clBuildProgram(prog)
Fixes: bb2453c6495 ("rusticl/kernel: move most of the code in launch inside the closure")
(cherry picked from commit df344f12cc006fea8d9ce5780e06b2870c87886c)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
42726a2a
by Karol Herbst at 2025-11-13T08:10:26-08:00
rusticl/spirv: preserve signed zeroes by default
Cc: mesa-stable
(cherry picked from commit 92a4ae0ab2ad1494a5bf27d2d1dc86a2476e551e)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
b074ea9f
by Patrick Lerda at 2025-11-13T08:10:27-08:00
r600: limit pre-evergreen predicate ready size
With the current stack configuration the rv770 seems to be unable
to go beyond three with the "vs-output-array-float-index-wr-before-gs.shader_test"
test. Anyway, the value four seems to be sufficient for the other tests.
This issue was triggered on rv770, for instance, with:
"piglit/bin/shader_runner tests/spec/glsl-1.50/execution/variable-indexing/gs-output-array-float-index-wr.shader_test -auto -fbo"
"piglit/bin/shader_runner tests/spec/glsl-1.50/execution/variable-indexing/vs-output-array-float-index-wr-before-gs.shader_test -auto -fbo"
Fixes: 713edb59982c ("r600/sfn: handle the IF predicate in the scheduler")
Signed-off-by: Patrick Lerda <patrick9876@free.fr>
(cherry picked from commit ae049f6fea2b5abc8efbae434b9ab860f134733b)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
2cb191d7
by Sagar Ghuge at 2025-11-13T08:10:28-08:00
intel/common: Consider 0 threads while setting TG
In ray tracing dispatch, we have dispatch.threads set to 0 since we
calculate the local_size_x/y/z based on the launch sizes.
This change takes 0 threads into an account and returh the TG size 8 in
such scenarios. Before this change, we were setting TG size to 2.
Fixes: 0c4e1c9efcf4 ("intel/common: Add helper for compute thread group dispatch size")
Signed-off-by: Sagar Ghuge <sagar.ghuge@intel.com>
Reviewed-by: José Roberto de Souza <jose.souza@intel.com>
(cherry picked from commit 16f66ffe55d7264b4b401dc31dcd91fdb615143b)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
f0aeb824
by Timothy Arceri at 2025-11-13T08:10:29-08:00
glsl: assign block indices in the order they appear
The hash lookup should be negligible. This makes things
predictable rather than having hash table modifications causing
the order to change, and fixes things for some seemingly buggy games.
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/13802
Fixes: be5a15f11d77 ("util/hash_table: start with 16 entries to reduce reallocations")
Reviewed-by: Marek Olšák <marek.olsak@amd.com>
(cherry picked from commit 595a2fdbd2a922ff5ba5ccc9e173ea871fbca51c)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
de44196b
by Tapani Pälli at 2025-11-13T08:10:30-08:00
anv: fix issues found with indirect data stride
Use tristate for the aligned setting, otherwise it is always
first disabled which contributes to the condition if we set the
new stride active.
v2: set ByteStride in dword units and take secondary cmdbuf
in to account (Lionel)
Cc: mesa-stable
Signed-off-by: Tapani Pälli <tapani.palli@intel.com>
Reviewed-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Tested-by: Nataraj Deshpande <nataraj.deshpande@intel.com>
(cherry picked from commit 2741ddd75ab258d1ef5ee9b160d4c20a1b0dc756)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
8ffc19f9
by Faith Ekstrand at 2025-11-13T08:10:30-08:00
nir: Add a couple panfrost sysvals to divergence analysis
Fixes: 2af6e4beeb39 ("pan: Don't pretend we support load_{vertex_id_zero_base,first_vertex}")
Reviewed-by: Lars-Ivar Hesselberg Simonsen <lars-ivar.simonsen@arm.com>
Reviewed-by: Christoph Pillmayer <christoph.pillmayern@arm.com>
(cherry picked from commit 0e9fcb33c33e01d5ec06cad101148c956d27ae3e)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
4a0cb910
by Sviatoslav Peleshko at 2025-11-13T08:10:31-08:00
mesa,driconf: Add WA to initialize vertex program outputs to vec4(0,0,0,1)
Per ARB_vertex_program spec result registers are 4-component and initially
undefined, and the FF fragment program expects its intputs to be
4-component too. So, if the client's vertex program does not write the
whole vector it will cause misrenderings unless the same client also
supplies fragment program that expects less than 4 componens.
This commit adds a workaround that initializes results to vec4(0, 0, 0, 1)
which seems to be an expected behavior for such clients.
Cc: mesa-stable
Signed-off-by: Sviatoslav Peleshko <sviatoslav.peleshko@globallogic.com>
Reviewed-by: Timothy Arceri <tarceri@itsqueeze.com>
(cherry picked from commit f03432c81a268ad2cf683f176cf0b97c24a617b2)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
a407dc6d
by Sviatoslav Peleshko at 2025-11-13T08:10:32-08:00
driconf: Add vertex_program_default_out option for Penumbra: Overture
Penumbra's vertex program Diffuse_EnvMap_Reflect_vp.cg produces 3-component
texture coordinates and primitive colors while using the FF fragment
program. Add this WA to fix the misrenderings.
Cc: mesa-stable
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14170
Signed-off-by: Sviatoslav Peleshko <sviatoslav.peleshko@globallogic.com>
Reviewed-by: Timothy Arceri <tarceri@itsqueeze.com>
(cherry picked from commit 5af8abbf8ba10e6ff56b258c2928d1ed56d9c940)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
feccefbc
by Natalie Vock at 2025-11-13T08:10:33-08:00
radv: Fix PSO history with RT pipelines
1. The prolog needs to have a null check. Libraries don't have prologs.
2. We only need to print the shaders actually included in this pipeline.
Libraries were already printed separately.
3. The traversal shader was wrongly omitted from the output.
Cc: mesa-stable
(cherry picked from commit 73a31dafbcbf390dc2427e37a1cc17ef20a42c29)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
7f68450a
by Dmitry Baryshkov at 2025-11-13T08:10:34-08:00
ci: drop google-freedreno remnants
Drop remnants of the google-freedreno lab entries.
Fixes: 6541b911bd7a ("freedreno/ci: Remove baremetal job templates")
Signed-off-by: Dmitry Baryshkov <dmitry.baryshkov@oss.qualcomm.com>
(cherry picked from commit 9a33edca35248426b94d4b6c2b3bae0f96c6bdec)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
e5f9980d
by Christian Gmeiner at 2025-11-13T08:10:35-08:00
meson: require sysprof-capture-4 >= 4.49.0
When Mesa is compiled with sysprof support, applications can crash with a
segfault during shutdown. This happens because sysprof_collector_mark()
registers thread-local storage destructors that get called after the library
containing the destructor code has been unloaded.
The problem was fixed in sysprof https://gitlab.gnome.org/GNOME/sysprof/-/merge_requests/152
CC: mesa-stable
Closes: mesa/mesa#13571
Signed-off-by: Christian Gmeiner <cgmeiner@igalia.com>
(cherry picked from commit e9341568fa9e4af1084db6702174ed4b4881bc73)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
09b856c3
by Timur Kristóf at 2025-11-13T08:10:36-08:00
ac/nir/ngg: Fix scratch space for NGG GS streamout
For GS streamout, we need the following LDS scratch space:
- Repacking streamout vertices takes 1 dword per 4 waves per stream
(max 16 bytes for Wave64, max 32 bytes for Wave32)
- 1 dword per stream for buffer info
(16 bytes)
- 1 dword per buffer for buffer info
(16 bytes)
Previously, the space used for buffer info aliased with the
space for repacking the output vertices in ngg_gs_finale(),
and there was no barrier in between, which caused a race
condition, resulting in random failure.
Fix this by allocating a few more LDS dwords so that aliasing
is not required, which also allows us to remove an extra
workgroup barrier.
Cc: mesa-stable
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/12705
Signed-off-by: Timur Kristóf <timur.kristof@gmail.com>
Reviewed-by: Marek Olšák <marek.olsak@amd.com>
Reviewed-by: Pierre-Eric Pelloux-Prayer <pierre-eric.pelloux-prayer@amd.com>
(cherry picked from commit 8f99d736d09a88713b2aac969a793c3461e6f759)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
76d66b72
by Lionel Landwerlin at 2025-11-13T08:10:37-08:00
anv: disable software detiling on Xe2+ for image atomics 64bits
This is what happens when you leave MR unreviewed for months.
Signed-off-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Fixes: d39e443ef8 ("anv: add infrastructure for common vk_pipeline")
Reviewed-by: Alyssa Rosenzweig <alyssa.rosenzweig@intel.com>
(cherry picked from commit c4e28785370bfd7f1f36ffbbc0d27885b0beca60)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
b5a42451
by Marek Olšák at 2025-11-13T08:10:37-08:00
gallium/noop: don't unref buffers passed to set_vertex_buffers to fix crashes
this code is invalid after the refcounting rework
Fixes: b3133e250e1 - gallium: add pipe_context::resource_release to eliminate buffer refcounting
Reviewed-by: Pierre-Eric Pelloux-Prayer <pierre-eric.pelloux-prayer@amd.com>
(cherry picked from commit 7d22e4c7ba81d12b5184786e3c0f5a5a2ad6c150)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
f651443a
by Joshua Simmons at 2025-11-13T08:10:38-08:00
vtn: Fix OpCopyLogical destination type
Previously the type info for nested values was copied from the source
operand, rather than propagating the new type from the destination
operand.
Fixes: 4c363acf94a ("vtn: Allow for OpCopyLogical with different but compatible types")
Reviewed-by: Georg Lehmann <dadschoorse@gmail.com>
(cherry picked from commit 7ac1f7777d21587e401727cf3218978aed30ec96)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
e2164fbc
by Gert Wollny at 2025-11-13T08:10:39-08:00
r600/sfn: Don't start a new ALU-CF if LDS pipeline loads are pending
Fixes: e57643cf (r600/sfn: Add handling for R600 indirect access alias handling)
Signed-off-by: Gert Wollny <gert.wollny@collabora.com>
(cherry picked from commit 79e4323cf0c258cf48d7ace96a35c8812e01b39b)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
0fbf00af
by Ludvig Lindau at 2025-11-13T08:10:40-08:00
panfrost: Make instrs_equal check res table/index
Add resource table and index check to instruction equality function.
This prevents CSE from mistakenly eliminating LEA_BUF_IMM instructions
that load from different resources, but with the same buffer offset.
Cc: mesa-stable
Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
(cherry picked from commit 00b5275fe889ceb92173d09b771af29b1a559c7b)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
b7ce6abb
by Lars-Ivar Hesselberg Simonsen at 2025-11-13T08:37:59-08:00
pan/format: Fix mapping for I16F
This was mapped to RG16F, while R16F should be correct.
Cc: mesa-stable
Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
(cherry picked from commit 1e2ca4dad6dd42a2953c30daf240b99955372b07)
Conflicts:
src/panfrost/ci/panfrost-g610-fails.txt
src/panfrost/ci/panfrost-g610-flakes.txt
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
23665f9b
by Lars-Ivar Hesselberg Simonsen at 2025-11-13T08:38:00-08:00
pan/format: Disable PAN_BIND_STORAGE_IMAGE for RGBA4/BGRA4
The RGBA4/BGRA4 formats had the PAN_BIND_STORAGE_IMAGE set, but we
cannot support that.
Fixes: d95423686fd ("pan/format: Add PAN_BIND_STORAGE_IMAGE flag")
Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
(cherry picked from commit 15868cf6e9aa2fe8a8d3f431b3e89924a72f3529)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
28ca4a48
by Mario Kleiner at 2025-11-13T08:38:01-08:00
wsi/wayland: Zero min_luminance, max_luminance HDR light levels are valid.
CTA-861-G section 6.9.1 Static Metadata Type 1 declares that zero values
for different groups of HDR Metadata properties are allowed, including
zero nits values for max display mastering luminance, max content light
level, max frame-average light level and min display mastering luminance.
A zero value is meant to be treated by the video sink as "undefined" /
"unknown", and handled accordingly. This is common for dynamically
generated visual content.
The is_hdr_metadata_legal() function in the Vulkan/WSI/Wayland HDR backend
currently declares HDR light level metadata as invalid if the mastering
display min_luminance and max_luminance light levels are set to the legal
level of zero nits. This causes valid HDR metadata as set by the client
via vkSetHdrMetadata() to be not sent to the compositor.
Fix this by skipping checks that don't apply if min_luminance or
max_luminance are zero. If max_luminance is zero then we skip sending
of mastering display min/max luminance to Wayland, as sending a a
max_luminance <= min_luminance would trigger a protocol error. All
other valid data is still send, ie. color primaries, white-point,
content light levels.
Fixes: cb7726bb2cf ("vulkan/wsi: validate HDR metadata to not cause protocol errors")
Signed-off-by: Mario Kleiner <mario.kleiner.de@gmail.com>
Co-authored-by: Michel Dänzer <michel@daenzer.net>
Reviewed-by: Xaver Hugl <xaver.hugl@kde.org>
(cherry picked from commit 490f05f82ced94d0a2893946aad96083447cac38)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
25abf47e
by Dylan Baker at 2025-11-14T08:36:53-08:00
.pick_status.json: Update to 8f13905c5e38ac3921c4804b19fc0f50531b0317
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
48b0dd28
by Samuel Pitoiset at 2025-11-14T08:36:53-08:00
radv: add vk_wsi_disable_unordered_submits and enable for GTK
GTK is missing a semaphore between QueueSubmit() and QueuePresent()
causing the WSI submit to be "unordered" and to immediately signal the
semaphores (because it's missing a wait semaphore in QueuePresent()).
The workaround is to disable unordered WSI submits until GTK fixes it
properly.
Cc: "25.3"
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14087
Signed-off-by: Samuel Pitoiset <samuel.pitoiset@gmail.com>
(cherry picked from commit 0d9d45db4e1b6d00747bf635ba3222146a899468)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38432>
-
523eea18
by Dylan Baker at 2025-11-14T13:24:41-08:00
docs: add release notes for 25.3.0
-
f7aeb0d6
by Dylan Baker at 2025-11-14T13:25:42-08:00
VERSION: bump for 25.3.0
Signed-off-by: Dylan Baker <dylan.c.baker@intel.com>