| // Copyright 2023 The Tint Authors. |
| // |
| // Licensed under the Apache License, Version 2.0 (the "License"); |
| // you may not use this file except in compliance with the License. |
| // You may obtain a copy of the License at |
| // |
| // http://www.apache.org/licenses/LICENSE-2.0 |
| // |
| // Unless required by applicable law or agreed to in writing, software |
| // distributed under the License is distributed on an "AS IS" BASIS, |
| // WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied. |
| // See the License for the specific language governing permissions and |
| // limitations under the License. |
| |
| #include "src/tint/lang/glsl/writer/ast_raise/texture_builtins_from_uniform.h" |
| |
| #include <utility> |
| |
| #include "src/tint/lang/wgsl/ast/transform/helper_test.h" |
| |
| namespace tint::glsl::writer { |
| namespace { |
| |
| using TextureBuiltinsFromUniformTest = ast::transform::TransformTest; |
| |
| TEST_F(TextureBuiltinsFromUniformTest, ShouldRunEmptyModule) { |
| auto* src = R"()"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| EXPECT_FALSE(ShouldRun<TextureBuiltinsFromUniform>(src, data)); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, ShouldRunNoTextureNumLevels) { |
| auto* src = R"( |
| @group(0) @binding(0) var t : texture_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| _ = textureDimensions(t); |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| EXPECT_FALSE(ShouldRun<TextureBuiltinsFromUniform>(src, data)); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, ShouldRunWithTextureNumLevels) { |
| auto* src = R"( |
| @group(0) @binding(0) var t : texture_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = textureNumLevels(t); |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| EXPECT_TRUE(ShouldRun<TextureBuiltinsFromUniform>(src, data)); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, Error_MissingTransformData) { |
| auto* src = R"( |
| @group(0) @binding(0) var t : texture_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = textureNumLevels(t); |
| } |
| )"; |
| |
| auto* expect = |
| "error: missing transform data for tint::glsl::writer::TextureBuiltinsFromUniform"; |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src); |
| |
| EXPECT_EQ(expect, str(got)); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, BasicTextureNumLevels) { |
| auto* src = R"( |
| @group(0) @binding(0) var t : texture_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = textureNumLevels(t); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol { |
| texture_builtin_value_0 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_1 : tint_symbol; |
| |
| @group(0) @binding(0) var t : texture_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = tint_symbol_1.texture_builtin_value_0; |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| // Note: Using the following EXPECT_EQ directly on BindingPointToFieldAndOffset seems to cause |
| // compiler to hang. EXPECT_EQ( |
| // TextureBuiltinsFromUniformOptions::BindingPointToFieldAndOffset{ |
| // {BindgPoint{0u, 0u}, |
| // std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 0u)}}, |
| // val->bindpoint_to_data); |
| EXPECT_EQ(1u, val->bindpoint_to_data.size()); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, BasicTextureNumSamples) { |
| auto* src = R"( |
| @group(0) @binding(0) var t : texture_multisampled_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var samples : u32 = textureNumSamples(t); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol { |
| texture_builtin_value_0 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_1 : tint_symbol; |
| |
| @group(0) @binding(0) var t : texture_multisampled_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var samples : u32 = tint_symbol_1.texture_builtin_value_0; |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| EXPECT_EQ(1u, val->bindpoint_to_data.size()); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumSamples, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, SameBuiltinCalledMultipleTimes) { |
| auto* src = R"( |
| @group(0) @binding(0) var tex : texture_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = textureNumLevels(tex); |
| len = textureNumLevels(tex); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol { |
| texture_builtin_value_0 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_1 : tint_symbol; |
| |
| @group(0) @binding(0) var tex : texture_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = tint_symbol_1.texture_builtin_value_0; |
| len = tint_symbol_1.texture_builtin_value_0; |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| EXPECT_EQ(1u, val->bindpoint_to_data.size()); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, SameBuiltinCalledMultipleTimesTextureNumSamples) { |
| auto* src = R"( |
| @group(0) @binding(0) var tex : texture_multisampled_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = textureNumSamples(tex); |
| len = textureNumSamples(tex); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol { |
| texture_builtin_value_0 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_1 : tint_symbol; |
| |
| @group(0) @binding(0) var tex : texture_multisampled_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = tint_symbol_1.texture_builtin_value_0; |
| len = tint_symbol_1.texture_builtin_value_0; |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| EXPECT_EQ(1u, val->bindpoint_to_data.size()); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumSamples, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, TextureAsFunctionParameterBasic) { |
| auto* src = R"( |
| @group(0) @binding(0) var tex : texture_2d<f32>; |
| |
| fn f(t: texture_2d<f32>) -> u32 { |
| return textureNumLevels(t); |
| } |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = f(tex); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol_1 { |
| texture_builtin_value_0 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_2 : tint_symbol_1; |
| |
| @group(0) @binding(0) var tex : texture_2d<f32>; |
| |
| fn f(t : texture_2d<f32>, tint_symbol : u32) -> u32 { |
| return tint_symbol; |
| } |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = f(tex, tint_symbol_2.texture_builtin_value_0); |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| EXPECT_EQ(1u, val->bindpoint_to_data.size()); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, TextureAsFunctionParameterUsedTwice) { |
| auto* src = R"( |
| @group(0) @binding(0) var tex : texture_2d<f32>; |
| |
| fn f(t: texture_2d<f32>) -> u32 { |
| var len = textureNumLevels(t); |
| len += textureNumLevels(t); |
| return len; |
| } |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = f(tex); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol_1 { |
| texture_builtin_value_0 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_2 : tint_symbol_1; |
| |
| @group(0) @binding(0) var tex : texture_2d<f32>; |
| |
| fn f(t : texture_2d<f32>, tint_symbol : u32) -> u32 { |
| var len = tint_symbol; |
| len += tint_symbol; |
| return len; |
| } |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = f(tex, tint_symbol_2.texture_builtin_value_0); |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| EXPECT_EQ(1u, val->bindpoint_to_data.size()); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, TextureAsFunctionParameterMultipleParameters) { |
| auto* src = R"( |
| @group(0) @binding(0) var tex1 : texture_2d<f32>; |
| @group(0) @binding(1) var tex2 : texture_2d<f32>; |
| @group(0) @binding(2) var tex3 : texture_2d<f32>; |
| |
| fn f(t1: texture_2d<f32>, t2: texture_2d<f32>, t3: texture_2d<f32>) -> u32 { |
| return textureNumLevels(t1) + textureNumLevels(t2) + textureNumLevels(t3); |
| } |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = f(tex1, tex2, tex3); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol_3 { |
| texture_builtin_value_0 : u32, |
| texture_builtin_value_1 : u32, |
| texture_builtin_value_2 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_4 : tint_symbol_3; |
| |
| @group(0) @binding(0) var tex1 : texture_2d<f32>; |
| |
| @group(0) @binding(1) var tex2 : texture_2d<f32>; |
| |
| @group(0) @binding(2) var tex3 : texture_2d<f32>; |
| |
| fn f(t1 : texture_2d<f32>, t2 : texture_2d<f32>, t3 : texture_2d<f32>, tint_symbol : u32, tint_symbol_1 : u32, tint_symbol_2 : u32) -> u32 { |
| return ((tint_symbol + tint_symbol_1) + tint_symbol_2); |
| } |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = f(tex1, tex2, tex3, tint_symbol_4.texture_builtin_value_0, tint_symbol_4.texture_builtin_value_1, tint_symbol_4.texture_builtin_value_2); |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| EXPECT_EQ(3u, val->bindpoint_to_data.size()); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 4u), |
| val->bindpoint_to_data.at(BindingPoint{0, 1})); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 8u), |
| val->bindpoint_to_data.at(BindingPoint{0, 2})); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, TextureAsFunctionParameterNested) { |
| auto* src = R"( |
| @group(0) @binding(0) var tex : texture_2d<f32>; |
| |
| fn f2(tt: texture_2d<f32>) -> u32 { |
| return textureNumLevels(tt); |
| } |
| |
| fn f1(t: texture_2d<f32>) -> u32 { |
| return f2(t); |
| } |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = f1(tex); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol_2 { |
| texture_builtin_value_0 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_3 : tint_symbol_2; |
| |
| @group(0) @binding(0) var tex : texture_2d<f32>; |
| |
| fn f2(tt : texture_2d<f32>, tint_symbol : u32) -> u32 { |
| return tint_symbol; |
| } |
| |
| fn f1(t : texture_2d<f32>, tint_symbol_1 : u32) -> u32 { |
| return f2(t, tint_symbol_1); |
| } |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = f1(tex, tint_symbol_3.texture_builtin_value_0); |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| EXPECT_EQ(1u, val->bindpoint_to_data.size()); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, TextureAsFunctionParameterMixed) { |
| auto* src = R"( |
| @group(0) @binding(0) var tex0 : texture_2d<f32>; |
| @group(0) @binding(1) var tex1 : texture_2d<f32>; |
| @group(0) @binding(2) var tex2 : texture_2d<f32>; |
| @group(0) @binding(3) var tex3 : texture_2d<f32>; |
| @group(0) @binding(4) var tex4 : texture_2d_array<f32>; // unused for textureNumLevels |
| |
| fn f_nested(t1: texture_2d<f32>, t2: texture_2d<f32>) -> u32 { |
| return textureNumLevels(t1) + textureNumLevels(t2); |
| } |
| |
| fn f1(a: u32, t: texture_2d<f32>) -> u32 { |
| return a + f_nested(t, tex1) + textureNumLevels(tex3); |
| } |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| _ = textureNumLayers(tex4); |
| _ = f1(9u, tex0); |
| _ = f_nested(tex2, tex2); |
| _ = f_nested(tex1, tex0); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol_3 { |
| texture_builtin_value_0 : u32, |
| texture_builtin_value_1 : u32, |
| texture_builtin_value_2 : u32, |
| texture_builtin_value_3 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_4 : tint_symbol_3; |
| |
| @group(0) @binding(0) var tex0 : texture_2d<f32>; |
| |
| @group(0) @binding(1) var tex1 : texture_2d<f32>; |
| |
| @group(0) @binding(2) var tex2 : texture_2d<f32>; |
| |
| @group(0) @binding(3) var tex3 : texture_2d<f32>; |
| |
| @group(0) @binding(4) var tex4 : texture_2d_array<f32>; |
| |
| fn f_nested(t1 : texture_2d<f32>, t2 : texture_2d<f32>, tint_symbol : u32, tint_symbol_1 : u32) -> u32 { |
| return (tint_symbol + tint_symbol_1); |
| } |
| |
| fn f1(a : u32, t : texture_2d<f32>, tint_symbol_2 : u32) -> u32 { |
| return ((a + f_nested(t, tex1, tint_symbol_2, tint_symbol_4.texture_builtin_value_0)) + tint_symbol_4.texture_builtin_value_1); |
| } |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| _ = textureNumLayers(tex4); |
| _ = f1(9u, tex0, tint_symbol_4.texture_builtin_value_2); |
| _ = f_nested(tex2, tex2, tint_symbol_4.texture_builtin_value_3, tint_symbol_4.texture_builtin_value_3); |
| _ = f_nested(tex1, tex0, tint_symbol_4.texture_builtin_value_0, tint_symbol_4.texture_builtin_value_2); |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| EXPECT_EQ(4u, val->bindpoint_to_data.size()); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 1})); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 4u), |
| val->bindpoint_to_data.at(BindingPoint{0, 3})); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 8u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 12u), |
| val->bindpoint_to_data.at(BindingPoint{0, 2})); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, MultipleTextures) { |
| auto* src = R"( |
| @group(0) @binding(0) var t0 : texture_2d<f32>; |
| @group(0) @binding(1) var t1 : texture_multisampled_2d<f32>; |
| @group(0) @binding(2) var t2 : texture_2d_array<f32>; |
| @group(0) @binding(3) var t3 : texture_cube<f32>; |
| @group(0) @binding(4) var t4 : texture_depth_2d; |
| @group(1) @binding(0) var t5 : texture_depth_multisampled_2d; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| _ = textureNumLevels(t0); |
| _ = textureNumSamples(t1); |
| _ = textureNumLevels(t2); |
| _ = textureNumLevels(t3); |
| _ = textureNumLevels(t4); |
| _ = textureNumSamples(t5); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol { |
| texture_builtin_value_0 : u32, |
| texture_builtin_value_1 : u32, |
| texture_builtin_value_2 : u32, |
| texture_builtin_value_3 : u32, |
| texture_builtin_value_4 : u32, |
| texture_builtin_value_5 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_1 : tint_symbol; |
| |
| @group(0) @binding(0) var t0 : texture_2d<f32>; |
| |
| @group(0) @binding(1) var t1 : texture_multisampled_2d<f32>; |
| |
| @group(0) @binding(2) var t2 : texture_2d_array<f32>; |
| |
| @group(0) @binding(3) var t3 : texture_cube<f32>; |
| |
| @group(0) @binding(4) var t4 : texture_depth_2d; |
| |
| @group(1) @binding(0) var t5 : texture_depth_multisampled_2d; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| _ = tint_symbol_1.texture_builtin_value_0; |
| _ = tint_symbol_1.texture_builtin_value_1; |
| _ = tint_symbol_1.texture_builtin_value_2; |
| _ = tint_symbol_1.texture_builtin_value_3; |
| _ = tint_symbol_1.texture_builtin_value_4; |
| _ = tint_symbol_1.texture_builtin_value_5; |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| EXPECT_EQ(6u, val->bindpoint_to_data.size()); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumSamples, 4u), |
| val->bindpoint_to_data.at(BindingPoint{0, 1})); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 8u), |
| val->bindpoint_to_data.at(BindingPoint{0, 2})); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 12u), |
| val->bindpoint_to_data.at(BindingPoint{0, 3})); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 16u), |
| val->bindpoint_to_data.at(BindingPoint{0, 4})); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumSamples, 20u), |
| val->bindpoint_to_data.at(BindingPoint{1, 0})); |
| } |
| |
| TEST_F(TextureBuiltinsFromUniformTest, BindingPointExist) { |
| auto* src = R"( |
| struct tint_symbol { |
| foo : array<vec4<u32>, 1u>, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_1 : tint_symbol; |
| |
| @group(0) @binding(0) var t : texture_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = textureNumLevels(t); |
| } |
| )"; |
| |
| auto* expect = R"( |
| struct tint_symbol { |
| foo : array<vec4<u32>, 1u>, |
| texture_builtin_value_0 : u32, |
| } |
| |
| @group(0) @binding(30) var<uniform> tint_symbol_1 : tint_symbol; |
| |
| @group(0) @binding(0) var t : texture_2d<f32>; |
| |
| @compute @workgroup_size(1) |
| fn main() { |
| var len : u32 = tint_symbol_1.texture_builtin_value_0; |
| } |
| )"; |
| |
| TextureBuiltinsFromUniform::Config cfg({0, 30u}); |
| |
| ast::transform::DataMap data; |
| data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg)); |
| |
| auto got = Run<TextureBuiltinsFromUniform>(src, data); |
| |
| EXPECT_EQ(expect, str(got)); |
| auto* val = got.data.Get<TextureBuiltinsFromUniform::Result>(); |
| ASSERT_NE(val, nullptr); |
| EXPECT_EQ(std::make_pair(TextureBuiltinsFromUniformOptions::Field::TextureNumLevels, 0u), |
| val->bindpoint_to_data.at(BindingPoint{0, 0})); |
| } |
| |
| } // namespace |
| } // namespace tint::glsl::writer |