AlexIndustrial/mesa
1
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
192,525 Commits 1 Branch 0 Tags
a8a15dc5b585b99f823c2ef2f2edb7906d0b35d1
Commit Graph

178365 Commits

Author SHA1 Message Date
Rhys Perry a8a15dc5b5 aco: add struct and helpers for exec potentially empty 
Signed-off-by: Rhys Perry <pendingchaos02@gmail.com>
Reviewed-by: Daniel Schürmann <daniel@schuermann.dev>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30320>
 2024-07-26 11:08:27 +00:00
Rhys Perry 39264a90c3 aco: consider exec empty after divergent continue then divergent break 
For:
loop {
   if (divergent)
      continue
   if (divergent)
      break
   //exec is potentially empty here
   loop {
      if (divergent)
         break
   }
}
If a subset of invocations take the continue and then the rest take the
break, then exec will be empty after the break.

Signed-off-by: Rhys Perry <pendingchaos02@gmail.com>
Reviewed-by: Daniel Schürmann <daniel@schuermann.dev>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30320>
 2024-07-26 11:08:27 +00:00
Mary Guillemard e863acb318 panvk: Pass attrib_buf_idx_offset to desc_copy_info 
This was missing from the original fix and was causing MMU falults on
"dEQP-VK.memory.pipeline_barrier.host_write_uniform_texel_buffer.*".

Fixes: cec45cac84 ("panvk: Fix image support in vertex jobs")
Signed-off-by: Mary Guillemard <mary.guillemard@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30378>
 2024-07-26 08:55:26 +00:00
Mary Guillemard 4c1c169e54 panfrost: Add B8G8R8A8_SNORM in panfrost_pipe_format 
Was missing and causing a DATA_INVALID_FAULT on panvk with
"dEQP-VK.texture.texel_buffer.uniform.snorm.b8g8r8a8-snorm" test.

Signed-off-by: Mary Guillemard <mary.guillemard@collabora.com>
Reviewed-by: Boris Brezillon <boris.brezillon@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30378>
 2024-07-26 08:55:26 +00:00
Juan A. Suarez Romero 8f8b520c78 vc4: fix typo in simulator conditional declaration 
Fixes: f1f8c465d5 ("vc4,v3d,v3dv: avoid compiling in unused `sim_file` field in the {vc4,v3d}_screen/v3dv_physical_device struct")
Reviewed-by: Eric Engestrom <eric@igalia.com>
Signed-off-by: Juan A. Suarez Romero <jasuarez@igalia.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30357>
 2024-07-26 07:33:00 +00:00
GKraats ad02bfe41d i915g: fix max_lod at mipmap-sampling 
At update_map at i915_state_sampler.c max_lod is no longer set to 1
for npots. This almost totally disabled mipmapping.
Max_lod should still be set to 1, but only if it is still 0,
because no mipmap-levels are present.
According to existing comment at update_map this is needed, to
avoid problems at sampling,
if MIN_FILTER and MAX_FILTER differ.

Cc: mesa-stable

Signed-off-by: GKraats <vd.kraats@hccnet.nl>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/28638>
 2024-07-26 04:26:54 +00:00
GKraats bb95d744ca i915g: fix mipmap-layout for npots 
Remove at i945_texture_layout_2d() call of  util_next_power_of_two(),
which oversized the npot-blocks for every level to get power of 2
for width and height. Hardware doesnot expect these oversized
npot-blocks, causing mangled mipmapping.
This also is done at i915_texture_layout_2d(), which is
used by older gen3-gpus.

Cc: mesa-stable

Signed-off-by: GKraats <vd.kraats@hccnet.nl>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/28638>
 2024-07-26 04:26:54 +00:00
GKraats a1a301488b i915g: fix generation of large mipmaps 
Generation of mipmaps was failing for large heights.
If height > 1365 LEVEL 1 couldnot be generated because of
the max texture size limit (2048). This is solved by using an
offset at the texture-buffer at overflow situations.
The height of the offset must be multiple of 8.
This solves the problem mentioned at MR !27561 (closed).

