| // Copyright 2017 The Dawn & Tint Authors |
| // |
| // Redistribution and use in source and binary forms, with or without |
| // modification, are permitted provided that the following conditions are met: |
| // |
| // 1. Redistributions of source code must retain the above copyright notice, this |
| // list of conditions and the following disclaimer. |
| // |
| // 2. Redistributions in binary form must reproduce the above copyright notice, |
| // this list of conditions and the following disclaimer in the documentation |
| // and/or other materials provided with the distribution. |
| // |
| // 3. Neither the name of the copyright holder nor the names of its |
| // contributors may be used to endorse or promote products derived from |
| // this software without specific prior written permission. |
| // |
| // THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS "AS IS" |
| // AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT LIMITED TO, THE |
| // IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR A PARTICULAR PURPOSE ARE |
| // DISCLAIMED. IN NO EVENT SHALL THE COPYRIGHT HOLDER OR CONTRIBUTORS BE LIABLE |
| // FOR ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL, EXEMPLARY, OR CONSEQUENTIAL |
| // DAMAGES (INCLUDING, BUT NOT LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR |
| // SERVICES; LOSS OF USE, DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER |
| // CAUSED AND ON ANY THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY, |
| // OR TORT (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE |
| // OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. |
| |
| #include <tuple> |
| #include <utility> |
| #include <vector> |
| |
| #include "dawn/common/Assert.h" |
| #include "dawn/common/Constants.h" |
| #include "dawn/tests/unittests/validation/ValidationTest.h" |
| #include "dawn/utils/ComboRenderBundleEncoderDescriptor.h" |
| #include "dawn/utils/ComboRenderPipelineDescriptor.h" |
| #include "dawn/utils/WGPUHelpers.h" |
| |
| namespace dawn { |
| namespace { |
| |
| class BindGroupValidationTest : public ValidationTest { |
| public: |
| wgpu::Texture CreateTexture(wgpu::TextureUsage usage, |
| wgpu::TextureFormat format, |
| uint32_t layerCount) { |
| wgpu::TextureDescriptor descriptor; |
| descriptor.dimension = wgpu::TextureDimension::e2D; |
| descriptor.size = {kWidth, kHeight, layerCount}; |
| descriptor.sampleCount = 1; |
| descriptor.mipLevelCount = 1; |
| descriptor.usage = usage; |
| descriptor.format = format; |
| |
| return device.CreateTexture(&descriptor); |
| } |
| |
| void SetUp() override { |
| ValidationTest::SetUp(); |
| |
| // Create objects to use as resources inside test bind groups. |
| { |
| wgpu::BufferDescriptor descriptor; |
| descriptor.size = 1024; |
| descriptor.usage = wgpu::BufferUsage::Uniform; |
| mUBO = device.CreateBuffer(&descriptor); |
| } |
| { |
| wgpu::BufferDescriptor descriptor; |
| descriptor.size = 1024; |
| descriptor.usage = wgpu::BufferUsage::Storage; |
| mSSBO = device.CreateBuffer(&descriptor); |
| } |
| { mSampler = device.CreateSampler(); } |
| { |
| mSampledTexture = |
| CreateTexture(wgpu::TextureUsage::TextureBinding, kDefaultTextureFormat, 1); |
| mSampledTextureView = mSampledTexture.CreateView(); |
| |
| wgpu::ExternalTextureDescriptor externalTextureDesc = |
| CreateDefaultExternalTextureDescriptor(); |
| externalTextureDesc.plane0 = mSampledTextureView; |
| mExternalTexture = device.CreateExternalTexture(&externalTextureDesc); |
| mExternalTextureBindingEntry.externalTexture = mExternalTexture; |
| } |
| } |
| |
| protected: |
| wgpu::ExternalTextureDescriptor CreateDefaultExternalTextureDescriptor() { |
| wgpu::ExternalTextureDescriptor desc; |
| desc.yuvToRgbConversionMatrix = mPlaceholderConstantArray.data(); |
| desc.gamutConversionMatrix = mPlaceholderConstantArray.data(); |
| desc.srcTransferFunctionParameters = mPlaceholderConstantArray.data(); |
| desc.dstTransferFunctionParameters = mPlaceholderConstantArray.data(); |
| desc.visibleSize = {kWidth, kHeight}; |
| return desc; |
| } |
| |
| WGPUDevice CreateTestDevice(native::Adapter dawnAdapter, |
| wgpu::DeviceDescriptor descriptor) override { |
| wgpu::FeatureName requiredFeatures[1] = {wgpu::FeatureName::Depth32FloatStencil8}; |
| descriptor.requiredFeatures = requiredFeatures; |
| descriptor.requiredFeatureCount = 1; |
| return dawnAdapter.CreateDevice(&descriptor); |
| } |
| |
| void DoTextureSampleTypeTest(bool success, |
| wgpu::TextureFormat format, |
| wgpu::TextureSampleType sampleType, |
| wgpu::TextureAspect aspect = wgpu::TextureAspect::All) { |
| wgpu::BindGroupLayout layout = |
| utils::MakeBindGroupLayout(device, {{0, wgpu::ShaderStage::Fragment, sampleType}}); |
| |
| wgpu::TextureDescriptor descriptor; |
| descriptor.size = {4, 4, 1}; |
| descriptor.usage = wgpu::TextureUsage::TextureBinding; |
| descriptor.format = format; |
| |
| wgpu::TextureViewDescriptor viewDescriptor; |
| viewDescriptor.aspect = aspect; |
| wgpu::TextureView view = device.CreateTexture(&descriptor).CreateView(&viewDescriptor); |
| |
| if (success) { |
| utils::MakeBindGroup(device, layout, {{0, view}}); |
| } else { |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, view}})); |
| } |
| } |
| |
| wgpu::Buffer mUBO; |
| wgpu::Buffer mSSBO; |
| wgpu::Sampler mSampler; |
| wgpu::Texture mSampledTexture; |
| wgpu::TextureView mSampledTextureView; |
| wgpu::ExternalTextureBindingEntry mExternalTextureBindingEntry; |
| |
| static constexpr wgpu::TextureFormat kDefaultTextureFormat = wgpu::TextureFormat::RGBA8Unorm; |
| |
| private: |
| uint32_t kWidth = 16; |
| uint32_t kHeight = 16; |
| wgpu::ExternalTexture mExternalTexture; |
| std::array<float, 12> mPlaceholderConstantArray; |
| }; |
| |
| // Test the validation of BindGroupDescriptor::nextInChain |
| TEST_F(BindGroupValidationTest, NextInChainNullptr) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout(device, {}); |
| |
| wgpu::BindGroupDescriptor descriptor; |
| descriptor.layout = layout; |
| descriptor.entryCount = 0; |
| descriptor.entries = nullptr; |
| |
| // Control case: check that nextInChain = nullptr is valid |
| descriptor.nextInChain = nullptr; |
| device.CreateBindGroup(&descriptor); |
| |
| // Check that nextInChain != nullptr is an error. |
| wgpu::ChainedStruct chainedDescriptor; |
| chainedDescriptor.sType = wgpu::SType::Invalid; |
| descriptor.nextInChain = &chainedDescriptor; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| } |
| |
| // Check constraints on entryCount |
| TEST_F(BindGroupValidationTest, EntryCountMismatch) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::SamplerBindingType::Filtering}}); |
| |
| // Control case: check that a descriptor with one binding is ok |
| utils::MakeBindGroup(device, layout, {{0, mSampler}}); |
| |
| // Check that entryCount != layout.entryCount fails. |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {})); |
| } |
| |
| // Check constraints on BindGroupEntry::binding |
| TEST_F(BindGroupValidationTest, WrongBindings) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::SamplerBindingType::Filtering}}); |
| |
| // Control case: check that a descriptor with a binding matching the layout's is ok |
| utils::MakeBindGroup(device, layout, {{0, mSampler}}); |
| |
| // Check that binding must be present in the layout |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{1, mSampler}})); |
| } |
| |
| // Check that the same binding cannot be set twice |
| TEST_F(BindGroupValidationTest, BindingSetTwice) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::SamplerBindingType::Filtering}, |
| {1, wgpu::ShaderStage::Fragment, wgpu::SamplerBindingType::Filtering}}); |
| |
| // Control case: check that different bindings work |
| utils::MakeBindGroup(device, layout, {{0, mSampler}, {1, mSampler}}); |
| |
| // Check that setting the same binding twice is invalid |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, mSampler}, {0, mSampler}})); |
| } |
| |
| // Check that a sampler binding must contain exactly one sampler |
| TEST_F(BindGroupValidationTest, SamplerBindingType) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::SamplerBindingType::Filtering}}); |
| |
| wgpu::BindGroupEntry binding; |
| binding.binding = 0; |
| binding.sampler = nullptr; |
| binding.textureView = nullptr; |
| binding.buffer = nullptr; |
| binding.offset = 0; |
| binding.size = 0; |
| |
| wgpu::BindGroupDescriptor descriptor; |
| descriptor.layout = layout; |
| descriptor.entryCount = 1; |
| descriptor.entries = &binding; |
| |
| // Not setting anything fails |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| |
| // Control case: setting just the sampler works |
| binding.sampler = mSampler; |
| device.CreateBindGroup(&descriptor); |
| |
| // Setting the texture view as well is an error |
| binding.textureView = mSampledTextureView; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.textureView = nullptr; |
| |
| // Setting the buffer as well is an error |
| binding.buffer = mUBO; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.buffer = nullptr; |
| |
| // Setting the external texture view as well is an error |
| binding.nextInChain = &mExternalTextureBindingEntry; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.nextInChain = nullptr; |
| |
| // Setting the sampler to an error sampler is an error. |
| { |
| wgpu::SamplerDescriptor samplerDesc; |
| samplerDesc.minFilter = static_cast<wgpu::FilterMode>(0xFFFFFFFF); |
| |
| wgpu::Sampler errorSampler; |
| ASSERT_DEVICE_ERROR(errorSampler = device.CreateSampler(&samplerDesc)); |
| |
| binding.sampler = errorSampler; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.sampler = nullptr; |
| } |
| } |
| |
| // Check that a texture binding must contain exactly a texture view |
| TEST_F(BindGroupValidationTest, TextureBindingType) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::TextureSampleType::Float}}); |
| |
| wgpu::BindGroupEntry binding; |
| binding.binding = 0; |
| binding.sampler = nullptr; |
| binding.textureView = nullptr; |
| binding.buffer = nullptr; |
| binding.offset = 0; |
| binding.size = 0; |
| |
| wgpu::BindGroupDescriptor descriptor; |
| descriptor.layout = layout; |
| descriptor.entryCount = 1; |
| descriptor.entries = &binding; |
| |
| // Not setting anything fails |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| |
| // Control case: setting just the texture view works |
| binding.textureView = mSampledTextureView; |
| device.CreateBindGroup(&descriptor); |
| |
| // Setting the sampler as well is an error |
| binding.sampler = mSampler; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.sampler = nullptr; |
| |
| // Setting the buffer as well is an error |
| binding.buffer = mUBO; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.buffer = nullptr; |
| |
| // Setting the external texture view as well is an error |
| binding.nextInChain = &mExternalTextureBindingEntry; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.nextInChain = nullptr; |
| |
| // Setting the texture view to an error texture view is an error. |
| { |
| wgpu::TextureViewDescriptor viewDesc; |
| viewDesc.format = kDefaultTextureFormat; |
| viewDesc.dimension = wgpu::TextureViewDimension::e2D; |
| viewDesc.baseMipLevel = 0; |
| viewDesc.mipLevelCount = 0; |
| viewDesc.baseArrayLayer = 0; |
| viewDesc.arrayLayerCount = 1000; |
| |
| wgpu::TextureView errorView; |
| ASSERT_DEVICE_ERROR(errorView = mSampledTexture.CreateView(&viewDesc)); |
| |
| binding.textureView = errorView; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.textureView = nullptr; |
| } |
| } |
| |
| // Check that a buffer binding must contain exactly a buffer |
| TEST_F(BindGroupValidationTest, BufferBindingType) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Uniform}}); |
| |
| wgpu::BindGroupEntry binding; |
| binding.binding = 0; |
| binding.sampler = nullptr; |
| binding.textureView = nullptr; |
| binding.buffer = nullptr; |
| binding.offset = 0; |
| binding.size = 1024; |
| |
| wgpu::BindGroupDescriptor descriptor; |
| descriptor.layout = layout; |
| descriptor.entryCount = 1; |
| descriptor.entries = &binding; |
| |
| // Not setting anything fails |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| |
| // Control case: setting just the buffer works |
| binding.buffer = mUBO; |
| device.CreateBindGroup(&descriptor); |
| |
| // Setting the texture view as well is an error |
| binding.textureView = mSampledTextureView; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.textureView = nullptr; |
| |
| // Setting the sampler as well is an error |
| binding.sampler = mSampler; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.sampler = nullptr; |
| |
| // Setting the external texture view as well is an error |
| binding.nextInChain = &mExternalTextureBindingEntry; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.nextInChain = nullptr; |
| |
| // Setting the buffer to an error buffer is an error. |
| { |
| wgpu::BufferDescriptor bufferDesc; |
| bufferDesc.size = 1024; |
| bufferDesc.usage = static_cast<wgpu::BufferUsage>(0xFFFFFFFF); |
| |
| wgpu::Buffer errorBuffer; |
| ASSERT_DEVICE_ERROR(errorBuffer = device.CreateBuffer(&bufferDesc)); |
| |
| binding.buffer = errorBuffer; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.buffer = nullptr; |
| } |
| } |
| |
| // Check that an external texture binding must contain exactly an external texture |
| TEST_F(BindGroupValidationTest, ExternalTextureBindingType) { |
| // Create an external texture |
| wgpu::Texture texture = |
| CreateTexture(wgpu::TextureUsage::TextureBinding, kDefaultTextureFormat, 1); |
| wgpu::ExternalTextureDescriptor externalDesc = CreateDefaultExternalTextureDescriptor(); |
| externalDesc.plane0 = texture.CreateView(); |
| wgpu::ExternalTexture externalTexture = device.CreateExternalTexture(&externalDesc); |
| |
| // Create a bind group layout for a single external texture |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, &utils::kExternalTextureBindingLayout}}); |
| |
| wgpu::BindGroupEntry binding; |
| binding.binding = 0; |
| binding.sampler = nullptr; |
| binding.textureView = nullptr; |
| binding.buffer = nullptr; |
| binding.offset = 0; |
| binding.size = 0; |
| |
| wgpu::BindGroupDescriptor descriptor; |
| descriptor.layout = layout; |
| descriptor.entryCount = 1; |
| descriptor.entries = &binding; |
| |
| // Not setting anything fails |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| |
| // Control case: setting just the external texture works |
| wgpu::ExternalTextureBindingEntry externalBindingEntry; |
| externalBindingEntry.externalTexture = externalTexture; |
| binding.nextInChain = &externalBindingEntry; |
| device.CreateBindGroup(&descriptor); |
| |
| // Setting the texture view as well is an error |
| binding.textureView = mSampledTextureView; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.textureView = nullptr; |
| |
| // Setting the sampler as well is an error |
| binding.sampler = mSampler; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.sampler = nullptr; |
| |
| // Setting the buffer as well is an error |
| binding.buffer = mUBO; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.buffer = nullptr; |
| |
| // Setting the external texture to an error external texture is an error. |
| { |
| wgpu::Texture errorTexture = |
| CreateTexture(wgpu::TextureUsage::TextureBinding, wgpu::TextureFormat::R8Unorm, 1); |
| wgpu::ExternalTextureDescriptor errorExternalDescriptor = |
| CreateDefaultExternalTextureDescriptor(); |
| errorExternalDescriptor.plane0 = errorTexture.CreateView(); |
| |
| wgpu::ExternalTexture errorExternalTexture; |
| ASSERT_DEVICE_ERROR(errorExternalTexture = |
| device.CreateExternalTexture(&errorExternalDescriptor)); |
| |
| wgpu::ExternalTextureBindingEntry errorExternalBindingEntry; |
| errorExternalBindingEntry.externalTexture = errorExternalTexture; |
| binding.nextInChain = &errorExternalBindingEntry; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.nextInChain = nullptr; |
| } |
| |
| // Setting an external texture with another external texture chained is an error. |
| { |
| wgpu::ExternalTexture externalTexture2 = device.CreateExternalTexture(&externalDesc); |
| wgpu::ExternalTextureBindingEntry externalBindingEntry2; |
| externalBindingEntry2.externalTexture = externalTexture2; |
| externalBindingEntry.nextInChain = &externalBindingEntry2; |
| |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| } |
| |
| // Chaining a struct that isn't an external texture binding entry is an error. |
| { |
| wgpu::ExternalTextureBindingLayout externalBindingLayout; |
| binding.nextInChain = &externalBindingLayout; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| } |
| } |
| |
| // Check that a texture binding must have the correct usage |
| TEST_F(BindGroupValidationTest, TextureUsage) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::TextureSampleType::Float}}); |
| |
| // Control case: setting a sampleable texture view works. |
| utils::MakeBindGroup(device, layout, {{0, mSampledTextureView}}); |
| |
| // Make an render attachment texture and try to set it for a SampledTexture binding |
| wgpu::Texture outputTexture = |
| CreateTexture(wgpu::TextureUsage::RenderAttachment, wgpu::TextureFormat::RGBA8Unorm, 1); |
| wgpu::TextureView outputTextureView = outputTexture.CreateView(); |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, outputTextureView}})); |
| } |
| |
| // Check that a storage texture binding must have the correct usage |
| TEST_F(BindGroupValidationTest, StorageTextureUsage) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Compute, wgpu::StorageTextureAccess::WriteOnly, |
| wgpu::TextureFormat::RGBA8Uint}}); |
| |
| wgpu::TextureDescriptor descriptor; |
| descriptor.dimension = wgpu::TextureDimension::e2D; |
| descriptor.size = {16, 16, 1}; |
| descriptor.sampleCount = 1; |
| descriptor.mipLevelCount = 1; |
| descriptor.usage = wgpu::TextureUsage::StorageBinding; |
| descriptor.format = wgpu::TextureFormat::RGBA8Uint; |
| |
| wgpu::TextureView view = device.CreateTexture(&descriptor).CreateView(); |
| |
| // Control case: setting a storage texture view works. |
| utils::MakeBindGroup(device, layout, {{0, view}}); |
| |
| // Sampled texture is invalid with storage buffer binding |
| descriptor.usage = wgpu::TextureUsage::TextureBinding; |
| descriptor.format = wgpu::TextureFormat::RGBA8Unorm; |
| view = device.CreateTexture(&descriptor).CreateView(); |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, view}})); |
| |
| // Multisampled texture is invalid with storage buffer binding |
| // Regression case for crbug.com/dawn/614 where this hit an DAWN_ASSERT. |
| descriptor.sampleCount = 4; |
| descriptor.usage |= wgpu::TextureUsage::RenderAttachment; |
| view = device.CreateTexture(&descriptor).CreateView(); |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, view}})); |
| } |
| |
| // Check that a texture must have the correct sample type |
| TEST_F(BindGroupValidationTest, TextureSampleType) { |
| // Test that RGBA8Unorm is only compatible with float/unfilterable-float. |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::RGBA8Unorm, wgpu::TextureSampleType::Float); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::RGBA8Unorm, |
| wgpu::TextureSampleType::UnfilterableFloat); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::RGBA8Unorm, wgpu::TextureSampleType::Depth); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::RGBA8Unorm, wgpu::TextureSampleType::Uint); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::RGBA8Unorm, wgpu::TextureSampleType::Sint); |
| |
| // Test that float32 formats are only compatible with unfilterable-float (without the |
| // float32-filterable feature enabled). |
| for (const auto f32Format : {wgpu::TextureFormat::R32Float, wgpu::TextureFormat::RG32Float, |
| wgpu::TextureFormat::RGBA32Float}) { |
| DoTextureSampleTypeTest(false, f32Format, wgpu::TextureSampleType::Float); |
| DoTextureSampleTypeTest(true, f32Format, wgpu::TextureSampleType::UnfilterableFloat); |
| DoTextureSampleTypeTest(false, f32Format, wgpu::TextureSampleType::Depth); |
| DoTextureSampleTypeTest(false, f32Format, wgpu::TextureSampleType::Uint); |
| DoTextureSampleTypeTest(false, f32Format, wgpu::TextureSampleType::Sint); |
| } |
| |
| // Test that Depth16Unorm is only compatible with depth/unfilterable-float. |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth16Unorm, |
| wgpu::TextureSampleType::Float); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth16Unorm, |
| wgpu::TextureSampleType::UnfilterableFloat); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth16Unorm, |
| wgpu::TextureSampleType::Depth); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth16Unorm, |
| wgpu::TextureSampleType::Uint); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth16Unorm, |
| wgpu::TextureSampleType::Sint); |
| |
| // Test that Depth24Plus is only compatible with depth/unfilterable-float. |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth24Plus, |
| wgpu::TextureSampleType::Float); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth24Plus, |
| wgpu::TextureSampleType::UnfilterableFloat); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth24Plus, wgpu::TextureSampleType::Depth); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth24Plus, wgpu::TextureSampleType::Uint); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth24Plus, wgpu::TextureSampleType::Sint); |
| |
| // Test that Depth24PlusStencil8 with depth aspect is only compatible with |
| // depth/unfilterable-float. |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth24PlusStencil8, |
| wgpu::TextureSampleType::Float, wgpu::TextureAspect::DepthOnly); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth24PlusStencil8, |
| wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureAspect::DepthOnly); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth24PlusStencil8, |
| wgpu::TextureSampleType::Depth, wgpu::TextureAspect::DepthOnly); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth24PlusStencil8, |
| wgpu::TextureSampleType::Uint, wgpu::TextureAspect::DepthOnly); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth24PlusStencil8, |
| wgpu::TextureSampleType::Sint, wgpu::TextureAspect::DepthOnly); |
| |
| // Test that Depth24PlusStencil8 with stencil aspect is only compatible with uint. |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth24PlusStencil8, |
| wgpu::TextureSampleType::Float, wgpu::TextureAspect::StencilOnly); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth24PlusStencil8, |
| wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureAspect::StencilOnly); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth24PlusStencil8, |
| wgpu::TextureSampleType::Depth, wgpu::TextureAspect::StencilOnly); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth24PlusStencil8, |
| wgpu::TextureSampleType::Uint, wgpu::TextureAspect::StencilOnly); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth24PlusStencil8, |
| wgpu::TextureSampleType::Sint, wgpu::TextureAspect::StencilOnly); |
| |
| // Test that Depth32Float is only compatible with depth/unfilterable-float. |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth32Float, |
| wgpu::TextureSampleType::Float); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth32Float, |
| wgpu::TextureSampleType::UnfilterableFloat); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth32Float, |
| wgpu::TextureSampleType::Depth); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth32Float, |
| wgpu::TextureSampleType::Uint); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth32Float, |
| wgpu::TextureSampleType::Sint); |
| |
| // Test that Depth32FloatStencil8 with depth aspect is only compatible with |
| // depth/unfilterable-float. |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth32FloatStencil8, |
| wgpu::TextureSampleType::Float, wgpu::TextureAspect::DepthOnly); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth32FloatStencil8, |
| wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureAspect::DepthOnly); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth32FloatStencil8, |
| wgpu::TextureSampleType::Depth, wgpu::TextureAspect::DepthOnly); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth32FloatStencil8, |
| wgpu::TextureSampleType::Uint, wgpu::TextureAspect::DepthOnly); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth32FloatStencil8, |
| wgpu::TextureSampleType::Sint, wgpu::TextureAspect::DepthOnly); |
| |
| // Test that Depth32FloatStencil8 with stencil aspect is only compatible with uint. |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth32FloatStencil8, |
| wgpu::TextureSampleType::Float, wgpu::TextureAspect::StencilOnly); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth32FloatStencil8, |
| wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureAspect::StencilOnly); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth32FloatStencil8, |
| wgpu::TextureSampleType::Depth, wgpu::TextureAspect::StencilOnly); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::Depth32FloatStencil8, |
| wgpu::TextureSampleType::Uint, wgpu::TextureAspect::StencilOnly); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::Depth32FloatStencil8, |
| wgpu::TextureSampleType::Sint, wgpu::TextureAspect::StencilOnly); |
| |
| // Test that RG8Uint is only compatible with uint. |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::RG8Uint, wgpu::TextureSampleType::Float); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::RG8Uint, |
| wgpu::TextureSampleType::UnfilterableFloat); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::RG8Uint, wgpu::TextureSampleType::Depth); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::RG8Uint, wgpu::TextureSampleType::Uint); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::RG8Uint, wgpu::TextureSampleType::Sint); |
| |
| // Test that R16Sint is only compatible with sint. |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::R16Sint, wgpu::TextureSampleType::Float); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::R16Sint, |
| wgpu::TextureSampleType::UnfilterableFloat); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::R16Sint, wgpu::TextureSampleType::Depth); |
| DoTextureSampleTypeTest(false, wgpu::TextureFormat::R16Sint, wgpu::TextureSampleType::Uint); |
| DoTextureSampleTypeTest(true, wgpu::TextureFormat::R16Sint, wgpu::TextureSampleType::Sint); |
| } |
| |
| class BindGroupValidationTest_Float32Filterable : public BindGroupValidationTest { |
| protected: |
| WGPUDevice CreateTestDevice(dawn::native::Adapter dawnAdapter, |
| wgpu::DeviceDescriptor descriptor) override { |
| wgpu::FeatureName requiredFeatures[1] = {wgpu::FeatureName::Float32Filterable}; |
| descriptor.requiredFeatures = requiredFeatures; |
| descriptor.requiredFeatureCount = 1; |
| return dawnAdapter.CreateDevice(&descriptor); |
| } |
| }; |
| |
| // Checks that float32 texture formats have the correct sample type when float32-filterable feature |
| // enabled. |
| TEST_F(BindGroupValidationTest_Float32Filterable, TextureSampleType) { |
| // With the feature enabled, float32 formats should be compatible with both float and |
| // unfilterable-float. |
| for (const auto f32Format : {wgpu::TextureFormat::R32Float, wgpu::TextureFormat::RG32Float, |
| wgpu::TextureFormat::RGBA32Float}) { |
| DoTextureSampleTypeTest(true, f32Format, wgpu::TextureSampleType::Float); |
| DoTextureSampleTypeTest(true, f32Format, wgpu::TextureSampleType::UnfilterableFloat); |
| DoTextureSampleTypeTest(false, f32Format, wgpu::TextureSampleType::Depth); |
| DoTextureSampleTypeTest(false, f32Format, wgpu::TextureSampleType::Uint); |
| DoTextureSampleTypeTest(false, f32Format, wgpu::TextureSampleType::Sint); |
| } |
| } |
| |
| // Test which depth-stencil formats are allowed to be sampled (all). |
| TEST_F(BindGroupValidationTest, SamplingDepthStencilTexture) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::TextureSampleType::Depth}}); |
| |
| wgpu::TextureDescriptor desc; |
| desc.size = {1, 1, 1}; |
| desc.usage = wgpu::TextureUsage::TextureBinding; |
| |
| // Depth32Float is allowed to be sampled. |
| { |
| desc.format = wgpu::TextureFormat::Depth32Float; |
| wgpu::Texture texture = device.CreateTexture(&desc); |
| |
| utils::MakeBindGroup(device, layout, {{0, texture.CreateView()}}); |
| } |
| |
| // Depth24Plus is allowed to be sampled. |
| { |
| desc.format = wgpu::TextureFormat::Depth24Plus; |
| wgpu::Texture texture = device.CreateTexture(&desc); |
| |
| utils::MakeBindGroup(device, layout, {{0, texture.CreateView()}}); |
| } |
| |
| // Depth24PlusStencil8 is allowed to be sampled, if the depth or stencil aspect is selected. |
| { |
| desc.format = wgpu::TextureFormat::Depth24PlusStencil8; |
| wgpu::Texture texture = device.CreateTexture(&desc); |
| wgpu::TextureViewDescriptor viewDesc = {}; |
| |
| viewDesc.aspect = wgpu::TextureAspect::DepthOnly; |
| utils::MakeBindGroup(device, layout, {{0, texture.CreateView(&viewDesc)}}); |
| |
| layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::TextureSampleType::Uint}}); |
| |
| viewDesc.aspect = wgpu::TextureAspect::StencilOnly; |
| utils::MakeBindGroup(device, layout, {{0, texture.CreateView(&viewDesc)}}); |
| } |
| } |
| |
| // Check that a texture must have the correct dimension |
| TEST_F(BindGroupValidationTest, TextureDimension) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::TextureSampleType::Float}}); |
| |
| // Control case: setting a 2D texture view works. |
| utils::MakeBindGroup(device, layout, {{0, mSampledTextureView}}); |
| |
| // Make a 2DArray texture and try to set it to a 2D binding. |
| wgpu::Texture arrayTexture = |
| CreateTexture(wgpu::TextureUsage::TextureBinding, wgpu::TextureFormat::RGBA8Uint, 2); |
| wgpu::TextureView arrayTextureView = arrayTexture.CreateView(); |
| |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, arrayTextureView}})); |
| } |
| |
| // Check that a storage texture binding must have a texture view with a mipLevelCount of 1 |
| TEST_F(BindGroupValidationTest, StorageTextureViewLayerCount) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Compute, wgpu::StorageTextureAccess::WriteOnly, |
| wgpu::TextureFormat::RGBA8Uint}}); |
| |
| wgpu::TextureDescriptor descriptor; |
| descriptor.dimension = wgpu::TextureDimension::e2D; |
| descriptor.size = {16, 16, 1}; |
| descriptor.sampleCount = 1; |
| descriptor.mipLevelCount = 1; |
| descriptor.usage = wgpu::TextureUsage::StorageBinding; |
| descriptor.format = wgpu::TextureFormat::RGBA8Uint; |
| |
| wgpu::Texture textureNoMip = device.CreateTexture(&descriptor); |
| |
| descriptor.mipLevelCount = 3; |
| wgpu::Texture textureMip = device.CreateTexture(&descriptor); |
| |
| // Control case: setting a storage texture view on a texture with only one mip level works |
| { |
| wgpu::TextureView view = textureNoMip.CreateView(); |
| utils::MakeBindGroup(device, layout, {{0, view}}); |
| } |
| |
| // Setting a storage texture view with mipLevelCount=1 on a texture of multiple mip levels is |
| // valid |
| { |
| wgpu::TextureViewDescriptor viewDesc = {}; |
| viewDesc.aspect = wgpu::TextureAspect::All; |
| viewDesc.dimension = wgpu::TextureViewDimension::e2D; |
| viewDesc.format = wgpu::TextureFormat::RGBA8Uint; |
| viewDesc.baseMipLevel = 0; |
| viewDesc.mipLevelCount = 1; |
| |
| // Setting texture view with lod 0 is valid |
| wgpu::TextureView view = textureMip.CreateView(&viewDesc); |
| utils::MakeBindGroup(device, layout, {{0, view}}); |
| |
| // Setting texture view with other lod is also valid |
| viewDesc.baseMipLevel = 2; |
| view = textureMip.CreateView(&viewDesc); |
| utils::MakeBindGroup(device, layout, {{0, view}}); |
| } |
| |
| // Texture view with mipLevelCount > 1 is invalid |
| { |
| wgpu::TextureViewDescriptor viewDesc = {}; |
| viewDesc.aspect = wgpu::TextureAspect::All; |
| viewDesc.dimension = wgpu::TextureViewDimension::e2D; |
| viewDesc.format = wgpu::TextureFormat::RGBA8Uint; |
| viewDesc.baseMipLevel = 0; |
| viewDesc.mipLevelCount = 2; |
| |
| // Setting texture view with lod 0 and 1 is invalid |
| wgpu::TextureView view = textureMip.CreateView(&viewDesc); |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, view}})); |
| |
| // Setting texture view with lod 1 and 2 is invalid |
| viewDesc.baseMipLevel = 1; |
| view = textureMip.CreateView(&viewDesc); |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, view}})); |
| } |
| } |
| |
| // Check that a UBO must have the correct usage |
| TEST_F(BindGroupValidationTest, BufferUsageUBO) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Uniform}}); |
| |
| // Control case: using a buffer with the uniform usage works |
| utils::MakeBindGroup(device, layout, {{0, mUBO, 0, 256}}); |
| |
| // Using a buffer without the uniform usage fails |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, mSSBO, 0, 256}})); |
| } |
| |
| // Check that a SSBO must have the correct usage |
| TEST_F(BindGroupValidationTest, BufferUsageSSBO) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Storage}}); |
| |
| // Control case: using a buffer with the storage usage works |
| utils::MakeBindGroup(device, layout, {{0, mSSBO, 0, 256}}); |
| |
| // Using a buffer without the storage usage fails |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, mUBO, 0, 256}})); |
| } |
| |
| // Check that a readonly SSBO must have the correct usage |
| TEST_F(BindGroupValidationTest, BufferUsageReadonlySSBO) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::ReadOnlyStorage}}); |
| |
| // Control case: using a buffer with the storage usage works |
| utils::MakeBindGroup(device, layout, {{0, mSSBO, 0, 256}}); |
| |
| // Using a buffer without the storage usage fails |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, mUBO, 0, 256}})); |
| } |
| |
| // Check that a resolve buffer with internal storge usage cannot be used as SSBO |
| TEST_F(BindGroupValidationTest, BufferUsageQueryResolve) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Storage}}); |
| |
| // Control case: using a buffer with the storage usage works |
| utils::MakeBindGroup(device, layout, {{0, mSSBO, 0, 256}}); |
| |
| // Using a resolve buffer with the internal storage usage fails |
| wgpu::BufferDescriptor descriptor; |
| descriptor.size = 1024; |
| descriptor.usage = wgpu::BufferUsage::QueryResolve; |
| wgpu::Buffer buffer = device.CreateBuffer(&descriptor); |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, buffer, 0, 256}})); |
| } |
| |
| // Tests constraints on the buffer offset for bind groups. |
| TEST_F(BindGroupValidationTest, BufferOffsetAlignment) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}, |
| }); |
| |
| // Check that offset 0 is valid |
| utils::MakeBindGroup(device, layout, {{0, mUBO, 0, 512}}); |
| |
| // Check that offset 256 (aligned) is valid |
| utils::MakeBindGroup(device, layout, {{0, mUBO, 256, 256}}); |
| |
| // Check cases where unaligned buffer offset is invalid |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, mUBO, 1, 256}})); |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, mUBO, 128, 256}})); |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, mUBO, 255, 256}})); |
| } |
| |
| // Tests constraints on the texture for MultisampledTexture bindings |
| TEST_F(BindGroupValidationTest, MultisampledTexture) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureViewDimension::e2D, true}}); |
| |
| wgpu::BindGroupEntry binding; |
| binding.binding = 0; |
| binding.sampler = nullptr; |
| binding.textureView = nullptr; |
| binding.buffer = nullptr; |
| binding.offset = 0; |
| binding.size = 0; |
| |
| wgpu::BindGroupDescriptor descriptor; |
| descriptor.layout = layout; |
| descriptor.entryCount = 1; |
| descriptor.entries = &binding; |
| |
| // Not setting anything fails |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| |
| // Control case: setting a multisampled 2D texture works |
| wgpu::TextureDescriptor textureDesc; |
| textureDesc.sampleCount = 4; |
| textureDesc.usage = wgpu::TextureUsage::TextureBinding | wgpu::TextureUsage::RenderAttachment; |
| textureDesc.dimension = wgpu::TextureDimension::e2D; |
| textureDesc.format = wgpu::TextureFormat::RGBA8Unorm; |
| textureDesc.size = {1, 1, 1}; |
| wgpu::Texture msTexture = device.CreateTexture(&textureDesc); |
| |
| binding.textureView = msTexture.CreateView(); |
| device.CreateBindGroup(&descriptor); |
| binding.textureView = nullptr; |
| |
| // Error case: setting a single sampled 2D texture is an error. |
| binding.textureView = mSampledTextureView; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&descriptor)); |
| binding.textureView = nullptr; |
| } |
| |
| // Tests dafault offset and size of bind group entry work as expected |
| TEST_F(BindGroupValidationTest, BufferBindingDefaultOffsetAndSize) { |
| wgpu::BufferDescriptor bufferDesc; |
| bufferDesc.size = 768; // 768 = 256 x 3 |
| bufferDesc.usage = wgpu::BufferUsage::Uniform; |
| wgpu::Buffer buffer = device.CreateBuffer(&bufferDesc); |
| |
| bufferDesc.size = 260; |
| wgpu::Buffer bufferSized260 = device.CreateBuffer(&bufferDesc); |
| bufferDesc.size = 256; |
| wgpu::Buffer bufferSized256 = device.CreateBuffer(&bufferDesc); |
| |
| // Create a layout requiring minimium buffer binding size of 260 |
| wgpu::BufferBindingLayout bufferBindingLayout; |
| bufferBindingLayout.type = wgpu::BufferBindingType::Uniform; |
| bufferBindingLayout.hasDynamicOffset = false; |
| bufferBindingLayout.minBindingSize = 260; |
| |
| wgpu::BindGroupLayoutEntry bindGroupLayoutEntry; |
| bindGroupLayoutEntry.binding = 0; |
| bindGroupLayoutEntry.visibility = wgpu::ShaderStage::Vertex; |
| bindGroupLayoutEntry.buffer = bufferBindingLayout; |
| |
| wgpu::BindGroupLayoutDescriptor bindGroupLayoutDescriptor; |
| bindGroupLayoutDescriptor.entryCount = 1; |
| bindGroupLayoutDescriptor.entries = &bindGroupLayoutEntry; |
| wgpu::BindGroupLayout layout = device.CreateBindGroupLayout(&bindGroupLayoutDescriptor); |
| |
| // Default offset should be 0 |
| { |
| wgpu::BindGroupEntry binding; |
| binding.binding = 0; |
| binding.sampler = nullptr; |
| binding.textureView = nullptr; |
| binding.buffer = buffer; |
| // binding.offset omitted. |
| binding.size = 768; |
| |
| wgpu::BindGroupDescriptor bgDesc; |
| bgDesc.layout = layout; |
| bgDesc.entryCount = 1; |
| bgDesc.entries = &binding; |
| |
| // Offset 0 and size 768 should work. |
| device.CreateBindGroup(&bgDesc); |
| |
| // Offset 0 and size 260 should work. |
| binding.size = 260; |
| device.CreateBindGroup(&bgDesc); |
| |
| // Offset 0 and size 256 go smaller than minBindingSize and validation error. |
| binding.size = 256; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&bgDesc)); |
| |
| // Offset 0 and size 769 should be OOB and validation error. |
| binding.size = 769; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&bgDesc)); |
| } |
| |
| // Default size should be whole size - offset |
| { |
| wgpu::BindGroupEntry binding; |
| binding.binding = 0; |
| binding.sampler = nullptr; |
| binding.textureView = nullptr; |
| binding.buffer = buffer; |
| binding.offset = 0; |
| // binding.size omitted |
| |
| wgpu::BindGroupDescriptor bgDesc; |
| bgDesc.layout = layout; |
| bgDesc.entryCount = 1; |
| bgDesc.entries = &binding; |
| |
| // Offset 0 and default size = 768 should work. |
| device.CreateBindGroup(&bgDesc); |
| |
| // Offset 256 and default size = 512 should work. |
| binding.offset = 256; |
| device.CreateBindGroup(&bgDesc); |
| |
| // Offset 512 and default size = 256 go smaller than minBindingSize and validation error. |
| binding.offset = 512; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&bgDesc)); |
| |
| // Offset 1024 should be OOB and validation error. |
| binding.offset = 1024; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&bgDesc)); |
| } |
| |
| // Both offset and size are default, should be offset = 0 and size = whole size |
| { |
| wgpu::BindGroupEntry binding; |
| binding.binding = 0; |
| binding.sampler = nullptr; |
| binding.textureView = nullptr; |
| binding.buffer = buffer; |
| // binding.offset omitted |
| // binding.size omitted |
| |
| wgpu::BindGroupDescriptor bgDesc; |
| bgDesc.layout = layout; |
| bgDesc.entryCount = 1; |
| bgDesc.entries = &binding; |
| |
| // Offset 0 and default size = 768 should work. |
| device.CreateBindGroup(&bgDesc); |
| |
| // Use a buffer with size 260, offset 0 and default size = 260 should work. |
| binding.buffer = bufferSized260; |
| device.CreateBindGroup(&bgDesc); |
| |
| // Use a buffer with size 256, offset 0 and default size = 256 go smaller than |
| // minBindingSize and validation error. |
| binding.buffer = bufferSized256; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroup(&bgDesc)); |
| } |
| } |
| |
| // Tests constraints to be sure the buffer binding fits in the buffer |
| TEST_F(BindGroupValidationTest, BufferBindingOOB) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}, |
| }); |
| |
| wgpu::BufferDescriptor descriptor; |
| descriptor.size = 1024; |
| descriptor.usage = wgpu::BufferUsage::Uniform; |
| wgpu::Buffer buffer = device.CreateBuffer(&descriptor); |
| |
| // Success case, touching the start of the buffer works |
| utils::MakeBindGroup(device, layout, {{0, buffer, 0, 256}}); |
| |
| // Success case, touching the end of the buffer works |
| utils::MakeBindGroup(device, layout, {{0, buffer, 3 * 256, 256}}); |
| |
| // Error case, zero size is invalid. |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, buffer, 1024, 0}})); |
| |
| // Success case, touching the full buffer works |
| utils::MakeBindGroup(device, layout, {{0, buffer, 0, 1024}}); |
| utils::MakeBindGroup(device, layout, {{0, buffer, 0, wgpu::kWholeSize}}); |
| |
| // Success case, whole size causes the rest of the buffer to be used but not beyond. |
| utils::MakeBindGroup(device, layout, {{0, buffer, 256, wgpu::kWholeSize}}); |
| |
| // Error case, offset is OOB |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, buffer, 256 * 5, 0}})); |
| |
| // Error case, size is OOB |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, buffer, 0, 256 * 5}})); |
| |
| // Error case, offset+size is OOB |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, buffer, 1024, 256}})); |
| |
| // Error case, offset+size overflows to be 0 |
| ASSERT_DEVICE_ERROR( |
| utils::MakeBindGroup(device, layout, {{0, buffer, 256, uint32_t(0) - uint32_t(256)}})); |
| } |
| |
| // Tests constraints to be sure the uniform buffer binding isn't too large |
| TEST_F(BindGroupValidationTest, MaxUniformBufferBindingSize) { |
| wgpu::Limits supportedLimits = GetSupportedLimits().limits; |
| |
| wgpu::BufferDescriptor descriptor; |
| descriptor.size = 2 * supportedLimits.maxUniformBufferBindingSize; |
| descriptor.usage = wgpu::BufferUsage::Uniform | wgpu::BufferUsage::Storage; |
| wgpu::Buffer buffer = device.CreateBuffer(&descriptor); |
| |
| wgpu::BindGroupLayout uniformLayout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}}); |
| |
| // Success case, this is exactly the limit |
| utils::MakeBindGroup(device, uniformLayout, |
| {{0, buffer, 0, supportedLimits.maxUniformBufferBindingSize}}); |
| |
| wgpu::BindGroupLayout doubleUniformLayout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}, |
| {1, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}}); |
| |
| // Success case, individual bindings don't exceed the limit |
| utils::MakeBindGroup(device, doubleUniformLayout, |
| {{0, buffer, 0, supportedLimits.maxUniformBufferBindingSize}, |
| {1, buffer, supportedLimits.maxUniformBufferBindingSize, |
| supportedLimits.maxUniformBufferBindingSize}}); |
| |
| // Error case, this is above the limit |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup( |
| device, uniformLayout, {{0, buffer, 0, supportedLimits.maxUniformBufferBindingSize + 1}})); |
| |
| // Making sure the constraint doesn't apply to storage buffers |
| wgpu::BindGroupLayout readonlyStorageLayout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::ReadOnlyStorage}}); |
| wgpu::BindGroupLayout storageLayout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Storage}}); |
| |
| // Success case, storage buffer can still be created. |
| utils::MakeBindGroup(device, readonlyStorageLayout, |
| {{0, buffer, 0, 2 * supportedLimits.maxUniformBufferBindingSize}}); |
| utils::MakeBindGroup(device, storageLayout, |
| {{0, buffer, 0, 2 * supportedLimits.maxUniformBufferBindingSize}}); |
| } |
| |
| // Tests constraints to be sure the storage buffer binding isn't too large |
| TEST_F(BindGroupValidationTest, MaxStorageBufferBindingSize) { |
| wgpu::Limits supportedLimits = GetSupportedLimits().limits; |
| |
| wgpu::BufferDescriptor descriptor; |
| descriptor.size = 2 * supportedLimits.maxStorageBufferBindingSize; |
| descriptor.usage = wgpu::BufferUsage::Storage; |
| wgpu::Buffer buffer = device.CreateBuffer(&descriptor); |
| |
| wgpu::BindGroupLayout uniformLayout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Storage}}); |
| |
| // Success case, this is exactly the limit |
| utils::MakeBindGroup(device, uniformLayout, |
| {{0, buffer, 0, supportedLimits.maxStorageBufferBindingSize}}); |
| |
| // Success case, this is one less than the limit (check it is not an alignment constraint) |
| utils::MakeBindGroup(device, uniformLayout, |
| {{0, buffer, 0, supportedLimits.maxStorageBufferBindingSize - 4}}); |
| |
| wgpu::BindGroupLayout doubleUniformLayout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Storage}, |
| {1, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Storage}}); |
| |
| // Success case, individual bindings don't exceed the limit |
| utils::MakeBindGroup(device, doubleUniformLayout, |
| {{0, buffer, 0, supportedLimits.maxStorageBufferBindingSize}, |
| {1, buffer, supportedLimits.maxStorageBufferBindingSize, |
| supportedLimits.maxStorageBufferBindingSize}}); |
| |
| // Error case, this is above the limit |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup( |
| device, uniformLayout, {{0, buffer, 0, supportedLimits.maxStorageBufferBindingSize + 4}})); |
| } |
| |
| // Test constraints to be sure the effective storage and read-only storage buffer binding size must |
| // be a multiple of 4. |
| TEST_F(BindGroupValidationTest, EffectiveStorageBufferBindingSize) { |
| wgpu::BufferDescriptor descriptor; |
| descriptor.size = 262; |
| descriptor.usage = wgpu::BufferUsage::Storage; |
| wgpu::Buffer buffer = device.CreateBuffer(&descriptor); |
| |
| constexpr std::array<wgpu::BufferBindingType, 2> kStorageBufferBindingTypes = { |
| {wgpu::BufferBindingType::Storage, wgpu::BufferBindingType::ReadOnlyStorage}}; |
| |
| for (wgpu::BufferBindingType bufferBindingType : kStorageBufferBindingTypes) { |
| wgpu::BindGroupLayout layout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Compute, bufferBindingType}}); |
| |
| // Error case, as the effective buffer binding size (262) isn't a multiple of 4. |
| { |
| constexpr uint32_t kOffset = 0; |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, buffer, kOffset}})); |
| } |
| |
| // Error case, as the effective buffer binding size (6) isn't a multiple of 4. |
| { |
| constexpr uint32_t kOffset = 256; |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, layout, {{0, buffer, kOffset}})); |
| } |
| |
| // Error case, as the effective buffer binding size (2) isn't a multiple of 4. |
| { |
| constexpr uint32_t kOffset = 0; |
| constexpr uint32_t kBindingSize = 2; |
| ASSERT_DEVICE_ERROR( |
| utils::MakeBindGroup(device, layout, {{0, buffer, kOffset, kBindingSize}})); |
| } |
| |
| // Success case, as the effective buffer binding size (4) is a multiple of 4. |
| { |
| constexpr uint32_t kOffset = 0; |
| constexpr uint32_t kBindingSize = 4; |
| utils::MakeBindGroup(device, layout, {{0, buffer, kOffset, kBindingSize}}); |
| } |
| } |
| } |
| |
| // Test what happens when the layout is an error. |
| TEST_F(BindGroupValidationTest, ErrorLayout) { |
| wgpu::BindGroupLayout goodLayout = utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}, |
| }); |
| |
| wgpu::BindGroupLayout errorLayout; |
| ASSERT_DEVICE_ERROR( |
| errorLayout = utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}, |
| {0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}, |
| })); |
| |
| // Control case, creating with the good layout works |
| utils::MakeBindGroup(device, goodLayout, {{0, mUBO, 0, 256}}); |
| |
| // Creating with an error layout fails |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, errorLayout, {{0, mUBO, 0, 256}})); |
| } |
| |
| class BindGroupLayoutValidationTest : public ValidationTest { |
| public: |
| wgpu::BindGroupLayout MakeBindGroupLayout(wgpu::BindGroupLayoutEntry* binding, uint32_t count) { |
| wgpu::BindGroupLayoutDescriptor descriptor; |
| descriptor.entryCount = count; |
| descriptor.entries = binding; |
| return device.CreateBindGroupLayout(&descriptor); |
| } |
| |
| void TestCreateBindGroupLayout(wgpu::BindGroupLayoutEntry* binding, |
| uint32_t count, |
| bool expected) { |
| wgpu::BindGroupLayoutDescriptor descriptor; |
| |
| descriptor.entryCount = count; |
| descriptor.entries = binding; |
| |
| if (!expected) { |
| ASSERT_DEVICE_ERROR(device.CreateBindGroupLayout(&descriptor)); |
| } else { |
| device.CreateBindGroupLayout(&descriptor); |
| } |
| } |
| |
| void TestCreatePipelineLayout(wgpu::BindGroupLayout* bgl, uint32_t count, bool expected) { |
| wgpu::PipelineLayoutDescriptor descriptor; |
| |
| descriptor.bindGroupLayoutCount = count; |
| descriptor.bindGroupLayouts = bgl; |
| |
| if (!expected) { |
| ASSERT_DEVICE_ERROR(device.CreatePipelineLayout(&descriptor)); |
| } else { |
| device.CreatePipelineLayout(&descriptor); |
| } |
| } |
| }; |
| |
| // Tests setting storage buffer and readonly storage buffer bindings in vertex and fragment shader. |
| TEST_F(BindGroupLayoutValidationTest, BindGroupLayoutStorageBindingsInVertexShader) { |
| // Checks that storage buffer binding is not supported in vertex shader. |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Storage}})); |
| |
| utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::ReadOnlyStorage}}); |
| |
| utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Storage}}); |
| |
| utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::ReadOnlyStorage}}); |
| } |
| |
| // Tests setting that bind group layout bindings numbers may be very large. |
| TEST_F(BindGroupLayoutValidationTest, BindGroupLayoutEntryMax) { |
| // Check that up to kMaxBindingsPerBindGroup-1 is valid. |
| utils::MakeBindGroupLayout(device, {{kMaxBindingsPerBindGroup - 1, wgpu::ShaderStage::Vertex, |
| wgpu::BufferBindingType::Uniform}}); |
| |
| // But after is an error. |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroupLayout( |
| device, |
| {{kMaxBindingsPerBindGroup, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}})); |
| } |
| |
| // This test verifies that the BindGroupLayout bindings are correctly validated, even if the |
| // binding ids are out-of-order. |
| TEST_F(BindGroupLayoutValidationTest, BindGroupEntry) { |
| utils::MakeBindGroupLayout(device, |
| { |
| {1, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}, |
| {0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}, |
| }); |
| } |
| |
| // Check that dynamic = true is only allowed buffer bindings. |
| TEST_F(BindGroupLayoutValidationTest, DynamicAndTypeCompatibility) { |
| utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::BufferBindingType::Uniform, true}, |
| }); |
| |
| utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::BufferBindingType::Storage, true}, |
| }); |
| |
| utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::BufferBindingType::ReadOnlyStorage, true}, |
| }); |
| } |
| |
| // Test that it is invalid to create a BGL with more than one binding type set. |
| TEST_F(BindGroupLayoutValidationTest, BindGroupLayoutEntryTooManySet) { |
| wgpu::BindGroupLayoutEntry entry = {}; |
| entry.binding = 0; |
| entry.visibility = wgpu::ShaderStage::Fragment; |
| entry.buffer.type = wgpu::BufferBindingType::Uniform; |
| entry.sampler.type = wgpu::SamplerBindingType::Filtering; |
| |
| wgpu::BindGroupLayoutDescriptor descriptor; |
| descriptor.entryCount = 1; |
| descriptor.entries = &entry; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroupLayout(&descriptor), |
| testing::HasSubstr("had more than one of")); |
| } |
| |
| // Test that it is invalid to create a BGL with none one of buffer, |
| // sampler, texture, storageTexture, or externalTexture set. |
| TEST_F(BindGroupLayoutValidationTest, BindGroupLayoutEntryNoneSet) { |
| wgpu::BindGroupLayoutEntry entry = {}; |
| |
| wgpu::BindGroupLayoutDescriptor descriptor; |
| descriptor.entryCount = 1; |
| descriptor.entries = &entry; |
| ASSERT_DEVICE_ERROR(device.CreateBindGroupLayout(&descriptor), |
| testing::HasSubstr("had none of")); |
| } |
| |
| // This test verifies that visibility of bindings in BindGroupLayout can be none |
| TEST_F(BindGroupLayoutValidationTest, BindGroupLayoutVisibilityNone) { |
| utils::MakeBindGroupLayout(device, |
| { |
| {0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}, |
| }); |
| |
| wgpu::BindGroupLayoutEntry entry; |
| entry.binding = 0; |
| entry.visibility = wgpu::ShaderStage::None; |
| entry.buffer.type = wgpu::BufferBindingType::Uniform; |
| wgpu::BindGroupLayoutDescriptor descriptor; |
| descriptor.entryCount = 1; |
| descriptor.entries = &entry; |
| device.CreateBindGroupLayout(&descriptor); |
| } |
| |
| // This test verifies that binding with none visibility in bind group layout can be supported in |
| // bind group |
| TEST_F(BindGroupLayoutValidationTest, BindGroupLayoutVisibilityNoneExpectsBindGroupEntry) { |
| wgpu::BindGroupLayout bgl = utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Vertex, wgpu::BufferBindingType::Uniform}, |
| {1, wgpu::ShaderStage::None, wgpu::BufferBindingType::Uniform}, |
| }); |
| wgpu::BufferDescriptor descriptor; |
| descriptor.size = 4; |
| descriptor.usage = wgpu::BufferUsage::Uniform; |
| wgpu::Buffer buffer = device.CreateBuffer(&descriptor); |
| |
| utils::MakeBindGroup(device, bgl, {{0, buffer}, {1, buffer}}); |
| |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroup(device, bgl, {{0, buffer}})); |
| } |
| |
| #define BGLEntryType(...) \ |
| utils::BindingLayoutEntryInitializationHelper(0, wgpu::ShaderStage::Compute, __VA_ARGS__) |
| |
| TEST_F(BindGroupLayoutValidationTest, PerStageLimits) { |
| struct TestInfo { |
| uint32_t maxCount; |
| wgpu::BindGroupLayoutEntry entry; |
| wgpu::BindGroupLayoutEntry otherEntry; |
| }; |
| |
| wgpu::Limits limits = GetSupportedLimits().limits; |
| |
| std::array<TestInfo, 7> kTestInfos = { |
| TestInfo{limits.maxSampledTexturesPerShaderStage, |
| BGLEntryType(wgpu::TextureSampleType::Float), |
| BGLEntryType(wgpu::BufferBindingType::Uniform)}, |
| TestInfo{limits.maxSamplersPerShaderStage, |
| BGLEntryType(wgpu::SamplerBindingType::Filtering), |
| BGLEntryType(wgpu::BufferBindingType::Uniform)}, |
| TestInfo{limits.maxSamplersPerShaderStage, |
| BGLEntryType(wgpu::SamplerBindingType::Comparison), |
| BGLEntryType(wgpu::BufferBindingType::Uniform)}, |
| TestInfo{limits.maxStorageBuffersPerShaderStage, |
| BGLEntryType(wgpu::BufferBindingType::Storage), |
| BGLEntryType(wgpu::BufferBindingType::Uniform)}, |
| TestInfo{ |
| limits.maxStorageTexturesPerShaderStage, |
| BGLEntryType(wgpu::StorageTextureAccess::WriteOnly, wgpu::TextureFormat::RGBA8Unorm), |
| BGLEntryType(wgpu::BufferBindingType::Uniform)}, |
| TestInfo{limits.maxUniformBuffersPerShaderStage, |
| BGLEntryType(wgpu::BufferBindingType::Uniform), |
| BGLEntryType(wgpu::TextureSampleType::Float)}, |
| // External textures use multiple bindings (3 sampled textures, 1 sampler, 1 uniform buffer) |
| // that count towards the per stage binding limits. The number of external textures are |
| // currently restricted by the maximum number of sampled textures. |
| TestInfo{limits.maxSampledTexturesPerShaderStage / kSampledTexturesPerExternalTexture, |
| BGLEntryType(&utils::kExternalTextureBindingLayout), |
| BGLEntryType(wgpu::BufferBindingType::Uniform)}}; |
| |
| for (TestInfo info : kTestInfos) { |
| wgpu::BindGroupLayout bgl[2]; |
| std::vector<utils::BindingLayoutEntryInitializationHelper> maxBindings; |
| |
| for (uint32_t i = 0; i < info.maxCount; ++i) { |
| wgpu::BindGroupLayoutEntry entry = info.entry; |
| entry.binding = i; |
| maxBindings.push_back(entry); |
| } |
| |
| // Creating with the maxes works. |
| bgl[0] = MakeBindGroupLayout(maxBindings.data(), maxBindings.size()); |
| |
| // Adding an extra binding of a different type works. |
| { |
| std::vector<utils::BindingLayoutEntryInitializationHelper> bindings = maxBindings; |
| wgpu::BindGroupLayoutEntry entry = info.otherEntry; |
| entry.binding = info.maxCount; |
| bindings.push_back(entry); |
| MakeBindGroupLayout(bindings.data(), bindings.size()); |
| } |
| |
| // Adding an extra binding of the maxed type in a different stage works |
| { |
| std::vector<utils::BindingLayoutEntryInitializationHelper> bindings = maxBindings; |
| wgpu::BindGroupLayoutEntry entry = info.entry; |
| entry.binding = info.maxCount; |
| entry.visibility = wgpu::ShaderStage::Fragment; |
| bindings.push_back(entry); |
| MakeBindGroupLayout(bindings.data(), bindings.size()); |
| } |
| |
| // Adding an extra binding of the maxed type and stage exceeds the per stage limit. |
| { |
| std::vector<utils::BindingLayoutEntryInitializationHelper> bindings = maxBindings; |
| wgpu::BindGroupLayoutEntry entry = info.entry; |
| entry.binding = info.maxCount; |
| bindings.push_back(entry); |
| ASSERT_DEVICE_ERROR(MakeBindGroupLayout(bindings.data(), bindings.size())); |
| } |
| |
| // Creating a pipeline layout from the valid BGL works. |
| TestCreatePipelineLayout(bgl, 1, true); |
| |
| // Adding an extra binding of a different type in a different BGL works |
| bgl[1] = utils::MakeBindGroupLayout(device, {info.otherEntry}); |
| TestCreatePipelineLayout(bgl, 2, true); |
| |
| { |
| // Adding an extra binding of the maxed type in a different stage works |
| wgpu::BindGroupLayoutEntry entry = info.entry; |
| entry.visibility = wgpu::ShaderStage::Fragment; |
| bgl[1] = utils::MakeBindGroupLayout(device, {entry}); |
| TestCreatePipelineLayout(bgl, 2, true); |
| } |
| |
| // Adding an extra binding of the maxed type in a different BGL exceeds the per stage limit. |
| bgl[1] = utils::MakeBindGroupLayout(device, {info.entry}); |
| TestCreatePipelineLayout(bgl, 2, false); |
| } |
| } |
| |
| // External textures require multiple binding slots (3 sampled texture, 1 uniform buffer, 1 |
| // sampler), so ensure that these count towards the limit when combined non-external texture |
| // bindings. |
| TEST_F(BindGroupLayoutValidationTest, PerStageLimitsWithExternalTexture) { |
| struct TestInfo { |
| uint32_t maxCount; |
| uint32_t bindingsPerExternalTexture; |
| wgpu::BindGroupLayoutEntry entry; |
| wgpu::BindGroupLayoutEntry otherEntry; |
| }; |
| |
| wgpu::Limits limits = GetSupportedLimits().limits; |
| |
| std::array<TestInfo, 3> kTestInfos = { |
| TestInfo{limits.maxSampledTexturesPerShaderStage, kSampledTexturesPerExternalTexture, |
| BGLEntryType(wgpu::TextureSampleType::Float), |
| BGLEntryType(wgpu::BufferBindingType::Uniform)}, |
| TestInfo{limits.maxSamplersPerShaderStage, kSamplersPerExternalTexture, |
| BGLEntryType(wgpu::SamplerBindingType::Filtering), |
| BGLEntryType(wgpu::BufferBindingType::Uniform)}, |
| TestInfo{limits.maxUniformBuffersPerShaderStage, kUniformsPerExternalTexture, |
| BGLEntryType(wgpu::BufferBindingType::Uniform), |
| BGLEntryType(wgpu::TextureSampleType::Float)}, |
| }; |
| |
| for (TestInfo info : kTestInfos) { |
| wgpu::BindGroupLayout bgl[2]; |
| std::vector<utils::BindingLayoutEntryInitializationHelper> maxBindings; |
| |
| // Create an external texture binding layout entry |
| wgpu::BindGroupLayoutEntry firstEntry = BGLEntryType(&utils::kExternalTextureBindingLayout); |
| firstEntry.binding = 0; |
| maxBindings.push_back(firstEntry); |
| |
| // Create the other bindings such that we reach the max bindings per stage when including |
| // the external texture. |
| for (uint32_t i = 1; i <= info.maxCount - info.bindingsPerExternalTexture; ++i) { |
| wgpu::BindGroupLayoutEntry entry = info.entry; |
| entry.binding = i; |
| maxBindings.push_back(entry); |
| } |
| |
| // Ensure that creation without the external texture works. |
| bgl[0] = MakeBindGroupLayout(maxBindings.data(), maxBindings.size()); |
| |
| // Adding an extra binding of a different type works. |
| { |
| std::vector<utils::BindingLayoutEntryInitializationHelper> bindings = maxBindings; |
| wgpu::BindGroupLayoutEntry entry = info.otherEntry; |
| entry.binding = info.maxCount; |
| bindings.push_back(entry); |
| MakeBindGroupLayout(bindings.data(), bindings.size()); |
| } |
| |
| // Adding an extra binding of the maxed type in a different stage works |
| { |
| std::vector<utils::BindingLayoutEntryInitializationHelper> bindings = maxBindings; |
| wgpu::BindGroupLayoutEntry entry = info.entry; |
| entry.binding = info.maxCount; |
| entry.visibility = wgpu::ShaderStage::Fragment; |
| bindings.push_back(entry); |
| MakeBindGroupLayout(bindings.data(), bindings.size()); |
| } |
| |
| // Adding an extra binding of the maxed type and stage exceeds the per stage limit. |
| { |
| std::vector<utils::BindingLayoutEntryInitializationHelper> bindings = maxBindings; |
| wgpu::BindGroupLayoutEntry entry = info.entry; |
| entry.binding = info.maxCount; |
| bindings.push_back(entry); |
| ASSERT_DEVICE_ERROR(MakeBindGroupLayout(bindings.data(), bindings.size())); |
| } |
| |
| // Creating a pipeline layout from the valid BGL works. |
| TestCreatePipelineLayout(bgl, 1, true); |
| |
| // Adding an extra binding of a different type in a different BGL works |
| bgl[1] = utils::MakeBindGroupLayout(device, {info.otherEntry}); |
| TestCreatePipelineLayout(bgl, 2, true); |
| |
| { |
| // Adding an extra binding of the maxed type in a different stage works |
| wgpu::BindGroupLayoutEntry entry = info.entry; |
| entry.visibility = wgpu::ShaderStage::Fragment; |
| bgl[1] = utils::MakeBindGroupLayout(device, {entry}); |
| TestCreatePipelineLayout(bgl, 2, true); |
| } |
| |
| // Adding an extra binding of the maxed type in a different BGL exceeds the per stage limit. |
| bgl[1] = utils::MakeBindGroupLayout(device, {info.entry}); |
| TestCreatePipelineLayout(bgl, 2, false); |
| } |
| } |
| |
| // Check that dynamic buffer numbers exceed maximum value in one bind group layout. |
| TEST_F(BindGroupLayoutValidationTest, DynamicBufferNumberLimit) { |
| wgpu::BindGroupLayout bgl[2]; |
| std::vector<wgpu::BindGroupLayoutEntry> maxUniformDB; |
| std::vector<wgpu::BindGroupLayoutEntry> maxStorageDB; |
| std::vector<wgpu::BindGroupLayoutEntry> maxReadonlyStorageDB; |
| |
| wgpu::Limits limits = GetSupportedLimits().limits; |
| |
| // In this test, we use all the same shader stage. Ensure that this does not exceed the |
| // per-stage limit. |
| DAWN_ASSERT(limits.maxDynamicUniformBuffersPerPipelineLayout <= |
| limits.maxUniformBuffersPerShaderStage); |
| DAWN_ASSERT(limits.maxDynamicStorageBuffersPerPipelineLayout <= |
| limits.maxStorageBuffersPerShaderStage); |
| |
| for (uint32_t i = 0; i < limits.maxDynamicUniformBuffersPerPipelineLayout; ++i) { |
| maxUniformDB.push_back(utils::BindingLayoutEntryInitializationHelper( |
| i, wgpu::ShaderStage::Compute, wgpu::BufferBindingType::Uniform, true)); |
| } |
| |
| for (uint32_t i = 0; i < limits.maxDynamicStorageBuffersPerPipelineLayout; ++i) { |
| maxStorageDB.push_back(utils::BindingLayoutEntryInitializationHelper( |
| i, wgpu::ShaderStage::Compute, wgpu::BufferBindingType::Storage, true)); |
| } |
| |
| for (uint32_t i = 0; i < limits.maxDynamicStorageBuffersPerPipelineLayout; ++i) { |
| maxReadonlyStorageDB.push_back(utils::BindingLayoutEntryInitializationHelper( |
| i, wgpu::ShaderStage::Compute, wgpu::BufferBindingType::ReadOnlyStorage, true)); |
| } |
| |
| // Test creating with the maxes works |
| { |
| bgl[0] = MakeBindGroupLayout(maxUniformDB.data(), maxUniformDB.size()); |
| TestCreatePipelineLayout(bgl, 1, true); |
| |
| bgl[0] = MakeBindGroupLayout(maxStorageDB.data(), maxStorageDB.size()); |
| TestCreatePipelineLayout(bgl, 1, true); |
| |
| bgl[0] = MakeBindGroupLayout(maxReadonlyStorageDB.data(), maxReadonlyStorageDB.size()); |
| TestCreatePipelineLayout(bgl, 1, true); |
| } |
| |
| // The following tests exceed the per-pipeline layout limits. We use the Fragment stage to |
| // ensure we don't hit the per-stage limit. |
| |
| // Check dynamic uniform buffers exceed maximum in pipeline layout. |
| { |
| bgl[0] = MakeBindGroupLayout(maxUniformDB.data(), maxUniformDB.size()); |
| bgl[1] = utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Uniform, true}, |
| }); |
| |
| TestCreatePipelineLayout(bgl, 2, false); |
| } |
| |
| // Check dynamic storage buffers exceed maximum in pipeline layout |
| { |
| bgl[0] = MakeBindGroupLayout(maxStorageDB.data(), maxStorageDB.size()); |
| bgl[1] = utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::Storage, true}, |
| }); |
| |
| TestCreatePipelineLayout(bgl, 2, false); |
| } |
| |
| // Check dynamic readonly storage buffers exceed maximum in pipeline layout |
| { |
| bgl[0] = MakeBindGroupLayout(maxReadonlyStorageDB.data(), maxReadonlyStorageDB.size()); |
| bgl[1] = utils::MakeBindGroupLayout( |
| device, |
| { |
| {0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::ReadOnlyStorage, true}, |
| }); |
| |
| TestCreatePipelineLayout(bgl, 2, false); |
| } |
| |
| // Check dynamic storage buffers + dynamic readonly storage buffers exceed maximum storage |
| // buffers in pipeline layout |
| { |
| bgl[0] = MakeBindGroupLayout(maxStorageDB.data(), maxStorageDB.size()); |
| bgl[1] = utils::MakeBindGroupLayout( |
| device, |
| { |
| {0, wgpu::ShaderStage::Fragment, wgpu::BufferBindingType::ReadOnlyStorage, true}, |
| }); |
| |
| TestCreatePipelineLayout(bgl, 2, false); |
| } |
| |
| // Check dynamic uniform buffers exceed maximum in bind group layout. |
| { |
| maxUniformDB.push_back(utils::BindingLayoutEntryInitializationHelper( |
| limits.maxDynamicUniformBuffersPerPipelineLayout, wgpu::ShaderStage::Fragment, |
| wgpu::BufferBindingType::Uniform, true)); |
| TestCreateBindGroupLayout(maxUniformDB.data(), maxUniformDB.size(), false); |
| } |
| |
| // Check dynamic storage buffers exceed maximum in bind group layout. |
| { |
| maxStorageDB.push_back(utils::BindingLayoutEntryInitializationHelper( |
| limits.maxDynamicStorageBuffersPerPipelineLayout, wgpu::ShaderStage::Fragment, |
| wgpu::BufferBindingType::Storage, true)); |
| TestCreateBindGroupLayout(maxStorageDB.data(), maxStorageDB.size(), false); |
| } |
| |
| // Check dynamic readonly storage buffers exceed maximum in bind group layout. |
| { |
| maxReadonlyStorageDB.push_back(utils::BindingLayoutEntryInitializationHelper( |
| limits.maxDynamicStorageBuffersPerPipelineLayout, wgpu::ShaderStage::Fragment, |
| wgpu::BufferBindingType::ReadOnlyStorage, true)); |
| TestCreateBindGroupLayout(maxReadonlyStorageDB.data(), maxReadonlyStorageDB.size(), false); |
| } |
| } |
| |
| // Test that multisampled textures must be 2D sampled textures |
| TEST_F(BindGroupLayoutValidationTest, MultisampledTextureViewDimension) { |
| // Multisampled 2D texture works. |
| utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureViewDimension::e2D, true}, |
| }); |
| |
| // Multisampled 2D (defaulted) texture works. |
| utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureViewDimension::Undefined, true}, |
| }); |
| |
| // Multisampled 2D array texture is invalid. |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureViewDimension::e2DArray, true}, |
| })); |
| |
| // Multisampled cube texture is invalid. |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureViewDimension::Cube, true}, |
| })); |
| |
| // Multisampled cube array texture is invalid. |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureViewDimension::CubeArray, true}, |
| })); |
| |
| // Multisampled 3D texture is invalid. |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureViewDimension::e3D, true}, |
| })); |
| |
| // Multisampled 1D texture is invalid. |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureViewDimension::e1D, true}, |
| })); |
| } |
| |
| // Test that multisampled texture bindings are valid |
| TEST_F(BindGroupLayoutValidationTest, MultisampledTextureSampleType) { |
| // Multisampled float sample type is not supported. |
| ASSERT_DEVICE_ERROR(utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::Float, |
| wgpu::TextureViewDimension::e2D, true}, |
| })); |
| |
| // Multisampled unfilterable float sample type works. |
| utils::MakeBindGroupLayout( |
| device, { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::UnfilterableFloat, |
| wgpu::TextureViewDimension::e2D, true}, |
| }); |
| |
| // Multisampled uint sample type works. |
| utils::MakeBindGroupLayout(device, |
| { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::Uint, |
| wgpu::TextureViewDimension::e2D, true}, |
| }); |
| |
| // Multisampled sint sample type works. |
| utils::MakeBindGroupLayout(device, |
| { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::Sint, |
| wgpu::TextureViewDimension::e2D, true}, |
| }); |
| |
| // Multisampled depth sample type works. |
| utils::MakeBindGroupLayout(device, |
| { |
| {0, wgpu::ShaderStage::Compute, wgpu::TextureSampleType::Depth, |
| wgpu::TextureViewDimension::e2D, true}, |
| }); |
| } |
| |
| // Tests that creating a bind group layout with a valid static sampler raises an error |
| // if the required feature is not enabled. |
| TEST_F(BindGroupLayoutValidationTest, StaticSamplerNotSupportedWithoutFeatureEnabled) { |
| wgpu::BindGroupLayoutEntry binding = {}; |
| binding.binding = 0; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| staticSamplerBinding.sampler = device.CreateSampler(); |
| binding.nextInChain = &staticSamplerBinding; |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 1; |
| desc.entries = &binding; |
| |
| ASSERT_DEVICE_ERROR(device.CreateBindGroupLayout(&desc)); |
| } |
| |
| class BindGroupLayoutWithStaticSamplersValidationTest : public BindGroupLayoutValidationTest { |
| WGPUDevice CreateTestDevice(native::Adapter dawnAdapter, |
| wgpu::DeviceDescriptor descriptor) override { |
| wgpu::FeatureName requiredFeatures[1] = {wgpu::FeatureName::StaticSamplers}; |
| descriptor.requiredFeatures = requiredFeatures; |
| descriptor.requiredFeatureCount = 1; |
| return dawnAdapter.CreateDevice(&descriptor); |
| } |
| }; |
| |
| // Tests that creating a bind group layout with a valid static sampler succeeds if the |
| // required feature is enabled. |
| TEST_F(BindGroupLayoutWithStaticSamplersValidationTest, StaticSamplerSupportedWhenFeatureEnabled) { |
| wgpu::BindGroupLayoutEntry binding = {}; |
| binding.binding = 0; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| staticSamplerBinding.sampler = device.CreateSampler(); |
| binding.nextInChain = &staticSamplerBinding; |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 1; |
| desc.entries = &binding; |
| |
| device.CreateBindGroupLayout(&desc); |
| } |
| |
| // Tests that creating a bind group layout with a static sampler that has an |
| // invalid sampler object fails. |
| TEST_F(BindGroupLayoutWithStaticSamplersValidationTest, StaticSamplerWithInvalidSamplerObject) { |
| wgpu::BindGroupLayoutEntry binding = {}; |
| binding.binding = 0; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| |
| wgpu::SamplerDescriptor samplerDesc; |
| samplerDesc.minFilter = static_cast<wgpu::FilterMode>(0xFFFFFFFF); |
| |
| wgpu::Sampler errorSampler; |
| ASSERT_DEVICE_ERROR(errorSampler = device.CreateSampler(&samplerDesc)); |
| |
| staticSamplerBinding.sampler = errorSampler; |
| binding.nextInChain = &staticSamplerBinding; |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 1; |
| desc.entries = &binding; |
| |
| ASSERT_DEVICE_ERROR(device.CreateBindGroupLayout(&desc)); |
| } |
| |
| // Verifies that creation of a bind group with no entry for a static sampler |
| // succeeds. |
| TEST_F(BindGroupLayoutWithStaticSamplersValidationTest, CreateBindGroupWithStaticSamplerSupported) { |
| wgpu::BindGroupLayoutEntry binding = {}; |
| binding.binding = 0; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| staticSamplerBinding.sampler = device.CreateSampler(); |
| binding.nextInChain = &staticSamplerBinding; |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 1; |
| desc.entries = &binding; |
| |
| wgpu::BindGroupLayout layout = device.CreateBindGroupLayout(&desc); |
| |
| wgpu::BindGroupDescriptor descriptor; |
| descriptor.layout = layout; |
| descriptor.entryCount = 0; |
| |
| device.CreateBindGroup(&descriptor); |
| } |
| |
| // Verifies that creation of a correctly-specified bind group for a layout that |
| // has a static sampler and a sampler succeeds. |
| TEST_F(BindGroupLayoutWithStaticSamplersValidationTest, |
| CreateBindGroupWithStaticSamplerAndSamplerSupported) { |
| std::vector<wgpu::BindGroupLayoutEntry> entries; |
| |
| wgpu::BindGroupLayoutEntry binding0 = {}; |
| binding0.binding = 0; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| staticSamplerBinding.sampler = device.CreateSampler(); |
| binding0.nextInChain = &staticSamplerBinding; |
| entries.push_back(binding0); |
| |
| wgpu::BindGroupLayoutEntry binding1 = {}; |
| binding1.binding = 1; |
| binding1.sampler.type = wgpu::SamplerBindingType::Filtering; |
| entries.push_back(binding1); |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 2; |
| desc.entries = entries.data(); |
| |
| wgpu::BindGroupLayout layout = device.CreateBindGroupLayout(&desc); |
| |
| wgpu::SamplerDescriptor samplerDesc; |
| samplerDesc.minFilter = wgpu::FilterMode::Linear; |
| utils::MakeBindGroup(device, layout, {{1, device.CreateSampler(&samplerDesc)}}); |
| } |
| |
| // Verifies that creation of a correctly-specified bind group for a layout that |
| // has a sampler and a static sampler succeeds. |
| TEST_F(BindGroupLayoutWithStaticSamplersValidationTest, |
| CreateBindGroupWithSamplerAndStaticSamplerSupported) { |
| std::vector<wgpu::BindGroupLayoutEntry> entries; |
| |
| wgpu::BindGroupLayoutEntry binding0 = {}; |
| binding0.binding = 0; |
| binding0.sampler.type = wgpu::SamplerBindingType::Filtering; |
| entries.push_back(binding0); |
| |
| wgpu::BindGroupLayoutEntry binding1 = {}; |
| binding1.binding = 1; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| staticSamplerBinding.sampler = device.CreateSampler(); |
| binding1.nextInChain = &staticSamplerBinding; |
| entries.push_back(binding1); |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 2; |
| desc.entries = entries.data(); |
| |
| wgpu::BindGroupLayout layout = device.CreateBindGroupLayout(&desc); |
| |
| wgpu::SamplerDescriptor samplerDesc; |
| samplerDesc.minFilter = wgpu::FilterMode::Linear; |
| utils::MakeBindGroup(device, layout, {{0, device.CreateSampler(&samplerDesc)}}); |
| } |
| |
| // Verifies that creating a bind group with an entry for a static sampler causes |
| // an error. |
| TEST_F(BindGroupLayoutWithStaticSamplersValidationTest, |
| EntryForStaticSamplerInBindGroupCausesError) { |
| wgpu::BindGroupLayoutEntry binding = {}; |
| binding.binding = 0; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| staticSamplerBinding.sampler = device.CreateSampler(); |
| binding.nextInChain = &staticSamplerBinding; |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 1; |
| desc.entries = &binding; |
| |
| wgpu::BindGroupLayout layout = device.CreateBindGroupLayout(&desc); |
| |
| wgpu::SamplerDescriptor samplerDesc; |
| samplerDesc.minFilter = wgpu::FilterMode::Linear; |
| ASSERT_DEVICE_ERROR( |
| utils::MakeBindGroup(device, layout, {{0, device.CreateSampler(&samplerDesc)}})); |
| } |
| |
| // Verifies that creation of a bind group with the correct number of entries for a layout that has a |
| // sampler and a static sampler raises an error if the entry is specified at the |
| // index of the static sampler rather than that of the sampler. |
| TEST_F(BindGroupLayoutWithStaticSamplersValidationTest, |
| CorrectNumberOfEntriesButEntryForStaticSamplerAtSecondIndexInBindGroupCausesError) { |
| std::vector<wgpu::BindGroupLayoutEntry> entries; |
| |
| wgpu::BindGroupLayoutEntry binding0 = {}; |
| binding0.binding = 0; |
| binding0.sampler.type = wgpu::SamplerBindingType::Filtering; |
| entries.push_back(binding0); |
| |
| wgpu::BindGroupLayoutEntry binding1 = {}; |
| binding1.binding = 1; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| staticSamplerBinding.sampler = device.CreateSampler(); |
| binding1.nextInChain = &staticSamplerBinding; |
| entries.push_back(binding1); |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 2; |
| desc.entries = entries.data(); |
| |
| wgpu::BindGroupLayout layout = device.CreateBindGroupLayout(&desc); |
| |
| wgpu::SamplerDescriptor samplerDesc; |
| samplerDesc.minFilter = wgpu::FilterMode::Linear; |
| ASSERT_DEVICE_ERROR( |
| utils::MakeBindGroup(device, layout, {{1, device.CreateSampler(&samplerDesc)}})); |
| } |
| |
| // Verifies that creation of a bind group with the correct number of entries for a layout that has a |
| // static sampler and a sampler raises an error if the entry is specified at the |
| // index of the static sampler rather than that of the sampler. |
| TEST_F(BindGroupLayoutWithStaticSamplersValidationTest, |
| CorrectNumberOfEntriesButEntryForStaticSamplerInBindGroupCausesError) { |
| std::vector<wgpu::BindGroupLayoutEntry> entries; |
| |
| wgpu::BindGroupLayoutEntry binding0 = {}; |
| binding0.binding = 0; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| staticSamplerBinding.sampler = device.CreateSampler(); |
| binding0.nextInChain = &staticSamplerBinding; |
| entries.push_back(binding0); |
| |
| wgpu::BindGroupLayoutEntry binding1 = {}; |
| binding1.binding = 1; |
| binding1.sampler.type = wgpu::SamplerBindingType::Filtering; |
| entries.push_back(binding1); |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 2; |
| desc.entries = entries.data(); |
| |
| wgpu::BindGroupLayout layout = device.CreateBindGroupLayout(&desc); |
| |
| wgpu::SamplerDescriptor samplerDesc; |
| samplerDesc.minFilter = wgpu::FilterMode::Linear; |
| ASSERT_DEVICE_ERROR( |
| utils::MakeBindGroup(device, layout, {{0, device.CreateSampler(&samplerDesc)}})); |
| } |
| |
| constexpr uint32_t kBindingSize = 8; |
| |
| class SetBindGroupValidationTest : public ValidationTest { |
| public: |
| WGPUDevice CreateTestDevice(native::Adapter dawnAdapter, |
| wgpu::DeviceDescriptor descriptor) override { |
| wgpu::FeatureName requiredFeatures[1] = {wgpu::FeatureName::StaticSamplers}; |
| descriptor.requiredFeatures = requiredFeatures; |
| descriptor.requiredFeatureCount = 1; |
| return dawnAdapter.CreateDevice(&descriptor); |
| } |
| |
| void SetUp() override { |
| ValidationTest::SetUp(); |
| |
| mBindGroupLayout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Compute | wgpu::ShaderStage::Fragment, |
| wgpu::BufferBindingType::Uniform, true}, |
| {1, wgpu::ShaderStage::Compute | wgpu::ShaderStage::Fragment, |
| wgpu::BufferBindingType::Uniform, false}, |
| {2, wgpu::ShaderStage::Compute | wgpu::ShaderStage::Fragment, |
| wgpu::BufferBindingType::Storage, true}, |
| {3, wgpu::ShaderStage::Compute | wgpu::ShaderStage::Fragment, |
| wgpu::BufferBindingType::ReadOnlyStorage, true}}); |
| mMinUniformBufferOffsetAlignment = |
| GetSupportedLimits().limits.minUniformBufferOffsetAlignment; |
| mBufferSize = 3 * mMinUniformBufferOffsetAlignment + 8; |
| } |
| |
| wgpu::Buffer CreateBuffer(uint64_t bufferSize, wgpu::BufferUsage usage) { |
| wgpu::BufferDescriptor bufferDescriptor; |
| bufferDescriptor.size = bufferSize; |
| bufferDescriptor.usage = usage; |
| |
| return device.CreateBuffer(&bufferDescriptor); |
| } |
| |
| wgpu::BindGroupLayout mBindGroupLayout; |
| |
| wgpu::RenderPipeline CreateRenderPipeline() { |
| wgpu::ShaderModule vsModule = utils::CreateShaderModule(device, R"( |
| @vertex fn main() -> @builtin(position) vec4f { |
| return vec4f(); |
| })"); |
| |
| wgpu::ShaderModule fsModule = utils::CreateShaderModule(device, R"( |
| struct S { |
| value : vec2f |
| } |
| |
| @group(0) @binding(0) var<uniform> uBufferDynamic : S; |
| @group(0) @binding(1) var<uniform> uBuffer : S; |
| @group(0) @binding(2) var<storage, read_write> sBufferDynamic : S; |
| @group(0) @binding(3) var<storage, read> sReadonlyBufferDynamic : S; |
| |
| @fragment fn main() { |
| })"); |
| |
| utils::ComboRenderPipelineDescriptor pipelineDescriptor; |
| pipelineDescriptor.vertex.module = vsModule; |
| pipelineDescriptor.cFragment.module = fsModule; |
| pipelineDescriptor.cTargets[0].writeMask = wgpu::ColorWriteMask::None; |
| wgpu::PipelineLayout pipelineLayout = |
| utils::MakeBasicPipelineLayout(device, &mBindGroupLayout); |
| pipelineDescriptor.layout = pipelineLayout; |
| return device.CreateRenderPipeline(&pipelineDescriptor); |
| } |
| |
| wgpu::ComputePipeline CreateComputePipeline() { |
| wgpu::ShaderModule csModule = utils::CreateShaderModule(device, R"( |
| struct S { |
| value : vec2f |
| } |
| |
| @group(0) @binding(0) var<uniform> uBufferDynamic : S; |
| @group(0) @binding(1) var<uniform> uBuffer : S; |
| @group(0) @binding(2) var<storage, read_write> sBufferDynamic : S; |
| @group(0) @binding(3) var<storage, read> sReadonlyBufferDynamic : S; |
| |
| @compute @workgroup_size(4, 4, 1) fn main() { |
| })"); |
| |
| wgpu::PipelineLayout pipelineLayout = |
| utils::MakeBasicPipelineLayout(device, &mBindGroupLayout); |
| |
| wgpu::ComputePipelineDescriptor csDesc; |
| csDesc.layout = pipelineLayout; |
| csDesc.compute.module = csModule; |
| |
| return device.CreateComputePipeline(&csDesc); |
| } |
| |
| wgpu::BindGroup CreateAllTypesBindGroup(uint32_t bindingSize) { |
| wgpu::Buffer uniformBuffer = CreateBuffer(mBufferSize, wgpu::BufferUsage::Uniform); |
| wgpu::Buffer storageBuffer = CreateBuffer(mBufferSize, wgpu::BufferUsage::Storage); |
| wgpu::Buffer readonlyStorageBuffer = CreateBuffer(mBufferSize, wgpu::BufferUsage::Storage); |
| return utils::MakeBindGroup(device, mBindGroupLayout, |
| {{0, uniformBuffer, 0, bindingSize}, |
| {1, uniformBuffer, 0, bindingSize}, |
| {2, storageBuffer, 0, bindingSize}, |
| {3, readonlyStorageBuffer, 0, bindingSize}}); |
| } |
| |
| void TestRenderPassBindGroup(wgpu::BindGroup bindGroup, |
| uint32_t* offsets, |
| uint32_t count, |
| bool expectation) { |
| wgpu::RenderPipeline renderPipeline = CreateRenderPipeline(); |
| PlaceholderRenderPass renderPass(device); |
| |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::RenderPassEncoder renderPassEncoder = commandEncoder.BeginRenderPass(&renderPass); |
| renderPassEncoder.SetPipeline(renderPipeline); |
| if (bindGroup != nullptr) { |
| renderPassEncoder.SetBindGroup(0, bindGroup, count, offsets); |
| } |
| renderPassEncoder.Draw(3); |
| renderPassEncoder.End(); |
| if (!expectation) { |
| ASSERT_DEVICE_ERROR(commandEncoder.Finish()); |
| } else { |
| commandEncoder.Finish(); |
| } |
| } |
| |
| void TestComputePassBindGroup(wgpu::BindGroup bindGroup, |
| uint32_t* offsets, |
| uint32_t count, |
| bool expectation) { |
| wgpu::ComputePipeline computePipeline = CreateComputePipeline(); |
| |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder computePassEncoder = commandEncoder.BeginComputePass(); |
| computePassEncoder.SetPipeline(computePipeline); |
| if (bindGroup != nullptr) { |
| computePassEncoder.SetBindGroup(0, bindGroup, count, offsets); |
| } |
| computePassEncoder.DispatchWorkgroups(1); |
| computePassEncoder.End(); |
| if (!expectation) { |
| ASSERT_DEVICE_ERROR(commandEncoder.Finish()); |
| } else { |
| commandEncoder.Finish(); |
| } |
| } |
| |
| protected: |
| uint32_t mMinUniformBufferOffsetAlignment; |
| uint64_t mBufferSize; |
| }; |
| |
| // This is the test case that should work. |
| TEST_F(SetBindGroupValidationTest, Basic) { |
| // Set up the bind group. |
| wgpu::BindGroup bindGroup = CreateAllTypesBindGroup(kBindingSize); |
| |
| std::array<uint32_t, 3> offsets = {512, 256, 0}; |
| |
| TestRenderPassBindGroup(bindGroup, offsets.data(), 3, true); |
| |
| TestComputePassBindGroup(bindGroup, offsets.data(), 3, true); |
| } |
| |
| // Draw/dispatch with a bind group missing is invalid |
| TEST_F(SetBindGroupValidationTest, MissingBindGroup) { |
| TestRenderPassBindGroup(nullptr, nullptr, 0, false); |
| TestComputePassBindGroup(nullptr, nullptr, 0, false); |
| } |
| |
| // Unset the bind group required by current pipeline is invalid. |
| TEST_F(SetBindGroupValidationTest, UnsetBindGroupWhenNeeded) { |
| // Set up the bind group. |
| wgpu::BindGroup bindGroup = CreateAllTypesBindGroup(kBindingSize); |
| |
| std::array<uint32_t, 3> offsets = {512, 256, 0}; |
| |
| // render pass case |
| { |
| wgpu::RenderPipeline renderPipeline = CreateRenderPipeline(); |
| PlaceholderRenderPass renderPass(device); |
| |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::RenderPassEncoder renderPassEncoder = commandEncoder.BeginRenderPass(&renderPass); |
| renderPassEncoder.SetPipeline(renderPipeline); |
| renderPassEncoder.SetBindGroup(0, bindGroup, offsets.size(), offsets.data()); |
| // Unset the bind group which is required by the current pipeline. |
| renderPassEncoder.SetBindGroup(0, nullptr); |
| renderPassEncoder.Draw(3); |
| renderPassEncoder.End(); |
| ASSERT_DEVICE_ERROR(commandEncoder.Finish()); |
| } |
| |
| // compute pass case |
| { |
| wgpu::ComputePipeline computePipeline = CreateComputePipeline(); |
| |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder computePassEncoder = commandEncoder.BeginComputePass(); |
| computePassEncoder.SetPipeline(computePipeline); |
| computePassEncoder.SetBindGroup(0, bindGroup, offsets.size(), offsets.data()); |
| // The pipeline in compute pass requires an appropriate bindgroup, which is missing. |
| computePassEncoder.SetBindGroup(0, nullptr); |
| computePassEncoder.DispatchWorkgroups(1); |
| computePassEncoder.End(); |
| ASSERT_DEVICE_ERROR(commandEncoder.Finish()); |
| } |
| } |
| |
| // Regression test for the validation aspect caching not being invalidated when unsetting a |
| // bind group. |
| TEST_F(SetBindGroupValidationTest, UnsetInvalidatesBindGroupValidationCache) { |
| // Set up the bind group. |
| wgpu::BindGroup bindGroup = CreateAllTypesBindGroup(kBindingSize); |
| |
| std::array<uint32_t, 3> offsets = {512, 256, 0}; |
| |
| // Render pass case |
| { |
| wgpu::RenderPipeline renderPipeline = CreateRenderPipeline(); |
| PlaceholderRenderPass renderPass(device); |
| |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::RenderPassEncoder renderPassEncoder = commandEncoder.BeginRenderPass(&renderPass); |
| renderPassEncoder.SetPipeline(renderPipeline); |
| renderPassEncoder.SetBindGroup(0, bindGroup, 3, offsets.data()); |
| renderPassEncoder.Draw(3); |
| // Unset the bindgroup after draw. The bindgroup might be cached by the previous draw. |
| renderPassEncoder.SetBindGroup(0, nullptr); |
| renderPassEncoder.Draw(3); |
| renderPassEncoder.End(); |
| ASSERT_DEVICE_ERROR(commandEncoder.Finish()); |
| } |
| |
| // Compute pass case |
| { |
| wgpu::ComputePipeline computePipeline = CreateComputePipeline(); |
| |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder computePassEncoder = commandEncoder.BeginComputePass(); |
| computePassEncoder.SetPipeline(computePipeline); |
| computePassEncoder.SetBindGroup(0, bindGroup, 3, offsets.data()); |
| computePassEncoder.DispatchWorkgroups(1); |
| // Unset the bindgroup after dispatch. The bindgroup might be cached by the previous |
| // dispatch. |
| computePassEncoder.SetBindGroup(0, nullptr); |
| computePassEncoder.DispatchWorkgroups(1); |
| computePassEncoder.End(); |
| ASSERT_DEVICE_ERROR(commandEncoder.Finish()); |
| } |
| } |
| |
| // Setting bind group after a draw / dispatch should re-verify the layout is compatible |
| TEST_F(SetBindGroupValidationTest, VerifyGroupIfChangedAfterAction) { |
| // Set up the bind group |
| wgpu::Buffer uniformBuffer = CreateBuffer(mBufferSize, wgpu::BufferUsage::Uniform); |
| wgpu::Buffer storageBuffer = CreateBuffer(mBufferSize, wgpu::BufferUsage::Storage); |
| wgpu::Buffer readonlyStorageBuffer = CreateBuffer(mBufferSize, wgpu::BufferUsage::Storage); |
| wgpu::BindGroup bindGroup = utils::MakeBindGroup(device, mBindGroupLayout, |
| {{0, uniformBuffer, 0, kBindingSize}, |
| {1, uniformBuffer, 0, kBindingSize}, |
| {2, storageBuffer, 0, kBindingSize}, |
| {3, readonlyStorageBuffer, 0, kBindingSize}}); |
| |
| std::array<uint32_t, 3> offsets = {512, 256, 0}; |
| |
| // Set up bind group that is incompatible |
| wgpu::BindGroupLayout invalidLayout = utils::MakeBindGroupLayout( |
| device, {{0, wgpu::ShaderStage::Compute | wgpu::ShaderStage::Fragment, |
| wgpu::BufferBindingType::Storage}}); |
| wgpu::BindGroup invalidGroup = |
| utils::MakeBindGroup(device, invalidLayout, {{0, storageBuffer, 0, kBindingSize}}); |
| |
| { |
| wgpu::ComputePipeline computePipeline = CreateComputePipeline(); |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder computePassEncoder = commandEncoder.BeginComputePass(); |
| computePassEncoder.SetPipeline(computePipeline); |
| computePassEncoder.SetBindGroup(0, bindGroup, 3, offsets.data()); |
| computePassEncoder.DispatchWorkgroups(1); |
| computePassEncoder.SetBindGroup(0, invalidGroup, 0, nullptr); |
| computePassEncoder.DispatchWorkgroups(1); |
| computePassEncoder.End(); |
| ASSERT_DEVICE_ERROR(commandEncoder.Finish()); |
| } |
| { |
| wgpu::RenderPipeline renderPipeline = CreateRenderPipeline(); |
| PlaceholderRenderPass renderPass(device); |
| |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::RenderPassEncoder renderPassEncoder = commandEncoder.BeginRenderPass(&renderPass); |
| renderPassEncoder.SetPipeline(renderPipeline); |
| renderPassEncoder.SetBindGroup(0, bindGroup, 3, offsets.data()); |
| renderPassEncoder.Draw(3); |
| renderPassEncoder.SetBindGroup(0, invalidGroup, 0, nullptr); |
| renderPassEncoder.Draw(3); |
| renderPassEncoder.End(); |
| ASSERT_DEVICE_ERROR(commandEncoder.Finish()); |
| } |
| } |
| |
| // Test cases that test dynamic offsets count mismatch with bind group layout. |
| TEST_F(SetBindGroupValidationTest, DynamicOffsetsMismatch) { |
| // Set up bind group. |
| wgpu::BindGroup bindGroup = CreateAllTypesBindGroup(kBindingSize); |
| |
| // Number of offsets mismatch. |
| std::array<uint32_t, 4> mismatchOffsets = {768, 512, 256, 0}; |
| |
| TestRenderPassBindGroup(bindGroup, mismatchOffsets.data(), 1, false); |
| TestRenderPassBindGroup(bindGroup, mismatchOffsets.data(), 2, false); |
| TestRenderPassBindGroup(bindGroup, mismatchOffsets.data(), 4, false); |
| |
| TestComputePassBindGroup(bindGroup, mismatchOffsets.data(), 1, false); |
| TestComputePassBindGroup(bindGroup, mismatchOffsets.data(), 2, false); |
| TestComputePassBindGroup(bindGroup, mismatchOffsets.data(), 4, false); |
| } |
| |
| // Test cases that test dynamic offsets not aligned |
| TEST_F(SetBindGroupValidationTest, DynamicOffsetsNotAligned) { |
| // Set up bind group. |
| wgpu::BindGroup bindGroup = CreateAllTypesBindGroup(kBindingSize); |
| |
| // Dynamic offsets are not aligned. |
| std::array<uint32_t, 3> notAlignedOffsets = {512, 128, 0}; |
| |
| TestRenderPassBindGroup(bindGroup, notAlignedOffsets.data(), 3, false); |
| |
| TestComputePassBindGroup(bindGroup, notAlignedOffsets.data(), 3, false); |
| } |
| |
| // Test cases that test dynamic uniform buffer out of bound situation. |
| TEST_F(SetBindGroupValidationTest, OffsetOutOfBoundDynamicUniformBuffer) { |
| // Set up bind group. |
| wgpu::BindGroup bindGroup = CreateAllTypesBindGroup(kBindingSize); |
| |
| // Dynamic offset + offset is larger than buffer size. |
| std::array<uint32_t, 3> overFlowOffsets = {1024, 256, 0}; |
| |
| TestRenderPassBindGroup(bindGroup, overFlowOffsets.data(), 3, false); |
| |
| TestComputePassBindGroup(bindGroup, overFlowOffsets.data(), 3, false); |
| } |
| |
| // Test cases that test dynamic storage buffer out of bound situation. |
| TEST_F(SetBindGroupValidationTest, OffsetOutOfBoundDynamicStorageBuffer) { |
| // Set up bind group. |
| wgpu::BindGroup bindGroup = CreateAllTypesBindGroup(kBindingSize); |
| |
| // Dynamic offset + offset is larger than buffer size. |
| std::array<uint32_t, 3> overFlowOffsets = {0, 256, 1024}; |
| |
| TestRenderPassBindGroup(bindGroup, overFlowOffsets.data(), 3, false); |
| |
| TestComputePassBindGroup(bindGroup, overFlowOffsets.data(), 3, false); |
| } |
| |
| // Test cases that test dynamic uniform buffer out of bound situation because of binding size. |
| TEST_F(SetBindGroupValidationTest, BindingSizeOutOfBoundDynamicUniformBuffer) { |
| // Set up bind group, but binding size is larger than (mBufferSize - DynamicOffset). |
| constexpr uint32_t kLargeBindingSize = kBindingSize + 4u; |
| wgpu::BindGroup bindGroup = CreateAllTypesBindGroup(kLargeBindingSize); |
| |
| // c + offset isn't larger than buffer size. |
| // But with binding size, it will trigger OOB error. |
| std::array<uint32_t, 3> offsets = {768, 256, 0}; |
| |
| TestRenderPassBindGroup(bindGroup, offsets.data(), 3, false); |
| |
| TestComputePassBindGroup(bindGroup, offsets.data(), 3, false); |
| } |
| |
| // Test cases that test dynamic storage buffer out of bound situation because of binding size. |
| TEST_F(SetBindGroupValidationTest, BindingSizeOutOfBoundDynamicStorageBuffer) { |
| constexpr uint32_t kLargeBindingSize = kBindingSize + 4u; |
| wgpu::BindGroup bindGroup = CreateAllTypesBindGroup(kLargeBindingSize); |
| |
| // Dynamic offset + offset isn't larger than buffer size. |
| // But with binding size, it will trigger OOB error. |
| std::array<uint32_t, 3> offsets = {0, 256, 768}; |
| |
| TestRenderPassBindGroup(bindGroup, offsets.data(), 3, false); |
| |
| TestComputePassBindGroup(bindGroup, offsets.data(), 3, false); |
| } |
| |
| // Regression test for crbug.com/dawn/408 where dynamic offsets were applied in the wrong order. |
| // Dynamic offsets should be applied in increasing order of binding number. |
| TEST_F(SetBindGroupValidationTest, DynamicOffsetOrder) { |
| // Note: The order of the binding numbers of the bind group and bind group layout are |
| // intentionally different and not in increasing order. |
| // This test uses both storage and uniform buffers to ensure buffer bindings are sorted first by |
| // binding number before type. |
| wgpu::BindGroupLayout bgl = utils::MakeBindGroupLayout( |
| device, { |
| {3, wgpu::ShaderStage::Compute, wgpu::BufferBindingType::ReadOnlyStorage, true}, |
| {0, wgpu::ShaderStage::Compute, wgpu::BufferBindingType::ReadOnlyStorage, true}, |
| {2, wgpu::ShaderStage::Compute, wgpu::BufferBindingType::Uniform, true}, |
| }); |
| |
| // Create buffers which are 3x, 2x, and 1x the size of the minimum buffer offset, plus 4 bytes |
| // to spare (to avoid zero-sized bindings). We will offset the bindings so they reach the very |
| // end of the buffer. Any mismatch applying too-large of an offset to a smaller buffer will hit |
| // the out-of-bounds condition during validation. |
| wgpu::Buffer buffer3x = |
| CreateBuffer(3 * mMinUniformBufferOffsetAlignment + 4, wgpu::BufferUsage::Storage); |
| wgpu::Buffer buffer2x = |
| CreateBuffer(2 * mMinUniformBufferOffsetAlignment + 4, wgpu::BufferUsage::Storage); |
| wgpu::Buffer buffer1x = |
| CreateBuffer(1 * mMinUniformBufferOffsetAlignment + 4, wgpu::BufferUsage::Uniform); |
| wgpu::BindGroup bindGroup = utils::MakeBindGroup(device, bgl, |
| { |
| {0, buffer3x, 0, 4}, |
| {3, buffer2x, 0, 4}, |
| {2, buffer1x, 0, 4}, |
| }); |
| |
| std::array<uint32_t, 3> offsets; |
| { |
| // Base case works. |
| offsets = {/* binding 0 */ 0, |
| /* binding 2 */ 0, |
| /* binding 3 */ 0}; |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder computePassEncoder = commandEncoder.BeginComputePass(); |
| computePassEncoder.SetBindGroup(0, bindGroup, offsets.size(), offsets.data()); |
| computePassEncoder.End(); |
| commandEncoder.Finish(); |
| } |
| { |
| // Offset the first binding to touch the end of the buffer. Should succeed. |
| // Will fail if the offset is applied to the first or second bindings since their buffers |
| // are too small. |
| offsets = {/* binding 0 */ 3 * mMinUniformBufferOffsetAlignment, |
| /* binding 2 */ 0, |
| /* binding 3 */ 0}; |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder computePassEncoder = commandEncoder.BeginComputePass(); |
| computePassEncoder.SetBindGroup(0, bindGroup, offsets.size(), offsets.data()); |
| computePassEncoder.End(); |
| commandEncoder.Finish(); |
| } |
| { |
| // Offset the second binding to touch the end of the buffer. Should succeed. |
| offsets = {/* binding 0 */ 0, |
| /* binding 2 */ 1 * mMinUniformBufferOffsetAlignment, |
| /* binding 3 */ 0}; |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder computePassEncoder = commandEncoder.BeginComputePass(); |
| computePassEncoder.SetBindGroup(0, bindGroup, offsets.size(), offsets.data()); |
| computePassEncoder.End(); |
| commandEncoder.Finish(); |
| } |
| { |
| // Offset the third binding to touch the end of the buffer. Should succeed. |
| // Will fail if the offset is applied to the second binding since its buffer |
| // is too small. |
| offsets = {/* binding 0 */ 0, |
| /* binding 2 */ 0, |
| /* binding 3 */ 2 * mMinUniformBufferOffsetAlignment}; |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder computePassEncoder = commandEncoder.BeginComputePass(); |
| computePassEncoder.SetBindGroup(0, bindGroup, offsets.size(), offsets.data()); |
| computePassEncoder.End(); |
| commandEncoder.Finish(); |
| } |
| { |
| // Offset each binding to touch the end of their buffer. Should succeed. |
| offsets = {/* binding 0 */ 3 * mMinUniformBufferOffsetAlignment, |
| /* binding 2 */ 1 * mMinUniformBufferOffsetAlignment, |
| /* binding 3 */ 2 * mMinUniformBufferOffsetAlignment}; |
| wgpu::CommandEncoder commandEncoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder computePassEncoder = commandEncoder.BeginComputePass(); |
| computePassEncoder.SetBindGroup(0, bindGroup, offsets.size(), offsets.data()); |
| computePassEncoder.End(); |
| commandEncoder.Finish(); |
| } |
| } |
| |
| // Test that an error is produced (and no ASSERTs fired) when using an error bindgroup in |
| // SetBindGroup |
| TEST_F(SetBindGroupValidationTest, ErrorBindGroup) { |
| // Bindgroup creation fails because not all bindings are specified. |
| wgpu::BindGroup bindGroup; |
| ASSERT_DEVICE_ERROR(bindGroup = utils::MakeBindGroup(device, mBindGroupLayout, {})); |
| |
| TestRenderPassBindGroup(bindGroup, nullptr, 0, false); |
| |
| TestComputePassBindGroup(bindGroup, nullptr, 0, false); |
| } |
| |
| // Test validation of the bindgroup slot for OOB. |
| TEST_F(SetBindGroupValidationTest, BindGroupSlotBoundary) { |
| wgpu::BindGroupLayout emptyBGL = utils::MakeBindGroupLayout(device, {}); |
| wgpu::BindGroup emptyBindGroup = utils::MakeBindGroup(device, emptyBGL, {}); |
| |
| PlaceholderRenderPass renderPass(device); |
| |
| auto TestIndex = [=](wgpu::BindGroup bg, uint32_t i, bool valid) { |
| { |
| wgpu::CommandEncoder encoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder cp = encoder.BeginComputePass(); |
| cp.SetBindGroup(i, bg); |
| cp.End(); |
| if (valid) { |
| encoder.Finish(); |
| } else { |
| ASSERT_DEVICE_ERROR(encoder.Finish()); |
| } |
| } |
| |
| { |
| wgpu::CommandEncoder encoder = device.CreateCommandEncoder(); |
| wgpu::RenderPassEncoder rp = encoder.BeginRenderPass(&renderPass); |
| rp.SetBindGroup(i, bg); |
| rp.End(); |
| if (valid) { |
| encoder.Finish(); |
| } else { |
| ASSERT_DEVICE_ERROR(encoder.Finish()); |
| } |
| } |
| |
| { |
| utils::ComboRenderBundleEncoderDescriptor renderBundleDesc = {}; |
| renderBundleDesc.colorFormatCount = 1; |
| renderBundleDesc.cColorFormats[0] = wgpu::TextureFormat::RGBA8Unorm; |
| wgpu::RenderBundleEncoder rb = device.CreateRenderBundleEncoder(&renderBundleDesc); |
| rb.SetBindGroup(i, bg); |
| if (valid) { |
| rb.Finish(); |
| } else { |
| ASSERT_DEVICE_ERROR(rb.Finish()); |
| } |
| } |
| }; |
| |
| // Base |
| TestIndex(emptyBindGroup, 0, true); |
| // Set the last bind group slot is valid |
| TestIndex(emptyBindGroup, kMaxBindGroups - 1, true); |
| // Set pass the last bind group slot is invalid |
| TestIndex(emptyBindGroup, kMaxBindGroups, false); |
| |
| // Unset the slot which is not set before is valid |
| TestIndex(nullptr, 0, true); |
| // Unset the last bind group slot is valid |
| TestIndex(nullptr, kMaxBindGroups - 1, true); |
| // Unset pass the last bind group slot is invalid |
| TestIndex(nullptr, kMaxBindGroups, false); |
| } |
| |
| // Test that dynamic offset count must be zero when unsetting a bindgroup. |
| TEST_F(SetBindGroupValidationTest, UnsetWithDynamicOffsetIsInvalid) { |
| auto TestDynamicOffsetCount = [=](uint32_t count, uint32_t* offsets, bool valid) { |
| { |
| wgpu::CommandEncoder encoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder cp = encoder.BeginComputePass(); |
| cp.SetBindGroup(0, nullptr, count, offsets); |
| cp.End(); |
| if (valid) { |
| encoder.Finish(); |
| } else { |
| ASSERT_DEVICE_ERROR(encoder.Finish()); |
| } |
| } |
| |
| { |
| PlaceholderRenderPass renderPass(device); |
| wgpu::CommandEncoder encoder = device.CreateCommandEncoder(); |
| wgpu::RenderPassEncoder rp = encoder.BeginRenderPass(&renderPass); |
| rp.SetBindGroup(0, nullptr, count, offsets); |
| rp.End(); |
| if (valid) { |
| encoder.Finish(); |
| } else { |
| ASSERT_DEVICE_ERROR(encoder.Finish()); |
| } |
| } |
| |
| { |
| utils::ComboRenderBundleEncoderDescriptor renderBundleDesc = {}; |
| renderBundleDesc.colorFormatCount = 1; |
| renderBundleDesc.cColorFormats[0] = wgpu::TextureFormat::RGBA8Unorm; |
| wgpu::RenderBundleEncoder rb = device.CreateRenderBundleEncoder(&renderBundleDesc); |
| rb.SetBindGroup(0, nullptr, count, offsets); |
| if (valid) { |
| rb.Finish(); |
| } else { |
| ASSERT_DEVICE_ERROR(rb.Finish()); |
| } |
| } |
| }; |
| |
| std::array<uint32_t, 2> offsets = {256, 0}; |
| |
| // When unsetting bindgroup, it is invalid if dynamicOffsetsCount > 0. |
| TestDynamicOffsetCount(2, offsets.data(), false); |
| |
| // When unsetting bindgroup, it is valid if dynamicOffsets is non-null and dynamicOffsetsCount |
| // is 0. |
| TestDynamicOffsetCount(0, offsets.data(), true); |
| } |
| |
| // Test that a pipeline with empty bindgroups layouts requires empty bindgroups to be set. |
| TEST_F(SetBindGroupValidationTest, EmptyBindGroupsAreRequired) { |
| wgpu::BindGroupLayout emptyBGL = utils::MakeBindGroupLayout(device, {}); |
| wgpu::PipelineLayout pl = |
| utils::MakePipelineLayout(device, {emptyBGL, emptyBGL, emptyBGL, emptyBGL}); |
| |
| wgpu::ComputePipelineDescriptor pipelineDesc; |
| pipelineDesc.layout = pl; |
| pipelineDesc.compute.module = utils::CreateShaderModule(device, R"( |
| @compute @workgroup_size(1) fn main() { |
| } |
| )"); |
| wgpu::ComputePipeline pipeline = device.CreateComputePipeline(&pipelineDesc); |
| |
| wgpu::BindGroup emptyBindGroup = utils::MakeBindGroup(device, emptyBGL, {}); |
| |
| // Control case, setting 4 empty bindgroups works. |
| { |
| wgpu::CommandEncoder encoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder pass = encoder.BeginComputePass(); |
| pass.SetPipeline(pipeline); |
| pass.SetBindGroup(0, emptyBindGroup); |
| pass.SetBindGroup(1, emptyBindGroup); |
| pass.SetBindGroup(2, emptyBindGroup); |
| pass.SetBindGroup(3, emptyBindGroup); |
| pass.DispatchWorkgroups(1); |
| pass.End(); |
| encoder.Finish(); |
| } |
| |
| // Error case, setting only the first three empty bindgroups. |
| { |
| wgpu::CommandEncoder encoder = device.CreateCommandEncoder(); |
| wgpu::ComputePassEncoder pass = encoder.BeginComputePass(); |
| pass.SetPipeline(pipeline); |
| pass.SetBindGroup(0, emptyBindGroup); |
| pass.SetBindGroup(1, emptyBindGroup); |
| pass.SetBindGroup(2, emptyBindGroup); |
| pass.DispatchWorkgroups(1); |
| pass.End(); |
| ASSERT_DEVICE_ERROR(encoder.Finish()); |
| } |
| } |
| |
| // Test that a static sampler is valid to access from a shader module. |
| TEST_F(SetBindGroupValidationTest, StaticSamplerAccessedFromShader) { |
| wgpu::BindGroupLayoutEntry binding = {}; |
| binding.binding = 0; |
| binding.visibility = wgpu::ShaderStage::Compute; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| staticSamplerBinding.sampler = device.CreateSampler(); |
| binding.nextInChain = &staticSamplerBinding; |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 1; |
| desc.entries = &binding; |
| |
| wgpu::BindGroupLayout layout = device.CreateBindGroupLayout(&desc); |
| |
| wgpu::PipelineLayout pl = utils::MakePipelineLayout(device, {layout}); |
| |
| wgpu::ComputePipelineDescriptor pipelineDesc; |
| pipelineDesc.layout = pl; |
| pipelineDesc.compute.module = utils::CreateShaderModule(device, R"( |
| @group(0) @binding(0) var s : sampler; |
| @compute @workgroup_size(1) fn main() { |
| _ = s; |
| } |
| )"); |
| device.CreateComputePipeline(&pipelineDesc); |
| } |
| |
| // Test that a static sampler cannot be accessed from a shader module as a |
| // non-sampler variable type. |
| TEST_F(SetBindGroupValidationTest, StaticSamplerAccessedFromShaderAsNonSamplerTypeCausesError) { |
| wgpu::BindGroupLayoutEntry binding = {}; |
| binding.binding = 0; |
| binding.visibility = wgpu::ShaderStage::Compute; |
| wgpu::StaticSamplerBindingLayout staticSamplerBinding = {}; |
| staticSamplerBinding.sampler = device.CreateSampler(); |
| binding.nextInChain = &staticSamplerBinding; |
| |
| wgpu::BindGroupLayoutDescriptor desc = {}; |
| desc.entryCount = 1; |
| desc.entries = &binding; |
| |
| wgpu::BindGroupLayout layout = device.CreateBindGroupLayout(&desc); |
| |
| wgpu::PipelineLayout pl = utils::MakePipelineLayout(device, {layout}); |
| |
| wgpu::ComputePipelineDescriptor pipelineDesc; |
| pipelineDesc.layout = pl; |
| pipelineDesc.compute.module = utils::CreateShaderModule(device, R"( |
| @group(0) @binding(0) var t : texture_2d<f32>; |
| @compute @workgroup_size(1) fn main() { |
| _ = textureDimensions(t); |
| } |
| )"); |
| ASSERT_DEVICE_ERROR(device.CreateComputePipeline(&pipelineDesc)); |
| } |
| |
| class SetBindGroupPersistenceValidationTest : public ValidationTest { |
| protected: |
| void SetUp() override { |
| ValidationTest::SetUp(); |
| |
| mVsModule = utils::CreateShaderModule(device, R"( |
| @vertex fn main() -> @builtin(position) vec4f { |
| return vec4f(); |
| })"); |
| |
| mBufferSize = 3 * GetSupportedLimits().limits.minUniformBufferOffsetAlignment + 8; |
| } |
| |
| wgpu::Buffer CreateBuffer(uint64_t bufferSize, wgpu::BufferUsage usage) { |
| wgpu::BufferDescriptor bufferDescriptor; |
| bufferDescriptor.size = bufferSize; |
| bufferDescriptor.usage = usage; |
| |
| return device.CreateBuffer(&bufferDescriptor); |
| } |
| |
| // Generates bind group layouts and a pipeline from a 2D list of binding types. |
| std::tuple<std::vector<wgpu::BindGroupLayout>, wgpu::RenderPipeline> SetUpLayoutsAndPipeline( |
| std::vector<std::vector<wgpu::BufferBindingType>> layouts) { |
| std::vector<wgpu::BindGroupLayout> bindGroupLayouts(layouts.size()); |
| |
| // Iterate through the desired bind group layouts. |
| for (uint32_t l = 0; l < layouts.size(); ++l) { |
| const auto& layout = layouts[l]; |
| std::vector<wgpu::BindGroupLayoutEntry> bindings(layout.size()); |
| |
| // Iterate through binding types and populate a list of BindGroupLayoutEntrys. |
| for (uint32_t b = 0; b < layout.size(); ++b) { |
| bindings[b] = utils::BindingLayoutEntryInitializationHelper( |
| b, wgpu::ShaderStage::Fragment, layout[b]); |
| } |
| |
| // Create the bind group layout. |
| wgpu::BindGroupLayoutDescriptor bglDescriptor; |
| bglDescriptor.entryCount = bindings.size(); |
| bglDescriptor.entries = bindings.data(); |
| bindGroupLayouts[l] = device.CreateBindGroupLayout(&bglDescriptor); |
| } |
| |
| // Create a pipeline layout from the list of bind group layouts. |
| wgpu::PipelineLayoutDescriptor pipelineLayoutDescriptor; |
|