AlexIndustrial/mesa
1
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
214,640 Commits 1 Branch 0 Tags
0216f09e45280e040bef410bb5d49f67bccd4bcd
Commit Graph

214640 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Marek Olšák 0216f09e45 nir/lower_interpolation: check IO location correctly 
Vangogh timed out.

Reviewed-by: Alyssa Rosenzweig <alyssa.rosenzweig@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38337>
 2025-11-10 16:44:36 +00:00
Sergi Blanch Torne 9e63a8a5d0 Revert "ci: disable Collabora's farm due to maintenance" 
This reverts commit a21cd9d60c.

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38344>
 2025-11-10 14:24:01 +00:00
Ahmed Hesham 6901bb0c6c panfrost/lima/panvk: Define a common vendor ID 
Rusticl reports `CL_DEVICE_VENDOR_ID` using the `vendor_id` property
defined in Panfrost. The value is not set so a `0` is reported
instead.

Initialise the value to `0x13B5`, which is Arm's PCI vendor ID.

Add the definition in `lib/pan_props.h` so it can be shared with
Gallium Lima, Panfrost and PanVK.

Signed-off-by: Ahmed Hesham <ahmed.hesham@arm.com>
Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38283>
 2025-11-10 14:01:40 +00:00
Valentine Burley e91832739b venus/ci: Add missing Collabora farm rules to ANV jobs 
Signed-off-by: Valentine Burley <valentine.burley@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38348>
 2025-11-10 12:47:26 +00:00
Patrick Lerda ae049f6fea 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: 713edb5998 ("r600/sfn: handle the IF predicate in the scheduler")
Signed-off-by: Patrick Lerda <patrick9876@free.fr>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38213>
 2025-11-10 12:25:38 +00:00
Karol Herbst 92a4ae0ab2 rusticl/spirv: preserve signed zeroes by default 
Cc: mesa-stable
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38327>
 2025-11-10 10:52:56 +00:00
Karol Herbst df344f12cc 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: bb2453c649 ("rusticl/kernel: move most of the code in launch inside the closure")
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38327>
 2025-11-10 10:52:56 +00:00
Karol Herbst c0f0baeaca rusticl/queue: fix error code for invalid sampler kernel arg 
Fixes: 5795ee0e08 ("rusticl: translate spirv to nir and first steps to kernel arg handling")
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38327>
 2025-11-10 10:52:56 +00:00
Karol Herbst e98abe35c0 rusticl/queue: fix error code for invalid queue properties part 2 
Fixes: 2c202eb787 ("rusticl: verify validity of property names and values")
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38327>
 2025-11-10 10:52:56 +00:00
Karol Herbst e83400cab2 rusticl/queue: fix error code for invalid queue properties part 1 
Cc: mesa-stable
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38327>
 2025-11-10 10:52:56 +00:00
Lucas Fryzek a824754de0 lvp: Enable VK_FORMAT_R4G4B4A4_UNORM_PACK16 
Reviewed-by: Christian Gmeiner <cgmeiner@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36558>
 2025-11-10 10:10:07 +00:00
Eric Engestrom f689322d27 ci: track src/android_stub/ changes 
Fixes: 932f51d593 ("ci: Include enough Android headers to let us compile test EGL")
Suggested-by: Yonggang Luo <luoyonggang@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38346>
 2025-11-10 09:27:07 +00:00
Eric Engestrom 2ec3e536fd ci: track src/c11/ changes 
It's used by mesa_util, so let's just consider changes to it can affect
any job.

Fixes: b2ddec4e98 ("c11: Implement c11/time.h with c11/impl/time.c")
Reviewed-by: Yonggang Luo <luoyonggang@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38346>
 2025-11-10 09:27:07 +00:00
Erik Faye-Lund d607082b90 radeonsi/ci: document flake 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38345>
 2025-11-10 09:13:07 +00:00
Lionel Landwerlin c478b6355a 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>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38306>
 2025-11-10 08:57:06 +00:00
Christian Gmeiner 0c31313b6e etnaviv: Disable trilinear filtering for shadow samplers 
The Vivante GPUs have a hardware bug where trilinear filtering
(MIP=LINEAR) produces incorrect results when used with depth/stencil
textures that have shadow comparison enabled, leading to GPU hangs.

Work around this by forcing MIP=NEAREST for depth/stencil formats,
downgrading from trilinear to bilinear filtering as done by binary blob
too.

Fixes dEQP-GLES3.functional.texture.shadow.*.linear_mipmap_linear.*
except DEPTH32F ones on all GPUs I have access to.

Signed-off-by: Christian Gmeiner <cgmeiner@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38308>
 2025-11-10 08:20:53 +00:00
Sergi Blanch Torne a21cd9d60c ci: disable Collabora's farm due to maintenance 
Planned downtime in the farm:
* Start: 2025-11-10 08:00 UTC
* End: 2025-11-10 14:00 UTC

