mesa/src/amd/vulkan
Rhys Perry 61ac5acca3 radv,ac/nir: lower global access to _amd global access intrinsics
fossil-db (Sienna Cichlid):
Totals from 400 (0.30% of 134621) affected shaders:
VGPRs: 18696 -> 18688 (-0.04%)
CodeSize: 2031348 -> 1946640 (-4.17%)
Instrs: 374703 -> 360226 (-3.86%)
Latency: 4200727 -> 4108628 (-2.19%); split: -2.20%, +0.01%
InvThroughput: 1059935 -> 1029441 (-2.88%); split: -2.88%, +0.00%
VClause: 5777 -> 5771 (-0.10%)
SClause: 11890 -> 10891 (-8.40%); split: -8.57%, +0.17%
Copies: 34035 -> 33259 (-2.28%); split: -2.98%, +0.70%
Branches: 11108 -> 11100 (-0.07%); split: -0.08%, +0.01%
PreSGPRs: 15999 -> 15942 (-0.36%); split: -0.44%, +0.08%
PreVGPRs: 16994 -> 16970 (-0.14%)

fossil-db (Polaris10):
Totals from 400 (0.29% of 135668) affected shaders:
SGPRs: 23799 -> 22919 (-3.70%); split: -4.30%, +0.61%
VGPRs: 18480 -> 18472 (-0.04%)
CodeSize: 2090316 -> 2041592 (-2.33%)
Instrs: 395461 -> 385747 (-2.46%); split: -2.46%, +0.00%
Latency: 5045768 -> 5020196 (-0.51%); split: -0.53%, +0.02%
InvThroughput: 2694320 -> 2689886 (-0.16%); split: -0.23%, +0.07%
VClause: 5982 -> 5968 (-0.23%)
SClause: 12064 -> 10823 (-10.29%); split: -10.33%, +0.04%
Copies: 48233 -> 48322 (+0.18%); split: -0.47%, +0.65%
PreSGPRs: 16409 -> 16358 (-0.31%); split: -0.39%, +0.08%

fossil-db (Pitcairn):
Totals from 400 (0.29% of 135668) affected shaders:
SGPRs: 22431 -> 22215 (-0.96%); split: -2.60%, +1.64%
VGPRs: 18776 -> 18560 (-1.15%); split: -1.21%, +0.06%
CodeSize: 2104440 -> 2017708 (-4.12%)
MaxWaves: 2363 -> 2367 (+0.17%)
Instrs: 413099 -> 397446 (-3.79%)
Latency: 5507707 -> 5450251 (-1.04%); split: -1.12%, +0.07%
InvThroughput: 2838867 -> 2786903 (-1.83%); split: -1.83%, +0.00%
VClause: 10334 -> 10097 (-2.29%)
SClause: 12346 -> 11005 (-10.86%); split: -10.89%, +0.02%
Copies: 54034 -> 52065 (-3.64%); split: -3.99%, +0.35%
PreSGPRs: 17916 -> 17857 (-0.33%); split: -0.40%, +0.07%
PreVGPRs: 16917 -> 16893 (-0.14%)