Closes: https://gitlab.freedesktop.org/mesa/mesa/-/issues/10410

Cc: mesa-stable

Signed-off-by: GKraats <vd.kraats@hccnet.nl>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/28638>
 2024-07-26 04:26:53 +00:00
Mike Blumenkrantz c71c1d2a01 st/interop: return unsupported without screen hooks 
this will enable some refactoring

Reviewed-by: Jesse Natalie <jenatali@microsoft.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30377>
 2024-07-26 02:42:28 +00:00
Mike Blumenkrantz ed2ec808b1 glx: delete tests 
nobody needs these and they complicate glx interfaces by existing

Reviewed-by: Adam Jackson <ajax@redhat.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30365>
 2024-07-26 02:11:33 +00:00
Mike Blumenkrantz bb5145bcb8 llvmpipe: only use vma allocations on linux 
this was broken on other platforms

Fixes: a062544d3d ("llvmpipe: Use an anonymous file for memory allocations")

Reviewed-by: Konstantin Seurer <konstantin.seurer@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30229>
 2024-07-25 21:24:36 +00:00
Mike Blumenkrantz a8ff1bdc83 llvmpipe: handle vma allocation failure 
Fixes: a062544d3d ("llvmpipe: Use an anonymous file for memory allocations")

Reviewed-by: Konstantin Seurer <konstantin.seurer@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30229>
 2024-07-25 21:24:36 +00:00
Dave Airlie 3e01422a16 gallivm/sample: fix sampling indirect from vertex shaders 
When doing indirect sampling, we just fetch one value per lane,
but type.length == 1 caused num_quads to be 0 which caused things
to crash.

Fixes dEQP-GLES31.functional.shaders.opaque_type_indexing.sampler.uniform.vertex.sampler2d

Cc: mesa-stable
Reviewed-by: Konstantin Seurer <konstantin.seurer@gmail.com>
Reviewed-by: Roland Scheidegger <roland.scheidegger@broadcom.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30358>
 2024-07-25 20:45:58 +00:00
Georg Lehmann 97aa3464b9 radv/rt: remove one VALU from traversal loop 
Not much, but something, I guess?

Foz-DB Navi31:
Totals from 93 (0.12% of 79395) affected shaders:
MaxWaves: 1338 -> 1354 (+1.20%)
Instrs: 3689907 -> 3689721 (-0.01%); split: -0.01%, +0.00%
CodeSize: 18921812 -> 18922920 (+0.01%); split: -0.00%, +0.01%
VGPRs: 9012 -> 8988 (-0.27%)
Latency: 23153748 -> 23167640 (+0.06%)
InvThroughput: 4490882 -> 4493136 (+0.05%)
Copies: 287888 -> 287728 (-0.06%)
VALU: 2022082 -> 2021916 (-0.01%)
SALU: 458904 -> 459064 (+0.03%)

Reviewed-by: Konstantin Seurer <konstantin.seurer@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30342>
 2024-07-25 20:24:23 +00:00
Gurchetan Singh 7cc199502f vulkan/runtime: introduce vk_meta_object_list 
Code movement: Move the object list + destroy_object
function to separate files.

This allows vk_command_buffer.{h, c} to not depend on all
of vk_meta, which depends on vk_pipeline, which depends on
NIR.

Reviewed-by: Yonggang Luo <luoyonggang@gmail.com>
Reviewed-by: Yiwei Zhang <zzyiwei@chromium.org>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30355>
 2024-07-25 19:14:31 +00:00
Renato Pereyra 97ed2e4d4b egl: Refactor init of CPU tracing in EGL for Android 
eglGetPlatformDisplay is called by Android's Zygote when preloading
EGL at boot. When Perfetto is initialized by `util_cpu_trace_init`, it
launches side threads to handle tasks. Unfortunately, Zygote does not
tolerate unexpected threads created within its PID. As a result, Zygote
aborts and Android devices fail to boot.

