Timo Aaltonen pushed to branch upstream-unstable at X Strike Force / lib / mesa
Commits: 78d8a5e1 by Eric Engestrom at 2025-10-15T18:37:47+02:00 docs: add sha sum for 25.2.5 - - - - - 3fb338b7 by Eric Engestrom at 2025-10-17T15:23:51+02:00 .pick_status.json: Mark !36883 commits as denominated As well as several commits nominated because they fix these commits. https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36883#note_3064958 - - - - - 47dbff68 by Eric Engestrom at 2025-10-29T17:42:18+01:00 .pick_status.json: Update to b82044c31b0be1c7682548a8e10905a4ff5b13d7 - - - - - 64892b23 by Eric Engestrom at 2025-10-29T17:42:19+01:00 .pick_status.json: Mark 77fb8fb062457dad73bd763e97bf757b6cd04080 as denominated - - - - - f28e0f74 by Eric Engestrom at 2025-10-29T17:42:19+01:00 .pick_status.json: Mark bca29b1c92320dea0004341a08cc76a18e3edaf3 as denominated - - - - - 4bde951b by Eric Engestrom at 2025-10-29T17:42:19+01:00 .pick_status.json: Mark 8d05b7b72e70fe35d6ff6b5d65272ec520a707f3 as denominated - - - - - 1ba32911 by Eric Engestrom at 2025-10-29T17:42:19+01:00 .pick_status.json: Mark 006085e6769c3697c29cd5087dfabe7b5b8d046a as denominated - - - - - 4eb8d969 by Eric Engestrom at 2025-10-29T17:42:19+01:00 .pick_status.json: Mark 343eef990e54d974d811f7414e79a8854b8c97f9 as denominated - - - - - ff252238 by Lionel Landwerlin at 2025-10-29T17:42:19+01:00 brw: fix invalid sparse bitfield offset computation dest_size is the number of outputs to be provided into the IR, but the location of the sparse bitfield in the dst temporary SEND destination might be different (shorter due to masking of unused components computed above). Signed-off-by: Lionel Landwerlin <[email protected]> Cc: mesa-stable Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14094 Reviewed-by: Alyssa Rosenzweig <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37876> (cherry picked from commit 49226692e50cf272d7425c82c5c48016ffc23b56) - - - - - a3290bb5 by Lionel Landwerlin at 2025-10-29T17:42:19+01:00 brw: prevent LOAD_REG modifications on MOV_INDIRECT/BROADCAST Due to those opcode reading variable amount of data in src0, it's not possible to easily figure out what builder SIMD size should be used to produce the LOAD_REG replacement. Signed-off-by: Lionel Landwerlin <[email protected]> Fixes: 2d13acf9d9 ("brw: Add passes to generate and lower load_reg") Fixes: 93996c07e2 ("brw: fix broadcast opcode") Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14054 Reviewed-by: Ian Romanick <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37756> (cherry picked from commit acf953757ef6c567dded4987599502780412a1f2) - - - - - b5c32aa2 by Gert Wollny at 2025-10-29T17:42:19+01:00 r600: Fix comparison of strides array when emitting vertex buffers The comparison was only comparing a number of bytes where we actually have to compare a number of dwords (Thanks QuadShader for digging into this) Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14067 Fixes: 659b7eb2799 ("r600: better tracking for vertex buffer emission") v2: use element size instead of type size (Vitaly) Signed-off-by: Gert Wollny <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37856> (cherry picked from commit 673351bbf32e87349a926380bc65afd233a068ef) - - - - - f19d3d5b by Mike Blumenkrantz at 2025-10-29T17:42:19+01:00 zink: defer swapchain updates for interval changes if acquired image is active in the case where an app triggers a swap interval change mid-frame, this handling previously triggered an immediate swapchain retire and then presented the new swapchain which had yet to be rendered to instead, defer swapchain updates to immediately after present when things are safe to ensure that the right image is always presented Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14104 cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37894> (cherry picked from commit db9dbcbec0002ed87e825927983b841d1e90f163) - - - - - c7be587b by José Roberto de Souza at 2025-10-29T17:42:19+01:00 gallium/llvmpipe/test: Rename rsqrtf() to _rsqrtf() Some versions of math.h exports rsqrtf() while others don't, so this was causing compilation to fail when it is supported. I have not found a easy way to detect if rsqrtf() is supported and as this is only used in a llvmpipe tests it is not worthy do changes in Meson files to detected if it is supported. So here just renaming the Mesa function to _rsqrtf() and fixing the build for both math.h versions. Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/13797 Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/12934 Reviewed-by: Roland Scheidegger <[email protected]> Signed-off-by: José Roberto de Souza <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37515> (cherry picked from commit 5a482a7a3d1973f9c86a22f31050e2d2acbc8450) - - - - - c936c018 by Mel Henning at 2025-10-29T17:42:19+01:00 nvk: Fix maxVariableDescriptorCount with iub Otherwise, we would report very high values for inline uniform block since NVK_MAX_DESCRIPTOR_SET_SIZE is a lot larger than NVK_MAX_INLINE_UNIFORM_BLOCK_SIZE. Fixes dEQP-VK.api.maintenance3_check.support_count_inline_uniform_block_nonzero_binding_offset on vulkan-cts-1.4.4.0 Fixes: 6a74b3e3118 ("nvk: Support VkDescriptorSetVariableDescriptorCountLayoutSupport") Reviewed-by: Mohamed Ahmed <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37878> (cherry picked from commit ff7f785f09ce72bbc56a8fd1f879d09ab814c08e) - - - - - 747df8a6 by Timur Kristóf at 2025-10-29T17:42:19+01:00 radeonsi: Don't use compute queue with regalloc hang bug It already didn't use compute queues on GFX6, but some GFX7 chips are also affected by the same bug. Compute queues may run compute dispatches in parallel with the graphics queue, even from other processes/apps. At the moment we don't have a way to restrict all workgroups to 256 invocations, so instead let's make sure not to use the compute queue. Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37885> (cherry picked from commit 765a748840e6a67d64c2b29b149f6aadee3a39fd) - - - - - 78c83d09 by Timur Kristóf at 2025-10-29T17:42:19+01:00 radv: Disable compute queues when the regalloc bug is present Compute queues may run compute dispatches in parallel with the graphics queue, even from other processes/apps. At the moment we can't make sure that all compute shaders use a workgroup size of 256 to mitigate the regalloc hang, so disable compute queues on affected chips. Can be reverted if a better mitigation is found in the future. Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37885> (cherry picked from commit 6f499141f5b25de4def889b4151e954cf044a3a6) - - - - - b0814ec8 by Timur Kristóf at 2025-10-29T17:42:19+01:00 radv: Mitigate GPU hang on Hawaii in Dota 2 and RotTR Mitigate a GPU hang in Dota 2 and Rise of the Tomb Raider by reducing the primitive rate for triangle lists. This workaround is not documented by AMD and may not be correct. The problem isn't well understood and needs further investigation to narrow down what the root cause is. Until then, it's better to give users something that works, even if not optimal. Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37885> (cherry picked from commit 8ea08747b86bba88998333dc04d983c2a2391e48) - - - - - 2e40c0be by Danylo Piliaiev at 2025-10-29T17:42:20+01:00 tu: Destroy all mutexes used for device We never destroyed most of mutexes we used, it was likely fine on platforms turnip is running on, but still not correct. Signed-off-by: Danylo Piliaiev <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37465> (cherry picked from commit ea849b55570416e0e6054384340482308103f563) - - - - - 2cc59fc5 by Danylo Piliaiev at 2025-10-29T17:42:20+01:00 tu: Synchronize access to copy_timestamp_cs_pool tu_u_trace_submission_data_finish happens on the other thread than tu_create_copy_timestamp_cs. Fixes: 6e5944ec4b5 ("tu: Cache copy timestamp cs to avoid allocations on submit") Signed-off-by: Danylo Piliaiev <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37848> (cherry picked from commit 9f85c8897acc8c5d1e88934f411fefcf7d152516) - - - - - 057423c7 by Ruijing Dong at 2025-10-29T17:42:20+01:00 radeonsi/vcn: Correct a typo condition for jpeg decoding Checking dec->jctx[i] instead of sctx->ctx Cc: mesa-stable Reviewed-by: David Rosca <[email protected]> Signed-off-by: Ruijing Dong <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37875> (cherry picked from commit 6e1988e3ed7c104514b0f76cd1c327dcb17c90de) - - - - - 0ea4ca0f by Xaver Hugl at 2025-10-29T17:42:20+01:00 vulkan/wsi: require extended target volume support for scRGB It's hardly going to be useful without that Signed-off-by: Xaver Hugl <[email protected]> Fixes: 4b663d56 ("vulkan/wsi: implement support for VK_EXT_hdr_metadata on Wayland") Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37920> (cherry picked from commit 892cf427a0f62538a6943fd7500a9b23f0dd91ea) - - - - - ebcd616b by Marek Olšák at 2025-10-29T17:42:20+01:00 r300: fix DXTC blits Fixes: 9d359c6d10ad - gallium: delete pipe_surface::width and pipe_surface::height Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37912> (cherry picked from commit 733ba77bfe7fc200257eae6eac098b6577c705e3) - - - - - 190eab96 by Mike Blumenkrantz at 2025-10-29T17:42:20+01:00 zink: consistently set/unset msrtss in begin_rendering this has to always be set or unset, never persistent from previous renderpass Fixes: 5080f2b6f55 ("zink: disable msrtss handling when blitting") Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37923> (cherry picked from commit f74cf450782509d9e386a83a3f8221a3d1bdb701) - - - - - 0183b1aa by Job Noorman at 2025-10-29T17:42:20+01:00 nir: mark fneg distribution through fadd/ffma as nsz df1876f615a ("nir: Mark negative re-distribution on fadd as imprecise") fixed the fadd case by marking it as imprecise. This commit fixes the ffma case for the same reason. However, "imprecise" isn't necessary and nowadays we have "nsz" which is more accurate here. Use that for both fadd and ffma. Signed-off-by: Job Noorman <[email protected]> Fixes: 62795475e8f ("nir/algebraic: Distribute source modifiers into instructions") Reviewed-by: Georg Lehmann <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37930> (cherry picked from commit ad421cdf2e68a1ccef80cb810c012c8469579cb6) - - - - - 60194f00 by Marek Olšák at 2025-10-29T17:42:20+01:00 winsys/radeon: fix completely broken tessellation for gfx6-7 The info was moved to radeon_info, but it was only set for the amdgpu kernel driver. It was uninitialized for radeon. Fixes: d82eda72a1fe3932 - ac/gpu_info: move HS info into radeon_info Acked-by: Pierre-Eric Pelloux-Prayer <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37910> (cherry picked from commit f5b648f6d30697363d3326f408a50ae87587b1bc) - - - - - 57711bc0 by Timur Kristóf at 2025-10-29T17:42:20+01:00 ac/nir/ngg_mesh: Lower num_subgroups to constant Mesh shader workgroups always have the same amount of subgroups. When the API workgroup size is the same as the real workgroup size, this is a small optimization (using a constant instead of a shader arg). When the API workgroup size is smaller than the real workgroup size (eg. when the number of output vertices or primitves is greater than the API workgroup size on RDNA 2), this fixes a potential bug because num_subgroups would return the "real" workgroup size instead of the API one. Cc: mesa-stable Signed-off-by: Timur Kristóf <[email protected]> Reviewed-by: Marek Olšák <[email protected]> Reviewed-by: Qiang Yu <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37947> (cherry picked from commit d20049b430b60e1ece5bef504a3b3f694a83aa1c) - - - - - 118b7d39 by Yiwei Zhang at 2025-10-29T17:42:20+01:00 panvk: fix to advance vs driver_set properly Should only set once outside the multidraw loop so that per draw can patch its own own desc attribs when needed. Fixes: a5a0dd3ccc0 ("panvk: Implement multiDrawIndirect for v10+") Reviewed-by: Boris Brezillon <[email protected]> Acked-by: Christoph Pillmayer <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37951> (cherry picked from commit 800c4d34306efb1e67734cefb1e75bf2b8ef2013) - - - - - fd29ba54 by Yiwei Zhang at 2025-10-29T17:42:20+01:00 panvk: fix to advance vs res_table properly Fix a regression from an unfortunate typo. Fixes: 48e8d6d207a ("panfrost, panvk: The size of resource tables needs to be a multiple of 4.") Reviewed-by: Boris Brezillon <[email protected]> Reviewed-by: Christoph Pillmayer <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37951> (cherry picked from commit 387f75f43ddbc036c2070e8386deb180282f420a) - - - - - b20ae278 by Connor Abbott at 2025-10-29T17:42:20+01:00 tu: Don't patch GMEM for input attachments never in GMEM This can happen if we resolve to a resolve attachment and then use that resolve attachment as an input attachment in a later subpass. We don't need to put it in GMEM, but it's still considered "written" because input attachment reads need a dependency after the resolve. MSRTSS input attachment tests effectively created such a scenario after lowering to transient multisample attachments and inserting resolves. Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37919> (cherry picked from commit d491a79027b175f2b13536b5db67b471ba58bd28) - - - - - 2b8d7ec8 by Connor Abbott at 2025-10-29T17:42:21+01:00 tu: Fix 3d load path with D24S8 on a7xx We need to always use the FMT6_Z24S8_AS_R8G8B8A8 format for GMEM even if UBWC is disabled, as already done for the 2d store path. Because we use the pre-baked RB_MRT_BUF_INFO register value, this means we have to override it. Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37919> (cherry picked from commit 9417ce287c29495090ce88df3084a58542db6966) - - - - - 84d7289a by Connor Abbott at 2025-10-29T17:42:21+01:00 tu: Also disable stencil load for attachments not in GMEM We were accidentally still emitting loads for D32S8 resolve attachments. Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37919> (cherry picked from commit a3652af380cc1d4ec55fe3f784b7c66082fa2be1) - - - - - 2f0f0ba0 by Emma Anholt at 2025-10-29T17:42:21+01:00 nir/shrink_stores: Don't shrink stores to an invalid num_components. Avoids a regression in the CL CTS on the next commit. Fixes: 2dba7e60567f ("nir: split nir_opt_shrink_stores from nir_opt_shrink_vectors") Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37313> (cherry picked from commit 537cc4e0ffc1b8c3f1b6a9857749102723775a78) - - - - - 6b3cce40 by Mel Henning at 2025-10-29T17:42:21+01:00 nvk: Really fix maxVariableDescriptorCount w/ iub I didn't test "nvk: Fix maxVariableDescriptorCount with iub" as thoroughly as I should have and it regressed dEQP-VK.api.maintenance3_check.descriptor_set because we were then violating the requirement that maxPerSetDescriptors describes a limit that's guaranteed to be supported (and reported as supported in GetDescriptorSetLayoutSupport). That commit was also based on a misreading of nvk_nir_lower_descriptors.c where I thought that the end offset of an inline uniform block needed to be less than the size of a UBO. That is not the case - on closer inspection that code gracefully falls back to placing IUBs in globablmem if necessary. So, we can afford to be less strict about our IUB sizing and only require that IUBs follow the existing limit imposed by maxInlineUniformBlockSize. Fixes: ff7f785f09ce ("nvk: Fix maxVariableDescriptorCount with iub") Reviewed-by: Faith Ekstrand <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37922> (cherry picked from commit 77cd629b34f67b7035ae9c167ce1fedefe75ce32) - - - - - 74e2818d by Lionel Landwerlin at 2025-10-29T17:42:21+01:00 brw: only consider cross lane access on non scalar VGRFs Signed-off-by: Lionel Landwerlin <[email protected]> Fixes: 1bff4f93ca ("brw: Basic infrastructure to store convergent values as scalars") Reviewed-by: Francisco Jerez <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37939> (cherry picked from commit 70aa028f274f5c25a4d38ba64f327557dbbb0c9e) - - - - - b1b03725 by Lionel Landwerlin at 2025-10-29T17:42:21+01:00 brw: fix ballot() type operations in shaders with HALT instructions Fixes dEQP-VK.reconvergence.terminate_invocation.bit_count LNL fossildb stats: Totals from 16489 (3.36% of 490184) affected shaders: Instrs: 3710499 -> 3710500 (+0.00%) Cycle count: 91601018 -> 90305642 (-1.41%); split: -1.81%, +0.40% Max dispatch width: 523936 -> 523952 (+0.00%); split: +0.02%, -0.01% Signed-off-by: Lionel Landwerlin <[email protected]> Cc: mesa-stable Reviewed-by: Francisco Jerez <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37939> (cherry picked from commit 757c042e39a3281999cd65ede1ad508159ae15d4) - - - - - a234f97c by Faith Ekstrand at 2025-10-29T17:42:21+01:00 panvk: Fix integer dot product properties We already set has_[su]dot_4x8[_sat] in nir_shader_compiler_options so we're already getting the opcodes. We just need to advertise the features properly. If bifrost_compile.h is to be believed, those are all available starting at gen 9. Closes: https://gitlab.freedesktop.org/panfrost/mesa/-/issues/218 Closes: https://gitlab.freedesktop.org/panfrost/mesa/-/issues/219 Fixes: f7f9b3d170f5 ("panvk: Move to vk_properties") Reviewed-by: Mary Guillemard <[email protected]> Reviewed-by: Lars-Ivar Hesselberg Simonsen <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37980> (cherry picked from commit 38950083ae9fe5650150614687c7c46342d71d02) - - - - - e790aed4 by Olivia Lee at 2025-10-29T17:42:21+01:00 panfrost: fix cl_local_size for precompiled shaders nir_lower_compute_system_values will attempt to lower load_workgroup_size unless workgroup_size_variable is set. For precomp shaders, the workgroup size is set statically for each entrypoint by nir_precompiled_build_variant. Because we call lower_compute_system_values early, it sets the workgroup size to zero. Temporarily setting workgroup_size_variable while we are still processing all the entrypoints together inhibits this. Signed-off-by: Olivia Lee <[email protected]> Fixes: 20970bcd965 ("panfrost: Add base of OpenCL C infrastructure") Reviewed-by: Eric R. Smith <[email protected]> Reviewed-by: Mary Guillemard <[email protected]> Acked-by: Alyssa Rosenzweig <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37799> (cherry picked from commit a410d90fd254dd4930e72547de430a8cf5daf13b) - - - - - 31c097e0 by Karol Herbst at 2025-10-29T17:42:21+01:00 nak: fix MMA latencies on Ampere Acked-by: Faith Ekstrand <[email protected]> Fixes: 7a01953a396 ("nak: Add Ampere and Ada latency information") Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37941> (cherry picked from commit e7dca5a6ca3ab4f2215d48292bfa3bbb3aab6d2c) - - - - - 2e100429 by Pierre-Eric Pelloux-Prayer at 2025-10-29T17:42:21+01:00 radeonsi: propagate shader updates for merged shaders In case of merged shaders (eg: VS+GS), a change to VS should trigger a GS update. Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/13935 Fixes: b1a34ac95df ("radeonsi: change do_update_shaders boolean to a bitmask") Reviewed-by: Marek Olšák <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37882> (cherry picked from commit 90103fe61862b8cd3703dea5d906244f1bc61e4f) - - - - - 8b860c7a by Benjamin Cheng at 2025-10-29T17:42:21+01:00 radv/video_enc: Cleanup slice count assert This was left over when first enabling multiple slice encoding. Fixes: 63e952ff2cc ("radv/video: Support encoding multiple slices") Reviewed-by: David Rosca <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37999> (cherry picked from commit b6d6c1af73b1e1cad5f84b59eaedad4faacd8dda) - - - - - ac45b8fd by Valentine Burley at 2025-10-29T17:42:21+01:00 tu: Fix indexing with variable descriptor count Based on RADV. The Vulkan spec says: "If bindingCount is zero or if this structure is not included in the pNext chain, the VkDescriptorBindingFlags for each descriptor set layout binding is considered to be zero. Otherwise, the descriptor set layout binding at VkDescriptorSetLayoutCreateInfo::pBindings[i] uses the flags in pBindingFlags[i]." Fixes dEQP-VK.api.maintenance3_check.* in VKCTS 1.4.4.0. Cc: mesa-stable Signed-off-by: Valentine Burley <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38002> (cherry picked from commit 17e25b4983dc333d971c7b6eed4bdae741a9bf03) - - - - - cdccd8a1 by Valentine Burley at 2025-10-29T17:42:21+01:00 tu: Fix maxVariableDescriptorCount with inline uniform blocks It must not be larger than maxInlineUniformBlockSize. Fixes VKCTS 1.4.4.0's dEQP-VK.api.maintenance3_check.support_count_inline_uniform_block*. Cc: mesa-stable Signed-off-by: Valentine Burley <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38002> (cherry picked from commit fd2fa0fbc93792bd9c588c61b1ba37fe05893bba) - - - - - b3b6bac3 by Faith Ekstrand at 2025-10-29T17:42:22+01:00 nvk: Include the chipset in the pipeline/binary cache UUID Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38018> (cherry picked from commit d1793c7a594f49f8870beeef99bd3edcdb1ddb9f) - - - - - 3c31f722 by Faith Ekstrand at 2025-10-29T17:42:22+01:00 nvk: Disable sampleLocationsSampleCounts for 1x MSAA Suggested-by: Mel Henning <[email protected]> Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14108 Fixes: a34edc7500c8 ("nvk: Fill out sample locations on Maxwell B+") Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38018> (cherry picked from commit aa0f404f7b7d2d0b10f5a7d8b9a98006a6b5835b) - - - - - 514e0665 by Konstantin Seurer at 2025-10-29T17:42:22+01:00 aco: Fixup out_launch_size_y in the RT prolog for 1D dispatch launch_size_y is set to ACO_RT_CONVERTED_2D_LAUNCH_SIZE for 1D dispatches. The prolog needs to set it to 1 so that the app shader loads the correct value. cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37974> (cherry picked from commit 47ffe2ecd42625405b16141868af81dc3f9006c6) - - - - - 3bb663fe by Xaver Hugl at 2025-10-29T17:42:22+01:00 vulkan/wsi: remove support for VK_COLOR_SPACE_EXTENDED_SRGB_NONLINEAR_EXT It's not really clear whether or not it should use gamma 2.2 or the piece-wise transfer function, or how clients would use it for wider gamut in general. Currently no compositors I know of support ext_srgb, so this shouldn't affect applications in practice. Signed-off-by: Xaver Hugl <[email protected]> Fixes: 4b663d56 ("vulkan/wsi: implement support for VK_EXT_hdr_metadata on Wayland") Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36444> (cherry picked from commit 14fcf145e3d95975b9d93d8c91b20331709b9d22) - - - - - 8d1294d6 by Lionel Landwerlin at 2025-10-29T17:42:22+01:00 anv: destroy sets when destroying pool Signed-off-by: Lionel Landwerlin <[email protected]> Cc: mesa-stable Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14169 Reviewed-by: Ivan Briano <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38035> (cherry picked from commit 2689056c82dde882238058d183f6455750d4e340) - - - - - 8c38ff74 by Connor Abbott at 2025-10-29T17:42:22+01:00 tu: Fix RT count with remapped color attachments The index of each RT is the remapped color attachment index, so we have to use the remapped indices when telling the HW the number of RTs. This fixes KHR-GLES3.framebuffer_blit.scissor_blit on ANGLE once we enabled VK_EXT_multisampled_render_to_single_sampled, which switched ANGLE to using dynamic rendering with VK_KHR_dynamic_rendering_local_read. Fixes: d50eef5b06f ("tu: Support color attachment remapping") Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37990> (cherry picked from commit 8d276e0d70151744509cbd7bb89ae8b58e8fed93) - - - - - c2609fad by Faith Ekstrand at 2025-10-29T17:42:22+01:00 nvk: Look at the right pointer in GetDescriptorInfo for SSBOs It doesn't actually matter but we shouldn't poke at the wrong union field. Fixes: 77db71db7dfc ("nvk: Implement GetDescriptorEXT") Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38040> (cherry picked from commit a13474939dffe2e710aa1d6a38c5c458fc7a0752) - - - - - 914864a5 by Faith Ekstrand at 2025-10-29T17:42:22+01:00 nvk: Capture/replay buffer addresses for EDB capture/replay Fixes: 3f1c3f04be93 ("nvk: Advertise VK_EXT_descriptor_buffer") Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38040> (cherry picked from commit 998dbd43d3c3dd7f2cc0953aa8c4aeb2151964dc) - - - - - 0f12956d by Faith Ekstrand at 2025-10-29T17:42:22+01:00 panvk/shader: [de]serialize desc_info.max_varying_loads Fixes: de86641d3f4f ("panvk: Limit AD allocation to max var loads in v9+") Acked-by: Eric R. Smith <[email protected]> Reviewed-by: Lars-Ivar Hesselberg Simonsen <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38019> (cherry picked from commit a546484ed9ed235674b5bba093def5c21f7dd151) - - - - - ea04b97d by Faith Ekstrand at 2025-10-29T17:42:22+01:00 panvk/shader: Use the right copy size for deserializing dynamic UBOs/SSBOs Fixes: 563823c9ca9e ("panvk: Implement vk_shader") Acked-by: Eric R. Smith <[email protected]> Reviewed-by: Lars-Ivar Hesselberg Simonsen <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38019> (cherry picked from commit 64ad337036cf38c007047f4cf185ead9dfe4568d) - - - - - df3274f6 by Mary Guillemard at 2025-10-29T17:42:22+01:00 hk: Fix maxVariableDescriptorCount with inline uniform block Same problem as NVK on VKCTS 1.4.4.0 Fixes: 5bc828481630 ("hk: add Vulkan driver for Apple GPUs") Signed-off-by: Mary Guillemard <[email protected]> Acked-by: Alyssa Rosenzweig <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38054> (cherry picked from commit 8447b99f61aa28d0bf233fe984b10e5a4368a1df) - - - - - 6ee5bb45 by Mary Guillemard at 2025-10-29T17:42:22+01:00 hk: Disable 1x in sampleLocationsSampleCounts We don't support it, everyone dropped support for that, let's not expose it. Fixes: 5bc828481630 ("hk: add Vulkan driver for Apple GPUs") Signed-off-by: Mary Guillemard <[email protected]> Acked-by: Alyssa Rosenzweig <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38054> (cherry picked from commit 7e636d52f17c03a909cfa348033cfe6e7c0dbcba) - - - - - 5a3f942b by Mary Guillemard at 2025-10-29T17:42:22+01:00 hk: Remove unused allocation in queue_submit Unused and leaking memory, found with address sanitizer. Fixes: c64a2bbff5a3 ("asahi: port to stable uAPI") Signed-off-by: Mary Guillemard <[email protected]> Acked-by: Alyssa Rosenzweig <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38054> (cherry picked from commit 64131475a8371105a923e021299f6d8306654c53) - - - - - 8a952759 by Mary Guillemard at 2025-10-29T17:42:23+01:00 hk: Make width and height per block in HIC We were assuming that every formats used for HIC had a block widgh and height of 1x1. This is wrong for compressed formats like BC5, ASTC, ect. Fixes: 5bc828481630 ("hk: add Vulkan driver for Apple GPUs") Signed-off-by: Mary Guillemard <[email protected]> Reviewed-by: Eric Engestrom <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38060> (cherry picked from commit 887f06a966f4ac650701b9d1421dd2f67fc23ae5) - - - - - f8010cf8 by Mary Guillemard at 2025-10-29T17:42:23+01:00 hk: Allocate the temp tile buffer in copy_image_to_image_cpu We may require a bigger more than 16KiB to handle the image copy. We now always allocate a buffer to handle it properly fixing the remaining failures on VKCTS 1.4.4.0 for HIC. Fixes: 5bc828481630 ("hk: add Vulkan driver for Apple GPUs") Signed-off-by: Mary Guillemard <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38060> (cherry picked from commit d37ba302d0055f72577a47dcc4eff5400e7ecdb1) - - - - - d098ab32 by Taras Pisetskyi at 2025-10-29T17:42:23+01:00 drirc/anv: force_vk_vendor=-1 for Wuthering Waves Cc: mesa-stable Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/12459 Signed-off-by: Taras Pisetskyi <[email protected]> Reviewed-by: Tapani Pälli <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38023> (cherry picked from commit dcd9b90affab27a99a6ee44ce6d0ac3f4b5990f1) - - - - - 27c1b2e7 by Natalie Vock at 2025-10-29T17:42:23+01:00 nir/lower_shader_calls: Repair SSA after wrap_instrs Wrapping jump instructions that are located inside ifs can break SSA invariants because the else block no longer dominates the merge block. Repair the SSA to make the validator happy again. Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37957> (cherry picked from commit 50e65dac794511fb392fd9103f50c553d69a56d2) - - - - - 9b825e08 by Sagar Ghuge at 2025-10-29T17:42:23+01:00 brw/rt: Move nir_build_vec3_mat_mult_col_major helper to header Signed-off-by: Sagar Ghuge <[email protected]> Reviewed-by: Lionel Landwerlin <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36853> (cherry picked from commit 3edeb1e191980f1293f12a5515843b5f97fc249c) - - - - - c5494221 by Sagar Ghuge at 2025-10-29T17:42:23+01:00 brw/rt: fix ray_object_(direction|origin) for closest-hit shaders We were returning world BVH level for origin/direction, this commit fixes by retuning correct object BVH level origin/direction. Fixes: aaff19135644 ("brw/rt: fix ray_object_(direction|origin) for closest-hit shaders") Signed-off-by: Sagar Ghuge <[email protected]> Reviewed-by: Lionel Landwerlin <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36853> (cherry picked from commit 89fbcc8c3413016a23720d82ffb82d47d819912c) - - - - - 0c3b1a4c by Connor Abbott at 2025-10-29T17:42:23+01:00 tu: Rename tu_render_pass_attachment::clear_views to used_views It's not just used for clears, it was already used for loads and it needs to be used for stores too so clear_views was a confusing name. Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38064> (cherry picked from commit 6c3ed74ed27c8fb42c00c0c5c657d9197bc8a71d) - - - - - 39c26eef by Connor Abbott at 2025-10-29T17:42:23+01:00 tu: Fix attachment stores with subpasses with partial views Subpasses can have different view masks, although this isn't often used. So we can't use the view mask of the last subpass when deciding what to store, instead we have to use the same used_views field that's used by loads and clears. Noticed by upcoming tests for VK_QCOM_multiview_per_view_render_areas. Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38064> (cherry picked from commit c0b5c04b844b3772f1347703c9f95a1ae82ec68b) - - - - - c7be5c92 by Lionel Landwerlin at 2025-10-29T17:42:23+01:00 vulkan/render_pass: Add a missing sType Fixes: 3a204d5cf370 ("vulkan/render_pass: Add a better helper for render pass inheritance") Reviewed-by: Faith Ekstrand <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38045> (cherry picked from commit c5740c2548a023f4e03eae6ff53b598536ed2704) - - - - - 376823b0 by Benjamin Cheng at 2025-10-29T17:42:23+01:00 radv/video: Override H265 SPS block size parameters VCN only supports this set of parameters. Reviewed-by: Ruijing Dong <[email protected]> Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38061> (cherry picked from commit 84b6d8e0d7789ea18867aa36fe4fa9f4eeed9475) - - - - - 3bb5242f by Benjamin Cheng at 2025-10-29T17:42:23+01:00 radv/video: Override H265 SPS unaligned resolutions VCN requires 64x16 alignment for HEVC. When the app requests non-aligned resolutions, make up for it with conformance window cropping. Reviewed-by: Ruijing Dong <[email protected]> Cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38061> (cherry picked from commit cef8eff74d3f05a2cf5208f42c20c46c09678785) - - - - - 86ea3471 by Job Noorman at 2025-10-29T17:42:23+01:00 spirv: don't set in_bounds for structs The arr::in_bounds field was set unconditionally for every deref created for a chain. For struct derefs, which don't have this field, this would write to an unused memory location, which is probably why this never caused issues. Signed-off-by: Job Noorman <[email protected]> Fixes: f19cbe98e32 ("nir,spirv: Preserve inbounds access information") Reviewed-by: Alyssa Rosenzweig <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38110> (cherry picked from commit 0ac55b786ac357a468ca918fc848c7fe68edfc6c) - - - - - 7a20c05e by Alyssa Rosenzweig at 2025-10-29T17:42:23+01:00 anv: use D3D-compatible texturing for Proton Intel & AMD Direct3D drivers modify their rounding behaviour for texturing to match Direct3D expectations. Such behaviour is not conformant in Vulkan, and Intel hardware lacks a reasonable way to get NVIDIA's behaviour (which uniquely works for Vulkan & Direct3D). The second best choice is to use Direct3D-compatible behaviour for Proton (via driconf) and our current Vulkan-conformant behaviour everywhere else. Given the APIs diverge and there is no Vulkan extension to control the behaviour explicitly, driconf'ing on the engineName is the reasonable solution. anv already has a anv_force_filter_addr_rounding driconf option to force Direct3D behaviour for certain Direct3D titles. Here we simply apply it to all D3D10+ titles, aligning us with the Windows driver. Note that D3D9 does not have this behaviour. We therefore use standard Vulkan behaviour for D3D9 to avoid breaking D3D9 titles, even though the engineName is the same as D3D10+. This is the same solution radv uses, they call it radv_disable_trunc_coord. We could unify the driconf entries later. See https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38098#note_3166306 for a more detailed analysis, as well as the linked references: https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/27337 https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/25911 https://github.com/HansKristian-Work/vkd3d-proton/pull/1884 This fixes misrendering in piles of Direct3D games run on anv via Proton, including Assassin's Creed Valhalla. Cc: mesa-stable Closes: #13886 Signed-off-by: Alyssa Rosenzweig <[email protected]> Co-authored-by: Calder Young <[email protected]> Reviewed-by: Sagar Ghuge <[email protected]> Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38114> (cherry picked from commit 7a719527626313d18a3d41d009d3e05c98348aa2) - - - - - cbeb80c1 by Mike Blumenkrantz at 2025-10-29T17:42:24+01:00 zink: collapse gfx pipeline fetching and binding conditionals this avoids taking the wrong conditional if a pipeline fetch fails cc: mesa-stable Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38134> (cherry picked from commit 0b24fd174a8cf9543b07bdfa150d868d673ce44a) - - - - - 6ecfc443 by Eric Engestrom at 2025-10-29T18:08:35+01:00 docs: add release notes for 25.2.6 - - - - - 3f12436d by Eric Engestrom at 2025-10-29T18:08:35+01:00 VERSION: bump for 25.2.6 - - - - - 62 changed files: - .pick_status.json - VERSION - docs/relnotes.rst - docs/relnotes/25.2.5.rst - + docs/relnotes/25.2.6.rst - src/amd/common/nir/ac_nir_lower_ngg_mesh.c - src/amd/compiler/instruction_selection/aco_select_rt_prolog.cpp - src/amd/vulkan/radv_cmd_buffer.c - src/amd/vulkan/radv_physical_device.c - src/amd/vulkan/radv_video_enc.c - src/asahi/vulkan/hk_descriptor_set_layout.c - src/asahi/vulkan/hk_image.c - src/asahi/vulkan/hk_physical_device.c - src/asahi/vulkan/hk_private.h - src/asahi/vulkan/hk_queue.c - src/compiler/nir/nir_lower_shader_calls.c - src/compiler/nir/nir_opt_algebraic.py - src/compiler/nir/nir_opt_shrink_stores.c - src/compiler/nir/nir_precompiled.h - src/compiler/spirv/vtn_variables.c - src/freedreno/vulkan/tu_clear_blit.cc - src/freedreno/vulkan/tu_cmd_buffer.cc - src/freedreno/vulkan/tu_descriptor_set.cc - src/freedreno/vulkan/tu_device.cc - src/freedreno/vulkan/tu_device.h - src/freedreno/vulkan/tu_pass.cc - src/freedreno/vulkan/tu_pass.h - src/freedreno/vulkan/tu_pipeline.cc - src/gallium/drivers/llvmpipe/lp_test_arit.c - src/gallium/drivers/r300/ci/r300-rv410-fails.txt - src/gallium/drivers/r300/ci/r300-rv530-nohiz-fails.txt - src/gallium/drivers/r300/r300_state.c - src/gallium/drivers/r600/r600_state_common.c - src/gallium/drivers/radeonsi/radeon_vcn_dec.c - src/gallium/drivers/radeonsi/si_pipe.c - src/gallium/drivers/radeonsi/si_state_draw.cpp - src/gallium/drivers/zink/zink_context.c - src/gallium/drivers/zink/zink_draw.cpp - src/gallium/drivers/zink/zink_kopper.c - src/gallium/winsys/radeon/drm/meson.build - src/gallium/winsys/radeon/drm/radeon_drm_winsys.c - src/intel/compiler/brw_from_nir.cpp - src/intel/compiler/brw_load_reg.cpp - src/intel/compiler/brw_nir_lower_ray_queries.c - src/intel/compiler/brw_nir_lower_rt_intrinsics.c - src/intel/compiler/brw_nir_rt.h - src/intel/compiler/brw_schedule_instructions.cpp - src/intel/vulkan/anv_descriptor_set.c - src/intel/vulkan/anv_instance.c - src/nouveau/compiler/nak/sm80_instr_latencies.rs - src/nouveau/vulkan/nvk_buffer.c - src/nouveau/vulkan/nvk_descriptor_set.c - src/nouveau/vulkan/nvk_descriptor_set_layout.c - src/nouveau/vulkan/nvk_physical_device.c - src/nouveau/vulkan/nvk_private.h - src/panfrost/clc/pan_compile.c - src/panfrost/vulkan/csf/panvk_vX_cmd_draw.c - src/panfrost/vulkan/panvk_vX_physical_device.c - src/panfrost/vulkan/panvk_vX_shader.c - src/util/00-mesa-defaults.conf - src/vulkan/runtime/vk_render_pass.c - src/vulkan/wsi/wsi_common_wayland.c The diff was not included because it is too large. View it on GitLab: https://salsa.debian.org/xorg-team/lib/mesa/-/compare/84c1064eef19ee05a7f7f41ddaa4df830973fad7...3f12436d8018aa5f271ef67125807137995d5916 -- View it on GitLab: https://salsa.debian.org/xorg-team/lib/mesa/-/compare/84c1064eef19ee05a7f7f41ddaa4df830973fad7...3f12436d8018aa5f271ef67125807137995d5916 You're receiving this email because of your account on salsa.debian.org.