Signed-off-by: Rhys Perry <pendingchaos02@gmail.com>
Reviewed-by: Timur Kristóf <timur.kristof@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/14124>
2022-04-13 16:23:35 +00:00
..
layers radv: drop EXT or KHR suffixes for stuff promoted in Vulkan 1.3 2022-03-31 07:13:17 +00:00
winsys radv: improve failure logging for amdgpu on init 2022-04-07 13:48:34 +00:00
.editorconfig radv: Update editorconfig. 2021-04-10 03:31:58 +02:00
00-radv-defaults.conf radv: enable radv_disable_aniso_single_level for DXVK/vkd3d 2022-03-17 15:10:06 +00:00
meson.build radv: Remove radv_util.c 2022-04-05 15:53:46 +00:00
radv_acceleration_structure.c radv: Add more BVH vertex formats. 2022-04-01 21:00:20 +00:00
radv_acceleration_structure.h radv: Add copy/serialization info to accel struct headers. 2021-10-01 13:43:28 +00:00
radv_android.c radv: Move QueueSignalReleaseImageANDROID to common code 2022-01-05 16:36:10 +00:00
radv_check_va.py radv: add a Python script to check if a VA was ever valid 2020-12-30 08:40:21 +01:00
radv_cmd_buffer.c radv: allow holes in inline push constants 2022-04-12 11:44:30 +00:00
radv_constants.h radv: Use larger arena sizes. 2022-02-11 23:20:21 +00:00
radv_cs.h radv: apply spi_cu_en to CU_EN 2022-01-05 01:36:10 -05:00
radv_debug.c radv: abstract queue family away from queue family index. 2022-03-11 04:38:55 +00:00
radv_debug.h radv: use wave32 for raytracing 2022-01-21 16:25:16 +00:00
radv_descriptor_set.c radv: add few helpers to deal with pipeline layout 2022-04-12 06:31:33 +00:00
radv_descriptor_set.h radv: add few helpers to deal with pipeline layout 2022-04-12 06:31:33 +00:00
radv_device.c radv: Refactor ray tracing support checks 2022-04-12 16:13:38 +00:00
radv_formats.c radv: set read/write without format flags for supported texel buffers 2022-04-12 15:52:03 +00:00
radv_image.c radv: rework the workaround that disables DCC for incompatible copies 2022-04-01 08:21:52 +02:00
radv_llvm_helper.cpp radv: Rename radv_shader_helper.h to radv_llvm_helper.h 2021-10-01 10:40:18 +02:00
radv_llvm_helper.h radv: Rename radv_shader_helper.h to radv_llvm_helper.h 2021-10-01 10:40:18 +02:00
radv_meta.c radv: use radv_dynamic_state for saving/restoring meta operations 2022-04-05 07:54:52 +00:00
radv_meta.h radv: use radv_dynamic_state for saving/restoring meta operations 2022-04-05 07:54:52 +00:00
radv_meta_blit.c radv: only declare dynamic states that are used by internal operations 2022-04-05 07:54:52 +00:00
radv_meta_blit2d.c radv: only declare dynamic states that are used by internal operations 2022-04-05 07:54:52 +00:00
radv_meta_buffer.c radv: drop EXT or KHR suffixes for stuff promoted in Vulkan 1.3 2022-03-31 07:13:17 +00:00
radv_meta_bufimage.c radv: initialize workgroup_size in radv_meta_init_shader 2021-12-08 11:07:40 +00:00
radv_meta_clear.c radv: only declare dynamic states that are used by internal operations 2022-04-05 07:54:52 +00:00
radv_meta_copy.c radv: drop EXT or KHR suffixes for stuff promoted in Vulkan 1.3 2022-03-31 07:13:17 +00:00
radv_meta_copy_vrs_htile.c radv: drop EXT or KHR suffixes for stuff promoted in Vulkan 1.3 2022-03-31 07:13:17 +00:00
radv_meta_dcc_retile.c radv: drop EXT or KHR suffixes for stuff promoted in Vulkan 1.3 2022-03-31 07:13:17 +00:00
radv_meta_decompress.c radv: convert the meta depth decompression path to dynamic rendering 2022-04-01 08:21:52 +02:00
radv_meta_etc_decode.c radv: Add ETC2 decode shader. 2021-12-14 11:30:48 +00:00
radv_meta_fast_clear.c radv: convert the meta fast clear flush path to dynamic rendering 2022-04-01 08:21:52 +02:00
radv_meta_fmask_copy.c radv: fix optimized MSAA copies with suballocated images 2022-01-26 10:54:33 +00:00
radv_meta_fmask_expand.c radv: drop EXT or KHR suffixes for stuff promoted in Vulkan 1.3 2022-03-31 07:13:17 +00:00
radv_meta_resolve.c radv: use the common vk_framebuffer 2022-04-01 08:21:59 +02:00
radv_meta_resolve_cs.c radv: use the common vk_framebuffer 2022-04-01 08:21:59 +02:00
radv_meta_resolve_fs.c radv: only declare dynamic states that are used by internal operations 2022-04-05 07:54:52 +00:00
radv_nir_apply_pipeline_layout.c radv: assert that the arg is declared when used in get_scalar_arg() 2022-04-08 06:40:52 +00:00
radv_nir_lower_ray_queries.c radv: Refactor ray tracing support checks 2022-04-12 16:13:38 +00:00
radv_nir_lower_ycbcr_textures.c radv: Don't hash ycbcr sampler base object. 2022-03-18 17:56:15 +00:00
radv_nir_to_llvm.c radv: lower has_multiview_view_index in NIR 2022-03-31 07:34:21 +00:00
radv_pass.c radv: drop EXT or KHR suffixes for stuff promoted in Vulkan 1.3 2022-03-31 07:13:17 +00:00
radv_perfcounter.c amd: add a workaround for an SQ perf counter bug 2022-02-22 11:41:04 +00:00
radv_pipeline.c radv,ac/nir: lower global access to _amd global access intrinsics 2022-04-13 16:23:35 +00:00
radv_pipeline_cache.c radv: store the shader sha1 to radv_pipeline_stage 2022-04-12 06:13:24 +00:00
radv_pipeline_rt.c radv: Refactor ray tracing support checks 2022-04-12 16:13:38 +00:00
radv_private.h radv: Refactor ray tracing support checks 2022-04-12 16:13:38 +00:00
radv_query.c radv: suspend/resume queries during internal driver operations 2022-03-31 11:47:22 +00:00
radv_radeon_winsys.h radv/winsys: add support for new CTX OP to set/get stable pstates 2022-02-21 11:16:11 +00:00
radv_rt_common.c radv: Refactor ray tracing support checks 2022-04-12 16:13:38 +00:00
radv_rt_common.h radv: Replace magic constants with enum values 2022-04-03 12:43:00 +00:00
radv_sdma_copy_image.c radv: drop EXT or KHR suffixes for stuff promoted in Vulkan 1.3 2022-03-31 07:13:17 +00:00
radv_shader.c radv: Only use TES vertex offset 2 for triangles and quads. 2022-04-13 15:04:26 +00:00
radv_shader.h radv: allow holes in inline push constants 2022-04-12 11:44:30 +00:00
radv_shader_args.c radv: increase inline push constant limit if we can inline all constants 2022-04-12 11:44:30 +00:00
radv_shader_args.h radv: add missing multi inclusion define to radv_shader_args.h 2022-04-08 16:38:30 +00:00
radv_shader_info.c radv,aco: implement 64-bit inline push constants 2022-04-12 11:44:30 +00:00
radv_spm.c radv: add initial SPM support on GFX10+ 2021-12-08 08:40:51 +00:00
radv_sqtt.c radv: abstract queue family away from queue family index. 2022-03-11 04:38:55 +00:00
radv_wsi.c radv: try and fix internal transfer queue mapping 2022-03-13 02:37:19 +00:00
si_cmd_buffer.c radv: abstract queue family away from queue family index. 2022-03-11 04:38:55 +00:00
vk_format.h vulkan: Move common format function to vulkan/util/vk_format.h 2022-03-31 17:18:22 +00:00
vulkan.sym radv: Add Android module info to linker script. 2021-01-12 20:17:52 +00:00
vulkan_radv.def radv: fix build with mingw 2021-08-13 12:13:21 +02:00