Signed-off-by: Renato Pereyra <renatopereyra@chromium.org>
Reviewed-by: Yiwei Zhang <zzyiwei@chromium.org>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30360>
 2024-07-25 18:37:37 +00:00
Yiwei Zhang f788c87d02 venus: fix a race condition between gem close and gem handle tracking 
After using sparse array to manager virtgpu bo, we set gem_handle to 0
to indicate that the bo is invalid. However, the gem handle gets closed
before that and can be reused by another newly created bo, leading to
the tracked gem handle being unexpectedly zero'ed out.

Fixes: 88f481dd74 ("venus: make sure gem_handle and vn_renderer_bo are 1:1")
Signed-off-by: Yiwei Zhang <zzyiwei@chromium.org>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30362>
 2024-07-25 18:13:21 +00:00
Caio Oliveira 23b0798551 intel/brw: Move interp_reg and per_primitive_reg out of fs_visitor 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira a5cc8c4807 intel/brw: Move VARYING_PULL_CONSTANT_LOAD from fs_visitor to fs_builder 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira 8a39231e4f intel/brw: Move calculate_cfg out of fs_visitor 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira b98930c770 intel/brw: Move regalloc and scheduling functions out of fs_visitor 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira 5cb1f46fd1 intel/brw: Remove workgroup_size() helper from fs_visitor 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira 17b7e49089 intel/brw: Move out of fs_visitor and rename print instructions 
They use the brw_print prefix now.

Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira bb7f2db5a2 intel/brw: Move printing functions to its own file 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira cdbee4156e intel/brw: Reduce scope of some MESH specific functions 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira 67ead4edff intel/brw: Reduce scope of some TES specific functions 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira f9ddf51b70 intel/brw: Reduce scope of some TCS specific functions 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira 47b9dc9070 intel/brw: Reduce scope of some GS specific functions 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira 28858b3ad1 intel/brw: Reduce scope of some FS specific functions 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira a8b4b9dd51 intel/brw: Reduce scope of some VS specific functions 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira fdb029fe1b intel/brw: Move and reduce scope of run_*() functions 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Caio Oliveira c92b8a802e intel/brw: Move remaining compile stages to their own files 
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30169>
 2024-07-25 15:37:13 +00:00
Matt Turner a3714b55f4 intel/elk: Use REG_CLASS_COUNT 
Fixes: d44462c08d ("intel/elk: Fork Gfx8- compiler by copying existing code")
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30314>
 2024-07-25 14:55:09 +00:00
Matt Turner 5e24c21625 intel/brw: Use REG_CLASS_COUNT 
Fixes: 5d87f41a54 ("intel/fs/ra: Define REG_CLASS_COUNT constant specifying the number of register classes.")
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30314>
 2024-07-25 14:55:09 +00:00
X512 2e70757dc0 egl/haiku: fix double free of BBitmap 
Cc: mesa-stable
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30364>
 2024-07-25 14:20:42 +00:00
Karol Herbst 80da990f22 rusticl/spirv: do not add additional new lines when joining logs 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30029>
 2024-07-25 13:25:02 +00:00
Karol Herbst f283c38f9c clc: force linking of spirvs with mismatching pointer types in signatures 
With LLVM-17 and opaque pointers, sometimes the compiled spirvs lose all
their information in regards to what specific pointer type a function
parameter has.

To workaround this, we can tell the spirv linker to insert casts to handle
those cases.

See https://github.com/KhronosGroup/SPIRV-Tools/pull/5534

Cc: mesa-stable
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30029>
 2024-07-25 13:25:02 +00:00
Karol Herbst ec46d2a8f2 rusticl/kernel: move internal_args into NirKernelBuild 
This let's us support different internel arugments between devices

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30351>
 2024-07-25 10:59:00 +00:00