Signed-off-by: Sergi Blanch Torne <sergi.blanch.torne@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37938>
 2025-11-10 07:09:36 +00:00
spencer-lunarg f8e5e7cd7d lavapipe: Fix crash when using zero queues 
When using VK_KHR_maintenance9 the user can pass a null pointer
to VkDeviceQueueCreateInfo and we will create a dummy queue for
them.

Tested with new dEQP-VK.pipeline.no_queues.*
https://gerrit.khronos.org/c/vk-gl-cts/+/18717

Signed-off-by: spencer-lunarg <spencer@lunarg.com>
Reviewed-by: Konstantin Seurer <konstantin.seurer@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38288>
 2025-11-10 02:10:43 +00:00
Dave Airlie 179e744f75 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>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38298>
 2025-11-10 07:01:50 +10:00
Vinson Lee 1889f1a779 gfxstream: Fix GfxStreamVulkanMapper.cpp build error 
../src/gfxstream/guest/platform/kumquat/vulkan-mapper/GfxStreamVulkanMapper.cpp: In static member function ‘static GfxStreamVulkanMapper* GfxStreamVulkanMapper::getInstance(std::optional<DeviceId>)’:
../src/gfxstream/guest/platform/kumquat/vulkan-mapper/GfxStreamVulkanMapper.cpp:208:30: error: ‘os_get_option’ was not declared in this scope
  208 |         const char* driver = os_get_option(VK_ICD_FILENAMES);
      |

Fixes: 222b85328e ("mesa: replace most occurrences of getenv() with os_get_option()")
Signed-off-by: Vinson Lee <vlee@freedesktop.org>
Reviewed-by: Yonggang Luo <luoyonggang@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38331>
 2025-11-09 03:10:37 +00:00
Yiwei Zhang 894c47e384 pps/meson: minor refactor for pps_deps 
Reviewed-by: Yonggang Luo <luoyonggang@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38332>
 2025-11-08 18:39:00 -08:00
Yiwei Zhang 07a182a4bc pps/meson: amend missing util deps for os_get_option usage 
..otherwise -Dperfetto=true fails to build

Fixes: 222b85328e ("mesa: replace most occurrences of getenv() with os_get_option()")
Reviewed-by: Yonggang Luo <luoyonggang@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38332>
 2025-11-08 18:38:52 -08:00
Karol Herbst 87550fc657 st/interop: fix fence leak 
Cc: mesa-stable
Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/14050
Fixes: 1396dc1c38 ("mesa/st, dri2, wgl, glx: Modify flush_objects interop func to export a fence_fd")
Tested-by: Dmitry Baryshkov <dmitry.baryshkov@oss.qualcomm.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38310>
 2025-11-08 18:22:41 +00:00
Mel Henning 6e936ebc9c docs/nvk: Fix description of supported GPUs 
This description was incorrect in that it impiled we supported Hopper
and Blackwell A, which is not currently the case (see nvk_is_conformant
in nvk_physical_device.c).

Fixes: edd0cb6d56 ("docs/nvk: Update hardware support")
Reviewed-by: Mary Guillemard <mary@mary.zone>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38320>
 2025-11-08 17:23:58 +00:00
Mel Henning c33e278fc0 nak/nvdisasm_tests: Skip SM70 on cuda 13 
cuda 13 drops support for sm70, including nvdisasm support. This matches
the default sm list to the detected nvdisasm version.

Reviewed-by: Mary Guillemard <mary@mary.zone>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38322>
 2025-11-08 17:08:10 +00:00
Mel Henning 31e47c178d nak/nvdisasm_tests: Turn sm_list() into a function 
Reviewed-by: Mary Guillemard <mary@mary.zone>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38322>
 2025-11-08 17:08:10 +00:00
Faith Ekstrand f1cb63a21d nil: Add support for Blackwell 8 and 16-bit modifiers 
Backport-to: 25.2
Reviewed-by: James Jones <jajones@nvidia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36336>
 2025-11-07 23:00:31 +00:00
Faith Ekstrand 3247452b2c 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>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/36336>
 2025-11-07 23:00:31 +00:00
Sagar Ghuge 14194e59a4 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>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38291>
 2025-11-07 22:04:25 +00:00
Ian Romanick 4687bd43d2 vulkan: Fix incorrect assert 
You can have a group with 0 shaders in it. See also febe90e109
("vulkan: remove incorrect assert"). Fixes assertion failure while
compiling fossils/q2rtx/q2rtx-rt-pipeline.976f4ab1c0fee975.1.foz on
Intel platforms.

Fixes: e05a9b77b6 ("vulkan/runtime: split rt shaders hashing from compile")
Reviewed-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38318>
 2025-11-07 21:10:14 +00:00
