Move the Extension builtin to the builtin/ folder.
This CL moves Extension from ast:: to builtin::
Change-Id: Ica1e6f4f9229341b547011389d47ae3be9830b0d
Reviewed-on: https://dawn-review.googlesource.com/c/dawn/+/120362
Commit-Queue: Dan Sinclair <dsinclair@chromium.org>
Reviewed-by: Ben Clayton <bclayton@google.com>
Kokoro: Kokoro <noreply+kokoro@google.com>
diff --git a/src/tint/resolver/address_space_layout_validation_test.cc b/src/tint/resolver/address_space_layout_validation_test.cc
index 4a2411b..041e566 100644
--- a/src/tint/resolver/address_space_layout_validation_test.cc
+++ b/src/tint/resolver/address_space_layout_validation_test.cc
@@ -371,7 +371,7 @@
// @group(0) @binding(0)
// var<uniform> a : ScalarPackedAtEndOfVec3;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("ScalarPackedAtEndOfVec3", utils::Vector{
Member("v", ty.vec3(ty.f16())),
@@ -568,7 +568,7 @@
// @align(1) b : f32;
// };
// var<push_constant> a : S;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
Structure(
Source{{12, 34}}, "S",
utils::Vector{Member("a", ty.f32(), utils::Vector{MemberSize(5_a)}),
@@ -595,7 +595,7 @@
// @align(4) b : f32;
// };
// var<push_constant> a : S;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
Structure("S", utils::Vector{Member("a", ty.f32(), utils::Vector{MemberSize(5_a)}),
Member("b", ty.f32(), utils::Vector{MemberAlign(4_i)})});
GlobalVar("a", ty("S"), type::AddressSpace::kPushConstant);
diff --git a/src/tint/resolver/address_space_validation_test.cc b/src/tint/resolver/address_space_validation_test.cc
index f96b29f..2c879de 100644
--- a/src/tint/resolver/address_space_validation_test.cc
+++ b/src/tint/resolver/address_space_validation_test.cc
@@ -249,7 +249,7 @@
TEST_F(ResolverAddressSpaceValidationTest, GlobalVariable_Storage_F16) {
// enable f16;
// var<storage> g : f16;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("g", ty.f16(), type::AddressSpace::kStorage, Binding(0_a), Group(0_a));
@@ -259,7 +259,7 @@
TEST_F(ResolverAddressSpaceValidationTest, PointerAlias_Storage_F16) {
// enable f16;
// type t = ptr<storage, f16>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Alias("t", ty.pointer(ty.f16(), type::AddressSpace::kStorage));
@@ -270,7 +270,7 @@
// enable f16;
// type a = f16;
// var<storage, read> g : a;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Alias("a", ty.f16());
GlobalVar("g", ty("a"), type::AddressSpace::kStorage, Binding(0_a), Group(0_a));
@@ -282,7 +282,7 @@
// enable f16;
// type a = f16;
// type t = ptr<storage, a>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Alias("a", ty.f16());
Alias("t", ty.pointer(ty("a"), type::AddressSpace::kStorage));
@@ -306,7 +306,7 @@
TEST_F(ResolverAddressSpaceValidationTest, GlobalVariable_Storage_VectorF16) {
// var<storage> g : vec4<f16>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("g", ty.vec(ty.f16(), 4u), type::AddressSpace::kStorage, Binding(0_a), Group(0_a));
ASSERT_TRUE(r()->Resolve()) << r()->error();
@@ -314,7 +314,7 @@
TEST_F(ResolverAddressSpaceValidationTest, PointerAlias_Storage_VectorF16) {
// type t = ptr<storage, vec4<f16>>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Alias("t", ty.pointer(ty.vec(ty.f16(), 4u), type::AddressSpace::kStorage));
ASSERT_TRUE(r()->Resolve()) << r()->error();
@@ -343,7 +343,7 @@
// enable f16;
// struct S{ a : f16 };
// var<storage, read> g : array<S, 3u>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("a", ty.f16())});
GlobalVar("g", ty.array(ty("S"), 3_u), type::AddressSpace::kStorage, type::Access::kRead,
@@ -356,7 +356,7 @@
// enable f16;
// struct S{ a : f16 };
// type t = ptr<storage, read, array<S, 3u>>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("a", ty.f16())});
Alias("t",
@@ -412,7 +412,7 @@
TEST_F(ResolverAddressSpaceValidationTest, GlobalVariable_Storage_StructF16) {
// struct S { x : f16 };
// var<storage, read> g : S;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("x", ty.f16())});
GlobalVar("g", ty("S"), type::AddressSpace::kStorage, type::Access::kRead, Binding(0_a),
@@ -424,7 +424,7 @@
TEST_F(ResolverAddressSpaceValidationTest, PointerAlias_Storage_StructF16) {
// struct S { x : f16 };
// type t = ptr<storage, read, S>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("x", ty.f16())});
Alias("t", ty.pointer(ty("S"), type::AddressSpace::kStorage, type::Access::kRead));
@@ -436,7 +436,7 @@
// struct S { x : f16 };
// type a1 = S;
// var<storage, read> g : a1;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("x", ty.f16())});
Alias("a1", ty("S"));
@@ -451,7 +451,7 @@
// struct S { x : f16 };
// type a1 = S;
// type t = ptr<storage, read, a1>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("x", ty.f16())});
Alias("a1", ty("S"));
@@ -675,7 +675,7 @@
TEST_F(ResolverAddressSpaceValidationTest, GlobalVariable_UniformBufferF16) {
// enable f16;
// var<uniform> g : f16;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("g", ty.f16(), type::AddressSpace::kUniform, Binding(0_a), Group(0_a));
@@ -685,7 +685,7 @@
TEST_F(ResolverAddressSpaceValidationTest, PointerAlias_UniformBufferF16) {
// enable f16;
// type t = ptr<uniform, f16>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Alias("t", ty.pointer(ty.f16(), type::AddressSpace::kUniform));
@@ -709,7 +709,7 @@
TEST_F(ResolverAddressSpaceValidationTest, GlobalVariable_UniformBufferVectorF16) {
// enable f16;
// var<uniform> g : vec4<f16>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("g", ty.vec4<f16>(), type::AddressSpace::kUniform, Binding(0_a), Group(0_a));
@@ -719,7 +719,7 @@
TEST_F(ResolverAddressSpaceValidationTest, PointerAlias_UniformBufferVectorF16) {
// enable f16;
// type t = ptr<uniform, vec4<f16>>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Alias("t", ty.pointer(ty.vec4<f16>(), type::AddressSpace::kUniform));
@@ -754,7 +754,7 @@
// @size(16) f : f16;
// }
// var<uniform> g : array<S, 3u>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("a", ty.f16(), utils::Vector{MemberSize(16_a)})});
GlobalVar("g", ty.array(ty("S"), 3_u), type::AddressSpace::kUniform, Binding(0_a), Group(0_a));
@@ -768,7 +768,7 @@
// @size(16) f : f16;
// }
// type t = ptr<uniform, array<S, 3u>>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("a", ty.f16(), utils::Vector{MemberSize(16_a)})});
Alias("t", ty.pointer(ty.array(ty("S"), 3_u), type::AddressSpace::kUniform));
@@ -820,7 +820,7 @@
// enable f16;
// struct S { x : f16 };
// var<uniform> g : S;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("x", ty.f16())});
GlobalVar("g", ty("S"), type::AddressSpace::kUniform, Binding(0_a), Group(0_a));
@@ -832,7 +832,7 @@
// enable f16;
// struct S { x : f16 };
// type t = ptr<uniform, S>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("x", ty.f16())});
Alias("t", ty.pointer(ty("S"), type::AddressSpace::kUniform));
@@ -845,7 +845,7 @@
// struct S { x : f16 };
// type a1 = S;
// var<uniform> g : a1;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("x", ty.f16())});
Alias("a1", ty("S"));
@@ -859,7 +859,7 @@
// struct S { x : f16 };
// type a1 = S;
// type t = ptr<uniform, a1>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{Member("x", ty.f16())});
Alias("a1", ty("S"));
@@ -871,7 +871,7 @@
TEST_F(ResolverAddressSpaceValidationTest, GlobalVariable_PushConstantBool) {
// enable chromium_experimental_push_constant;
// var<push_constant> g : bool;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar(Source{{56, 78}}, "g", ty.bool_(Source{{12, 34}}), type::AddressSpace::kPushConstant);
ASSERT_FALSE(r()->Resolve());
@@ -884,7 +884,7 @@
TEST_F(ResolverAddressSpaceValidationTest, PointerAlias_PushConstantBool) {
// enable chromium_experimental_push_constant;
// type t = ptr<push_constant, bool>;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
Alias(Source{{56, 78}}, "t",
ty.pointer(ty.bool_(Source{{12, 34}}), type::AddressSpace::kPushConstant));
@@ -899,8 +899,8 @@
// enable f16;
// enable chromium_experimental_push_constant;
// var<push_constant> g : f16;
- Enable(ast::Extension::kF16);
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kF16);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar("g", ty.f16(Source{{56, 78}}), type::AddressSpace::kPushConstant);
ASSERT_FALSE(r()->Resolve());
@@ -912,8 +912,8 @@
// enable f16;
// enable chromium_experimental_push_constant;
// type t = ptr<push_constant, f16>;
- Enable(ast::Extension::kF16);
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kF16);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
Alias("t", ty.pointer(ty.f16(Source{{56, 78}}), type::AddressSpace::kPushConstant));
ASSERT_FALSE(r()->Resolve());
@@ -924,7 +924,7 @@
TEST_F(ResolverAddressSpaceValidationTest, GlobalVariable_PushConstantPointer) {
// enable chromium_experimental_push_constant;
// var<push_constant> g : ptr<private, f32>;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar(Source{{56, 78}}, "g",
ty.pointer(Source{{12, 34}}, ty.f32(), type::AddressSpace::kPrivate),
type::AddressSpace::kPushConstant);
@@ -939,7 +939,7 @@
TEST_F(ResolverAddressSpaceValidationTest, PointerAlias_PushConstantPointer) {
// enable chromium_experimental_push_constant;
// type t = ptr<push_constant, ptr<private, f32>>;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
Alias(Source{{56, 78}}, "t",
ty.pointer(ty.pointer(Source{{12, 34}}, ty.f32(), type::AddressSpace::kPrivate),
type::AddressSpace::kPushConstant));
@@ -954,7 +954,7 @@
TEST_F(ResolverAddressSpaceValidationTest, GlobalVariable_PushConstantIntScalar) {
// enable chromium_experimental_push_constant;
// var<push_constant> g : i32;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar("g", ty.i32(), type::AddressSpace::kPushConstant);
ASSERT_TRUE(r()->Resolve()) << r()->error();
@@ -963,7 +963,7 @@
TEST_F(ResolverAddressSpaceValidationTest, PointerAlias_PushConstantIntScalar) {
// enable chromium_experimental_push_constant;
// type t = ptr<push_constant, i32>;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
Alias("t", ty.pointer(ty.i32(), type::AddressSpace::kPushConstant));
ASSERT_TRUE(r()->Resolve()) << r()->error();
@@ -972,7 +972,7 @@
TEST_F(ResolverAddressSpaceValidationTest, GlobalVariable_PushConstantVectorF32) {
// enable chromium_experimental_push_constant;
// var<push_constant> g : vec4<f32>;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar("g", ty.vec4<f32>(), type::AddressSpace::kPushConstant);
ASSERT_TRUE(r()->Resolve()) << r()->error();
@@ -981,7 +981,7 @@
TEST_F(ResolverAddressSpaceValidationTest, PointerAlias_PushConstantVectorF32) {
// enable chromium_experimental_push_constant;
// var<push_constant> g : vec4<f32>;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
Alias("t", ty.pointer(ty.vec4<f32>(), type::AddressSpace::kPushConstant));
ASSERT_TRUE(r()->Resolve()) << r()->error();
@@ -991,7 +991,7 @@
// enable chromium_experimental_push_constant;
// struct S { a : f32}
// var<push_constant> g : array<S, 3u>;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
Structure("S", utils::Vector{Member("a", ty.f32())});
GlobalVar("g", ty.array(ty("S"), 3_u), type::AddressSpace::kPushConstant);
@@ -1002,7 +1002,7 @@
// enable chromium_experimental_push_constant;
// struct S { a : f32}
// type t = ptr<push_constant, array<S, 3u>>;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
Structure("S", utils::Vector{Member("a", ty.f32())});
Alias("t", ty.pointer(ty.array(ty("S"), 3_u), type::AddressSpace::kPushConstant));
diff --git a/src/tint/resolver/builtin_test.cc b/src/tint/resolver/builtin_test.cc
index dc49f3a..e3becab 100644
--- a/src/tint/resolver/builtin_test.cc
+++ b/src/tint/resolver/builtin_test.cc
@@ -471,7 +471,7 @@
TEST_P(ResolverBuiltinTest_FloatBuiltin_IdenticalType, OneParam_Scalar_f16) {
auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto val = 0.5_h;
if (param.name == std::string("acosh")) {
@@ -499,7 +499,7 @@
TEST_P(ResolverBuiltinTest_FloatBuiltin_IdenticalType, OneParam_Vector_f16) {
auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto val = param.name == std::string("acosh") ? vec3<f16>(1.0_h, 2.0_h, 3.0_h)
: vec3<f16>(0.5_h, 0.5_h, 0.8_h);
@@ -528,7 +528,7 @@
TEST_P(ResolverBuiltinTest_FloatBuiltin_IdenticalType, TwoParams_Scalar_f16) {
auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call(param.name, 1_h, 1_h);
WrapInFunction(call);
@@ -551,7 +551,7 @@
TEST_P(ResolverBuiltinTest_FloatBuiltin_IdenticalType, TwoParams_Vector_f16) {
auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call(param.name, vec3<f16>(1_h, 1_h, 3_h), vec3<f16>(1_h, 1_h, 3_h));
WrapInFunction(call);
@@ -577,7 +577,7 @@
TEST_P(ResolverBuiltinTest_FloatBuiltin_IdenticalType, ThreeParams_Scalar_f16) {
auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call(param.name, 0_h, 1_h, 2_h);
WrapInFunction(call);
@@ -600,7 +600,7 @@
TEST_P(ResolverBuiltinTest_FloatBuiltin_IdenticalType, ThreeParams_Vector_f16) {
auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call(param.name, vec3<f16>(0_h, 0_h, 0_h), vec3<f16>(1_h, 1_h, 1_h),
vec3<f16>(2_h, 2_h, 2_h));
@@ -628,7 +628,7 @@
TEST_P(ResolverBuiltinTest_FloatBuiltin_IdenticalType, FourParams_Scalar_f16) {
auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call(param.name, 1_h, 1_h, 1_h, 1_h);
WrapInFunction(call);
@@ -651,7 +651,7 @@
TEST_P(ResolverBuiltinTest_FloatBuiltin_IdenticalType, FourParams_Vector_f16) {
auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call(param.name, vec3<f16>(1_h, 1_h, 3_h), vec3<f16>(1_h, 1_h, 3_h),
vec3<f16>(1_h, 1_h, 3_h), vec3<f16>(1_h, 1_h, 3_h));
@@ -745,7 +745,7 @@
}
TEST_F(ResolverBuiltinFloatTest, Cross_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("cross", vec3<f16>(1_h, 2_h, 3_h), vec3<f16>(1_h, 2_h, 3_h));
WrapInFunction(call);
@@ -841,7 +841,7 @@
}
TEST_F(ResolverBuiltinFloatTest, Distance_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("distance", 1_h, 1_h);
WrapInFunction(call);
@@ -863,7 +863,7 @@
}
TEST_F(ResolverBuiltinFloatTest, Distance_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("distance", vec3<f16>(1_h, 1_h, 3_h), vec3<f16>(1_h, 1_h, 3_h));
WrapInFunction(call);
@@ -949,7 +949,7 @@
}
TEST_F(ResolverBuiltinFloatTest, FrexpScalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("frexp", 1_h);
WrapInFunction(call);
@@ -1013,7 +1013,7 @@
}
TEST_F(ResolverBuiltinFloatTest, FrexpVector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("frexp", vec3<f16>());
WrapInFunction(call);
@@ -1075,7 +1075,7 @@
}
TEST_F(ResolverBuiltinFloatTest, Length_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("length", 1_h);
WrapInFunction(call);
@@ -1097,7 +1097,7 @@
}
TEST_F(ResolverBuiltinFloatTest, Length_FloatVector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("length", vec3<f16>(1_h, 1_h, 3_h));
WrapInFunction(call);
@@ -1152,7 +1152,7 @@
}
TEST_F(ResolverBuiltinFloatTest, Mix_VectorScalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("mix", vec3<f16>(1_h, 1_h, 1_h), vec3<f16>(1_h, 1_h, 1_h), 4_h);
WrapInFunction(call);
@@ -1198,7 +1198,7 @@
}
TEST_F(ResolverBuiltinFloatTest, ModfScalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("modf", 1_h);
WrapInFunction(call);
@@ -1262,7 +1262,7 @@
}
TEST_F(ResolverBuiltinFloatTest, ModfVector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("modf", vec3<f16>());
WrapInFunction(call);
@@ -1372,7 +1372,7 @@
}
TEST_F(ResolverBuiltinFloatTest, Normalize_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("normalize", vec3<f16>(1_h, 1_h, 3_h));
WrapInFunction(call);
@@ -1835,7 +1835,7 @@
}
TEST_F(ResolverBuiltinTest, Determinant_2x2_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("var", ty.mat2x2<f16>(), type::AddressSpace::kPrivate);
@@ -1861,7 +1861,7 @@
}
TEST_F(ResolverBuiltinTest, Determinant_3x3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("var", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
@@ -1887,7 +1887,7 @@
}
TEST_F(ResolverBuiltinTest, Determinant_4x4_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("var", ty.mat4x4<f16>(), type::AddressSpace::kPrivate);
@@ -1948,7 +1948,7 @@
}
TEST_F(ResolverBuiltinTest, Dot_Vec2_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("my_var", ty.vec2<f16>(), type::AddressSpace::kPrivate);
diff --git a/src/tint/resolver/builtin_validation_test.cc b/src/tint/resolver/builtin_validation_test.cc
index b9c31c9..22e13c2 100644
--- a/src/tint/resolver/builtin_validation_test.cc
+++ b/src/tint/resolver/builtin_validation_test.cc
@@ -523,7 +523,7 @@
TEST_F(ResolverDP4aExtensionValidationTest, Dot4I8PackedWithExtension) {
// enable chromium_experimental_dp4a;
// fn func { return dot4I8Packed(1u, 2u); }
- Enable(ast::Extension::kChromiumExperimentalDp4A);
+ Enable(builtin::Extension::kChromiumExperimentalDp4A);
Func("func", utils::Empty, ty.i32(),
utils::Vector{
@@ -551,7 +551,7 @@
TEST_F(ResolverDP4aExtensionValidationTest, Dot4U8PackedWithExtension) {
// enable chromium_experimental_dp4a;
// fn func { return dot4U8Packed(1u, 2u); }
- Enable(ast::Extension::kChromiumExperimentalDp4A);
+ Enable(builtin::Extension::kChromiumExperimentalDp4A);
Func("func", utils::Empty, ty.u32(),
utils::Vector{
diff --git a/src/tint/resolver/call_test.cc b/src/tint/resolver/call_test.cc
index e5b245c..25f4814 100644
--- a/src/tint/resolver/call_test.cc
+++ b/src/tint/resolver/call_test.cc
@@ -82,7 +82,7 @@
};
TEST_F(ResolverCallTest, Valid) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
utils::Vector<const ast::Parameter*, 4> params;
utils::Vector<const ast::Expression*, 4> args;
diff --git a/src/tint/resolver/call_validation_test.cc b/src/tint/resolver/call_validation_test.cc
index 07e2271..b0b8cce 100644
--- a/src/tint/resolver/call_validation_test.cc
+++ b/src/tint/resolver/call_validation_test.cc
@@ -165,7 +165,7 @@
// var v : S;
// foo(&v.m);
// }
- Enable(ast::Extension::kChromiumExperimentalFullPtrParameters);
+ Enable(builtin::Extension::kChromiumExperimentalFullPtrParameters);
auto* S = Structure("S", utils::Vector{
Member("m", ty.i32()),
});
@@ -346,7 +346,7 @@
// let p: ptr<function, i32> = &(v[0]);
// x(p);
// }
- Enable(ast::Extension::kChromiumExperimentalFullPtrParameters);
+ Enable(builtin::Extension::kChromiumExperimentalFullPtrParameters);
Func("foo",
utils::Vector{
Param("p", ty.pointer<i32>(type::AddressSpace::kFunction)),
@@ -437,7 +437,7 @@
// let p3 = &(*p2)[0];
// foo(&*p);
// }
- Enable(ast::Extension::kChromiumExperimentalFullPtrParameters);
+ Enable(builtin::Extension::kChromiumExperimentalFullPtrParameters);
Func("foo",
utils::Vector{
Param("p", ty.pointer<i32>(type::AddressSpace::kFunction)),
diff --git a/src/tint/resolver/const_eval_binary_op_test.cc b/src/tint/resolver/const_eval_binary_op_test.cc
index e7f6f14..ef7453e 100644
--- a/src/tint/resolver/const_eval_binary_op_test.cc
+++ b/src/tint/resolver/const_eval_binary_op_test.cc
@@ -83,7 +83,7 @@
using ResolverConstEvalBinaryOpTest = ResolverTestWithParam<std::tuple<ast::BinaryOp, Case>>;
TEST_P(ResolverConstEvalBinaryOpTest, Test) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto op = std::get<0>(GetParam());
auto& c = std::get<1>(GetParam());
diff --git a/src/tint/resolver/const_eval_builtin_test.cc b/src/tint/resolver/const_eval_builtin_test.cc
index 76f8238..4e3cb5a 100644
--- a/src/tint/resolver/const_eval_builtin_test.cc
+++ b/src/tint/resolver/const_eval_builtin_test.cc
@@ -142,7 +142,7 @@
using ResolverConstEvalBuiltinTest = ResolverTestWithParam<std::tuple<sem::BuiltinType, Case>>;
TEST_P(ResolverConstEvalBuiltinTest, Test) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto builtin = std::get<0>(GetParam());
auto& c = std::get<1>(GetParam());
diff --git a/src/tint/resolver/const_eval_construction_test.cc b/src/tint/resolver/const_eval_construction_test.cc
index fbf7515..55c2cf5 100644
--- a/src/tint/resolver/const_eval_construction_test.cc
+++ b/src/tint/resolver/const_eval_construction_test.cc
@@ -102,7 +102,7 @@
}
TEST_F(ResolverConstEvalTest, Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = Expr(9.9_h);
WrapInFunction(expr);
@@ -146,7 +146,7 @@
}
using ResolverConstEvalZeroInitTest = ResolverTestWithParam<Case>;
TEST_P(ResolverConstEvalZeroInitTest, Test) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto& param = GetParam();
auto ty = param.type(*this);
auto* expr = Call(ty);
@@ -316,7 +316,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_ZeroInit_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>();
WrapInFunction(expr);
@@ -483,7 +483,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_Splat_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>(9.9_h);
WrapInFunction(expr);
@@ -719,7 +719,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_FullConstruct_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>(1_h, 2_h, 3_h);
WrapInFunction(expr);
@@ -1018,7 +1018,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_MixConstruct_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>(1_h, vec2<f16>(2_h, 3_h));
WrapInFunction(expr);
@@ -1053,7 +1053,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_MixConstruct_f16_all_10) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>(10_h, vec2<f16>(10_h, 10_h));
WrapInFunction(expr);
@@ -1088,7 +1088,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_MixConstruct_f16_all_positive_0) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>(0_h, vec2<f16>(0_h, 0_h));
WrapInFunction(expr);
@@ -1123,7 +1123,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_MixConstruct_f16_all_negative_0) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>(vec2<f16>(-0_h, -0_h), -0_h);
WrapInFunction(expr);
@@ -1158,7 +1158,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_MixConstruct_f16_mixed_sign_0) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>(0_h, vec2<f16>(-0_h, 0_h));
WrapInFunction(expr);
@@ -1341,7 +1341,7 @@
}
TEST_F(ResolverConstEvalTest, Mat2x3_ZeroInit_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = mat2x3<f16>();
WrapInFunction(expr);
@@ -1704,7 +1704,7 @@
using ResolverConstEvalArrayInitTest = ResolverTestWithParam<Case>;
TEST_P(ResolverConstEvalArrayInitTest, Test) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto& param = GetParam();
auto* expr = param.input.Expr(*this);
auto* a = Const("a", expr);
@@ -1892,7 +1892,7 @@
}
TEST_F(ResolverConstEvalTest, Struct_ZeroInit) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* s = Structure("S", utils::Vector{
Member("a", ty.i32()),
Member("b", ty.u32()),
@@ -1937,7 +1937,7 @@
}
TEST_F(ResolverConstEvalTest, Struct_Nested_ZeroInit) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* inner = Structure("Inner", utils::Vector{
Member("a", ty.i32()),
Member("b", ty.u32()),
@@ -2028,7 +2028,7 @@
}
TEST_F(ResolverConstEvalTest, Struct_MixedScalars_ZeroInit) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{
Member("m1", ty.i32()),
@@ -2138,7 +2138,7 @@
}
TEST_F(ResolverConstEvalTest, Struct_MixedVectors_ZeroInit) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{
Member("m1", ty.vec2<i32>()),
@@ -2258,7 +2258,7 @@
}
TEST_F(ResolverConstEvalTest, Struct_MixedScalars_Construct) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{
Member("m1", ty.i32()),
@@ -2315,7 +2315,7 @@
}
TEST_F(ResolverConstEvalTest, Struct_MixedVectors_Construct) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Structure("S", utils::Vector{
Member("m1", ty.vec2<i32>()),
diff --git a/src/tint/resolver/const_eval_conversion_test.cc b/src/tint/resolver/const_eval_conversion_test.cc
index e159b0e..bcad648 100644
--- a/src/tint/resolver/const_eval_conversion_test.cc
+++ b/src/tint/resolver/const_eval_conversion_test.cc
@@ -289,7 +289,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_Convert_f16_to_i32) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<i32>(vec3<f16>(1.1_h, 2.2_h, 3.3_h));
WrapInFunction(expr);
@@ -324,7 +324,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_Convert_u32_to_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>(vec3<u32>(10_u, 20_u, 30_u));
WrapInFunction(expr);
@@ -425,7 +425,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_Convert_Large_f32_to_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>(Source{{12, 34}}, vec3<f32>(1e10_f, 0_f, 0_f));
WrapInFunction(expr);
@@ -435,7 +435,7 @@
}
TEST_F(ResolverConstEvalTest, Vec3_Convert_Small_f32_to_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = vec3<f16>(vec3<f32>(1e-20_f, -2e-30_f, 3e-40_f));
WrapInFunction(expr);
diff --git a/src/tint/resolver/const_eval_indexing_test.cc b/src/tint/resolver/const_eval_indexing_test.cc
index 9776674..cfd7aa1 100644
--- a/src/tint/resolver/const_eval_indexing_test.cc
+++ b/src/tint/resolver/const_eval_indexing_test.cc
@@ -68,7 +68,7 @@
using ResolverConstEvalSwizzleTest = ResolverTestWithParam<Case>;
TEST_P(ResolverConstEvalSwizzleTest, Test) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto& param = GetParam();
auto* expr = MemberAccessor(param.input.Expr(*this), param.swizzle);
auto* a = Const("a", expr);
diff --git a/src/tint/resolver/const_eval_member_access_test.cc b/src/tint/resolver/const_eval_member_access_test.cc
index e93d63b..4fcba8b 100644
--- a/src/tint/resolver/const_eval_member_access_test.cc
+++ b/src/tint/resolver/const_eval_member_access_test.cc
@@ -263,7 +263,7 @@
using ResolverConstEvalArrayAccessTest = ResolverTestWithParam<Case>;
TEST_P(ResolverConstEvalArrayAccessTest, Test) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto& param = GetParam();
auto* expr = param.input.Expr(*this);
@@ -338,7 +338,7 @@
using ResolverConstEvalVectorAccessTest = ResolverTestWithParam<Case>;
TEST_P(ResolverConstEvalVectorAccessTest, Test) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto& param = GetParam();
auto* expr = param.input.Expr(*this);
diff --git a/src/tint/resolver/const_eval_unary_op_test.cc b/src/tint/resolver/const_eval_unary_op_test.cc
index f9a1e57..8b9b7c8 100644
--- a/src/tint/resolver/const_eval_unary_op_test.cc
+++ b/src/tint/resolver/const_eval_unary_op_test.cc
@@ -42,7 +42,7 @@
using ResolverConstEvalUnaryOpTest = ResolverTestWithParam<std::tuple<ast::UnaryOp, Case>>;
TEST_P(ResolverConstEvalUnaryOpTest, Test) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto op = std::get<0>(GetParam());
auto& c = std::get<1>(GetParam());
diff --git a/src/tint/resolver/dependency_graph_test.cc b/src/tint/resolver/dependency_graph_test.cc
index 8d61599..31e484e 100644
--- a/src/tint/resolver/dependency_graph_test.cc
+++ b/src/tint/resolver/dependency_graph_test.cc
@@ -1094,7 +1094,7 @@
// a transform may produce such a AST tree that has some declarations before directive nodes.
// DependencyGraph should deal with these cases.
auto* var_1 = GlobalVar("SYMBOL1", ty.i32());
- auto* enable = Enable(ast::Extension::kF16);
+ auto* enable = Enable(builtin::Extension::kF16);
auto* var_2 = GlobalVar("SYMBOL2", ty.f32());
auto* diagnostic = DiagnosticDirective(ast::DiagnosticSeverity::kWarning, "foo");
diff --git a/src/tint/resolver/entry_point_validation_test.cc b/src/tint/resolver/entry_point_validation_test.cc
index ebf2c93..98012ad 100644
--- a/src/tint/resolver/entry_point_validation_test.cc
+++ b/src/tint/resolver/entry_point_validation_test.cc
@@ -455,7 +455,7 @@
TEST_F(ResolverEntryPointValidationTest, PushConstantAllowedWithEnable) {
// enable chromium_experimental_push_constant;
// var<push_constant> a : u32;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar("a", ty.u32(), type::AddressSpace::kPushConstant);
EXPECT_TRUE(r()->Resolve());
@@ -485,7 +485,7 @@
// @compute @workgroup_size(1) fn main() {
// _ = a;
// }
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar("a", ty.u32(), type::AddressSpace::kPushConstant);
Func("main", {}, ty.void_(), utils::Vector{Assign(Phony(), "a")},
@@ -503,7 +503,7 @@
// _ = a;
// _ = b;
// }
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar(Source{{1, 2}}, "a", ty.u32(), type::AddressSpace::kPushConstant);
GlobalVar(Source{{3, 4}}, "b", ty.u32(), type::AddressSpace::kPushConstant);
@@ -534,7 +534,7 @@
// uses_a();
// uses_b();
// }
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar(Source{{1, 2}}, "a", ty.u32(), type::AddressSpace::kPushConstant);
GlobalVar(Source{{3, 4}}, "b", ty.u32(), type::AddressSpace::kPushConstant);
@@ -567,7 +567,7 @@
// @compute @workgroup_size(1) fn uses_b() {
// _ = a;
// }
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar("a", ty.u32(), type::AddressSpace::kPushConstant);
GlobalVar("b", ty.u32(), type::AddressSpace::kPushConstant);
@@ -624,7 +624,7 @@
// fn main(@location(0) @interpolate(flat) a : *) {}
auto params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* a = Param("a", params.create_ast_type(*this),
utils::Vector{
@@ -655,7 +655,7 @@
// fn main(a : Input) {}
auto params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* input = Structure("Input", utils::Vector{
Member("a", params.create_ast_type(*this),
@@ -685,7 +685,7 @@
// }
auto params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Func(Source{{12, 34}}, "main", utils::Empty, params.create_ast_type(*this),
utils::Vector{
@@ -715,7 +715,7 @@
// }
auto params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* output = Structure(
"Output", utils::Vector{
diff --git a/src/tint/resolver/expression_kind_test.cc b/src/tint/resolver/expression_kind_test.cc
index c8cea54..dc3d8a8 100644
--- a/src/tint/resolver/expression_kind_test.cc
+++ b/src/tint/resolver/expression_kind_test.cc
@@ -220,7 +220,7 @@
GlobalVar("v", ty("texture_storage_2d", "rgba8unorm", expr), Group(0_u), Binding(0_u));
break;
case Use::kAddressSpace:
- Enable(ast::Extension::kChromiumExperimentalFullPtrParameters);
+ Enable(builtin::Extension::kChromiumExperimentalFullPtrParameters);
Func("f", utils::Vector{Param("p", ty("ptr", expr, ty.f32()))}, ty.void_(),
utils::Empty);
break;
diff --git a/src/tint/resolver/f16_extension_test.cc b/src/tint/resolver/f16_extension_test.cc
index f0d515f..d767919 100644
--- a/src/tint/resolver/f16_extension_test.cc
+++ b/src/tint/resolver/f16_extension_test.cc
@@ -27,7 +27,7 @@
TEST_F(ResolverF16ExtensionTest, TypeUsedWithExtension) {
// enable f16;
// var<private> v : f16;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("v", ty.f16(), type::AddressSpace::kPrivate);
@@ -45,7 +45,7 @@
TEST_F(ResolverF16ExtensionTest, Vec2TypeUsedWithExtension) {
// enable f16;
// var<private> v : vec2<f16>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("v", ty.vec2<f16>(), type::AddressSpace::kPrivate);
@@ -63,7 +63,7 @@
TEST_F(ResolverF16ExtensionTest, Vec2TypeInitUsedWithExtension) {
// enable f16;
// var<private> v = vec2<f16>();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("v", vec2<f16>(), type::AddressSpace::kPrivate);
@@ -81,7 +81,7 @@
TEST_F(ResolverF16ExtensionTest, Vec2TypeConvUsedWithExtension) {
// enable f16;
// var<private> v = vec2<f16>(vec2<f32>());
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("v", vec2<f16>(vec2<f32>()), type::AddressSpace::kPrivate);
@@ -99,7 +99,7 @@
TEST_F(ResolverF16ExtensionTest, F16LiteralUsedWithExtension) {
// enable f16;
// var<private> v = 16h;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("v", Expr(16_h), type::AddressSpace::kPrivate);
@@ -119,7 +119,7 @@
TEST_P(ResolverF16ExtensionBuiltinTypeAliasTest, Vec2hTypeUsedWithExtension) {
// enable f16;
// var<private> v : vec2h;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("v", ty(Source{{12, 34}}, GetParam()), type::AddressSpace::kPrivate);
diff --git a/src/tint/resolver/function_validation_test.cc b/src/tint/resolver/function_validation_test.cc
index 961511d..7ef446a 100644
--- a/src/tint/resolver/function_validation_test.cc
+++ b/src/tint/resolver/function_validation_test.cc
@@ -1081,7 +1081,7 @@
auto& param = GetParam();
auto ptr_type = ty("ptr", Ident(Source{{12, 34}}, param.address_space), ty.i32());
auto* arg = Param(Source{{12, 34}}, "p", ptr_type);
- Enable(ast::Extension::kChromiumExperimentalFullPtrParameters);
+ Enable(builtin::Extension::kChromiumExperimentalFullPtrParameters);
Func("f", utils::Vector{arg}, ty.void_(), utils::Empty);
if (param.expectation == Expectation::kAlwaysPass ||
diff --git a/src/tint/resolver/host_shareable_validation_test.cc b/src/tint/resolver/host_shareable_validation_test.cc
index f6991358..b518b57 100644
--- a/src/tint/resolver/host_shareable_validation_test.cc
+++ b/src/tint/resolver/host_shareable_validation_test.cc
@@ -97,7 +97,7 @@
}
TEST_F(ResolverHostShareableValidationTest, NoError) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* i1 = Structure("I1", utils::Vector{
Member(Source{{1, 1}}, "w1", ty.f32()),
diff --git a/src/tint/resolver/materialize_test.cc b/src/tint/resolver/materialize_test.cc
index acd69a8..4824549 100644
--- a/src/tint/resolver/materialize_test.cc
+++ b/src/tint/resolver/materialize_test.cc
@@ -312,7 +312,7 @@
MaterializeTest<std::tuple<Expectation, Method, Data>>;
TEST_P(MaterializeAbstractNumericToConcreteType, Test) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
const auto& param = GetParam();
const auto& expectation = std::get<0>(param);
@@ -1282,7 +1282,7 @@
TEST_F(MaterializeAbstractStructure, Modf_Scalar_ExplicitType) {
// var v = modf(1_h); // v is __modf_result_f16
// v = modf(1); // __modf_result_f16 <- __modf_result_abstract
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("modf", 1_a);
WrapInFunction(Decl(Var("v", Call("modf", 1_h))), //
Assign("v", call));
@@ -1301,7 +1301,7 @@
TEST_F(MaterializeAbstractStructure, Modf_Vector_ExplicitType) {
// var v = modf(vec2(1_h)); // v is __modf_result_vec2_f16
// v = modf(vec2(1)); // __modf_result_vec2_f16 <- __modf_result_vec2_abstract
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("modf", Call(ty.vec2<Infer>(), 1_a));
WrapInFunction(Decl(Var("v", Call("modf", Call(ty.vec2<Infer>(), 1_h)))), Assign("v", call));
ASSERT_TRUE(r()->Resolve()) << r()->error();
@@ -1363,7 +1363,7 @@
TEST_F(MaterializeAbstractStructure, Frexp_Scalar_ExplicitType) {
// var v = frexp(1_h); // v is __frexp_result_f16
// v = frexp(1); // __frexp_result_f16 <- __frexp_result_abstract
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("frexp", 1_a);
WrapInFunction(Decl(Var("v", Call("frexp", 1_h))), //
Assign("v", call));
@@ -1384,7 +1384,7 @@
TEST_F(MaterializeAbstractStructure, Frexp_Vector_ExplicitType) {
// var v = frexp(vec2(1_h)); // v is __frexp_result_vec2_f16
// v = frexp(vec2(1)); // __frexp_result_vec2_f16 <- __frexp_result_vec2_abstract
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* call = Call("frexp", Call(ty.vec2<Infer>(), 1_a));
WrapInFunction(Decl(Var("v", Call("frexp", Call(ty.vec2<Infer>(), 1_h)))), Assign("v", call));
ASSERT_TRUE(r()->Resolve()) << r()->error();
diff --git a/src/tint/resolver/override_test.cc b/src/tint/resolver/override_test.cc
index 2fd48ed..a9518d2 100644
--- a/src/tint/resolver/override_test.cc
+++ b/src/tint/resolver/override_test.cc
@@ -103,7 +103,7 @@
}
TEST_F(ResolverOverrideTest, F16_TemporallyBan) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Override(Source{{12, 34}}, "a", ty.f16(), Expr(1_h), Id(1_u));
diff --git a/src/tint/resolver/resolver.cc b/src/tint/resolver/resolver.cc
index 352c5e4..8c36ad7 100644
--- a/src/tint/resolver/resolver.cc
+++ b/src/tint/resolver/resolver.cc
@@ -143,7 +143,7 @@
if (result) {
// Run the uniformity analysis, which requires a complete semantic module.
- if (!enabled_extensions_.Contains(ast::Extension::kChromiumDisableUniformityAnalysis)) {
+ if (!enabled_extensions_.Contains(builtin::Extension::kChromiumDisableUniformityAnalysis)) {
if (!AnalyzeUniformity(builder_, dependencies_)) {
return false;
}
diff --git a/src/tint/resolver/resolver.h b/src/tint/resolver/resolver.h
index c5223db..003fa3d 100644
--- a/src/tint/resolver/resolver.h
+++ b/src/tint/resolver/resolver.h
@@ -501,7 +501,7 @@
DependencyGraph dependencies_;
SemHelper sem_;
Validator validator_;
- ast::Extensions enabled_extensions_;
+ builtin::Extensions enabled_extensions_;
utils::Vector<sem::Function*, 8> entry_points_;
utils::Hashmap<const type::Type*, const Source*, 8> atomic_composite_info_;
utils::Bitset<0> marked_;
diff --git a/src/tint/resolver/side_effects_test.cc b/src/tint/resolver/side_effects_test.cc
index b4770e4..456b371 100644
--- a/src/tint/resolver/side_effects_test.cc
+++ b/src/tint/resolver/side_effects_test.cc
@@ -15,6 +15,7 @@
#include "src/tint/resolver/resolver.h"
#include "gtest/gtest.h"
+#include "src/tint/builtin/extension.h"
#include "src/tint/resolver/resolver_test_helper.h"
#include "src/tint/sem/index_accessor_expression.h"
#include "src/tint/sem/member_accessor_expression.h"
@@ -160,7 +161,7 @@
using SideEffectsBuiltinTest = resolver::ResolverTestWithParam<Case>;
TEST_P(SideEffectsBuiltinTest, Test) {
- Enable(ast::Extension::kChromiumExperimentalDp4A);
+ Enable(tint::builtin::Extension::kChromiumExperimentalDp4A);
auto& c = GetParam();
uint32_t next_binding = 0;
diff --git a/src/tint/resolver/struct_layout_test.cc b/src/tint/resolver/struct_layout_test.cc
index 7288449..33f7599 100644
--- a/src/tint/resolver/struct_layout_test.cc
+++ b/src/tint/resolver/struct_layout_test.cc
@@ -55,7 +55,7 @@
}
TEST_F(ResolverStructLayoutTest, ScalarsWithF16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* s = Structure("S", utils::Vector{
Member("a", ty.f32()),
@@ -134,7 +134,7 @@
}
TEST_F(ResolverStructLayoutTest, ImplicitStrideArrayStaticSize) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* s = Structure("S", utils::Vector{
Member("a", ty.array<i32, 3>()),
@@ -174,7 +174,7 @@
}
TEST_F(ResolverStructLayoutTest, ExplicitStrideArrayStaticSize) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* s = Structure("S", utils::Vector{
Member("a", ty.array<i32, 3>(utils::Vector{Stride(8)})),
@@ -335,7 +335,7 @@
}
TEST_F(ResolverStructLayoutTest, Matrix) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* s = Structure("S", utils::Vector{
Member("a_1", ty.mat2x2<f32>()),
diff --git a/src/tint/resolver/type_initializer_validation_test.cc b/src/tint/resolver/type_initializer_validation_test.cc
index 0f7144b..dde1a2e 100644
--- a/src/tint/resolver/type_initializer_validation_test.cc
+++ b/src/tint/resolver/type_initializer_validation_test.cc
@@ -85,7 +85,7 @@
// }
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* initializer_expr = params.create_rhs_ast_value(*this, 0);
@@ -186,7 +186,7 @@
// }
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Func("foo", utils::Empty, params.create_rhs_ast_type(*this),
utils::Vector{Return(Call(params.create_rhs_ast_type(*this)))}, {});
@@ -343,7 +343,7 @@
TEST_P(ConversionInitializerValidTest, All) {
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
// var a : <lhs_type1> = <lhs_type2>(<rhs_type>(<rhs_value_expr>));
auto lhs_type1 = params.lhs_type(*this);
@@ -449,7 +449,7 @@
<< FriendlyName(rhs_type) << "(<rhs value expr>))";
SCOPED_TRACE(ss.str());
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* a = Var("a", lhs_type1, Call(lhs_type2, Call(rhs_type, rhs_value_expr)));
@@ -944,7 +944,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, F16_Success) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = Call<f16>(Expr(1.5_h));
WrapInFunction(expr);
@@ -1000,7 +1000,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, Convert_u32_to_f16_Success) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = Call<f16>(123_u);
WrapInFunction(expr);
@@ -1020,7 +1020,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, Convert_f16_to_f32_Success) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = Call<f32>(123_h);
WrapInFunction(expr);
@@ -1052,7 +1052,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, Vec2F16_Error_ScalarArgumentTypeMismatch) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec2<f16>(Source{{12, 34}}, 1_h, 2_f));
@@ -1175,7 +1175,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, Vec2F16_Success_Scalar) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* tc = vec2<f16>(1_h, 1_h);
WrapInFunction(tc);
@@ -1309,7 +1309,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, Vec3F16_Error_ScalarArgumentTypeMismatch) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>(Source{{12, 34}}, 1_h, 2_h, 3_f));
@@ -1451,7 +1451,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, Vec3F16_Success_Scalar) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* tc = vec3<f16>(1_h, 1_h, 1_h);
WrapInFunction(tc);
@@ -1632,7 +1632,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, Vec4F16_Error_ScalarArgumentTypeMismatch) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec4<f16>(Source{{12, 34}}, 1_h, 1_h, 1_f, 1_h));
@@ -1799,7 +1799,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, Vec4F16_Success_Scalar) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* tc = vec4<f16>(1_h, 1_h, 1_h, 1_h);
WrapInFunction(tc);
@@ -2035,7 +2035,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, InferVec2ElementTypeFromScalars) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec2_bool = vec2<Infer>(true, false);
auto* vec2_i32 = vec2<Infer>(1_i, 2_i);
@@ -2064,7 +2064,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, InferVec2ElementTypeFromVec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec2_bool = vec2<Infer>(vec2<bool>(true, false));
auto* vec2_i32 = vec2<Infer>(vec2<i32>(1_i, 2_i));
@@ -2093,7 +2093,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, InferVec3ElementTypeFromScalars) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec3_bool = vec3<Infer>(Expr(true), Expr(false), Expr(true));
auto* vec3_i32 = vec3<Infer>(Expr(1_i), Expr(2_i), Expr(3_i));
@@ -2122,7 +2122,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, InferVec3ElementTypeFromVec3) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec3_bool = vec3<Infer>(vec3<bool>(true, false, true));
auto* vec3_i32 = vec3<Infer>(vec3<i32>(1_i, 2_i, 3_i));
@@ -2151,7 +2151,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, InferVec3ElementTypeFromScalarAndVec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec3_bool = vec3<Infer>(Expr(true), vec2<bool>(false, true));
auto* vec3_i32 = vec3<Infer>(Expr(1_i), vec2<i32>(2_i, 3_i));
@@ -2180,7 +2180,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, InferVec4ElementTypeFromScalars) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec4_bool = vec4<Infer>(Expr(true), Expr(false), Expr(true), Expr(false));
auto* vec4_i32 = vec4<Infer>(Expr(1_i), Expr(2_i), Expr(3_i), Expr(4_i));
@@ -2209,7 +2209,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, InferVec4ElementTypeFromVec4) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec4_bool = vec4<Infer>(vec4<bool>(true, false, true, false));
auto* vec4_i32 = vec4<Infer>(vec4<i32>(1_i, 2_i, 3_i, 4_i));
@@ -2238,7 +2238,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, InferVec4ElementTypeFromScalarAndVec3) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec4_bool = vec4<Infer>(Expr(true), vec3<bool>(false, true, false));
auto* vec4_i32 = vec4<Infer>(Expr(1_i), vec3<i32>(2_i, 3_i, 4_i));
@@ -2267,7 +2267,7 @@
}
TEST_F(ResolverTypeInitializerValidationTest, InferVec4ElementTypeFromVec2AndVec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec4_bool = vec4<Infer>(vec2<bool>(true, false), vec2<bool>(true, false));
auto* vec4_i32 = vec4<Infer>(vec2<i32>(1_i, 2_i), vec2<i32>(3_i, 4_i));
@@ -2406,7 +2406,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
const std::string element_type_name = param.get_element_type_name();
std::stringstream args_tys;
@@ -2435,7 +2435,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
const std::string element_type_name = param.get_element_type_name();
std::stringstream args_tys;
@@ -2463,7 +2463,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
const std::string element_type_name = param.get_element_type_name();
std::stringstream args_tys;
@@ -2492,7 +2492,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
const std::string element_type_name = param.get_element_type_name();
std::stringstream args_tys;
@@ -2520,7 +2520,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
std::stringstream args_tys;
utils::Vector<const ast::Expression*, 8> args;
@@ -2548,7 +2548,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
std::stringstream args_tys;
utils::Vector<const ast::Expression*, 8> args;
@@ -2580,7 +2580,7 @@
return;
}
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
const std::string element_type_name = param.get_element_type_name();
std::stringstream args_tys;
@@ -2618,7 +2618,7 @@
return;
}
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
const std::string element_type_name = param.get_element_type_name();
std::stringstream args_tys;
@@ -2650,7 +2650,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
ast::Type matrix_type = param.create_mat_ast_type(*this);
auto* tc = Call(Source{{12, 40}}, matrix_type);
@@ -2665,7 +2665,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
utils::Vector<const ast::Expression*, 4> args;
for (uint32_t i = 0; i < param.columns; i++) {
@@ -2686,7 +2686,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
utils::Vector<const ast::Expression*, 16> args;
for (uint32_t i = 0; i < param.columns * param.rows; i++) {
@@ -2706,7 +2706,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* elem_type_alias = Alias("ElemType", param.create_element_ast_type(*this));
@@ -2736,7 +2736,7 @@
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* elem_type_alias = Alias("ElemType", param.create_element_ast_type(*this));
@@ -2767,7 +2767,7 @@
TEST_P(MatrixInitializerTest, ArgumentTypeAlias_Success) {
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
ast::Type matrix_type = param.create_mat_ast_type(*this);
ast::Type vec_type = param.create_column_ast_type(*this);
@@ -2787,7 +2787,7 @@
TEST_P(MatrixInitializerTest, ArgumentElementTypeAlias_Error) {
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
ast::Type matrix_type = param.create_mat_ast_type(*this);
auto* u32_type_alias = Alias("UnsignedInt", ty.u32());
@@ -2814,7 +2814,7 @@
TEST_P(MatrixInitializerTest, ArgumentElementTypeAlias_Success) {
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* elem_type_alias = Alias("ElemType", param.create_element_ast_type(*this));
@@ -2834,7 +2834,7 @@
TEST_P(MatrixInitializerTest, InferElementTypeFromVectors) {
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
utils::Vector<const ast::Expression*, 8> args;
for (uint32_t i = 0; i < param.columns; i++) {
@@ -2851,7 +2851,7 @@
TEST_P(MatrixInitializerTest, InferElementTypeFromScalars) {
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
utils::Vector<const ast::Expression*, 8> args;
for (uint32_t i = 0; i < param.rows * param.columns; i++) {
@@ -2867,7 +2867,7 @@
TEST_P(MatrixInitializerTest, CannotInferElementTypeFromVectors_Mismatch) {
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
std::stringstream err;
err << "12:34 error: no matching initializer for mat" << param.columns << "x" << param.rows
@@ -2898,7 +2898,7 @@
TEST_P(MatrixInitializerTest, CannotInferElementTypeFromScalars_Mismatch) {
const auto param = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
std::stringstream err;
err << "12:34 error: no matching initializer for mat" << param.columns << "x" << param.rows
@@ -2988,7 +2988,7 @@
auto& str_params = std::get<0>(param);
uint32_t N = std::get<1>(param);
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
utils::Vector<const ast::StructMember*, 16> members;
utils::Vector<const ast::Expression*, 16> values;
@@ -3013,7 +3013,7 @@
auto& str_params = std::get<0>(param);
uint32_t N = std::get<1>(param);
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
utils::Vector<const ast::StructMember*, 16> members;
utils::Vector<const ast::Expression*, 8> values;
@@ -3046,7 +3046,7 @@
auto& ctor_params = std::get<1>(param);
uint32_t N = std::get<2>(param);
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
if (str_params.ast == ctor_params.ast) {
return;
diff --git a/src/tint/resolver/type_validation_test.cc b/src/tint/resolver/type_validation_test.cc
index 0e69da8..efc55f0 100644
--- a/src/tint/resolver/type_validation_test.cc
+++ b/src/tint/resolver/type_validation_test.cc
@@ -1005,7 +1005,7 @@
using SampledTextureTypeTest = ResolverTestWithParam<TypeParams>;
TEST_P(SampledTextureTypeTest, All) {
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar(
"a",
ty.sampled_texture(Source{{12, 34}}, type::TextureDimension::k2d, params.type_func(*this)),
@@ -1025,7 +1025,7 @@
using MultisampledTextureTypeTest = ResolverTestWithParam<TypeParams>;
TEST_P(MultisampledTextureTypeTest, All) {
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a",
ty.multisampled_texture(Source{{12, 34}}, type::TextureDimension::k2d,
params.type_func(*this)),
@@ -1231,7 +1231,7 @@
// var a : matNxM<EL_TY>;
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
ast::Type el_ty = params.elem_ty(*this);
@@ -1271,7 +1271,7 @@
// var a : matNxM<EL_TY>;
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
ast::Type el_ty = params.elem_ty(*this);
@@ -1316,7 +1316,7 @@
// var a : vecN<EL_TY>;
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a", ty.vec(params.elem_ty(*this), params.width), type::AddressSpace::kPrivate);
EXPECT_TRUE(r()->Resolve()) << r()->error();
@@ -1350,7 +1350,7 @@
// var a : vecN<EL_TY>;
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a", ty.vec(Source{{12, 34}}, params.elem_ty(*this), params.width),
type::AddressSpace::kPrivate);
@@ -1389,7 +1389,7 @@
// explicit = aliased;
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Var("aliased", ty(params.alias))),
Decl(Var("explicit", params.type(*this))), //
@@ -1401,7 +1401,7 @@
// var v : vecN<T> = vecTN();
auto& params = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Var("v", params.type(*this), Call(params.alias))));
EXPECT_TRUE(r()->Resolve()) << r()->error();
@@ -1449,7 +1449,7 @@
// enable f16;
// var<private> v : f32<true>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("v", type::AddressSpace::kPrivate, ty(Source{{12, 34}}, GetParam(), true));
EXPECT_FALSE(r()->Resolve());
@@ -1462,7 +1462,7 @@
// alias A = f32;
// var<private> v : A<true>;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Alias(Source{{56, 78}}, "A", ty(GetParam()));
GlobalVar("v", type::AddressSpace::kPrivate, ty(Source{{12, 34}}, "A", true));
diff --git a/src/tint/resolver/validator.cc b/src/tint/resolver/validator.cc
index 2a73bea..44d6c5b 100644
--- a/src/tint/resolver/validator.cc
+++ b/src/tint/resolver/validator.cc
@@ -149,7 +149,7 @@
Validator::Validator(
ProgramBuilder* builder,
SemHelper& sem,
- const ast::Extensions& enabled_extensions,
+ const builtin::Extensions& enabled_extensions,
const utils::Hashmap<const type::Type*, const Source*, 8>& atomic_composite_info,
utils::Hashset<TypeAndAddressSpace, 8>& valid_type_storage_layouts)
: symbols_(builder->Symbols()),
@@ -829,7 +829,7 @@
case type::AddressSpace::kUniform:
case type::AddressSpace::kWorkgroup:
ok = enabled_extensions_.Contains(
- ast::Extension::kChromiumExperimentalFullPtrParameters);
+ builtin::Extension::kChromiumExperimentalFullPtrParameters);
break;
default:
break;
@@ -1653,7 +1653,7 @@
}
const auto extension = builtin->RequiredExtension();
- if (extension == ast::Extension::kUndefined) {
+ if (extension == builtin::Extension::kUndefined) {
return true;
}
@@ -1669,7 +1669,7 @@
bool Validator::CheckF16Enabled(const Source& source) const {
// Validate if f16 type is allowed.
- if (!enabled_extensions_.Contains(ast::Extension::kF16)) {
+ if (!enabled_extensions_.Contains(builtin::Extension::kF16)) {
AddError("f16 type used without 'f16' extension enabled", source);
return false;
}
@@ -1719,7 +1719,8 @@
}
if (param_type->Is<type::Pointer>() &&
- !enabled_extensions_.Contains(ast::Extension::kChromiumExperimentalFullPtrParameters)) {
+ !enabled_extensions_.Contains(
+ builtin::Extension::kChromiumExperimentalFullPtrParameters)) {
// https://gpuweb.github.io/gpuweb/wgsl/#function-restriction
// Each argument of pointer type to a user-defined function must have the same memory
// view as its root identifier.
@@ -2512,7 +2513,7 @@
}
if (address_space == type::AddressSpace::kPushConstant &&
- !enabled_extensions_.Contains(ast::Extension::kChromiumExperimentalPushConstant) &&
+ !enabled_extensions_.Contains(builtin::Extension::kChromiumExperimentalPushConstant) &&
IsValidationEnabled(attributes, ast::DisabledValidation::kIgnoreAddressSpace)) {
AddError(
"use of variable address space 'push_constant' requires enabling extension "
diff --git a/src/tint/resolver/validator.h b/src/tint/resolver/validator.h
index dc1bea6..499dcda 100644
--- a/src/tint/resolver/validator.h
+++ b/src/tint/resolver/validator.h
@@ -102,7 +102,7 @@
/// @param valid_type_storage_layouts a set of validated type layouts by address space
Validator(ProgramBuilder* builder,
SemHelper& helper,
- const ast::Extensions& enabled_extensions,
+ const builtin::Extensions& enabled_extensions,
const utils::Hashmap<const type::Type*, const Source*, 8>& atomic_composite_info,
utils::Hashset<TypeAndAddressSpace, 8>& valid_type_storage_layouts);
~Validator();
@@ -550,7 +550,7 @@
diag::List& diagnostics_;
SemHelper& sem_;
DiagnosticFilterStack diagnostic_filters_;
- const ast::Extensions& enabled_extensions_;
+ const builtin::Extensions& enabled_extensions_;
const utils::Hashmap<const type::Type*, const Source*, 8>& atomic_composite_info_;
utils::Hashset<TypeAndAddressSpace, 8>& valid_type_storage_layouts_;
};
diff --git a/src/tint/resolver/variable_test.cc b/src/tint/resolver/variable_test.cc
index c5af49c..2239945 100644
--- a/src/tint/resolver/variable_test.cc
+++ b/src/tint/resolver/variable_test.cc
@@ -41,7 +41,7 @@
// var a : A;
// }
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* S = Structure("S", utils::Vector{Member("i", ty.i32())});
auto* A = Alias("A", ty.Of(S));
@@ -106,7 +106,7 @@
// var a : A = A(1);
// }
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* S = Structure("S", utils::Vector{Member("i", ty.i32())});
auto* A = Alias("A", ty.Of(S));
@@ -399,7 +399,7 @@
// let p : pointer<function, i32> = &v;
// }
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* S = Structure("S", utils::Vector{Member("i", ty.i32())});
auto* A = Alias("A", ty.Of(S));
diff --git a/src/tint/resolver/variable_validation_test.cc b/src/tint/resolver/variable_validation_test.cc
index 2649562..738d926 100644
--- a/src/tint/resolver/variable_validation_test.cc
+++ b/src/tint/resolver/variable_validation_test.cc
@@ -488,7 +488,7 @@
TEST_F(ResolverVariableValidationTest, GlobalVariable_PushConstantWithInitializer) {
// enable chromium_experimental_push_constant;
// var<push_constant> a : u32 = 0u;
- Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ Enable(builtin::Extension::kChromiumExperimentalPushConstant);
GlobalVar(Source{{1u, 2u}}, "a", ty.u32(), type::AddressSpace::kPushConstant,
Expr(Source{{3u, 4u}}, u32(0)));
