diff options
author | ReinUsesLisp <reinuseslisp@airmail.cc> | 2021-06-24 22:40:24 +0200 |
---|---|---|
committer | ameerj <52414509+ameerj@users.noreply.github.com> | 2021-07-23 03:51:39 +0200 |
commit | 8a3427a4c857aa08e365d1776d1f0d9f32639c9c (patch) | |
tree | 6436b8973fe9f97c131aea892885b61215b67e01 /src/shader_recompiler/backend/glasm/emit_glasm.cpp | |
parent | shader: Rework varyings and implement passthrough geometry shaders (diff) | |
download | yuzu-8a3427a4c857aa08e365d1776d1f0d9f32639c9c.tar yuzu-8a3427a4c857aa08e365d1776d1f0d9f32639c9c.tar.gz yuzu-8a3427a4c857aa08e365d1776d1f0d9f32639c9c.tar.bz2 yuzu-8a3427a4c857aa08e365d1776d1f0d9f32639c9c.tar.lz yuzu-8a3427a4c857aa08e365d1776d1f0d9f32639c9c.tar.xz yuzu-8a3427a4c857aa08e365d1776d1f0d9f32639c9c.tar.zst yuzu-8a3427a4c857aa08e365d1776d1f0d9f32639c9c.zip |
Diffstat (limited to '')
-rw-r--r-- | src/shader_recompiler/backend/glasm/emit_glasm.cpp | 28 |
1 files changed, 23 insertions, 5 deletions
diff --git a/src/shader_recompiler/backend/glasm/emit_glasm.cpp b/src/shader_recompiler/backend/glasm/emit_glasm.cpp index 2b96977b3..64787b353 100644 --- a/src/shader_recompiler/backend/glasm/emit_glasm.cpp +++ b/src/shader_recompiler/backend/glasm/emit_glasm.cpp @@ -304,6 +304,9 @@ void SetupOptions(const IR::Program& program, const Profile& profile, header += "OPTION NV_viewport_array2;"; } } + if (program.is_geometry_passthrough && profile.support_geometry_shader_passthrough) { + header += "OPTION NV_geometry_shader_passthrough;"; + } if (info.uses_typeless_image_reads && profile.support_typeless_image_loads) { header += "OPTION EXT_shader_image_load_formatted;"; } @@ -410,11 +413,26 @@ std::string EmitGLASM(const Profile& profile, const RuntimeInfo& runtime_info, I runtime_info.tess_clockwise ? "CW" : "CCW"); break; case Stage::Geometry: - header += fmt::format("PRIMITIVE_IN {};" - "PRIMITIVE_OUT {};" - "VERTICES_OUT {};", - InputPrimitive(runtime_info.input_topology), - OutputPrimitive(program.output_topology), program.output_vertices); + header += fmt::format("PRIMITIVE_IN {};", InputPrimitive(runtime_info.input_topology)); + if (program.is_geometry_passthrough) { + if (profile.support_geometry_shader_passthrough) { + for (size_t index = 0; index < IR::NUM_GENERICS; ++index) { + if (program.info.passthrough.Generic(index)) { + header += fmt::format("PASSTHROUGH result.attrib[{}];", index); + } + } + if (program.info.passthrough.AnyComponent(IR::Attribute::PositionX)) { + header += "PASSTHROUGH result.position;"; + } + } else { + LOG_WARNING(Shader_GLASM, "Passthrough geometry program used but not supported"); + } + } else { + header += + fmt::format("VERTICES_OUT {};" + "PRIMITIVE_OUT {};", + program.output_vertices, OutputPrimitive(program.output_topology)); + } break; case Stage::Compute: header += fmt::format("GROUP_SIZE {} {} {};", program.workgroup_size[0], |