Benjamin Cheng 82d944b388 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: d103b76ad6 ("radv/video: add VK_KHR_video_decode_av1 support.")
Reviewed-by: David Rosca <david.rosca@amd.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38311>
 2025-11-07 18:16:48 +00:00
Danylo Piliaiev 9c4d2a1f51 tu: Add a reason for concurrent binning disablement to RP tracepoint 
Signed-off-by: Danylo Piliaiev <dpiliaiev@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38258>
 2025-11-07 17:50:03 +00:00
Danylo Piliaiev 6b0df4b01a tu: Add concurrent_binning_barrier tracepoint 
Makes easy to spot the synchronization points for CB.

Signed-off-by: Danylo Piliaiev <dpiliaiev@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38258>
 2025-11-07 17:50:03 +00:00
Dylan Baker 829ff578e4 docs: update calendar for 25.3.0-rc4 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38309>
 2025-11-07 17:44:24 +00:00
Dylan Baker 678827cc43 docs: update calendar for 25.3.0-rc3 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38309>
 2025-11-07 17:44:24 +00:00
Dylan Baker e3996c3379 docs: update calendar for 25.3.0-rc2 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38309>
 2025-11-07 17:44:23 +00:00
Dylan Baker 8f1e7aaa3c docs: Extend calendar entries for 25.3 by 1 releases. 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38309>
 2025-11-07 17:44:21 +00:00
Ludvig Lindau 290c830416 pan/v9+: Change texel buffer limits 
Increase texel buffer size limit and lower uniform texel buffer
alignment limit.

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Ludvig Lindau 4573110e4e pan/v9+: Make texel buffers use BufferDescriptor 
Texel buffers are currently described by a TextureDescriptor,which leads
to restrictive limits on size and alignment.
These limits can be avoided by using a BufferDescriptor instead.

This requires first embedding a ConversionDescriptor into some of the
currently empty space of the BufferDescriptor, and modifying the
compiler so that instead of outputting TEX_FETCH, it will:

1. Load the ConversionDescriptor with LD_PKA
2. Get the buffer address with LEA_BUF[_IMM]
3. Use LD_CVT to get the value

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Lars-Ivar Hesselberg Simonsen af28c453ba panvk: Increase maxBufferSize to UINT32_MAX 
Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Lars-Ivar Hesselberg Simonsen 7408a09050 pan/format: Add PAN_BIND_TEXEL_BUFFER 
Expands the format table with a dedicated bit for texel buffer use. We
can fit this by setting the size of the hw-field to 21, which is fine as
we never encode more than 21 bits (see MALI_PACK_FMT).

This bit is set for all formats that support PAN_BIND_SAMPLER_VIEW and
PAN_BIND_STORAGE_IMAGE.

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Acked-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Lars-Ivar Hesselberg Simonsen c4ec6ea060 pan/va: Add late lowering passes for texel buffers 
Adds a pass that lowers texel buffer accesses for textures/images to use
BufferDescriptors. This needs to be done late in case the resource
indices must be lowered first.

Acked-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Lars-Ivar Hesselberg Simonsen b3b6fba548 nir: Add pan intrinsics for texel buffer access 
Will be used by panfrost to access texel buffers.

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Ludvig Lindau 6da1c1d025 pan/genxml: Add ConversionDesc to v9+ BufferDescriptor 
Add a field in BufferDescriptor to hold a ConversionDescriptor to
prepare for changing texel buffers to use BufferDescriptor instead of
TextureDescriptor

Also re-orders the descriptor based on word offset where appropriate.

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Ludvig Lindau 4a3d5acc1d pan/genxml: Move BufferDescriptor for v9+ 
This change is required by the next commit.

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Lars-Ivar Hesselberg Simonsen dfb6a101f1 pan/genxml: Remove reg_format from v9+ ConversionDesc 
The Register Format-field in ConversionDescriptor is not used since v9
and should be left as zero.

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Ludvig Lindau 6058cd2dfa pan/va: Add LD_CVT 
Adds LD_CVT instruction for loading memory with conversion.

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Lars-Ivar Hesselberg Simonsen a9e3b679f1 pan/va: Add LEA_BUF 
Adds the non-immediate version of LEA_BUF_IMM.

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Lars-Ivar Hesselberg Simonsen 68a14e8166 pan/va: Change LEA_BUF_IMM src description 
Gives the src for LEA_BUF_IMM a more descriptive name and specifies the
size of the register.

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00
Lars-Ivar Hesselberg Simonsen 3e3da8cf82 panfrost: Rename (LD|LEA)_BUFFER to (LD|LEA)_PKA 
This aligns with internal naming and removes confusion with
LEA_BUF[_IMM].

Reviewed-by: Erik Faye-Lund <erik.faye-lund@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37007>
 2025-11-07 17:03:53 +00:00