mesa/src/amd/vulkan
Timur Kristóf 8341af5109 radv, aco, ac/nir: Tweak position export scheduling for NGG culling.
The result is about +5-ish fps in Doom Eternal.

It turns out that the location of position exports matters more
than we thought, and it's actually better to keep them at the bottom
for culling shaders rather than schedule it up to the top.

Signed-off-by: Timur Kristóf <timur.kristof@gmail.com>
Reviewed-by: Daniel Schürmann <daniel@schuermann.dev>
Reviewed-by: Samuel Pitoiset <samuel.pitoiset@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/10525>
2021-07-13 23:56:33 +00:00
..
layers ac: add ac_thread_trace::data 2021-06-03 15:39:34 +00:00
winsys radv: Support address capture and replay. 2021-07-05 17:27:51 +00:00
.editorconfig radv: Update editorconfig. 2021-04-10 03:31:58 +02:00
meson.build radv: Add -Wpointer-arith. 2021-06-21 09:32:00 +00:00
radv_acceleration_structure.c radv: Implement device-side BVH building. 2021-06-18 22:16:27 +00:00
radv_android.c radv/winsys: Return vulkan errors for buffer creation. 2021-07-05 17:27:51 +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: New shader args for NGG culling settings and viewport. 2021-07-13 23:56:33 +00:00
radv_constants.h radv: Add support for RT bind point. 2021-05-18 18:29:36 +00:00
radv_cs.h radv: Format. 2021-04-10 03:31:58 +02:00
radv_debug.c radv/winsys: Add support for a fixed VA address for replay. 2021-07-05 17:27:51 +00:00
radv_debug.h radv: Support NGG culling with new perftest environment variable. 2021-07-13 23:56:33 +00:00
radv_descriptor_set.c radv/winsys: Add support for a fixed VA address for replay. 2021-07-05 17:27:51 +00:00
radv_descriptor_set.h Revert "radv: Do not access set layout during vkCmdBindDescriptorSets." 2021-05-20 13:38:33 +00:00
radv_device.c radv: Support NGG culling with new perftest environment variable. 2021-07-13 23:56:33 +00:00
radv_formats.c radv: allow VK_FORMAT_R8G8_SRGB sampling 2021-06-21 18:17:09 +00:00
radv_image.c radv/winsys: Add support for a fixed VA address for replay. 2021-07-05 17:27:51 +00:00
radv_llvm_helper.cpp ac/llvm: set target features per function instead of per target machine 2021-05-25 16:15:44 +00:00
radv_meta.c radv: implement VK_EXT_color_write_enable 2021-07-02 10:02:02 +00:00
radv_meta.h radv: implement VK_EXT_color_write_enable 2021-07-02 10:02:02 +00:00
radv_meta_blit.c radv: Format. 2021-04-10 03:31:58 +02:00
radv_meta_blit2d.c radv: Format. 2021-04-10 03:31:58 +02:00
radv_meta_buffer.c nir: Move workgroup_size and workgroup_variable_size into common shader_info 2021-06-08 09:23:55 -07:00
radv_meta_bufimage.c nir: Move workgroup_size and workgroup_variable_size into common shader_info 2021-06-08 09:23:55 -07:00
radv_meta_clear.c radv: allow more fast clears for depth surfaces without TC-compat HTILE 2021-07-02 13:23:38 +02:00
radv_meta_copy.c radv: pass an image range to radv_layout_dcc_compressed() 2021-05-26 06:59:35 +00:00
radv_meta_copy_vrs_htile.c nir: Move workgroup_size and workgroup_variable_size into common shader_info 2021-06-08 09:23:55 -07:00
radv_meta_dcc_retile.c nir: Move workgroup_size and workgroup_variable_size into common shader_info 2021-06-08 09:23:55 -07:00
radv_meta_decompress.c radv: create only one pipeline for decompressing depth/stencil images 2021-06-18 14:15:30 +02:00
radv_meta_fast_clear.c nir: Move workgroup_size and workgroup_variable_size into common shader_info 2021-06-08 09:23:55 -07:00
radv_meta_fmask_expand.c nir: Move workgroup_size and workgroup_variable_size into common shader_info 2021-06-08 09:23:55 -07:00
radv_meta_resolve.c radv: only init DCC if compressed in the HW resolve path 2021-05-26 06:59:35 +00:00
radv_meta_resolve_cs.c nir: Move workgroup_size and workgroup_variable_size into common shader_info 2021-06-08 09:23:55 -07:00
radv_meta_resolve_fs.c radv: Format. 2021-04-10 03:31:58 +02:00
radv_nir_lower_ycbcr_textures.c radv: Handle unnormalized samplers in YCbCr lowering 2021-05-15 18:15:52 +00:00
radv_nir_to_llvm.c radv: lower primitive shading rate in NIR 2021-07-12 17:54:07 +00:00
radv_pass.c radv: handle the VRS attachment subpass 2021-04-14 09:31:13 +00:00
radv_pipeline.c radv: Support NGG culling with new perftest environment variable. 2021-07-13 23:56:33 +00:00
radv_pipeline_cache.c radv: cleanup LLVM related includes 2021-04-23 11:52:01 +02:00
radv_private.h radv: Support NGG culling with new perftest environment variable. 2021-07-13 23:56:33 +00:00
radv_query.c radv/winsys: Add support for a fixed VA address for replay. 2021-07-05 17:27:51 +00:00
radv_radeon_winsys.h radv: Support address capture and replay. 2021-07-05 17:27:51 +00:00
radv_shader.c radv, aco, ac/nir: Tweak position export scheduling for NGG culling. 2021-07-13 23:56:33 +00:00
radv_shader.h radv, aco, ac/nir: Tweak position export scheduling for NGG culling. 2021-07-13 23:56:33 +00:00
radv_shader_args.c radv: New shader args for NGG culling settings and viewport. 2021-07-13 23:56:33 +00:00
radv_shader_args.h radv: New shader args for NGG culling settings and viewport. 2021-07-13 23:56:33 +00:00
radv_shader_helper.h radv: remove RADV_DEBUG=nothreadllvm 2021-04-23 11:26:48 +00:00
radv_shader_info.c nir: Move workgroup_size and workgroup_variable_size into common shader_info 2021-06-08 09:23:55 -07:00
radv_sqtt.c radv/winsys: Add support for a fixed VA address for replay. 2021-07-05 17:27:51 +00:00
radv_util.c radv: Format. 2021-04-10 03:31:58 +02:00
radv_wsi.c radv: Format. 2021-04-10 03:31:58 +02:00
radv_wsi_display.c radv: Implement VK_EXT_acquire_drm_display 2021-06-24 15:48:38 +00:00
radv_wsi_wayland.c radv: Format. 2021-04-10 03:31:58 +02:00
radv_wsi_x11.c radv: Format. 2021-04-10 03:31:58 +02:00
si_cmd_buffer.c radv: Expose radv_get_viewport_xform in radv_private.h 2021-07-13 23:56:33 +00:00
vk_format.h radv: Format. 2021-04-10 03:31:58 +02:00
vulkan.sym radv: Add Android module info to linker script. 2021-01-12 20:17:52 +00:00