src/tint/lang/glsl/writer/ast_raise/texture_builtins_from_uniform_test.cc - tint - Git at Google

 // Copyright 2023 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 "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, 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;
 }
 )";

     std::vector<BindingPoint> bps = {{0, 0}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);
     EXPECT_EQ(expect, str(got));
 }

 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;
 }
 )";

     std::vector<BindingPoint> bps = {{0, 0}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);
     EXPECT_EQ(expect, str(got));
 }

 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;
 }
 )";

     std::vector<BindingPoint> bps = {{0, 0}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);
     EXPECT_EQ(expect, str(got));
 }

 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;
 }
 )";

     std::vector<BindingPoint> bps = {{0, 0}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);
     EXPECT_EQ(expect, str(got));
 }

 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);
 }
 )";

     std::vector<BindingPoint> bps = {{0, 0}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);
     EXPECT_EQ(expect, str(got));
 }

 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);
 }
 )";

     std::vector<BindingPoint> bps = {{0, 0}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);
     EXPECT_EQ(expect, str(got));
 }

 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);
 }
 )";

     std::vector<BindingPoint> bps = {{0, 0}, {0, 1}, {0, 2}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);
     EXPECT_EQ(expect, str(got));
 }

 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);
 }
 )";

     std::vector<BindingPoint> bps = {{0, 0}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);
     EXPECT_EQ(expect, str(got));
 }

 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);
 }
 )";

     std::vector<BindingPoint> bps = {{0, 1}, {0, 3}, {0, 0}, {0, 2}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);
     EXPECT_EQ(expect, str(got));
 }

 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;
 }
 )";

     std::vector<BindingPoint> bps = {{0, 0}, {0, 1}, {0, 2}, {0, 3}, {0, 4}, {1, 0}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);

     EXPECT_EQ(expect, str(got));
 }

 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;
 }
 )";

     std::vector<BindingPoint> bps = {{0, 0}};
     TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

     ast::transform::DataMap data;
     data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

     auto got = Run<TextureBuiltinsFromUniform>(src, data);

     EXPECT_EQ(expect, str(got));
 }

 }  // namespace
 }  // namespace tint::glsl::writer
	// Copyright 2023 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 "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, 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;
	}
	)";

	std::vector<BindingPoint> bps = {{0, 0}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);
	EXPECT_EQ(expect, str(got));
	}

	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;
	}
	)";

	std::vector<BindingPoint> bps = {{0, 0}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);
	EXPECT_EQ(expect, str(got));
	}

	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;
	}
	)";

	std::vector<BindingPoint> bps = {{0, 0}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);
	EXPECT_EQ(expect, str(got));
	}

	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;
	}
	)";

	std::vector<BindingPoint> bps = {{0, 0}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);
	EXPECT_EQ(expect, str(got));
	}

	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);
	}
	)";

	std::vector<BindingPoint> bps = {{0, 0}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);
	EXPECT_EQ(expect, str(got));
	}

	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);
	}
	)";

	std::vector<BindingPoint> bps = {{0, 0}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);
	EXPECT_EQ(expect, str(got));
	}

	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);
	}
	)";

	std::vector<BindingPoint> bps = {{0, 0}, {0, 1}, {0, 2}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);
	EXPECT_EQ(expect, str(got));
	}

	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);
	}
	)";

	std::vector<BindingPoint> bps = {{0, 0}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);
	EXPECT_EQ(expect, str(got));
	}

	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);
	}
	)";

	std::vector<BindingPoint> bps = {{0, 1}, {0, 3}, {0, 0}, {0, 2}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);
	EXPECT_EQ(expect, str(got));
	}

	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;
	}
	)";

	std::vector<BindingPoint> bps = {{0, 0}, {0, 1}, {0, 2}, {0, 3}, {0, 4}, {1, 0}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);

	EXPECT_EQ(expect, str(got));
	}

	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;
	}
	)";

	std::vector<BindingPoint> bps = {{0, 0}};
	TextureBuiltinsFromUniform::Config cfg({0, 30u}, bps);

	ast::transform::DataMap data;
	data.Add<TextureBuiltinsFromUniform::Config>(std::move(cfg));

	auto got = Run<TextureBuiltinsFromUniform>(src, data);

	EXPECT_EQ(expect, str(got));
	}

	} // namespace
	} // namespace tint::glsl::writer