forked from suyu/suyu
91dddca26e
Constant attributes (in OpenGL known disabled attributes) are not supported on Vulkan, even with extensions. To emulate this behavior we return zero on reads from disabled vertex attributes in shader code. This has no caching cost because attribute formats are not dynamic state on Vulkan and we have to store it in the pipeline cache anyway. - Fixes Animal Crossing: New Horizons terrain borders
111 lines
3.1 KiB
C++
111 lines
3.1 KiB
C++
// Copyright 2019 yuzu Emulator Project
|
|
// Licensed under GPLv2 or any later version
|
|
// Refer to the license.txt file included.
|
|
|
|
#pragma once
|
|
|
|
#include <array>
|
|
#include <set>
|
|
#include <vector>
|
|
|
|
#include "common/common_types.h"
|
|
#include "video_core/engines/maxwell_3d.h"
|
|
#include "video_core/engines/shader_type.h"
|
|
#include "video_core/shader/registry.h"
|
|
#include "video_core/shader/shader_ir.h"
|
|
|
|
namespace Vulkan {
|
|
class VKDevice;
|
|
}
|
|
|
|
namespace Vulkan {
|
|
|
|
using Maxwell = Tegra::Engines::Maxwell3D::Regs;
|
|
using TexelBufferEntry = VideoCommon::Shader::Sampler;
|
|
using SamplerEntry = VideoCommon::Shader::Sampler;
|
|
using ImageEntry = VideoCommon::Shader::Image;
|
|
|
|
constexpr u32 DESCRIPTOR_SET = 0;
|
|
|
|
class ConstBufferEntry : public VideoCommon::Shader::ConstBuffer {
|
|
public:
|
|
explicit constexpr ConstBufferEntry(const VideoCommon::Shader::ConstBuffer& entry, u32 index)
|
|
: VideoCommon::Shader::ConstBuffer{entry}, index{index} {}
|
|
|
|
constexpr u32 GetIndex() const {
|
|
return index;
|
|
}
|
|
|
|
private:
|
|
u32 index{};
|
|
};
|
|
|
|
class GlobalBufferEntry {
|
|
public:
|
|
constexpr explicit GlobalBufferEntry(u32 cbuf_index, u32 cbuf_offset, bool is_written)
|
|
: cbuf_index{cbuf_index}, cbuf_offset{cbuf_offset}, is_written{is_written} {}
|
|
|
|
constexpr u32 GetCbufIndex() const {
|
|
return cbuf_index;
|
|
}
|
|
|
|
constexpr u32 GetCbufOffset() const {
|
|
return cbuf_offset;
|
|
}
|
|
|
|
constexpr bool IsWritten() const {
|
|
return is_written;
|
|
}
|
|
|
|
private:
|
|
u32 cbuf_index{};
|
|
u32 cbuf_offset{};
|
|
bool is_written{};
|
|
};
|
|
|
|
struct ShaderEntries {
|
|
u32 NumBindings() const {
|
|
return static_cast<u32>(const_buffers.size() + global_buffers.size() +
|
|
texel_buffers.size() + samplers.size() + images.size());
|
|
}
|
|
|
|
std::vector<ConstBufferEntry> const_buffers;
|
|
std::vector<GlobalBufferEntry> global_buffers;
|
|
std::vector<TexelBufferEntry> texel_buffers;
|
|
std::vector<SamplerEntry> samplers;
|
|
std::vector<ImageEntry> images;
|
|
std::set<u32> attributes;
|
|
std::array<bool, Maxwell::NumClipDistances> clip_distances{};
|
|
std::size_t shader_length{};
|
|
bool uses_warps{};
|
|
};
|
|
|
|
struct Specialization final {
|
|
u32 base_binding{};
|
|
|
|
// Compute specific
|
|
std::array<u32, 3> workgroup_size{};
|
|
u32 shared_memory_size{};
|
|
|
|
// Graphics specific
|
|
std::optional<float> point_size;
|
|
std::bitset<Maxwell::NumVertexAttributes> enabled_attributes;
|
|
std::array<Maxwell::VertexAttribute::Type, Maxwell::NumVertexAttributes> attribute_types{};
|
|
bool ndc_minus_one_to_one{};
|
|
};
|
|
// Old gcc versions don't consider this trivially copyable.
|
|
// static_assert(std::is_trivially_copyable_v<Specialization>);
|
|
|
|
struct SPIRVShader {
|
|
std::vector<u32> code;
|
|
ShaderEntries entries;
|
|
};
|
|
|
|
ShaderEntries GenerateShaderEntries(const VideoCommon::Shader::ShaderIR& ir);
|
|
|
|
std::vector<u32> Decompile(const VKDevice& device, const VideoCommon::Shader::ShaderIR& ir,
|
|
Tegra::Engines::ShaderType stage,
|
|
const VideoCommon::Shader::Registry& registry,
|
|
const Specialization& specialization);
|
|
|
|
} // namespace Vulkan
|