| // Copyright 2017 The Dawn Authors |
| // |
| // Licensed under the Apache License, Version 2.0 (the "License"); |
| // you may not use this file except in compliance with the License. |
| // You may obtain a copy of the License at |
| // |
| // http://www.apache.org/licenses/LICENSE-2.0 |
| // |
| // Unless required by applicable law or agreed to in writing, software |
| // distributed under the License is distributed on an "AS IS" BASIS, |
| // WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied. |
| // See the License for the specific language governing permissions and |
| // limitations under the License. |
| |
| #include "dawn_native/ShaderModule.h" |
| |
| #include "dawn_native/BindGroupLayout.h" |
| #include "dawn_native/Device.h" |
| #include "dawn_native/ObjectContentHasher.h" |
| #include "dawn_native/Pipeline.h" |
| #include "dawn_native/PipelineLayout.h" |
| #include "dawn_native/SpirvUtils.h" |
| |
| #include <spirv-tools/libspirv.hpp> |
| #include <spirv-tools/optimizer.hpp> |
| #include <spirv_cross.hpp> |
| |
| #ifdef DAWN_ENABLE_WGSL |
| // Tint include must be after spirv_cross.hpp, because spirv-cross has its own |
| // version of spirv_headers. We also need to undef SPV_REVISION because SPIRV-Cross |
| // is at 3 while spirv-headers is at 4. |
| # undef SPV_REVISION |
| # include <tint/tint.h> |
| #endif // DAWN_ENABLE_WGSL |
| |
| #include <sstream> |
| |
| namespace dawn_native { |
| |
| namespace { |
| |
| std::string GetShaderDeclarationString(BindGroupIndex group, BindingNumber binding) { |
| std::ostringstream ostream; |
| ostream << "the shader module declaration at set " << static_cast<uint32_t>(group) |
| << " binding " << static_cast<uint32_t>(binding); |
| return ostream.str(); |
| } |
| |
| #ifdef DAWN_ENABLE_WGSL |
| tint::transform::VertexFormat ToTintVertexFormat(wgpu::VertexFormat format) { |
| switch (format) { |
| case wgpu::VertexFormat::UChar2: |
| return tint::transform::VertexFormat::kVec2U8; |
| case wgpu::VertexFormat::UChar4: |
| return tint::transform::VertexFormat::kVec4U8; |
| case wgpu::VertexFormat::Char2: |
| return tint::transform::VertexFormat::kVec2I8; |
| case wgpu::VertexFormat::Char4: |
| return tint::transform::VertexFormat::kVec4I8; |
| case wgpu::VertexFormat::UChar2Norm: |
| return tint::transform::VertexFormat::kVec2U8Norm; |
| case wgpu::VertexFormat::UChar4Norm: |
| return tint::transform::VertexFormat::kVec4U8Norm; |
| case wgpu::VertexFormat::Char2Norm: |
| return tint::transform::VertexFormat::kVec2I8Norm; |
| case wgpu::VertexFormat::Char4Norm: |
| return tint::transform::VertexFormat::kVec4I8Norm; |
| case wgpu::VertexFormat::UShort2: |
| return tint::transform::VertexFormat::kVec2U16; |
| case wgpu::VertexFormat::UShort4: |
| return tint::transform::VertexFormat::kVec4U16; |
| case wgpu::VertexFormat::Short2: |
| return tint::transform::VertexFormat::kVec2I16; |
| case wgpu::VertexFormat::Short4: |
| return tint::transform::VertexFormat::kVec4I16; |
| case wgpu::VertexFormat::UShort2Norm: |
| return tint::transform::VertexFormat::kVec2U16Norm; |
| case wgpu::VertexFormat::UShort4Norm: |
| return tint::transform::VertexFormat::kVec4U16Norm; |
| case wgpu::VertexFormat::Short2Norm: |
| return tint::transform::VertexFormat::kVec2I16Norm; |
| case wgpu::VertexFormat::Short4Norm: |
| return tint::transform::VertexFormat::kVec4I16Norm; |
| case wgpu::VertexFormat::Half2: |
| return tint::transform::VertexFormat::kVec2F16; |
| case wgpu::VertexFormat::Half4: |
| return tint::transform::VertexFormat::kVec4F16; |
| case wgpu::VertexFormat::Float: |
| return tint::transform::VertexFormat::kF32; |
| case wgpu::VertexFormat::Float2: |
| return tint::transform::VertexFormat::kVec2F32; |
| case wgpu::VertexFormat::Float3: |
| return tint::transform::VertexFormat::kVec3F32; |
| case wgpu::VertexFormat::Float4: |
| return tint::transform::VertexFormat::kVec4F32; |
| case wgpu::VertexFormat::UInt: |
| return tint::transform::VertexFormat::kU32; |
| case wgpu::VertexFormat::UInt2: |
| return tint::transform::VertexFormat::kVec2U32; |
| case wgpu::VertexFormat::UInt3: |
| return tint::transform::VertexFormat::kVec3U32; |
| case wgpu::VertexFormat::UInt4: |
| return tint::transform::VertexFormat::kVec4U32; |
| case wgpu::VertexFormat::Int: |
| return tint::transform::VertexFormat::kI32; |
| case wgpu::VertexFormat::Int2: |
| return tint::transform::VertexFormat::kVec2I32; |
| case wgpu::VertexFormat::Int3: |
| return tint::transform::VertexFormat::kVec3I32; |
| case wgpu::VertexFormat::Int4: |
| return tint::transform::VertexFormat::kVec4I32; |
| } |
| } |
| |
| tint::transform::InputStepMode ToTintInputStepMode(wgpu::InputStepMode mode) { |
| switch (mode) { |
| case wgpu::InputStepMode::Vertex: |
| return tint::transform::InputStepMode::kVertex; |
| case wgpu::InputStepMode::Instance: |
| return tint::transform::InputStepMode::kInstance; |
| } |
| } |
| |
| SingleShaderStage PipelineStateToShaderStage(tint::ast::PipelineStage stage) { |
| switch (stage) { |
| case tint::ast::PipelineStage::kVertex: |
| return SingleShaderStage::Vertex; |
| case tint::ast::PipelineStage::kFragment: |
| return SingleShaderStage::Fragment; |
| case tint::ast::PipelineStage::kCompute: |
| return SingleShaderStage::Compute; |
| default: |
| UNREACHABLE(); |
| } |
| } |
| |
| #endif // DAWN_ENABLE_WGSL |
| |
| MaybeError ValidateSpirv(const uint32_t* code, uint32_t codeSize) { |
| spvtools::SpirvTools spirvTools(SPV_ENV_VULKAN_1_1); |
| |
| std::ostringstream errorStream; |
| errorStream << "SPIRV Validation failure:" << std::endl; |
| |
| spirvTools.SetMessageConsumer([&errorStream](spv_message_level_t level, const char*, |
| const spv_position_t& position, |
| const char* message) { |
| switch (level) { |
| case SPV_MSG_FATAL: |
| case SPV_MSG_INTERNAL_ERROR: |
| case SPV_MSG_ERROR: |
| errorStream << "error: line " << position.index << ": " << message |
| << std::endl; |
| break; |
| case SPV_MSG_WARNING: |
| errorStream << "warning: line " << position.index << ": " << message |
| << std::endl; |
| break; |
| case SPV_MSG_INFO: |
| errorStream << "info: line " << position.index << ": " << message |
| << std::endl; |
| break; |
| default: |
| break; |
| } |
| }); |
| |
| if (!spirvTools.Validate(code, codeSize)) { |
| std::string disassembly; |
| if (spirvTools.Disassemble(std::vector<uint32_t>(code, code + codeSize), |
| &disassembly)) { |
| errorStream << "disassembly:" << std::endl << disassembly; |
| } |
| |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| return {}; |
| } |
| |
| #ifdef DAWN_ENABLE_WGSL |
| ResultOrError<tint::ast::Module> ParseWGSL(const tint::Source::File* file) { |
| std::ostringstream errorStream; |
| errorStream << "Tint WGSL reader failure:" << std::endl; |
| |
| tint::reader::wgsl::Parser parser(file); |
| if (!parser.Parse()) { |
| auto err = tint::diag::Formatter{}.format(parser.diagnostics()); |
| errorStream << "Parser: " << err << std::endl |
| << "Shader: " << std::endl |
| << file->content << std::endl; |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| tint::ast::Module module = parser.module(); |
| if (!module.IsValid()) { |
| errorStream << "Invalid module generated..." << std::endl; |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| tint::TypeDeterminer typeDeterminer(&module); |
| if (!typeDeterminer.Determine()) { |
| errorStream << "Type Determination: " << typeDeterminer.error(); |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| return std::move(module); |
| } |
| |
| ResultOrError<tint::ast::Module> ParseSPIRV(const std::vector<uint32_t>& spirv) { |
| std::ostringstream errorStream; |
| errorStream << "Tint SPIRV reader failure:" << std::endl; |
| |
| tint::reader::spirv::Parser parser(spirv); |
| if (!parser.Parse()) { |
| errorStream << "Parser: " << parser.error() << std::endl; |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| tint::ast::Module module = parser.module(); |
| if (!module.IsValid()) { |
| errorStream << "Invalid module generated..." << std::endl; |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| tint::TypeDeterminer typeDeterminer(&module); |
| if (!typeDeterminer.Determine()) { |
| errorStream << "Type Determination: " << typeDeterminer.error(); |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| return std::move(module); |
| } |
| |
| MaybeError ValidateModule(tint::ast::Module* module) { |
| std::ostringstream errorStream; |
| errorStream << "Tint module validation" << std::endl; |
| |
| tint::Validator validator; |
| if (!validator.Validate(module)) { |
| auto err = tint::diag::Formatter{}.format(validator.diagnostics()); |
| errorStream << "Validation: " << err << std::endl; |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| return {}; |
| } |
| |
| ResultOrError<std::vector<uint32_t>> ModuleToSPIRV(tint::ast::Module module) { |
| std::ostringstream errorStream; |
| errorStream << "Tint SPIR-V writer failure:" << std::endl; |
| |
| tint::writer::spirv::Generator generator(std::move(module)); |
| if (!generator.Generate()) { |
| errorStream << "Generator: " << generator.error() << std::endl; |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| std::vector<uint32_t> spirv = generator.result(); |
| return std::move(spirv); |
| } |
| #endif // DAWN_ENABLE_WGSL |
| |
| std::vector<uint64_t> GetBindGroupMinBufferSizes( |
| const EntryPointMetadata::BindingGroupInfoMap& shaderBindings, |
| const BindGroupLayoutBase* layout) { |
| std::vector<uint64_t> requiredBufferSizes(layout->GetUnverifiedBufferCount()); |
| uint32_t packedIdx = 0; |
| |
| for (BindingIndex bindingIndex{0}; bindingIndex < layout->GetBufferCount(); |
| ++bindingIndex) { |
| const BindingInfo& bindingInfo = layout->GetBindingInfo(bindingIndex); |
| if (bindingInfo.buffer.minBindingSize != 0) { |
| // Skip bindings that have minimum buffer size set in the layout |
| continue; |
| } |
| |
| ASSERT(packedIdx < requiredBufferSizes.size()); |
| const auto& shaderInfo = shaderBindings.find(bindingInfo.binding); |
| if (shaderInfo != shaderBindings.end()) { |
| requiredBufferSizes[packedIdx] = shaderInfo->second.buffer.minBindingSize; |
| } else { |
| // We have to include buffers if they are included in the bind group's |
| // packed vector. We don't actually need to check these at draw time, so |
| // if this is a problem in the future we can optimize it further. |
| requiredBufferSizes[packedIdx] = 0; |
| } |
| ++packedIdx; |
| } |
| |
| return requiredBufferSizes; |
| } |
| |
| ResultOrError<std::vector<uint32_t>> RunRobustBufferAccessPass( |
| const std::vector<uint32_t>& spirv) { |
| spvtools::Optimizer opt(SPV_ENV_VULKAN_1_1); |
| |
| std::ostringstream errorStream; |
| errorStream << "SPIRV Optimizer failure:" << std::endl; |
| opt.SetMessageConsumer([&errorStream](spv_message_level_t level, const char*, |
| const spv_position_t& position, |
| const char* message) { |
| switch (level) { |
| case SPV_MSG_FATAL: |
| case SPV_MSG_INTERNAL_ERROR: |
| case SPV_MSG_ERROR: |
| errorStream << "error: line " << position.index << ": " << message |
| << std::endl; |
| break; |
| case SPV_MSG_WARNING: |
| errorStream << "warning: line " << position.index << ": " << message |
| << std::endl; |
| break; |
| case SPV_MSG_INFO: |
| errorStream << "info: line " << position.index << ": " << message |
| << std::endl; |
| break; |
| default: |
| break; |
| } |
| }); |
| opt.RegisterPass(spvtools::CreateGraphicsRobustAccessPass()); |
| |
| std::vector<uint32_t> result; |
| if (!opt.Run(spirv.data(), spirv.size(), &result, spvtools::ValidatorOptions(), |
| false)) { |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| return std::move(result); |
| } |
| |
| MaybeError ValidateCompatibilityWithBindGroupLayout(DeviceBase*, |
| BindGroupIndex group, |
| const EntryPointMetadata& entryPoint, |
| const BindGroupLayoutBase* layout) { |
| const BindGroupLayoutBase::BindingMap& layoutBindings = layout->GetBindingMap(); |
| |
| // Iterate over all bindings used by this group in the shader, and find the |
| // corresponding binding in the BindGroupLayout, if it exists. |
| for (const auto& it : entryPoint.bindings[group]) { |
| BindingNumber bindingNumber = it.first; |
| const EntryPointMetadata::ShaderBindingInfo& shaderInfo = it.second; |
| |
| const auto& bindingIt = layoutBindings.find(bindingNumber); |
| if (bindingIt == layoutBindings.end()) { |
| return DAWN_VALIDATION_ERROR("Missing bind group layout entry for " + |
| GetShaderDeclarationString(group, bindingNumber)); |
| } |
| BindingIndex bindingIndex(bindingIt->second); |
| const BindingInfo& layoutInfo = layout->GetBindingInfo(bindingIndex); |
| |
| if (layoutInfo.bindingType != shaderInfo.bindingType) { |
| return DAWN_VALIDATION_ERROR( |
| "The binding type of the bind group layout entry conflicts " + |
| GetShaderDeclarationString(group, bindingNumber)); |
| } |
| |
| if ((layoutInfo.visibility & StageBit(entryPoint.stage)) == 0) { |
| return DAWN_VALIDATION_ERROR("The bind group layout entry for " + |
| GetShaderDeclarationString(group, bindingNumber) + |
| " is not visible for the shader stage"); |
| } |
| |
| switch (layoutInfo.bindingType) { |
| case BindingInfoType::Texture: { |
| if (layoutInfo.texture.multisampled != shaderInfo.texture.multisampled) { |
| return DAWN_VALIDATION_ERROR( |
| "The texture multisampled flag of the bind group layout entry is " |
| "different from " + |
| GetShaderDeclarationString(group, bindingNumber)); |
| } |
| |
| if (layoutInfo.texture.sampleType != shaderInfo.texture.sampleType) { |
| return DAWN_VALIDATION_ERROR( |
| "The texture sampleType of the bind group layout entry is " |
| "different from " + |
| GetShaderDeclarationString(group, bindingNumber)); |
| } |
| |
| if (layoutInfo.texture.viewDimension != shaderInfo.texture.viewDimension) { |
| return DAWN_VALIDATION_ERROR( |
| "The texture viewDimension of the bind group layout entry is " |
| "different " |
| "from " + |
| GetShaderDeclarationString(group, bindingNumber)); |
| } |
| break; |
| } |
| |
| case BindingInfoType::StorageTexture: { |
| ASSERT(layoutInfo.storageTexture.format != wgpu::TextureFormat::Undefined); |
| ASSERT(shaderInfo.storageTexture.format != wgpu::TextureFormat::Undefined); |
| |
| if (layoutInfo.storageTexture.access != shaderInfo.storageTexture.access) { |
| return DAWN_VALIDATION_ERROR( |
| "The storageTexture access mode of the bind group layout entry is " |
| "different from " + |
| GetShaderDeclarationString(group, bindingNumber)); |
| } |
| |
| if (layoutInfo.storageTexture.format != shaderInfo.storageTexture.format) { |
| return DAWN_VALIDATION_ERROR( |
| "The storageTexture format of the bind group layout entry is " |
| "different from " + |
| GetShaderDeclarationString(group, bindingNumber)); |
| } |
| if (layoutInfo.storageTexture.viewDimension != |
| shaderInfo.storageTexture.viewDimension) { |
| return DAWN_VALIDATION_ERROR( |
| "The storageTexture viewDimension of the bind group layout entry " |
| "is different from " + |
| GetShaderDeclarationString(group, bindingNumber)); |
| } |
| break; |
| } |
| |
| case BindingInfoType::Buffer: { |
| // Binding mismatch between shader and bind group is invalid. For example, a |
| // writable binding in the shader with a readonly storage buffer in the bind |
| // group layout is invalid. However, a readonly binding in the shader with a |
| // writable storage buffer in the bind group layout is valid. |
| bool validBindingConversion = |
| layoutInfo.buffer.type == wgpu::BufferBindingType::Storage && |
| shaderInfo.buffer.type == wgpu::BufferBindingType::ReadOnlyStorage; |
| |
| if (layoutInfo.buffer.type != shaderInfo.buffer.type && |
| !validBindingConversion) { |
| return DAWN_VALIDATION_ERROR( |
| "The buffer type of the bind group layout entry conflicts " + |
| GetShaderDeclarationString(group, bindingNumber)); |
| } |
| |
| if (layoutInfo.buffer.minBindingSize != 0 && |
| shaderInfo.buffer.minBindingSize > layoutInfo.buffer.minBindingSize) { |
| return DAWN_VALIDATION_ERROR( |
| "The minimum buffer size of the bind group layout entry is smaller " |
| "than " + |
| GetShaderDeclarationString(group, bindingNumber)); |
| } |
| break; |
| } |
| |
| case BindingInfoType::Sampler: |
| // TODO(crbug.com/dawn/367): Temporarily allow using either a sampler or a |
| // comparison sampler until we can perform the proper shader analysis of |
| // what type is used in the shader module. |
| break; |
| } |
| } |
| |
| return {}; |
| } |
| |
| ResultOrError<std::unique_ptr<EntryPointMetadata>> ExtractSpirvInfo( |
| const DeviceBase* device, |
| const spirv_cross::Compiler& compiler, |
| const std::string& entryPointName, |
| SingleShaderStage stage) { |
| std::unique_ptr<EntryPointMetadata> metadata = std::make_unique<EntryPointMetadata>(); |
| metadata->stage = stage; |
| |
| // TODO(cwallez@chromium.org): make errors here creation errors |
| // currently errors here do not prevent the shadermodule from being used |
| const auto& resources = compiler.get_shader_resources(); |
| |
| if (resources.push_constant_buffers.size() > 0) { |
| return DAWN_VALIDATION_ERROR("Push constants aren't supported."); |
| } |
| |
| if (resources.sampled_images.size() > 0) { |
| return DAWN_VALIDATION_ERROR("Combined images and samplers aren't supported."); |
| } |
| |
| // Fill in bindingInfo with the SPIRV bindings |
| auto ExtractResourcesBinding = |
| [](const DeviceBase* device, |
| const spirv_cross::SmallVector<spirv_cross::Resource>& resources, |
| const spirv_cross::Compiler& compiler, BindingInfoType bindingType, |
| EntryPointMetadata::BindingInfo* metadataBindings, |
| bool isStorageBuffer = false) -> MaybeError { |
| for (const auto& resource : resources) { |
| if (!compiler.get_decoration_bitset(resource.id).get(spv::DecorationBinding)) { |
| return DAWN_VALIDATION_ERROR("No Binding decoration set for resource"); |
| } |
| |
| if (!compiler.get_decoration_bitset(resource.id) |
| .get(spv::DecorationDescriptorSet)) { |
| return DAWN_VALIDATION_ERROR("No Descriptor Decoration set for resource"); |
| } |
| |
| BindingNumber bindingNumber( |
| compiler.get_decoration(resource.id, spv::DecorationBinding)); |
| BindGroupIndex bindGroupIndex( |
| compiler.get_decoration(resource.id, spv::DecorationDescriptorSet)); |
| |
| if (bindGroupIndex >= kMaxBindGroupsTyped) { |
| return DAWN_VALIDATION_ERROR("Bind group index over limits in the SPIRV"); |
| } |
| |
| const auto& it = (*metadataBindings)[bindGroupIndex].emplace( |
| bindingNumber, EntryPointMetadata::ShaderBindingInfo{}); |
| if (!it.second) { |
| return DAWN_VALIDATION_ERROR("Shader has duplicate bindings"); |
| } |
| |
| EntryPointMetadata::ShaderBindingInfo* info = &it.first->second; |
| info->id = resource.id; |
| info->base_type_id = resource.base_type_id; |
| info->bindingType = bindingType; |
| |
| switch (bindingType) { |
| case BindingInfoType::Texture: { |
| spirv_cross::SPIRType::ImageType imageType = |
| compiler.get_type(info->base_type_id).image; |
| spirv_cross::SPIRType::BaseType textureComponentType = |
| compiler.get_type(imageType.type).basetype; |
| |
| info->texture.viewDimension = |
| SpirvDimToTextureViewDimension(imageType.dim, imageType.arrayed); |
| info->texture.sampleType = |
| SpirvBaseTypeToTextureSampleType(textureComponentType); |
| info->texture.multisampled = imageType.ms; |
| |
| if (imageType.depth) { |
| if (imageType.ms) { |
| return DAWN_VALIDATION_ERROR( |
| "Multisampled depth textures aren't supported"); |
| } |
| if (info->texture.sampleType != wgpu::TextureSampleType::Float) { |
| return DAWN_VALIDATION_ERROR( |
| "Depth textures must have a float type"); |
| } |
| info->texture.sampleType = wgpu::TextureSampleType::Depth; |
| } |
| break; |
| } |
| case BindingInfoType::Buffer: { |
| // Determine buffer size, with a minimum of 1 element in the runtime |
| // array |
| spirv_cross::SPIRType type = compiler.get_type(info->base_type_id); |
| info->buffer.minBindingSize = |
| compiler.get_declared_struct_size_runtime_array(type, 1); |
| |
| // Differentiate between readonly storage bindings and writable ones |
| // based on the NonWritable decoration. |
| // TODO(dawn:527): Could isStorageBuffer be determined by calling |
| // compiler.get_storage_class(resource.id)? |
| if (isStorageBuffer) { |
| spirv_cross::Bitset flags = |
| compiler.get_buffer_block_flags(resource.id); |
| if (flags.get(spv::DecorationNonWritable)) { |
| info->buffer.type = wgpu::BufferBindingType::ReadOnlyStorage; |
| } else { |
| info->buffer.type = wgpu::BufferBindingType::Storage; |
| } |
| } else { |
| info->buffer.type = wgpu::BufferBindingType::Uniform; |
| } |
| break; |
| } |
| case BindingInfoType::StorageTexture: { |
| spirv_cross::Bitset flags = compiler.get_decoration_bitset(resource.id); |
| if (flags.get(spv::DecorationNonReadable)) { |
| info->storageTexture.access = wgpu::StorageTextureAccess::WriteOnly; |
| } else if (flags.get(spv::DecorationNonWritable)) { |
| info->storageTexture.access = wgpu::StorageTextureAccess::ReadOnly; |
| } else { |
| return DAWN_VALIDATION_ERROR( |
| "Read-write storage textures are not supported"); |
| } |
| |
| spirv_cross::SPIRType::ImageType imageType = |
| compiler.get_type(info->base_type_id).image; |
| wgpu::TextureFormat storageTextureFormat = |
| SpirvImageFormatToTextureFormat(imageType.format); |
| if (storageTextureFormat == wgpu::TextureFormat::Undefined) { |
| return DAWN_VALIDATION_ERROR( |
| "Invalid image format declaration on storage image"); |
| } |
| const Format& format = |
| device->GetValidInternalFormat(storageTextureFormat); |
| if (!format.supportsStorageUsage) { |
| return DAWN_VALIDATION_ERROR( |
| "The storage texture format is not supported"); |
| } |
| if (imageType.ms) { |
| return DAWN_VALIDATION_ERROR( |
| "Multisampled storage textures aren't supported"); |
| } |
| if (imageType.depth) { |
| return DAWN_VALIDATION_ERROR( |
| "Depth storage textures aren't supported"); |
| } |
| info->storageTexture.format = storageTextureFormat; |
| info->storageTexture.viewDimension = |
| SpirvDimToTextureViewDimension(imageType.dim, imageType.arrayed); |
| break; |
| } |
| case BindingInfoType::Sampler: { |
| info->sampler.type = wgpu::SamplerBindingType::Filtering; |
| } |
| } |
| } |
| return {}; |
| }; |
| |
| DAWN_TRY(ExtractResourcesBinding(device, resources.uniform_buffers, compiler, |
| BindingInfoType::Buffer, &metadata->bindings)); |
| DAWN_TRY(ExtractResourcesBinding(device, resources.separate_images, compiler, |
| BindingInfoType::Texture, &metadata->bindings)); |
| DAWN_TRY(ExtractResourcesBinding(device, resources.separate_samplers, compiler, |
| BindingInfoType::Sampler, &metadata->bindings)); |
| DAWN_TRY(ExtractResourcesBinding(device, resources.storage_buffers, compiler, |
| BindingInfoType::Buffer, &metadata->bindings, true)); |
| // ReadonlyStorageTexture is used as a tag to do general storage texture handling. |
| DAWN_TRY(ExtractResourcesBinding(device, resources.storage_images, compiler, |
| BindingInfoType::StorageTexture, &metadata->bindings)); |
| |
| // Extract the vertex attributes |
| if (stage == SingleShaderStage::Vertex) { |
| for (const auto& attrib : resources.stage_inputs) { |
| if (!(compiler.get_decoration_bitset(attrib.id).get(spv::DecorationLocation))) { |
| return DAWN_VALIDATION_ERROR( |
| "Unable to find Location decoration for Vertex input"); |
| } |
| uint32_t location = compiler.get_decoration(attrib.id, spv::DecorationLocation); |
| |
| if (location >= kMaxVertexAttributes) { |
| return DAWN_VALIDATION_ERROR("Attribute location over limits in the SPIRV"); |
| } |
| |
| metadata->usedVertexAttributes.set(location); |
| } |
| |
| // Without a location qualifier on vertex outputs, spirv_cross::CompilerMSL gives |
| // them all the location 0, causing a compile error. |
| for (const auto& attrib : resources.stage_outputs) { |
| if (!compiler.get_decoration_bitset(attrib.id).get(spv::DecorationLocation)) { |
| return DAWN_VALIDATION_ERROR("Need location qualifier on vertex output"); |
| } |
| } |
| } |
| |
| if (stage == SingleShaderStage::Fragment) { |
| // Without a location qualifier on vertex inputs, spirv_cross::CompilerMSL gives |
| // them all the location 0, causing a compile error. |
| for (const auto& attrib : resources.stage_inputs) { |
| if (!compiler.get_decoration_bitset(attrib.id).get(spv::DecorationLocation)) { |
| return DAWN_VALIDATION_ERROR("Need location qualifier on fragment input"); |
| } |
| } |
| |
| for (const auto& fragmentOutput : resources.stage_outputs) { |
| if (!compiler.get_decoration_bitset(fragmentOutput.id) |
| .get(spv::DecorationLocation)) { |
| return DAWN_VALIDATION_ERROR( |
| "Unable to find Location decoration for Fragment output"); |
| } |
| uint32_t unsanitizedAttachment = |
| compiler.get_decoration(fragmentOutput.id, spv::DecorationLocation); |
| if (unsanitizedAttachment >= kMaxColorAttachments) { |
| return DAWN_VALIDATION_ERROR( |
| "Fragment output index must be less than max number of color " |
| "attachments"); |
| } |
| ColorAttachmentIndex attachment(static_cast<uint8_t>(unsanitizedAttachment)); |
| |
| spirv_cross::SPIRType::BaseType shaderFragmentOutputBaseType = |
| compiler.get_type(fragmentOutput.base_type_id).basetype; |
| metadata->fragmentOutputFormatBaseTypes[attachment] = |
| SpirvBaseTypeToTextureComponentType(shaderFragmentOutputBaseType); |
| metadata->fragmentOutputsWritten.set(attachment); |
| } |
| } |
| |
| if (stage == SingleShaderStage::Compute) { |
| const spirv_cross::SPIREntryPoint& spirEntryPoint = |
| compiler.get_entry_point(entryPointName, spv::ExecutionModelGLCompute); |
| metadata->localWorkgroupSize.x = spirEntryPoint.workgroup_size.x; |
| metadata->localWorkgroupSize.y = spirEntryPoint.workgroup_size.y; |
| metadata->localWorkgroupSize.z = spirEntryPoint.workgroup_size.z; |
| } |
| |
| return {std::move(metadata)}; |
| } |
| |
| #ifdef DAWN_ENABLE_WGSL |
| // Currently only partially populated the reflection data, needs to be |
| // completed using PopulateMetadataUsingSPIRVCross. In the future, once |
| // this function is complete, ReflectShaderUsingSPIRVCross and |
| // PopulateMetadataUsingSPIRVCross will be removed. |
| ResultOrError<EntryPointMetadataTable> ReflectShaderUsingTint( |
| DeviceBase*, |
| const tint::ast::Module& module) { |
| ASSERT(module.IsValid()); |
| |
| EntryPointMetadataTable result; |
| std::ostringstream errorStream; |
| errorStream << "Tint Reflection failure:" << std::endl; |
| |
| tint::inspector::Inspector inspector(module); |
| auto entryPoints = inspector.GetEntryPoints(); |
| if (inspector.has_error()) { |
| errorStream << "Inspector: " << inspector.error() << std::endl; |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| for (auto& entryPoint : entryPoints) { |
| ASSERT(result.count(entryPoint.name) == 0); |
| |
| auto metadata = std::make_unique<EntryPointMetadata>(); |
| |
| metadata->stage = PipelineStateToShaderStage(entryPoint.stage); |
| |
| if (metadata->stage == SingleShaderStage::Vertex) { |
| for (auto& stage_input : entryPoint.input_variables) { |
| if (!stage_input.has_location_decoration) { |
| return DAWN_VALIDATION_ERROR( |
| "Need Location decoration on Vertex input"); |
| } |
| uint32_t location = stage_input.location_decoration; |
| if (location >= kMaxVertexAttributes) { |
| return DAWN_VALIDATION_ERROR("Attribute location over limits"); |
| } |
| metadata->usedVertexAttributes.set(location); |
| } |
| |
| for (auto& stage_output : entryPoint.output_variables) { |
| if (!stage_output.has_location_decoration) { |
| return DAWN_VALIDATION_ERROR( |
| "Need Location decoration on Vertex output"); |
| } |
| } |
| } |
| |
| if (metadata->stage == SingleShaderStage::Compute) { |
| metadata->localWorkgroupSize.x = entryPoint.workgroup_size_x; |
| metadata->localWorkgroupSize.y = entryPoint.workgroup_size_y; |
| metadata->localWorkgroupSize.z = entryPoint.workgroup_size_z; |
| } |
| |
| result[entryPoint.name] = std::move(metadata); |
| } |
| return std::move(result); |
| } |
| #endif // DAWN_ENABLE_WGSL |
| |
| // Uses SPIRV-Cross, which is planned for removal, but until |
| // ReflectShaderUsingTint is completed, will be kept as a |
| // fallback/source of truth. |
| ResultOrError<EntryPointMetadataTable> ReflectShaderUsingSPIRVCross( |
| DeviceBase* device, |
| std::vector<uint32_t> spirv) { |
| EntryPointMetadataTable result; |
| spirv_cross::Compiler compiler(spirv); |
| for (const spirv_cross::EntryPoint& entryPoint : |
| compiler.get_entry_points_and_stages()) { |
| ASSERT(result.count(entryPoint.name) == 0); |
| |
| SingleShaderStage stage = ExecutionModelToShaderStage(entryPoint.execution_model); |
| compiler.set_entry_point(entryPoint.name, entryPoint.execution_model); |
| |
| std::unique_ptr<EntryPointMetadata> metadata; |
| DAWN_TRY_ASSIGN(metadata, |
| ExtractSpirvInfo(device, compiler, entryPoint.name, stage)); |
| result[entryPoint.name] = std::move(metadata); |
| } |
| return std::move(result); |
| } |
| |
| #ifdef DAWN_ENABLE_WGSL |
| // Temporary utility method that allows for polyfilling like behaviour, |
| // specifically data missing from the Tint implementation is filled in |
| // using the SPIRV-Cross implementation. Once the Tint implementation is |
| // completed, this function will be removed. |
| MaybeError PopulateMetadataUsingSPIRVCross(DeviceBase* device, |
| std::vector<uint32_t> spirv, |
| EntryPointMetadataTable* tintTable) { |
| EntryPointMetadataTable crossTable; |
| DAWN_TRY_ASSIGN(crossTable, ReflectShaderUsingSPIRVCross(device, spirv)); |
| if (tintTable->size() != crossTable.size()) { |
| return DAWN_VALIDATION_ERROR( |
| "Tint and SPIRV-Cross returned different number of entry points"); |
| } |
| for (auto& crossMember : crossTable) { |
| auto& name = crossMember.first; |
| auto& crossEntry = crossMember.second; |
| |
| auto tintMember = tintTable->find(name); |
| if (tintMember == tintTable->end()) { |
| return DAWN_VALIDATION_ERROR( |
| "Tint and SPIRV-Cross returned different entry point names"); |
| } |
| |
| auto& tintEntry = tintMember->second; |
| if (tintEntry->stage != crossEntry->stage) { |
| return DAWN_VALIDATION_ERROR( |
| "Tint and SPIRV-Cross returned different stages for entry point"); |
| } |
| |
| if (tintEntry->stage == SingleShaderStage::Vertex) { |
| if (tintEntry->usedVertexAttributes != crossEntry->usedVertexAttributes) { |
| return DAWN_VALIDATION_ERROR( |
| "Tint and SPIRV-Cross returned different used vertex attributes for " |
| "entry point"); |
| } |
| } |
| |
| if (tintEntry->stage == SingleShaderStage::Compute) { |
| if (tintEntry->localWorkgroupSize.x != crossEntry->localWorkgroupSize.x || |
| tintEntry->localWorkgroupSize.y != crossEntry->localWorkgroupSize.y || |
| tintEntry->localWorkgroupSize.z != crossEntry->localWorkgroupSize.z) { |
| return DAWN_VALIDATION_ERROR( |
| "Tint and SPIRV-Cross returned different values for local workgroup " |
| "size"); |
| } |
| } |
| |
| // TODO(rharrison): Use the Inspector to get this data. |
| tintEntry->bindings = crossEntry->bindings; |
| tintEntry->fragmentOutputFormatBaseTypes = |
| crossEntry->fragmentOutputFormatBaseTypes; |
| tintEntry->fragmentOutputsWritten = crossEntry->fragmentOutputsWritten; |
| } |
| return {}; |
| } |
| #endif // DAWN_ENABLE_WGSL |
| |
| } // anonymous namespace |
| |
| ShaderModuleParseResult::ShaderModuleParseResult() = default; |
| ShaderModuleParseResult::~ShaderModuleParseResult() = default; |
| |
| ShaderModuleParseResult::ShaderModuleParseResult(ShaderModuleParseResult&& rhs) = default; |
| |
| ShaderModuleParseResult& ShaderModuleParseResult::operator=(ShaderModuleParseResult&& rhs) = |
| default; |
| |
| ResultOrError<ShaderModuleParseResult> ValidateShaderModuleDescriptor( |
| DeviceBase* device, |
| const ShaderModuleDescriptor* descriptor) { |
| const ChainedStruct* chainedDescriptor = descriptor->nextInChain; |
| if (chainedDescriptor == nullptr) { |
| return DAWN_VALIDATION_ERROR("Shader module descriptor missing chained descriptor"); |
| } |
| // For now only a single SPIRV or WGSL subdescriptor is allowed. |
| if (chainedDescriptor->nextInChain != nullptr) { |
| return DAWN_VALIDATION_ERROR( |
| "Shader module descriptor chained nextInChain must be nullptr"); |
| } |
| |
| ShaderModuleParseResult parseResult = {}; |
| switch (chainedDescriptor->sType) { |
| case wgpu::SType::ShaderModuleSPIRVDescriptor: { |
| const auto* spirvDesc = |
| static_cast<const ShaderModuleSPIRVDescriptor*>(chainedDescriptor); |
| std::vector<uint32_t> spirv(spirvDesc->code, spirvDesc->code + spirvDesc->codeSize); |
| if (device->IsToggleEnabled(Toggle::UseTintGenerator)) { |
| #ifdef DAWN_ENABLE_WGSL |
| tint::ast::Module module; |
| DAWN_TRY_ASSIGN(module, ParseSPIRV(spirv)); |
| if (device->IsValidationEnabled()) { |
| DAWN_TRY(ValidateModule(&module)); |
| } |
| parseResult.tintModule = std::make_unique<tint::ast::Module>(std::move(module)); |
| #else |
| return DAWN_VALIDATION_ERROR("Using Tint is not enabled in this build."); |
| #endif // DAWN_ENABLE_WGSL |
| } else { |
| if (device->IsValidationEnabled()) { |
| DAWN_TRY(ValidateSpirv(spirv.data(), spirv.size())); |
| } |
| parseResult.spirv = std::move(spirv); |
| } |
| break; |
| } |
| |
| case wgpu::SType::ShaderModuleWGSLDescriptor: { |
| #ifdef DAWN_ENABLE_WGSL |
| const auto* wgslDesc = |
| static_cast<const ShaderModuleWGSLDescriptor*>(chainedDescriptor); |
| |
| tint::Source::File file("", wgslDesc->source); |
| |
| if (device->IsToggleEnabled(Toggle::UseTintGenerator)) { |
| tint::ast::Module module; |
| DAWN_TRY_ASSIGN(module, ParseWGSL(&file)); |
| if (device->IsValidationEnabled()) { |
| DAWN_TRY(ValidateModule(&module)); |
| } |
| parseResult.tintModule = std::make_unique<tint::ast::Module>(std::move(module)); |
| } else { |
| tint::ast::Module module; |
| DAWN_TRY_ASSIGN(module, ParseWGSL(&file)); |
| |
| { |
| tint::transform::Manager transformManager; |
| transformManager.append( |
| std::make_unique<tint::transform::EmitVertexPointSize>()); |
| DAWN_TRY_ASSIGN(module, RunTransforms(&transformManager, &module)); |
| } |
| |
| if (device->IsValidationEnabled()) { |
| DAWN_TRY(ValidateModule(&module)); |
| } |
| |
| // Keep the Tint module around. The Metal backend will use it for vertex |
| // pulling since we can't go WGSL->point size transform->spirv->Tint. |
| // Tint's spirv reader doesn't understand point size. crbug.com/tint/412. |
| auto tintModule = std::make_unique<tint::ast::Module>(module.Clone()); |
| |
| std::vector<uint32_t> spirv; |
| DAWN_TRY_ASSIGN(spirv, ModuleToSPIRV(std::move(module))); |
| DAWN_TRY(ValidateSpirv(spirv.data(), spirv.size())); |
| |
| parseResult.tintModule = std::move(tintModule); |
| parseResult.spirv = std::move(spirv); |
| } |
| break; |
| #else |
| return DAWN_VALIDATION_ERROR("Using Tint is not enabled in this build."); |
| #endif // DAWN_ENABLE_WGSL |
| } |
| default: |
| return DAWN_VALIDATION_ERROR("Unsupported sType"); |
| } |
| |
| return std::move(parseResult); |
| } |
| |
| RequiredBufferSizes ComputeRequiredBufferSizesForLayout(const EntryPointMetadata& entryPoint, |
| const PipelineLayoutBase* layout) { |
| RequiredBufferSizes bufferSizes; |
| for (BindGroupIndex group : IterateBitSet(layout->GetBindGroupLayoutsMask())) { |
| bufferSizes[group] = GetBindGroupMinBufferSizes(entryPoint.bindings[group], |
| layout->GetBindGroupLayout(group)); |
| } |
| |
| return bufferSizes; |
| } |
| |
| #ifdef DAWN_ENABLE_WGSL |
| ResultOrError<tint::ast::Module> RunTransforms(tint::transform::Manager* manager, |
| tint::ast::Module* module) { |
| tint::transform::Transform::Output output = manager->Run(module); |
| if (output.diagnostics.contains_errors()) { |
| std::string err = |
| "Tint transform failure: " + tint::diag::Formatter{}.format(output.diagnostics); |
| return DAWN_VALIDATION_ERROR(err.c_str()); |
| } |
| |
| if (!output.module.IsValid()) { |
| return DAWN_VALIDATION_ERROR("Tint transform did not produce valid module."); |
| } |
| return std::move(output.module); |
| } |
| |
| std::unique_ptr<tint::transform::VertexPulling> MakeVertexPullingTransform( |
| const VertexStateDescriptor& vertexState, |
| const std::string& entryPoint, |
| BindGroupIndex pullingBufferBindingSet) { |
| auto transform = std::make_unique<tint::transform::VertexPulling>(); |
| tint::transform::VertexStateDescriptor state; |
| for (uint32_t i = 0; i < vertexState.vertexBufferCount; ++i) { |
| const auto& vertexBuffer = vertexState.vertexBuffers[i]; |
| tint::transform::VertexBufferLayoutDescriptor layout; |
| layout.array_stride = vertexBuffer.arrayStride; |
| layout.step_mode = ToTintInputStepMode(vertexBuffer.stepMode); |
| |
| for (uint32_t j = 0; j < vertexBuffer.attributeCount; ++j) { |
| const auto& attribute = vertexBuffer.attributes[j]; |
| tint::transform::VertexAttributeDescriptor attr; |
| attr.format = ToTintVertexFormat(attribute.format); |
| attr.offset = attribute.offset; |
| attr.shader_location = attribute.shaderLocation; |
| |
| layout.attributes.push_back(std::move(attr)); |
| } |
| |
| state.push_back(std::move(layout)); |
| } |
| transform->SetVertexState(std::move(state)); |
| transform->SetEntryPoint(entryPoint); |
| transform->SetPullingBufferBindingSet(static_cast<uint32_t>(pullingBufferBindingSet)); |
| return transform; |
| } |
| #endif |
| |
| MaybeError ValidateCompatibilityWithPipelineLayout(DeviceBase* device, |
| const EntryPointMetadata& entryPoint, |
| const PipelineLayoutBase* layout) { |
| for (BindGroupIndex group : IterateBitSet(layout->GetBindGroupLayoutsMask())) { |
| DAWN_TRY(ValidateCompatibilityWithBindGroupLayout(device, group, entryPoint, |
| layout->GetBindGroupLayout(group))); |
| } |
| |
| for (BindGroupIndex group : IterateBitSet(~layout->GetBindGroupLayoutsMask())) { |
| if (entryPoint.bindings[group].size() > 0) { |
| std::ostringstream ostream; |
| ostream << "No bind group layout entry matches the declaration set " |
| << static_cast<uint32_t>(group) << " in the shader module"; |
| return DAWN_VALIDATION_ERROR(ostream.str()); |
| } |
| } |
| |
| return {}; |
| } |
| |
| // ShaderModuleBase |
| |
| ShaderModuleBase::ShaderModuleBase(DeviceBase* device, const ShaderModuleDescriptor* descriptor) |
| : CachedObject(device), mType(Type::Undefined) { |
| ASSERT(descriptor->nextInChain != nullptr); |
| switch (descriptor->nextInChain->sType) { |
| case wgpu::SType::ShaderModuleSPIRVDescriptor: { |
| mType = Type::Spirv; |
| const auto* spirvDesc = |
| static_cast<const ShaderModuleSPIRVDescriptor*>(descriptor->nextInChain); |
| mOriginalSpirv.assign(spirvDesc->code, spirvDesc->code + spirvDesc->codeSize); |
| break; |
| } |
| case wgpu::SType::ShaderModuleWGSLDescriptor: { |
| mType = Type::Wgsl; |
| const auto* wgslDesc = |
| static_cast<const ShaderModuleWGSLDescriptor*>(descriptor->nextInChain); |
| mWgsl = std::string(wgslDesc->source); |
| break; |
| } |
| default: |
| UNREACHABLE(); |
| } |
| } |
| |
| ShaderModuleBase::ShaderModuleBase(DeviceBase* device, ObjectBase::ErrorTag tag) |
| : CachedObject(device, tag), mType(Type::Undefined) { |
| } |
| |
| ShaderModuleBase::~ShaderModuleBase() { |
| if (IsCachedReference()) { |
| GetDevice()->UncacheShaderModule(this); |
| } |
| } |
| |
| // static |
| ShaderModuleBase* ShaderModuleBase::MakeError(DeviceBase* device) { |
| return new ShaderModuleBase(device, ObjectBase::kError); |
| } |
| |
| bool ShaderModuleBase::HasEntryPoint(const std::string& entryPoint) const { |
| return mEntryPoints.count(entryPoint) > 0; |
| } |
| |
| const EntryPointMetadata& ShaderModuleBase::GetEntryPoint(const std::string& entryPoint) const { |
| ASSERT(HasEntryPoint(entryPoint)); |
| return *mEntryPoints.at(entryPoint); |
| } |
| |
| size_t ShaderModuleBase::ComputeContentHash() { |
| ObjectContentHasher recorder; |
| recorder.Record(mType); |
| recorder.Record(mOriginalSpirv); |
| recorder.Record(mWgsl); |
| return recorder.GetContentHash(); |
| } |
| |
| bool ShaderModuleBase::EqualityFunc::operator()(const ShaderModuleBase* a, |
| const ShaderModuleBase* b) const { |
| return a->mType == b->mType && a->mOriginalSpirv == b->mOriginalSpirv && |
| a->mWgsl == b->mWgsl; |
| } |
| |
| const std::vector<uint32_t>& ShaderModuleBase::GetSpirv() const { |
| ASSERT(!GetDevice()->IsToggleEnabled(Toggle::UseTintGenerator)); |
| return mSpirv; |
| } |
| |
| #ifdef DAWN_ENABLE_WGSL |
| ResultOrError<std::vector<uint32_t>> ShaderModuleBase::GeneratePullingSpirv( |
| const std::vector<uint32_t>& spirv, |
| const VertexStateDescriptor& vertexState, |
| const std::string& entryPoint, |
| BindGroupIndex pullingBufferBindingSet) const { |
| tint::ast::Module module; |
| DAWN_TRY_ASSIGN(module, ParseSPIRV(spirv)); |
| |
| return GeneratePullingSpirv(&module, vertexState, entryPoint, pullingBufferBindingSet); |
| } |
| |
| ResultOrError<std::vector<uint32_t>> ShaderModuleBase::GeneratePullingSpirv( |
| tint::ast::Module* moduleIn, |
| const VertexStateDescriptor& vertexState, |
| const std::string& entryPoint, |
| BindGroupIndex pullingBufferBindingSet) const { |
| std::ostringstream errorStream; |
| errorStream << "Tint vertex pulling failure:" << std::endl; |
| |
| tint::transform::Manager transformManager; |
| transformManager.append( |
| MakeVertexPullingTransform(vertexState, entryPoint, pullingBufferBindingSet)); |
| transformManager.append(std::make_unique<tint::transform::EmitVertexPointSize>()); |
| if (GetDevice()->IsRobustnessEnabled()) { |
| // TODO(enga): Run the Tint BoundArrayAccessors transform instead of the SPIRV Tools |
| // one, but it appears to crash after running VertexPulling. |
| // transformManager.append(std::make_unique<tint::transform::BoundArrayAccessors>()); |
| } |
| |
| tint::ast::Module module; |
| DAWN_TRY_ASSIGN(module, RunTransforms(&transformManager, moduleIn)); |
| |
| tint::writer::spirv::Generator generator(std::move(module)); |
| if (!generator.Generate()) { |
| errorStream << "Generator: " << generator.error() << std::endl; |
| return DAWN_VALIDATION_ERROR(errorStream.str().c_str()); |
| } |
| |
| std::vector<uint32_t> spirv = generator.result(); |
| if (GetDevice()->IsRobustnessEnabled()) { |
| DAWN_TRY_ASSIGN(spirv, RunRobustBufferAccessPass(spirv)); |
| } |
| DAWN_TRY(ValidateSpirv(spirv.data(), spirv.size())); |
| return std::move(spirv); |
| } |
| #endif |
| |
| MaybeError ShaderModuleBase::InitializeBase(ShaderModuleParseResult* parseResult) { |
| #ifdef DAWN_ENABLE_WGSL |
| tint::ast::Module* module = parseResult->tintModule.get(); |
| #endif |
| mSpirv = std::move(parseResult->spirv); |
| |
| // If not using Tint to generate backend code, run the robust buffer access pass now since |
| // all backends will use this SPIR-V. If Tint is used, the robustness pass should be run |
| // per-backend. |
| if (!GetDevice()->IsToggleEnabled(Toggle::UseTintGenerator) && |
| GetDevice()->IsRobustnessEnabled()) { |
| DAWN_TRY_ASSIGN(mSpirv, RunRobustBufferAccessPass(mSpirv)); |
| } |
| |
| // We still need the spirv for reflection. Remove this when we use the Tint inspector |
| // completely. |
| std::vector<uint32_t>* spirvPtr = &mSpirv; |
| std::vector<uint32_t> localSpirv; |
| if (GetDevice()->IsToggleEnabled(Toggle::UseTintGenerator)) { |
| #ifdef DAWN_ENABLE_WGSL |
| ASSERT(module != nullptr); |
| tint::ast::Module clonedModule = module->Clone(); |
| tint::TypeDeterminer typeDeterminer(&clonedModule); |
| if (!typeDeterminer.Determine()) { |
| return DAWN_VALIDATION_ERROR(typeDeterminer.error().c_str()); |
| } |
| DAWN_TRY_ASSIGN(localSpirv, ModuleToSPIRV(std::move(clonedModule))); |
| DAWN_TRY(ValidateSpirv(localSpirv.data(), localSpirv.size())); |
| spirvPtr = &localSpirv; |
| #else |
| UNREACHABLE(); |
| #endif |
| } |
| |
| if (GetDevice()->IsToggleEnabled(Toggle::UseTintInspector)) { |
| #ifdef DAWN_ENABLE_WGSL |
| tint::ast::Module localModule; |
| |
| tint::ast::Module* modulePtr = module; |
| if (!GetDevice()->IsToggleEnabled(Toggle::UseTintGenerator)) { |
| // We have mSpirv, but no Tint module |
| DAWN_TRY_ASSIGN(localModule, ParseSPIRV(mSpirv)); |
| DAWN_TRY(ValidateModule(&localModule)); |
| modulePtr = &localModule; |
| } |
| |
| EntryPointMetadataTable table; |
| DAWN_TRY_ASSIGN(table, ReflectShaderUsingTint(GetDevice(), *modulePtr)); |
| DAWN_TRY(PopulateMetadataUsingSPIRVCross(GetDevice(), *spirvPtr, &table)); |
| mEntryPoints = std::move(table); |
| #else |
| return DAWN_VALIDATION_ERROR("Using Tint is not enabled in this build."); |
| #endif |
| } else { |
| DAWN_TRY_ASSIGN(mEntryPoints, ReflectShaderUsingSPIRVCross(GetDevice(), *spirvPtr)); |
| } |
| |
| return {}; |
| } |
| } // namespace dawn_native |
