// 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