diff options
author | Lioncash <mathew1800@gmail.com> | 2020-09-23 21:06:21 +0200 |
---|---|---|
committer | Lioncash <mathew1800@gmail.com> | 2020-09-23 21:06:25 +0200 |
commit | ffeb4ef83e731bb54a82080749ca22a263466788 (patch) | |
tree | 1e920ce312a2692c461e093f0a7875d4e2ee56d8 /src/video_core/shader | |
parent | Merge pull request #4698 from lioncash/optional-null (diff) | |
download | yuzu-ffeb4ef83e731bb54a82080749ca22a263466788.tar yuzu-ffeb4ef83e731bb54a82080749ca22a263466788.tar.gz yuzu-ffeb4ef83e731bb54a82080749ca22a263466788.tar.bz2 yuzu-ffeb4ef83e731bb54a82080749ca22a263466788.tar.lz yuzu-ffeb4ef83e731bb54a82080749ca22a263466788.tar.xz yuzu-ffeb4ef83e731bb54a82080749ca22a263466788.tar.zst yuzu-ffeb4ef83e731bb54a82080749ca22a263466788.zip |
Diffstat (limited to 'src/video_core/shader')
-rw-r--r-- | src/video_core/shader/registry.cpp | 36 |
1 files changed, 19 insertions, 17 deletions
diff --git a/src/video_core/shader/registry.cpp b/src/video_core/shader/registry.cpp index cdf274e54..de9a3df90 100644 --- a/src/video_core/shader/registry.cpp +++ b/src/video_core/shader/registry.cpp @@ -24,31 +24,33 @@ GraphicsInfo MakeGraphicsInfo(ShaderType shader_stage, ConstBufferEngineInterfac if (shader_stage == ShaderType::Compute) { return {}; } - auto& graphics = static_cast<Tegra::Engines::Maxwell3D&>(engine); - - GraphicsInfo info; - info.tfb_layouts = graphics.regs.tfb_layouts; - info.tfb_varying_locs = graphics.regs.tfb_varying_locs; - info.primitive_topology = graphics.regs.draw.topology; - info.tessellation_primitive = graphics.regs.tess_mode.prim; - info.tessellation_spacing = graphics.regs.tess_mode.spacing; - info.tfb_enabled = graphics.regs.tfb_enabled; - info.tessellation_clockwise = graphics.regs.tess_mode.cw; - return info; + + auto& graphics = dynamic_cast<Tegra::Engines::Maxwell3D&>(engine); + + return { + .tfb_layouts = graphics.regs.tfb_layouts, + .tfb_varying_locs = graphics.regs.tfb_varying_locs, + .primitive_topology = graphics.regs.draw.topology, + .tessellation_primitive = graphics.regs.tess_mode.prim, + .tessellation_spacing = graphics.regs.tess_mode.spacing, + .tfb_enabled = graphics.regs.tfb_enabled != 0, + .tessellation_clockwise = graphics.regs.tess_mode.cw.Value() != 0, + }; } ComputeInfo MakeComputeInfo(ShaderType shader_stage, ConstBufferEngineInterface& engine) { if (shader_stage != ShaderType::Compute) { return {}; } - auto& compute = static_cast<Tegra::Engines::KeplerCompute&>(engine); + + auto& compute = dynamic_cast<Tegra::Engines::KeplerCompute&>(engine); const auto& launch = compute.launch_description; - ComputeInfo info; - info.workgroup_size = {launch.block_dim_x, launch.block_dim_y, launch.block_dim_z}; - info.local_memory_size_in_words = launch.local_pos_alloc; - info.shared_memory_size_in_words = launch.shared_alloc; - return info; + return { + .workgroup_size = {launch.block_dim_x, launch.block_dim_y, launch.block_dim_z}, + .shared_memory_size_in_words = launch.shared_alloc, + .local_memory_size_in_words = launch.local_pos_alloc, + }; } } // Anonymous namespace |