Karol Herbst d6b38605c8 rusticl/kernel: add type for the convert_spirv_to_nir return value 
and also move all the (de)serialization into it

Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30351>
 2024-07-25 10:59:00 +00:00
Karol Herbst 06902ec7d2 rusticl: remove unsued serialization helpers 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30351>
 2024-07-25 10:59:00 +00:00
Karol Herbst b58390bca2 rusticl: use blob for all serialization 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30351>
 2024-07-25 10:59:00 +00:00
Karol Herbst dc896c31f9 rusticl/program: move attribute_str to the spirv module 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30351>
 2024-07-25 10:59:00 +00:00
Karol Herbst fcdf27de6b rusticl/kernel: move setting of nir metadata into lower_and_optimize_nir 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30351>
 2024-07-25 10:59:00 +00:00
Karol Herbst 629d6fc124 rusticl/kernel: make some types and fields private 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30351>
 2024-07-25 10:59:00 +00:00
Karol Herbst 3442db4106 rusticl: move more kernel related things into kernel.rs 
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30351>
 2024-07-25 10:59:00 +00:00
Christian Gmeiner c33d2db06a meson: Add missing inc's to idep_nir_headers 
nir.h includes:
 - "compiler/glsl_types.h" -> inc_src is needed
 - "util/u_atomic.h" -> "no_extern_c.h" -> inc_include needed

This makes it possible to use rust's bindgen with only nir.h
as specified include.

Signed-off-by: Christian Gmeiner <cgmeiner@igalia.com>
Acked-by: Caio Oliveira <caio.oliveira@intel.com>
Reviewed-by: Faith Ekstrand <faith.ekstrand@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30359>
 2024-07-25 05:51:19 +00:00
David Heidelberg 5f7eb8cff6 freedreno: support lua pkgconfig variants 
Distributions have different naming styles, detect all of them.

Example from Alpine / postmarketOS:
Run-time dependency lua54 found: NO (tried pkgconfig and cmake)
Run-time dependency lua5.4 found: YES 5.4.7

Signed-off-by: David Heidelberg <david@ixit.cz>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30352>
 2024-07-25 05:38:06 +00:00
Dave Airlie 76ae27efb3 llvmpipe/cs/orcjit: add stub function name for coro 
This fixes some debug
JIT session error: Unexpected definitions in module : [ cs_co_variant ]
Failed to materialize symbols: { (cs0_variant0_3, { cs_variant }) }

Fixes: bb0efdd4d8 ("llvmpipe: add shader cache support for ORCJIT implementation")
Reviewed-by: Icenowy Zheng <uwu@icenowy.me>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30335>
 2024-07-25 00:26:46 +00:00
Dave Airlie fcf9e33ec0 draw/orcjit: supply stub function for tcs coro 
This fixes a crash with shader cache enabled:
JIT session error: Unexpected definitions in module : [ draw_llvm_tcs_coro_variant ]
Failed to materialize symbols: { (draw_llvm_tcs_variant0_7, { draw_llvm_tcs_variant }) }

Fixes: bb0efdd4d8 ("llvmpipe: add shader cache support for ORCJIT implementation")
Reviewed-by: Icenowy Zheng <uwu@icenowy.me>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30335>
 2024-07-25 00:26:46 +00:00
Mike Blumenkrantz ec7afd2c24 dril: rework config creation 
the original implementation of config selection had a number of flaws:
* using eglChooseConfigs with lots of loops, which was okay for filtering but
  also added considerable complexity and made it difficult to correctly
  get all the configs
* not adding enough configs; there were a lot more color and zs formats
  which weren't in the base config list
* double buffer configs were never created
* srgb configs were also never created

there will now be fewer configs than there were pre-DRIL, but this is only
because accum buffers are now gone and not because anything of value is
missing

Fixes: 3de62b2f9a ("gallium/dril: Compatibility stub for the legacy DRI loader interface")

Acked-by: Daniel Stone <daniels@collabora.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30311>
 2024-07-24 23:42:05 +00:00