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/BUILD.gn b/src/tint/BUILD.gn
index d54b930..10358f0 100644
--- a/src/tint/BUILD.gn
+++ b/src/tint/BUILD.gn
@@ -277,6 +277,7 @@
deps = [
":libtint_ast_hdrs",
":libtint_base_src",
+ ":libtint_builtins_src",
":libtint_constant_src",
":libtint_sem_src",
":libtint_text_src",
@@ -310,6 +311,7 @@
deps = [
":libtint_ast_src",
":libtint_base_src",
+ ":libtint_builtins_src",
":libtint_program_src",
":libtint_sem_src",
":libtint_type_src",
@@ -468,7 +470,6 @@
"ast/discard_statement.h",
"ast/enable.h",
"ast/expression.h",
- "ast/extension.h",
"ast/float_literal_expression.h",
"ast/for_loop_statement.h",
"ast/function.h",
@@ -554,7 +555,6 @@
"ast/discard_statement.cc",
"ast/enable.cc",
"ast/expression.cc",
- "ast/extension.cc",
"ast/float_literal_expression.cc",
"ast/for_loop_statement.cc",
"ast/function.cc",
@@ -685,6 +685,7 @@
deps = [
":libtint_ast_hdrs",
":libtint_base_src",
+ ":libtint_builtins_src",
":libtint_constant_src",
":libtint_type_src",
]
@@ -694,7 +695,10 @@
sources = [
"builtin/builtin_value.cc",
"builtin/builtin_value.h",
+ "builtin/extension.cc",
+ "builtin/extension.h",
]
+ deps = [ ":libtint_base_src" ]
}
libtint_source_set("libtint_type_src") {
@@ -869,6 +873,7 @@
deps = [
":libtint_ast_src",
":libtint_base_src",
+ ":libtint_builtins_src",
":libtint_inspector_src",
":libtint_program_src",
":libtint_sem_src",
@@ -1232,7 +1237,6 @@
"ast/diagnostic_directive_test.cc",
"ast/discard_statement_test.cc",
"ast/enable_test.cc",
- "ast/extension_test.cc",
"ast/float_literal_expression_test.cc",
"ast/for_loop_statement_test.cc",
"ast/function_test.cc",
@@ -1282,7 +1286,10 @@
}
tint_unittests_source_set("tint_unittests_builtins_src") {
- sources = [ "builtin/builtin_value_test.cc" ]
+ sources = [
+ "builtin/builtin_value_test.cc",
+ "builtin/extension_test.cc",
+ ]
deps = [ ":libtint_builtins_src" ]
}
@@ -1373,6 +1380,7 @@
]
deps = [
":libtint_base_src",
+ ":libtint_builtins_src",
":libtint_transform_src",
":tint_unittests_ast_src",
]
diff --git a/src/tint/CMakeLists.txt b/src/tint/CMakeLists.txt
index 385e906..bdaf2f4 100644
--- a/src/tint/CMakeLists.txt
+++ b/src/tint/CMakeLists.txt
@@ -549,8 +549,8 @@
)
tint_generated(builtin/builtin_value BENCH TEST)
+tint_generated(builtin/extension BENCH TEST)
tint_generated(ast/diagnostic_control BENCH TEST)
-tint_generated(ast/extension BENCH TEST)
tint_generated(ast/interpolate_attribute BENCH TEST)
tint_generated(resolver/init_conv_intrinsic)
tint_generated(sem/builtin_type)
diff --git a/src/tint/ast/enable.cc b/src/tint/ast/enable.cc
index 896b019..6087a3e 100644
--- a/src/tint/ast/enable.cc
+++ b/src/tint/ast/enable.cc
@@ -20,7 +20,7 @@
namespace tint::ast {
-Enable::Enable(ProgramID pid, NodeID nid, const Source& src, Extension ext)
+Enable::Enable(ProgramID pid, NodeID nid, const Source& src, builtin::Extension ext)
: Base(pid, nid, src), extension(ext) {}
Enable::Enable(Enable&&) = default;
diff --git a/src/tint/ast/enable.h b/src/tint/ast/enable.h
index 4c27113..0c64df9 100644
--- a/src/tint/ast/enable.h
+++ b/src/tint/ast/enable.h
@@ -19,8 +19,8 @@
#include <utility>
#include <vector>
-#include "src/tint/ast/extension.h"
#include "src/tint/ast/node.h"
+#include "src/tint/builtin/extension.h"
namespace tint::ast {
@@ -36,7 +36,7 @@
/// @param nid the unique node identifier
/// @param src the source of this node
/// @param ext the extension
- Enable(ProgramID pid, NodeID nid, const Source& src, Extension ext);
+ Enable(ProgramID pid, NodeID nid, const Source& src, builtin::Extension ext);
/// Move constructor
Enable(Enable&&);
@@ -49,7 +49,7 @@
const Enable* Clone(CloneContext* ctx) const override;
/// The extension name
- const Extension extension;
+ const builtin::Extension extension;
};
} // namespace tint::ast
diff --git a/src/tint/ast/enable_test.cc b/src/tint/ast/enable_test.cc
index e8b6e5c..9215018 100644
--- a/src/tint/ast/enable_test.cc
+++ b/src/tint/ast/enable_test.cc
@@ -22,12 +22,12 @@
using EnableTest = TestHelper;
TEST_F(EnableTest, Creation) {
- auto* ext = create<ast::Enable>(Source{{{20, 2}, {20, 5}}}, Extension::kF16);
+ auto* ext = create<ast::Enable>(Source{{{20, 2}, {20, 5}}}, builtin::Extension::kF16);
EXPECT_EQ(ext->source.range.begin.line, 20u);
EXPECT_EQ(ext->source.range.begin.column, 2u);
EXPECT_EQ(ext->source.range.end.line, 20u);
EXPECT_EQ(ext->source.range.end.column, 5u);
- EXPECT_EQ(ext->extension, Extension::kF16);
+ EXPECT_EQ(ext->extension, builtin::Extension::kF16);
}
} // namespace
diff --git a/src/tint/ast/module_test.cc b/src/tint/ast/module_test.cc
index cd03781..24faaee 100644
--- a/src/tint/ast/module_test.cc
+++ b/src/tint/ast/module_test.cc
@@ -135,9 +135,9 @@
}
TEST_F(ModuleTest, Directives) {
- auto* enable_1 = Enable(ast::Extension::kF16);
+ auto* enable_1 = Enable(builtin::Extension::kF16);
auto* diagnostic_1 = DiagnosticDirective(DiagnosticSeverity::kWarning, "foo");
- auto* enable_2 = Enable(ast::Extension::kChromiumExperimentalFullPtrParameters);
+ auto* enable_2 = Enable(builtin::Extension::kChromiumExperimentalFullPtrParameters);
auto* diagnostic_2 = DiagnosticDirective(DiagnosticSeverity::kOff, "bar");
this->SetResolveOnBuild(false);
diff --git a/src/tint/ast/extension.cc b/src/tint/builtin/extension.cc
similarity index 94%
rename from src/tint/ast/extension.cc
rename to src/tint/builtin/extension.cc
index 31a8083..3d57867 100644
--- a/src/tint/ast/extension.cc
+++ b/src/tint/builtin/extension.cc
@@ -15,14 +15,14 @@
////////////////////////////////////////////////////////////////////////////////
// File generated by tools/src/cmd/gen
// using the template:
-// src/tint/ast/extension.cc.tmpl
+// src/tint/builtin/extension.cc.tmpl
//
// Do not modify this file directly
////////////////////////////////////////////////////////////////////////////////
-#include "src/tint/ast/extension.h"
+#include "src/tint/builtin/extension.h"
-namespace tint::ast {
+namespace tint::builtin {
/// ParseExtension parses a Extension from a string.
/// @param str the string to parse
@@ -64,4 +64,4 @@
return out << "<unknown>";
}
-} // namespace tint::ast
+} // namespace tint::builtin
diff --git a/src/tint/ast/extension.cc.tmpl b/src/tint/builtin/extension.cc.tmpl
similarity index 84%
rename from src/tint/ast/extension.cc.tmpl
rename to src/tint/builtin/extension.cc.tmpl
index e0f319e..5f00264 100644
--- a/src/tint/ast/extension.cc.tmpl
+++ b/src/tint/builtin/extension.cc.tmpl
@@ -11,12 +11,12 @@
{{- Import "src/tint/templates/enums.tmpl.inc" -}}
{{- $enum := (Sem.Enum "extension") -}}
-#include "src/tint/ast/extension.h"
+#include "src/tint/builtin/extension.h"
-namespace tint::ast {
+namespace tint::builtin {
{{ Eval "ParseEnum" $enum}}
{{ Eval "EnumOStream" $enum}}
-} // namespace tint::ast
+} // namespace tint::builtin
diff --git a/src/tint/ast/extension.h b/src/tint/builtin/extension.h
similarity index 89%
rename from src/tint/ast/extension.h
rename to src/tint/builtin/extension.h
index 062e3fc..f0ebeca 100644
--- a/src/tint/ast/extension.h
+++ b/src/tint/builtin/extension.h
@@ -15,19 +15,19 @@
////////////////////////////////////////////////////////////////////////////////
// File generated by tools/src/cmd/gen
// using the template:
-// src/tint/ast/extension.h.tmpl
+// src/tint/builtin/extension.h.tmpl
//
// Do not modify this file directly
////////////////////////////////////////////////////////////////////////////////
-#ifndef SRC_TINT_AST_EXTENSION_H_
-#define SRC_TINT_AST_EXTENSION_H_
+#ifndef SRC_TINT_BUILTIN_EXTENSION_H_
+#define SRC_TINT_BUILTIN_EXTENSION_H_
#include <ostream>
#include "src/tint/utils/unique_vector.h"
-namespace tint::ast {
+namespace tint::builtin {
/// An enumerator of WGSL extensions
/// @see src/tint/intrinsics.def for extension descriptions
@@ -61,6 +61,6 @@
// A unique vector of extensions
using Extensions = utils::UniqueVector<Extension, 4>;
-} // namespace tint::ast
+} // namespace tint::builtin
-#endif // SRC_TINT_AST_EXTENSION_H_
+#endif // SRC_TINT_BUILTIN_EXTENSION_H_
diff --git a/src/tint/ast/extension.h.tmpl b/src/tint/builtin/extension.h.tmpl
similarity index 81%
rename from src/tint/ast/extension.h.tmpl
rename to src/tint/builtin/extension.h.tmpl
index 29feff9..3051ad44 100644
--- a/src/tint/ast/extension.h.tmpl
+++ b/src/tint/builtin/extension.h.tmpl
@@ -11,14 +11,14 @@
{{- Import "src/tint/templates/enums.tmpl.inc" -}}
{{- $enum := (Sem.Enum "extension") -}}
-#ifndef SRC_TINT_AST_EXTENSION_H_
-#define SRC_TINT_AST_EXTENSION_H_
+#ifndef SRC_TINT_BUILTIN_EXTENSION_H_
+#define SRC_TINT_BUILTIN_EXTENSION_H_
#include <ostream>
#include "src/tint/utils/unique_vector.h"
-namespace tint::ast {
+namespace tint::builtin {
/// An enumerator of WGSL extensions
/// @see src/tint/intrinsics.def for extension descriptions
@@ -27,6 +27,6 @@
// A unique vector of extensions
using Extensions = utils::UniqueVector<Extension, 4>;
-} // namespace tint::ast
+} // namespace tint::builtin
-#endif // SRC_TINT_AST_EXTENSION_H_
+#endif // SRC_TINT_BUILTIN_EXTENSION_H_
diff --git a/src/tint/ast/extension_bench.cc b/src/tint/builtin/extension_bench.cc
similarity index 94%
rename from src/tint/ast/extension_bench.cc
rename to src/tint/builtin/extension_bench.cc
index 3bf35f6..4619ce2 100644
--- a/src/tint/ast/extension_bench.cc
+++ b/src/tint/builtin/extension_bench.cc
@@ -15,18 +15,18 @@
////////////////////////////////////////////////////////////////////////////////
// File generated by tools/src/cmd/gen
// using the template:
-// src/tint/ast/extension_bench.cc.tmpl
+// src/tint/builtin/extension_bench.cc.tmpl
//
// Do not modify this file directly
////////////////////////////////////////////////////////////////////////////////
-#include "src/tint/ast/extension.h"
+#include "src/tint/builtin/extension.h"
#include <array>
#include "benchmark/benchmark.h"
-namespace tint::ast {
+namespace tint::builtin {
namespace {
void ExtensionParser(::benchmark::State& state) {
@@ -78,4 +78,4 @@
BENCHMARK(ExtensionParser);
} // namespace
-} // namespace tint::ast
+} // namespace tint::builtin
diff --git a/src/tint/ast/extension_bench.cc.tmpl b/src/tint/builtin/extension_bench.cc.tmpl
similarity index 86%
rename from src/tint/ast/extension_bench.cc.tmpl
rename to src/tint/builtin/extension_bench.cc.tmpl
index af3dc95..5019b55 100644
--- a/src/tint/ast/extension_bench.cc.tmpl
+++ b/src/tint/builtin/extension_bench.cc.tmpl
@@ -11,16 +11,16 @@
{{- Import "src/tint/templates/enums.tmpl.inc" -}}
{{- $enum := (Sem.Enum "extension") -}}
-#include "src/tint/ast/extension.h"
+#include "src/tint/builtin/extension.h"
#include <array>
#include "benchmark/benchmark.h"
-namespace tint::ast {
+namespace tint::builtin {
namespace {
{{ Eval "BenchmarkParseEnum" $enum }}
} // namespace
-} // namespace tint::ast
+} // namespace tint::builtin
diff --git a/src/tint/ast/extension_test.cc b/src/tint/builtin/extension_test.cc
similarity index 94%
rename from src/tint/ast/extension_test.cc
rename to src/tint/builtin/extension_test.cc
index ea08dcc..01eb1ae 100644
--- a/src/tint/ast/extension_test.cc
+++ b/src/tint/builtin/extension_test.cc
@@ -15,19 +15,20 @@
////////////////////////////////////////////////////////////////////////////////
// File generated by tools/src/cmd/gen
// using the template:
-// src/tint/ast/extension_test.cc.tmpl
+// src/tint/builtin/extension_test.cc.tmpl
//
// Do not modify this file directly
////////////////////////////////////////////////////////////////////////////////
-#include "src/tint/ast/extension.h"
+#include "src/tint/builtin/extension.h"
+
+#include <gtest/gtest.h>
#include <string>
-#include "src/tint/ast/test_helper.h"
#include "src/tint/utils/string.h"
-namespace tint::ast {
+namespace tint::builtin {
namespace {
namespace parse_print_tests {
@@ -92,4 +93,4 @@
} // namespace parse_print_tests
} // namespace
-} // namespace tint::ast
+} // namespace tint::builtin
diff --git a/src/tint/ast/extension_test.cc.tmpl b/src/tint/builtin/extension_test.cc.tmpl
similarity index 83%
rename from src/tint/ast/extension_test.cc.tmpl
rename to src/tint/builtin/extension_test.cc.tmpl
index 8c7a6af..6b735b7 100644
--- a/src/tint/ast/extension_test.cc.tmpl
+++ b/src/tint/builtin/extension_test.cc.tmpl
@@ -11,17 +11,18 @@
{{- Import "src/tint/templates/enums.tmpl.inc" -}}
{{- $enum := (Sem.Enum "extension") -}}
-#include "src/tint/ast/extension.h"
+#include "src/tint/builtin/extension.h"
+
+#include <gtest/gtest.h>
#include <string>
-#include "src/tint/ast/test_helper.h"
#include "src/tint/utils/string.h"
-namespace tint::ast {
+namespace tint::builtin {
namespace {
{{ Eval "TestParsePrintEnum" $enum}}
} // namespace
-} // namespace tint::ast
+} // namespace tint::builtin
diff --git a/src/tint/cmd/main.cc b/src/tint/cmd/main.cc
index 49037a7..cd46885 100644
--- a/src/tint/cmd/main.cc
+++ b/src/tint/cmd/main.cc
@@ -734,7 +734,7 @@
auto enable_list = program->AST().Enables();
bool dxc_require_16bit_types = false;
for (auto enable : enable_list) {
- if (enable->extension == tint::ast::Extension::kF16) {
+ if (enable->extension == tint::builtin::Extension::kF16) {
dxc_require_16bit_types = true;
break;
}
diff --git a/src/tint/inspector/inspector.cc b/src/tint/inspector/inspector.cc
index 2a9c27d..40658db 100644
--- a/src/tint/inspector/inspector.cc
+++ b/src/tint/inspector/inspector.cc
@@ -19,7 +19,6 @@
#include "src/tint/ast/bool_literal_expression.h"
#include "src/tint/ast/call_expression.h"
-#include "src/tint/ast/extension.h"
#include "src/tint/ast/float_literal_expression.h"
#include "src/tint/ast/id_attribute.h"
#include "src/tint/ast/identifier.h"
@@ -29,6 +28,7 @@
#include "src/tint/ast/module.h"
#include "src/tint/ast/override.h"
#include "src/tint/ast/var.h"
+#include "src/tint/builtin/extension.h"
#include "src/tint/sem/call.h"
#include "src/tint/sem/function.h"
#include "src/tint/sem/module.h"
diff --git a/src/tint/inspector/inspector_test.cc b/src/tint/inspector/inspector_test.cc
index c9762a1..743f878 100644
--- a/src/tint/inspector/inspector_test.cc
+++ b/src/tint/inspector/inspector_test.cc
@@ -289,7 +289,7 @@
std::function<ast::Type()> tint_type = GetTypeFunction(component, composition);
if (component == ComponentType::kF16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
}
auto* in_var = Param("in_var", tint_type(),
diff --git a/src/tint/ir/builder_impl_test.cc b/src/tint/ir/builder_impl_test.cc
index 44c2a61..6430c58 100644
--- a/src/tint/ir/builder_impl_test.cc
+++ b/src/tint/ir/builder_impl_test.cc
@@ -1509,7 +1509,7 @@
}
TEST_F(IR_BuilderImplTest, EmitLiteral_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = Expr(1.2_h);
GlobalVar("a", ty.f16(), type::AddressSpace::kPrivate, expr);
diff --git a/src/tint/program_builder.h b/src/tint/program_builder.h
index cc57ed3..0f8a6ed 100644
--- a/src/tint/program_builder.h
+++ b/src/tint/program_builder.h
@@ -42,7 +42,6 @@
#include "src/tint/ast/disable_validation_attribute.h"
#include "src/tint/ast/discard_statement.h"
#include "src/tint/ast/enable.h"
-#include "src/tint/ast/extension.h"
#include "src/tint/ast/float_literal_expression.h"
#include "src/tint/ast/for_loop_statement.h"
#include "src/tint/ast/id_attribute.h"
@@ -74,6 +73,7 @@
#include "src/tint/ast/variable_decl_statement.h"
#include "src/tint/ast/while_statement.h"
#include "src/tint/ast/workgroup_attribute.h"
+#include "src/tint/builtin/extension.h"
#include "src/tint/constant/composite.h"
#include "src/tint/constant/splat.h"
#include "src/tint/constant/value.h"
@@ -2036,7 +2036,7 @@
/// Adds the extension to the list of enable directives at the top of the module.
/// @param ext the extension to enable
/// @return an `ast::Enable` enabling the given extension.
- const ast::Enable* Enable(ast::Extension ext) {
+ const ast::Enable* Enable(builtin::Extension ext) {
auto* enable = create<ast::Enable>(ext);
AST().AddEnable(enable);
return enable;
@@ -2046,7 +2046,7 @@
/// @param source the enable source
/// @param ext the extension to enable
/// @return an `ast::Enable` enabling the given extension.
- const ast::Enable* Enable(const Source& source, ast::Extension ext) {
+ const ast::Enable* Enable(const Source& source, builtin::Extension ext) {
auto* enable = create<ast::Enable>(source, ext);
AST().AddEnable(enable);
return enable;
diff --git a/src/tint/reader/wgsl/parser_impl.cc b/src/tint/reader/wgsl/parser_impl.cc
index 2fe2386..ac166b9 100644
--- a/src/tint/reader/wgsl/parser_impl.cc
+++ b/src/tint/reader/wgsl/parser_impl.cc
@@ -422,14 +422,15 @@
return add_error(t.source(), "enable directives don't take parenthesis");
}
- auto extension = ast::Extension::kUndefined;
+ auto extension = builtin::Extension::kUndefined;
if (t.Is(Token::Type::kF16)) {
// `f16` is a valid extension name and also a keyword
synchronized_ = true;
next();
- extension = ast::Extension::kF16;
+ extension = builtin::Extension::kF16;
} else {
- auto ext = expect_enum("extension", ast::ParseExtension, ast::kExtensionStrings);
+ auto ext =
+ expect_enum("extension", builtin::ParseExtension, builtin::kExtensionStrings);
if (ext.errored) {
return Failure::kErrored;
}
diff --git a/src/tint/reader/wgsl/parser_impl_enable_directive_test.cc b/src/tint/reader/wgsl/parser_impl_enable_directive_test.cc
index 260175d..529bc15 100644
--- a/src/tint/reader/wgsl/parser_impl_enable_directive_test.cc
+++ b/src/tint/reader/wgsl/parser_impl_enable_directive_test.cc
@@ -30,7 +30,7 @@
auto& ast = program.AST();
ASSERT_EQ(ast.Enables().Length(), 1u);
auto* enable = ast.Enables()[0];
- EXPECT_EQ(enable->extension, ast::Extension::kF16);
+ EXPECT_EQ(enable->extension, builtin::Extension::kF16);
ASSERT_EQ(ast.GlobalDeclarations().Length(), 1u);
EXPECT_EQ(ast.GlobalDeclarations()[0], enable);
}
@@ -48,8 +48,8 @@
ASSERT_EQ(ast.Enables().Length(), 2u);
auto* enable_a = ast.Enables()[0];
auto* enable_b = ast.Enables()[1];
- EXPECT_EQ(enable_a->extension, ast::Extension::kF16);
- EXPECT_EQ(enable_b->extension, ast::Extension::kF16);
+ EXPECT_EQ(enable_a->extension, builtin::Extension::kF16);
+ EXPECT_EQ(enable_b->extension, builtin::Extension::kF16);
ASSERT_EQ(ast.GlobalDeclarations().Length(), 2u);
EXPECT_EQ(ast.GlobalDeclarations()[0], enable_a);
EXPECT_EQ(ast.GlobalDeclarations()[1], enable_b);
@@ -168,7 +168,7 @@
// Accept the enable directive although it caused an error
ASSERT_EQ(ast.Enables().Length(), 1u);
auto* enable = ast.Enables()[0];
- EXPECT_EQ(enable->extension, ast::Extension::kF16);
+ EXPECT_EQ(enable->extension, builtin::Extension::kF16);
ASSERT_EQ(ast.GlobalDeclarations().Length(), 2u);
EXPECT_EQ(ast.GlobalDeclarations()[1], enable);
}
@@ -188,7 +188,7 @@
// Accept the enable directive although it cause an error
ASSERT_EQ(ast.Enables().Length(), 1u);
auto* enable = ast.Enables()[0];
- EXPECT_EQ(enable->extension, ast::Extension::kF16);
+ EXPECT_EQ(enable->extension, builtin::Extension::kF16);
ASSERT_EQ(ast.GlobalDeclarations().Length(), 1u);
EXPECT_EQ(ast.GlobalDeclarations()[0], enable);
}
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)));
diff --git a/src/tint/sem/builtin.cc b/src/tint/sem/builtin.cc
index 243e1b7..7d13190 100644
--- a/src/tint/sem/builtin.cc
+++ b/src/tint/sem/builtin.cc
@@ -179,11 +179,11 @@
return false;
}
-ast::Extension Builtin::RequiredExtension() const {
+builtin::Extension Builtin::RequiredExtension() const {
if (IsDP4a()) {
- return ast::Extension::kChromiumExperimentalDp4A;
+ return builtin::Extension::kChromiumExperimentalDp4A;
}
- return ast::Extension::kUndefined;
+ return builtin::Extension::kUndefined;
}
} // namespace tint::sem
diff --git a/src/tint/sem/builtin.h b/src/tint/sem/builtin.h
index a733131..71e5467 100644
--- a/src/tint/sem/builtin.h
+++ b/src/tint/sem/builtin.h
@@ -18,7 +18,7 @@
#include <string>
#include <vector>
-#include "src/tint/ast/extension.h"
+#include "src/tint/builtin/extension.h"
#include "src/tint/sem/builtin_type.h"
#include "src/tint/sem/call_target.h"
#include "src/tint/sem/pipeline_stage_set.h"
@@ -147,8 +147,8 @@
bool HasSideEffects() const;
/// @returns the required extension of this builtin function. Returns
- /// ast::Extension::kNone if no extension is required.
- ast::Extension RequiredExtension() const;
+ /// builtin::Extension::kNone if no extension is required.
+ builtin::Extension RequiredExtension() const;
private:
const BuiltinType type_;
diff --git a/src/tint/sem/module.cc b/src/tint/sem/module.cc
index 38f0ec6..971c7f2 100644
--- a/src/tint/sem/module.cc
+++ b/src/tint/sem/module.cc
@@ -21,7 +21,7 @@
namespace tint::sem {
-Module::Module(utils::VectorRef<const ast::Node*> dep_ordered_decls, ast::Extensions extensions)
+Module::Module(utils::VectorRef<const ast::Node*> dep_ordered_decls, builtin::Extensions extensions)
: dep_ordered_decls_(std::move(dep_ordered_decls)), extensions_(std::move(extensions)) {}
Module::~Module() = default;
diff --git a/src/tint/sem/module.h b/src/tint/sem/module.h
index 21b08f2..6bcd802 100644
--- a/src/tint/sem/module.h
+++ b/src/tint/sem/module.h
@@ -16,7 +16,7 @@
#define SRC_TINT_SEM_MODULE_H_
#include "src/tint/ast/diagnostic_control.h"
-#include "src/tint/ast/extension.h"
+#include "src/tint/builtin/extension.h"
#include "src/tint/sem/node.h"
#include "src/tint/utils/vector.h"
@@ -34,7 +34,7 @@
/// Constructor
/// @param dep_ordered_decls the dependency-ordered module-scope declarations
/// @param extensions the list of enabled extensions in the module
- Module(utils::VectorRef<const ast::Node*> dep_ordered_decls, ast::Extensions extensions);
+ Module(utils::VectorRef<const ast::Node*> dep_ordered_decls, builtin::Extensions extensions);
/// Destructor
~Module() override;
@@ -45,7 +45,7 @@
}
/// @returns the list of enabled extensions in the module
- const ast::Extensions& Extensions() const { return extensions_; }
+ const builtin::Extensions& Extensions() const { return extensions_; }
/// Modifies the severity of a specific diagnostic rule for this module.
/// @param rule the diagnostic rule
@@ -61,7 +61,7 @@
private:
const utils::Vector<const ast::Node*, 64> dep_ordered_decls_;
- ast::Extensions extensions_;
+ builtin::Extensions extensions_;
ast::DiagnosticRuleSeverities diagnostic_severities_;
};
diff --git a/src/tint/transform/builtin_polyfill.cc b/src/tint/transform/builtin_polyfill.cc
index e140fb3..917d418 100644
--- a/src/tint/transform/builtin_polyfill.cc
+++ b/src/tint/transform/builtin_polyfill.cc
@@ -45,7 +45,7 @@
State(CloneContext& c, Builtins p) : ctx(c), polyfill(p) {
has_full_ptr_params = false;
for (auto* enable : c.src->AST().Enables()) {
- if (enable->extension == ast::Extension::kChromiumExperimentalFullPtrParameters) {
+ if (enable->extension == builtin::Extension::kChromiumExperimentalFullPtrParameters) {
has_full_ptr_params = true;
}
}
@@ -673,7 +673,7 @@
/// @return the polyfill function name
Symbol workgroupUniformLoad(const type::Type* type) {
if (!has_full_ptr_params) {
- b.Enable(ast::Extension::kChromiumExperimentalFullPtrParameters);
+ b.Enable(builtin::Extension::kChromiumExperimentalFullPtrParameters);
has_full_ptr_params = true;
}
auto name = b.Symbols().New("tint_workgroupUniformLoad");
diff --git a/src/tint/transform/clamp_frag_depth.cc b/src/tint/transform/clamp_frag_depth.cc
index feacf82..57d9a40 100644
--- a/src/tint/transform/clamp_frag_depth.cc
+++ b/src/tint/transform/clamp_frag_depth.cc
@@ -117,7 +117,7 @@
// fn clamp_frag_depth(v : f32) -> f32 {
// return clamp(v, frag_depth_clamp_args.min, frag_depth_clamp_args.max);
// }
- b.Enable(ast::Extension::kChromiumExperimentalPushConstant);
+ b.Enable(builtin::Extension::kChromiumExperimentalPushConstant);
b.Structure(b.Symbols().New("FragDepthClampArgs"),
utils::Vector{b.Member("min", b.ty.f32()), b.Member("max", b.ty.f32())});
diff --git a/src/tint/transform/direct_variable_access.cc b/src/tint/transform/direct_variable_access.cc
index a8a1272..8ae3e22 100644
--- a/src/tint/transform/direct_variable_access.cc
+++ b/src/tint/transform/direct_variable_access.cc
@@ -203,7 +203,7 @@
/// @returns the ApplyResult
ApplyResult Run() {
if (!ctx.src->Sem().Module()->Extensions().Contains(
- ast::Extension::kChromiumExperimentalFullPtrParameters)) {
+ builtin::Extension::kChromiumExperimentalFullPtrParameters)) {
// If the 'chromium_experimental_full_ptr_parameters' extension is not enabled, then
// there's nothing for this transform to do.
return SkipTransform;
diff --git a/src/tint/transform/disable_uniformity_analysis.cc b/src/tint/transform/disable_uniformity_analysis.cc
index ffd0b18..7c26fb8 100644
--- a/src/tint/transform/disable_uniformity_analysis.cc
+++ b/src/tint/transform/disable_uniformity_analysis.cc
@@ -31,13 +31,13 @@
const DataMap&,
DataMap&) const {
if (src->Sem().Module()->Extensions().Contains(
- ast::Extension::kChromiumDisableUniformityAnalysis)) {
+ builtin::Extension::kChromiumDisableUniformityAnalysis)) {
return SkipTransform;
}
ProgramBuilder b;
CloneContext ctx{&b, src, /* auto_clone_symbols */ true};
- b.Enable(ast::Extension::kChromiumDisableUniformityAnalysis);
+ b.Enable(builtin::Extension::kChromiumDisableUniformityAnalysis);
ctx.Clone();
return Program(std::move(b));
diff --git a/src/tint/transform/preserve_padding.cc b/src/tint/transform/preserve_padding.cc
index 011e5c9..ba30933 100644
--- a/src/tint/transform/preserve_padding.cc
+++ b/src/tint/transform/preserve_padding.cc
@@ -66,7 +66,7 @@
[&](const ast::Enable* enable) {
// Check if the full pointer parameters extension is already enabled.
if (enable->extension ==
- ast::Extension::kChromiumExperimentalFullPtrParameters) {
+ builtin::Extension::kChromiumExperimentalFullPtrParameters) {
ext_enabled = true;
}
});
@@ -197,7 +197,7 @@
/// Enable the full pointer parameters extension, if we have not already done so.
void EnableExtension() {
if (!ext_enabled) {
- b.Enable(ast::Extension::kChromiumExperimentalFullPtrParameters);
+ b.Enable(builtin::Extension::kChromiumExperimentalFullPtrParameters);
ext_enabled = true;
}
}
diff --git a/src/tint/writer/check_supported_extensions.cc b/src/tint/writer/check_supported_extensions.cc
index 3bb16bf..bde86a5 100644
--- a/src/tint/writer/check_supported_extensions.cc
+++ b/src/tint/writer/check_supported_extensions.cc
@@ -26,8 +26,8 @@
bool CheckSupportedExtensions(std::string_view writer_name,
const ast::Module& module,
diag::List& diags,
- utils::VectorRef<ast::Extension> supported) {
- utils::Hashset<ast::Extension, 32> set;
+ utils::VectorRef<builtin::Extension> supported) {
+ utils::Hashset<builtin::Extension, 32> set;
for (auto ext : supported) {
set.Add(ext);
}
diff --git a/src/tint/writer/check_supported_extensions.h b/src/tint/writer/check_supported_extensions.h
index c1884d0..8776102 100644
--- a/src/tint/writer/check_supported_extensions.h
+++ b/src/tint/writer/check_supported_extensions.h
@@ -15,7 +15,7 @@
#ifndef SRC_TINT_WRITER_CHECK_SUPPORTED_EXTENSIONS_H_
#define SRC_TINT_WRITER_CHECK_SUPPORTED_EXTENSIONS_H_
-#include "src/tint/ast/extension.h"
+#include "src/tint/builtin/extension.h"
#include "src/tint/utils/vector.h"
namespace tint::ast {
@@ -36,7 +36,7 @@
bool CheckSupportedExtensions(std::string_view writer_name,
const ast::Module& module,
diag::List& diags,
- utils::VectorRef<ast::Extension> supported);
+ utils::VectorRef<builtin::Extension> supported);
} // namespace tint::writer
diff --git a/src/tint/writer/check_supported_extensions_test.cc b/src/tint/writer/check_supported_extensions_test.cc
index 97c3b32..4d5690b 100644
--- a/src/tint/writer/check_supported_extensions_test.cc
+++ b/src/tint/writer/check_supported_extensions_test.cc
@@ -24,21 +24,21 @@
class CheckSupportedExtensionsTest : public ::testing::Test, public ProgramBuilder {};
TEST_F(CheckSupportedExtensionsTest, Supported) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
ASSERT_TRUE(CheckSupportedExtensions("writer", AST(), Diagnostics(),
utils::Vector{
- ast::Extension::kF16,
- ast::Extension::kChromiumExperimentalDp4A,
+ builtin::Extension::kF16,
+ builtin::Extension::kChromiumExperimentalDp4A,
}));
}
TEST_F(CheckSupportedExtensionsTest, Unsupported) {
- Enable(Source{{12, 34}}, ast::Extension::kF16);
+ Enable(Source{{12, 34}}, builtin::Extension::kF16);
ASSERT_FALSE(CheckSupportedExtensions("writer", AST(), Diagnostics(),
utils::Vector{
- ast::Extension::kChromiumExperimentalDp4A,
+ builtin::Extension::kChromiumExperimentalDp4A,
}));
EXPECT_EQ(Diagnostics().str(), "12:34 error: writer backend does not support extension 'f16'");
}
diff --git a/src/tint/writer/glsl/generator_impl.cc b/src/tint/writer/glsl/generator_impl.cc
index 1ea30d4..a09af2f 100644
--- a/src/tint/writer/glsl/generator_impl.cc
+++ b/src/tint/writer/glsl/generator_impl.cc
@@ -326,7 +326,7 @@
bool GeneratorImpl::RecordExtension(const ast::Enable* ext) {
// Deal with extension node here, recording it within the generator for later emition.
- if (ext->extension == ast::Extension::kF16) {
+ if (ext->extension == builtin::Extension::kF16) {
requires_f16_extension_ = true;
}
diff --git a/src/tint/writer/glsl/generator_impl_binary_test.cc b/src/tint/writer/glsl/generator_impl_binary_test.cc
index 884cba0..72eddc7 100644
--- a/src/tint/writer/glsl/generator_impl_binary_test.cc
+++ b/src/tint/writer/glsl/generator_impl_binary_test.cc
@@ -69,7 +69,7 @@
return;
}
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("left", ty.f16(), type::AddressSpace::kPrivate);
GlobalVar("right", ty.f16(), type::AddressSpace::kPrivate);
@@ -167,7 +167,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, Multiply_VectorScalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a", vec3<f16>(1_h, 1_h, 1_h), type::AddressSpace::kPrivate);
auto* lhs = Expr("a");
@@ -201,7 +201,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, Multiply_ScalarVector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a", vec3<f16>(1_h, 1_h, 1_h), type::AddressSpace::kPrivate);
auto* lhs = Expr(1_h);
@@ -234,7 +234,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, Multiply_MatrixScalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("mat", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
auto* lhs = Expr("mat");
@@ -266,7 +266,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, Multiply_ScalarMatrix_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("mat", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
auto* lhs = Expr(1_h);
@@ -298,7 +298,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, Multiply_MatrixVector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("mat", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
auto* lhs = Expr("mat");
@@ -330,7 +330,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, Multiply_VectorMatrix_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("mat", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
auto* lhs = vec3<f16>(1_h, 1_h, 1_h);
@@ -361,7 +361,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, Multiply_MatrixMatrix_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("lhs", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
GlobalVar("rhs", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
@@ -391,7 +391,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, ModF16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a", ty.f16(), type::AddressSpace::kPrivate);
GlobalVar("b", ty.f16(), type::AddressSpace::kPrivate);
@@ -421,7 +421,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, ModVec3F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a", ty.vec3<f16>(), type::AddressSpace::kPrivate);
GlobalVar("b", ty.vec3<f16>(), type::AddressSpace::kPrivate);
@@ -451,7 +451,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, ModVec3F16ScalarF16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a", ty.vec3<f16>(), type::AddressSpace::kPrivate);
GlobalVar("b", ty.f16(), type::AddressSpace::kPrivate);
@@ -481,7 +481,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, ModScalarF16Vec3F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a", ty.f16(), type::AddressSpace::kPrivate);
GlobalVar("b", ty.vec3<f16>(), type::AddressSpace::kPrivate);
@@ -539,7 +539,7 @@
}
TEST_F(GlslGeneratorImplTest_Binary, ModMixedVec3ScalarF16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a", ty.vec3<f16>(), type::AddressSpace::kPrivate);
GlobalVar("b", ty.f16(), type::AddressSpace::kPrivate);
diff --git a/src/tint/writer/glsl/generator_impl_builtin_test.cc b/src/tint/writer/glsl/generator_impl_builtin_test.cc
index 33d2fa7..7526494 100644
--- a/src/tint/writer/glsl/generator_impl_builtin_test.cc
+++ b/src/tint/writer/glsl/generator_impl_builtin_test.cc
@@ -196,7 +196,7 @@
auto param = GetParam();
if (param.type == CallParamType::kF16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("h2", ty.vec2<f16>(), type::AddressSpace::kPrivate);
GlobalVar("h3", ty.vec3<f16>(), type::AddressSpace::kPrivate);
@@ -399,7 +399,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, FMA_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("a", ty.vec3<f16>(), type::AddressSpace::kPrivate);
GlobalVar("b", ty.vec3<f16>(), type::AddressSpace::kPrivate);
@@ -451,7 +451,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Runtime_Modf_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("f", Expr(1.5_h))), //
Decl(Let("v", Call("modf", "f"))));
@@ -522,7 +522,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Runtime_Modf_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("f", vec3<f16>(1.5_h, 2.5_h, 3.5_h))), //
Decl(Let("v", Call("modf", "f"))));
@@ -585,7 +585,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Const_Modf_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("modf", 1.5_h))));
@@ -640,7 +640,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Const_Modf_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("modf", vec3<f16>(1.5_h, 2.5_h, 3.5_h)))));
@@ -703,7 +703,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Runtime_Frexp_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Var("f", Expr(1_h)), //
Var("v", Call("frexp", "f")));
@@ -774,7 +774,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Runtime_Frexp_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Var("f", Expr(vec3<f16>())), //
Var("v", Call("frexp", "f")));
@@ -837,7 +837,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Const_Frexp_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("frexp", 1_h))));
@@ -892,7 +892,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Const_Frexp_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("frexp", vec3<f16>()))));
@@ -977,7 +977,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Degrees_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.f16());
auto* call = Call("degrees", val);
@@ -1008,7 +1008,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Degrees_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.vec3<f16>());
auto* call = Call("degrees", val);
@@ -1095,7 +1095,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Radians_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.f16());
auto* call = Call("radians", val);
@@ -1126,7 +1126,7 @@
}
TEST_F(GlslGeneratorImplTest_Builtin, Radians_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.vec3<f16>());
auto* call = Call("radians", val);
diff --git a/src/tint/writer/glsl/generator_impl_initializer_test.cc b/src/tint/writer/glsl/generator_impl_initializer_test.cc
index e9c4dc9..d62942d 100644
--- a/src/tint/writer/glsl/generator_impl_initializer_test.cc
+++ b/src/tint/writer/glsl/generator_impl_initializer_test.cc
@@ -62,7 +62,7 @@
}
TEST_F(GlslGeneratorImplTest_Initializer, EmitInitializer_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
// Use a number close to 1<<16 but whose decimal representation ends in 0.
WrapInFunction(Expr(f16((1 << 15) - 8)));
@@ -83,7 +83,7 @@
}
TEST_F(GlslGeneratorImplTest_Initializer, EmitInitializer_Type_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Call<f16>(-1.2e-3_h));
@@ -130,7 +130,7 @@
}
TEST_F(GlslGeneratorImplTest_Initializer, EmitInitializer_Type_Vec_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>(1_h, 2_h, 3_h));
@@ -150,7 +150,7 @@
}
TEST_F(GlslGeneratorImplTest_Initializer, EmitInitializer_Type_Vec_Empty_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>());
@@ -170,7 +170,7 @@
}
TEST_F(GlslGeneratorImplTest_Initializer, EmitInitializer_Type_Vec_SingleScalar_F16_Literal) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>(2_h));
@@ -193,7 +193,7 @@
}
TEST_F(GlslGeneratorImplTest_Initializer, EmitInitializer_Type_Vec_SingleScalar_F16_Var) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("v", Expr(2_h));
auto* cast = vec3<f16>(var);
@@ -244,7 +244,7 @@
}
TEST_F(GlslGeneratorImplTest_Initializer, EmitInitializer_Type_Mat_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(mat2x3<f16>(vec3<f16>(1_h, 2_h, 3_h), vec3<f16>(3_h, 4_h, 5_h)));
@@ -290,7 +290,7 @@
// vec4<f16>(7.0h),
// vec4<f16>(vec4<f16>(42.0h, 21.0h, 6.0h, -5.0h)),
// );
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vector_literal =
vec4<f16>(Expr(f16(2.0)), Expr(f16(3.0)), Expr(f16(4.0)), Expr(f16(8.0)));
@@ -324,7 +324,7 @@
}
TEST_F(GlslGeneratorImplTest_Initializer, EmitInitializer_Type_Mat_Empty_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(mat2x3<f16>());
@@ -360,7 +360,7 @@
// var m_2: mat4x4<f16> = mat4x4<f16>(m_1);
// }
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* m_1 = Var("m_1", ty.mat4x4(ty.f16()), mat4x4<f16>());
auto* m_2 = Var("m_2", ty.mat4x4(ty.f16()), mat4x4<f16>(m_1));
diff --git a/src/tint/writer/glsl/generator_impl_module_constant_test.cc b/src/tint/writer/glsl/generator_impl_module_constant_test.cc
index 9f0985d..dfbcecf 100644
--- a/src/tint/writer/glsl/generator_impl_module_constant_test.cc
+++ b/src/tint/writer/glsl/generator_impl_module_constant_test.cc
@@ -133,7 +133,7 @@
}
TEST_F(GlslGeneratorImplTest_ModuleConstant, Emit_GlobalConst_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalConst("G", Expr(1_h));
Func("f", utils::Empty, ty.void_(),
@@ -216,7 +216,7 @@
}
TEST_F(GlslGeneratorImplTest_ModuleConstant, Emit_GlobalConst_vec3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalConst("G", vec3<f16>(1_h, 2_h, 3_h));
Func("f", utils::Empty, ty.void_(),
@@ -279,7 +279,7 @@
}
TEST_F(GlslGeneratorImplTest_ModuleConstant, Emit_GlobalConst_mat2x3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalConst("G", mat2x3<f16>(1_h, 2_h, 3_h, 4_h, 5_h, 6_h));
Func("f", utils::Empty, ty.void_(),
diff --git a/src/tint/writer/glsl/generator_impl_type_test.cc b/src/tint/writer/glsl/generator_impl_type_test.cc
index 625c7d3..b538979 100644
--- a/src/tint/writer/glsl/generator_impl_type_test.cc
+++ b/src/tint/writer/glsl/generator_impl_type_test.cc
@@ -107,7 +107,7 @@
}
TEST_F(GlslGeneratorImplTest_Type, EmitType_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* f16 = create<type::F16>();
@@ -144,7 +144,7 @@
}
TEST_F(GlslGeneratorImplTest_Type, EmitType_Matrix_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* f16 = create<type::F16>();
auto* vec3 = create<type::Vector>(f16, 3u);
@@ -255,7 +255,7 @@
}
TEST_F(GlslGeneratorImplTest_Type, EmitType_Vector_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* f16 = create<type::F16>();
auto* vec3 = create<type::Vector>(f16, 3u);
diff --git a/src/tint/writer/glsl/generator_impl_variable_decl_statement_test.cc b/src/tint/writer/glsl/generator_impl_variable_decl_statement_test.cc
index 6511179..a4d11cb 100644
--- a/src/tint/writer/glsl/generator_impl_variable_decl_statement_test.cc
+++ b/src/tint/writer/glsl/generator_impl_variable_decl_statement_test.cc
@@ -170,7 +170,7 @@
}
TEST_F(GlslGeneratorImplTest_VariableDecl, Emit_VariableDeclStatement_Const_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", Expr(1_h));
Func("f", utils::Empty, ty.void_(),
@@ -257,7 +257,7 @@
}
TEST_F(GlslGeneratorImplTest_VariableDecl, Emit_VariableDeclStatement_Const_vec3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", vec3<f16>(1_h, 2_h, 3_h));
Func("f", utils::Empty, ty.void_(),
@@ -323,7 +323,7 @@
}
TEST_F(GlslGeneratorImplTest_VariableDecl, Emit_VariableDeclStatement_Const_mat2x3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", mat2x3<f16>(1_h, 2_h, 3_h, 4_h, 5_h, 6_h));
Func("f", utils::Empty, ty.void_(),
@@ -501,7 +501,7 @@
}
TEST_F(GlslGeneratorImplTest_VariableDecl, Emit_VariableDeclStatement_Initializer_ZeroVec_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("a", ty.vec3<f16>(), vec3<f16>());
@@ -530,7 +530,7 @@
}
TEST_F(GlslGeneratorImplTest_VariableDecl, Emit_VariableDeclStatement_Initializer_ZeroMat_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("a", ty.mat2x3<f16>(), mat2x3<f16>());
diff --git a/src/tint/writer/hlsl/generator_impl.cc b/src/tint/writer/hlsl/generator_impl.cc
index ad1d50d..4c036f9 100644
--- a/src/tint/writer/hlsl/generator_impl.cc
+++ b/src/tint/writer/hlsl/generator_impl.cc
@@ -297,11 +297,11 @@
bool GeneratorImpl::Generate() {
if (!CheckSupportedExtensions("HLSL", program_->AST(), diagnostics_,
utils::Vector{
- ast::Extension::kChromiumDisableUniformityAnalysis,
- ast::Extension::kChromiumExperimentalDp4A,
- ast::Extension::kChromiumExperimentalFullPtrParameters,
- ast::Extension::kChromiumExperimentalPushConstant,
- ast::Extension::kF16,
+ builtin::Extension::kChromiumDisableUniformityAnalysis,
+ builtin::Extension::kChromiumExperimentalDp4A,
+ builtin::Extension::kChromiumExperimentalFullPtrParameters,
+ builtin::Extension::kChromiumExperimentalPushConstant,
+ builtin::Extension::kF16,
})) {
return false;
}
diff --git a/src/tint/writer/hlsl/generator_impl_binary_test.cc b/src/tint/writer/hlsl/generator_impl_binary_test.cc
index afc6b8f..325ca67 100644
--- a/src/tint/writer/hlsl/generator_impl_binary_test.cc
+++ b/src/tint/writer/hlsl/generator_impl_binary_test.cc
@@ -80,7 +80,7 @@
return;
}
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("left", ty.f16(), type::AddressSpace::kPrivate);
GlobalVar("right", ty.f16(), type::AddressSpace::kPrivate);
@@ -188,7 +188,7 @@
}
TEST_F(HlslGeneratorImplTest_Binary, Multiply_VectorScalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* lhs = vec3<f16>(1_h, 1_h, 1_h);
auto* rhs = Expr(1_h);
@@ -220,7 +220,7 @@
}
TEST_F(HlslGeneratorImplTest_Binary, Multiply_ScalarVector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* lhs = Expr(1_h);
auto* rhs = vec3<f16>(1_h, 1_h, 1_h);
@@ -252,7 +252,7 @@
}
TEST_F(HlslGeneratorImplTest_Binary, Multiply_MatrixScalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("mat", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
auto* lhs = Expr("mat");
@@ -284,7 +284,7 @@
}
TEST_F(HlslGeneratorImplTest_Binary, Multiply_ScalarMatrix_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("mat", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
auto* lhs = Expr(1_h);
@@ -316,7 +316,7 @@
}
TEST_F(HlslGeneratorImplTest_Binary, Multiply_MatrixVector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("mat", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
auto* lhs = Expr("mat");
@@ -348,7 +348,7 @@
}
TEST_F(HlslGeneratorImplTest_Binary, Multiply_VectorMatrix_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("mat", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
auto* lhs = vec3<f16>(1_h, 1_h, 1_h);
@@ -379,7 +379,7 @@
}
TEST_F(HlslGeneratorImplTest_Binary, Multiply_MatrixMatrix_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("lhs", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
GlobalVar("rhs", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
diff --git a/src/tint/writer/hlsl/generator_impl_builtin_test.cc b/src/tint/writer/hlsl/generator_impl_builtin_test.cc
index d5c4188..9811b79 100644
--- a/src/tint/writer/hlsl/generator_impl_builtin_test.cc
+++ b/src/tint/writer/hlsl/generator_impl_builtin_test.cc
@@ -195,7 +195,7 @@
auto param = GetParam();
if (param.type == CallParamType::kF16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("h2", ty.vec2<f16>(), type::AddressSpace::kPrivate);
GlobalVar("h3", ty.vec3<f16>(), type::AddressSpace::kPrivate);
@@ -405,7 +405,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Runtime_Modf_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("f", Expr(1.5_h))), //
Decl(Let("v", Call("modf", "f"))));
@@ -459,7 +459,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Runtime_Modf_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("f", vec3<f16>(1.5_h, 2.5_h, 3.5_h))), //
Decl(Let("v", Call("modf", "f"))));
@@ -505,7 +505,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Const_Modf_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("modf", 1.5_h))));
@@ -543,7 +543,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Const_Modf_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("modf", vec3<f16>(1.5_h, 2.5_h, 3.5_h)))));
@@ -616,7 +616,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Runtime_Frexp_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Var("f", Expr(1_h)), //
Var("v", Call("frexp", "f")));
@@ -672,7 +672,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Runtime_Frexp_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Var("f", Expr(vec3<f16>())), //
Var("v", Call("frexp", "f")));
@@ -719,7 +719,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Const_Frexp_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("frexp", 1_h))));
@@ -757,7 +757,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Const_Frexp_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("frexp", vec3<f16>()))));
@@ -845,7 +845,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Degrees_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.f16());
auto* call = Call("degrees", val);
@@ -868,7 +868,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Degrees_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.vec3<f16>());
auto* call = Call("degrees", val);
@@ -933,7 +933,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Radians_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.f16());
auto* call = Call("radians", val);
@@ -956,7 +956,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Radians_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.vec3<f16>());
auto* call = Call("radians", val);
@@ -1047,7 +1047,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Sign_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.f16());
auto* call = Call("sign", val);
@@ -1066,7 +1066,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Sign_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.vec3<f16>());
auto* call = Call("sign", val);
@@ -1351,7 +1351,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Dot4I8Packed) {
- Enable(ast::Extension::kChromiumExperimentalDp4A);
+ Enable(builtin::Extension::kChromiumExperimentalDp4A);
auto* val1 = Var("val1", ty.u32());
auto* val2 = Var("val2", ty.u32());
@@ -1377,7 +1377,7 @@
}
TEST_F(HlslGeneratorImplTest_Builtin, Dot4U8Packed) {
- Enable(ast::Extension::kChromiumExperimentalDp4A);
+ Enable(builtin::Extension::kChromiumExperimentalDp4A);
auto* val1 = Var("val1", ty.u32());
auto* val2 = Var("val2", ty.u32());
diff --git a/src/tint/writer/hlsl/generator_impl_initializer_test.cc b/src/tint/writer/hlsl/generator_impl_initializer_test.cc
index 14f8c08..ebc206a 100644
--- a/src/tint/writer/hlsl/generator_impl_initializer_test.cc
+++ b/src/tint/writer/hlsl/generator_impl_initializer_test.cc
@@ -62,7 +62,7 @@
}
TEST_F(HlslGeneratorImplTest_Initializer, EmitInitializer_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
// Use a number close to 1<<16 but whose decimal representation ends in 0.
WrapInFunction(Expr(f16((1 << 15) - 8)));
@@ -83,7 +83,7 @@
}
TEST_F(HlslGeneratorImplTest_Initializer, EmitInitializer_Type_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Call<f16>(-1.2e-3_h));
@@ -130,7 +130,7 @@
}
TEST_F(HlslGeneratorImplTest_Initializer, EmitInitializer_Type_Vec_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>(1_h, 2_h, 3_h));
@@ -152,7 +152,7 @@
}
TEST_F(HlslGeneratorImplTest_Initializer, EmitInitializer_Type_Vec_Empty_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>());
@@ -172,7 +172,7 @@
}
TEST_F(HlslGeneratorImplTest_Initializer, EmitInitializer_Type_Vec_SingleScalar_F16_Literal) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>(2_h));
@@ -195,7 +195,7 @@
}
TEST_F(HlslGeneratorImplTest_Initializer, EmitInitializer_Type_Vec_SingleScalar_F16_Var) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("v", Expr(2_h));
auto* cast = vec3<f16>(var);
@@ -259,7 +259,7 @@
}
TEST_F(HlslGeneratorImplTest_Initializer, EmitInitializer_Type_Mat_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(mat2x3<f16>(vec3<f16>(1_h, 2_h, 3_h), vec3<f16>(3_h, 4_h, 5_h)));
@@ -307,7 +307,7 @@
// vec4<f16>(7.0h),
// vec4<f16>(vec4<f16>(42.0h, 21.0h, 6.0h, -5.0h)),
// );
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vector_literal =
vec4<f16>(Expr(f16(2.0)), Expr(f16(3.0)), Expr(f16(4.0)), Expr(f16(8.0)));
@@ -344,7 +344,7 @@
}
TEST_F(HlslGeneratorImplTest_Initializer, EmitInitializer_Type_Mat_Empty_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(mat2x3<f16>());
@@ -380,7 +380,7 @@
// var m_2: mat4x4<f16> = mat4x4<f16>(m_1);
// }
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* m_1 = Var("m_1", ty.mat4x4(ty.f16()), mat4x4<f16>());
auto* m_2 = Var("m_2", ty.mat4x4(ty.f16()), mat4x4<f16>(m_1));
diff --git a/src/tint/writer/hlsl/generator_impl_member_accessor_test.cc b/src/tint/writer/hlsl/generator_impl_member_accessor_test.cc
index 0bd7ae6..f2607c5 100644
--- a/src/tint/writer/hlsl/generator_impl_member_accessor_test.cc
+++ b/src/tint/writer/hlsl/generator_impl_member_accessor_test.cc
@@ -165,7 +165,7 @@
auto p = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
SetupStorageBuffer(utils::Vector{
Member("a", ty.i32()),
@@ -300,7 +300,7 @@
auto p = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* inner = Structure("Inner", utils::Vector{
Member("a", ty.i32()),
@@ -439,7 +439,7 @@
auto p = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
SetupUniformBuffer(utils::Vector{
Member("a", ty.i32()),
@@ -707,7 +707,7 @@
auto p = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* inner = Structure("Inner", utils::Vector{
Member("a", ty.i32()),
@@ -989,7 +989,7 @@
auto p = GetParam();
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
SetupStorageBuffer(utils::Vector{
Member("a", ty.i32()),
@@ -1192,7 +1192,7 @@
// var<storage> data : Data;
// data.a[2i][1i];
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
SetupStorageBuffer(utils::Vector{
Member("z", ty.f16()),
@@ -1258,7 +1258,7 @@
// var<uniform> data : Data;
// data.a[2i][1i];
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
SetupUniformBuffer(utils::Vector{
Member("z", ty.f16()),
diff --git a/src/tint/writer/hlsl/generator_impl_module_constant_test.cc b/src/tint/writer/hlsl/generator_impl_module_constant_test.cc
index 62f1d8ee..5a9327d 100644
--- a/src/tint/writer/hlsl/generator_impl_module_constant_test.cc
+++ b/src/tint/writer/hlsl/generator_impl_module_constant_test.cc
@@ -93,7 +93,7 @@
}
TEST_F(HlslGeneratorImplTest_ModuleConstant, Emit_GlobalConst_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalConst("G", Expr(1_h));
Func("f", utils::Empty, ty.void_(), utils::Vector{Decl(Let("l", Expr(var)))});
@@ -151,7 +151,7 @@
}
TEST_F(HlslGeneratorImplTest_ModuleConstant, Emit_GlobalConst_vec3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalConst("G", vec3<f16>(1_h, 2_h, 3_h));
Func("f", utils::Empty, ty.void_(), utils::Vector{Decl(Let("l", Expr(var)))});
@@ -195,7 +195,7 @@
}
TEST_F(HlslGeneratorImplTest_ModuleConstant, Emit_GlobalConst_mat2x3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalConst("G", mat2x3<f16>(1_h, 2_h, 3_h, 4_h, 5_h, 6_h));
Func("f", utils::Empty, ty.void_(), utils::Vector{Decl(Let("l", Expr(var)))});
diff --git a/src/tint/writer/hlsl/generator_impl_test.cc b/src/tint/writer/hlsl/generator_impl_test.cc
index 1f3801f..eeb9acb 100644
--- a/src/tint/writer/hlsl/generator_impl_test.cc
+++ b/src/tint/writer/hlsl/generator_impl_test.cc
@@ -29,7 +29,7 @@
}
TEST_F(HlslGeneratorImplTest, UnsupportedExtension) {
- Enable(Source{{12, 34}}, ast::Extension::kUndefined);
+ Enable(Source{{12, 34}}, builtin::Extension::kUndefined);
GeneratorImpl& gen = Build();
diff --git a/src/tint/writer/hlsl/generator_impl_variable_decl_statement_test.cc b/src/tint/writer/hlsl/generator_impl_variable_decl_statement_test.cc
index 170d993..fedf476 100644
--- a/src/tint/writer/hlsl/generator_impl_variable_decl_statement_test.cc
+++ b/src/tint/writer/hlsl/generator_impl_variable_decl_statement_test.cc
@@ -155,7 +155,7 @@
}
TEST_F(HlslGeneratorImplTest_VariableDecl, Emit_VariableDeclStatement_Const_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", Expr(1_h));
Func("f", utils::Empty, ty.void_(),
@@ -229,7 +229,7 @@
}
TEST_F(HlslGeneratorImplTest_VariableDecl, Emit_VariableDeclStatement_Const_vec3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", vec3<f16>(1_h, 2_h, 3_h));
Func("f", utils::Empty, ty.void_(),
@@ -285,7 +285,7 @@
}
TEST_F(HlslGeneratorImplTest_VariableDecl, Emit_VariableDeclStatement_Const_mat2x3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", mat2x3<f16>(1_h, 2_h, 3_h, 4_h, 5_h, 6_h));
Func("f", utils::Empty, ty.void_(),
@@ -383,7 +383,7 @@
}
TEST_F(HlslGeneratorImplTest_VariableDecl, Emit_VariableDeclStatement_Initializer_ZeroVec_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("a", ty.vec3<f16>(), vec3<f16>());
@@ -412,7 +412,7 @@
}
TEST_F(HlslGeneratorImplTest_VariableDecl, Emit_VariableDeclStatement_Initializer_ZeroMat_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("a", ty.mat2x3<f16>(), mat2x3<f16>());
diff --git a/src/tint/writer/msl/generator_impl.cc b/src/tint/writer/msl/generator_impl.cc
index 243fb11..87928b4 100644
--- a/src/tint/writer/msl/generator_impl.cc
+++ b/src/tint/writer/msl/generator_impl.cc
@@ -270,10 +270,10 @@
bool GeneratorImpl::Generate() {
if (!CheckSupportedExtensions("MSL", program_->AST(), diagnostics_,
utils::Vector{
- ast::Extension::kChromiumDisableUniformityAnalysis,
- ast::Extension::kChromiumExperimentalFullPtrParameters,
- ast::Extension::kChromiumExperimentalPushConstant,
- ast::Extension::kF16,
+ builtin::Extension::kChromiumDisableUniformityAnalysis,
+ builtin::Extension::kChromiumExperimentalFullPtrParameters,
+ builtin::Extension::kChromiumExperimentalPushConstant,
+ builtin::Extension::kF16,
})) {
return false;
}
diff --git a/src/tint/writer/msl/generator_impl_binary_test.cc b/src/tint/writer/msl/generator_impl_binary_test.cc
index 4916799..7519b61 100644
--- a/src/tint/writer/msl/generator_impl_binary_test.cc
+++ b/src/tint/writer/msl/generator_impl_binary_test.cc
@@ -155,7 +155,7 @@
}
TEST_F(MslBinaryTest, ModF16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* left = Var("left", ty.f16());
auto* right = Var("right", ty.f16());
@@ -183,7 +183,7 @@
}
TEST_F(MslBinaryTest, ModVec3F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* left = Var("left", ty.vec3<f16>());
auto* right = Var("right", ty.vec3<f16>());
diff --git a/src/tint/writer/msl/generator_impl_builtin_test.cc b/src/tint/writer/msl/generator_impl_builtin_test.cc
index c0f0ff3..0eabc02 100644
--- a/src/tint/writer/msl/generator_impl_builtin_test.cc
+++ b/src/tint/writer/msl/generator_impl_builtin_test.cc
@@ -214,7 +214,7 @@
auto param = GetParam();
if (param.type == CallParamType::kF16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
GlobalVar("h2", ty.vec2<f16>(), type::AddressSpace::kPrivate);
GlobalVar("h3", ty.vec3<f16>(), type::AddressSpace::kPrivate);
@@ -436,7 +436,7 @@
}
TEST_F(MslGeneratorImplTest, Runtime_Modf_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("f", Expr(1.5_h))), //
Decl(Let("v", Call("modf", "f"))));
@@ -498,7 +498,7 @@
}
TEST_F(MslGeneratorImplTest, Runtime_Modf_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("f", vec3<f16>(1.5_h, 2.5_h, 3.5_h))), //
Decl(Let("v", Call("modf", "f"))));
@@ -552,7 +552,7 @@
}
TEST_F(MslGeneratorImplTest, Const_Modf_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("modf", 1.5_h))));
@@ -598,7 +598,7 @@
}
TEST_F(MslGeneratorImplTest, Const_Modf_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("modf", vec3<f16>(1.5_h, 2.5_h, 3.5_h)))));
@@ -652,7 +652,7 @@
}
TEST_F(MslGeneratorImplTest, Runtime_Frexp_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Var("f", Expr(1_h)), //
Var("v", Call("frexp", "f")));
@@ -714,7 +714,7 @@
}
TEST_F(MslGeneratorImplTest, Runtime_Frexp_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Var("f", Expr(vec3<f16>())), //
Var("v", Call("frexp", "f")));
@@ -768,7 +768,7 @@
}
TEST_F(MslGeneratorImplTest, Const_Frexp_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("frexp", 1_h))));
@@ -814,7 +814,7 @@
}
TEST_F(MslGeneratorImplTest, Const_Frexp_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Decl(Let("v", Call("frexp", vec3<f16>()))));
@@ -888,7 +888,7 @@
}
TEST_F(MslGeneratorImplTest, Degrees_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.f16());
auto* call = Call("degrees", val);
@@ -915,7 +915,7 @@
}
TEST_F(MslGeneratorImplTest, Degrees_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.vec3<f16>());
auto* call = Call("degrees", val);
@@ -992,7 +992,7 @@
}
TEST_F(MslGeneratorImplTest, Radians_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.f16());
auto* call = Call("radians", val);
@@ -1019,7 +1019,7 @@
}
TEST_F(MslGeneratorImplTest, Radians_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* val = Var("val", ty.vec3<f16>());
auto* call = Call("radians", val);
diff --git a/src/tint/writer/msl/generator_impl_initializer_test.cc b/src/tint/writer/msl/generator_impl_initializer_test.cc
index bbcadfd..fbd1def 100644
--- a/src/tint/writer/msl/generator_impl_initializer_test.cc
+++ b/src/tint/writer/msl/generator_impl_initializer_test.cc
@@ -62,7 +62,7 @@
}
TEST_F(MslGeneratorImplTest, EmitInitializer_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
// Use a number close to 1<<16 but whose decimal representation ends in 0.
WrapInFunction(Expr(f16((1 << 15) - 8)));
@@ -83,7 +83,7 @@
}
TEST_F(MslGeneratorImplTest, EmitInitializer_Type_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Call<f16>(-1.2e-3_h));
@@ -130,7 +130,7 @@
}
TEST_F(MslGeneratorImplTest, EmitInitializer_Type_Vec_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>(1_h, 2_h, 3_h));
@@ -150,7 +150,7 @@
}
TEST_F(MslGeneratorImplTest, EmitInitializer_Type_Vec_Empty_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>());
@@ -170,7 +170,7 @@
}
TEST_F(MslGeneratorImplTest, EmitInitializer_Type_Vec_SingleScalar_F16_Literal) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>(2_h));
@@ -193,7 +193,7 @@
}
TEST_F(MslGeneratorImplTest, EmitInitializer_Type_Vec_SingleScalar_F16_Var) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("v", Expr(2_h));
auto* cast = vec3<f16>(var);
@@ -245,7 +245,7 @@
}
TEST_F(MslGeneratorImplTest, EmitInitializer_Type_Mat_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(mat2x3<f16>(vec3<f16>(1_h, 2_h, 3_h), vec3<f16>(3_h, 4_h, 5_h)));
@@ -291,7 +291,7 @@
// vec4<f16>(7.0h),
// vec4<f16>(vec4<f16>(42.0h, 21.0h, 6.0h, -5.0h)),
// );
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vector_literal =
vec4<f16>(Expr(f16(2.0)), Expr(f16(3.0)), Expr(f16(4.0)), Expr(f16(8.0)));
@@ -325,7 +325,7 @@
}
TEST_F(MslGeneratorImplTest, EmitInitializer_Type_Mat_Empty_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(mat2x3<f16>());
@@ -361,7 +361,7 @@
// var m_2: mat4x4<f16> = mat4x4<f16>(m_1);
// }
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* m_1 = Var("m_1", ty.mat4x4(ty.f16()), mat4x4<f16>());
auto* m_2 = Var("m_2", ty.mat4x4(ty.f16()), mat4x4<f16>(m_1));
diff --git a/src/tint/writer/msl/generator_impl_module_constant_test.cc b/src/tint/writer/msl/generator_impl_module_constant_test.cc
index e798364..8a326e2 100644
--- a/src/tint/writer/msl/generator_impl_module_constant_test.cc
+++ b/src/tint/writer/msl/generator_impl_module_constant_test.cc
@@ -113,7 +113,7 @@
}
TEST_F(MslGeneratorImplTest, Emit_GlobalConst_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalConst("G", Expr(1_h));
Func("f", utils::Empty, ty.void_(), utils::Vector{Decl(Let("l", Expr(var)))});
@@ -187,7 +187,7 @@
}
TEST_F(MslGeneratorImplTest, Emit_GlobalConst_vec3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalConst("G", vec3<f16>(1_h, 2_h, 3_h));
Func("f", utils::Empty, ty.void_(), utils::Vector{Decl(Let("l", Expr(var)))});
@@ -243,7 +243,7 @@
}
TEST_F(MslGeneratorImplTest, Emit_GlobalConst_mat2x3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalConst("G", mat2x3<f16>(1_h, 2_h, 3_h, 4_h, 5_h, 6_h));
Func("f", utils::Empty, ty.void_(), utils::Vector{Decl(Let("l", Expr(var)))});
diff --git a/src/tint/writer/msl/generator_impl_test.cc b/src/tint/writer/msl/generator_impl_test.cc
index a6d5cb7..71d5858 100644
--- a/src/tint/writer/msl/generator_impl_test.cc
+++ b/src/tint/writer/msl/generator_impl_test.cc
@@ -32,7 +32,7 @@
}
TEST_F(MslGeneratorImplTest, UnsupportedExtension) {
- Enable(Source{{12, 34}}, ast::Extension::kUndefined);
+ Enable(Source{{12, 34}}, builtin::Extension::kUndefined);
GeneratorImpl& gen = Build();
diff --git a/src/tint/writer/msl/generator_impl_variable_decl_statement_test.cc b/src/tint/writer/msl/generator_impl_variable_decl_statement_test.cc
index 927ae26..1386abb 100644
--- a/src/tint/writer/msl/generator_impl_variable_decl_statement_test.cc
+++ b/src/tint/writer/msl/generator_impl_variable_decl_statement_test.cc
@@ -155,7 +155,7 @@
}
TEST_F(MslGeneratorImplTest, Emit_VariableDeclStatement_Const_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", Expr(1_h));
Func("f", utils::Empty, ty.void_(), utils::Vector{Decl(C), Decl(Let("l", Expr(C)))});
@@ -229,7 +229,7 @@
}
TEST_F(MslGeneratorImplTest, Emit_VariableDeclStatement_Const_vec3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", vec3<f16>(1_h, 2_h, 3_h));
Func("f", utils::Empty, ty.void_(), utils::Vector{Decl(C), Decl(Let("l", Expr(C)))});
@@ -285,7 +285,7 @@
}
TEST_F(MslGeneratorImplTest, Emit_VariableDeclStatement_Const_mat2x3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", mat2x3<f16>(1_h, 2_h, 3_h, 4_h, 5_h, 6_h));
Func("f", utils::Empty, ty.void_(), utils::Vector{Decl(C), Decl(Let("l", Expr(C)))});
@@ -415,7 +415,7 @@
}
TEST_F(MslGeneratorImplTest, Emit_VariableDeclStatement_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("a", ty.vec2<f16>());
auto* stmt = Decl(var);
@@ -444,7 +444,7 @@
}
TEST_F(MslGeneratorImplTest, Emit_VariableDeclStatement_Matrix_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("a", ty.mat3x2<f16>());
@@ -473,7 +473,7 @@
}
TEST_F(MslGeneratorImplTest, Emit_VariableDeclStatement_Initializer_ZeroVec_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("a", ty.vec3<f16>(), vec3<f16>());
@@ -502,7 +502,7 @@
}
TEST_F(MslGeneratorImplTest, Emit_VariableDeclStatement_Initializer_ZeroMat_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("a", ty.mat2x3<f16>(), mat2x3<f16>());
diff --git a/src/tint/writer/spirv/builder.cc b/src/tint/writer/spirv/builder.cc
index 541bb37..7482558 100644
--- a/src/tint/writer/spirv/builder.cc
+++ b/src/tint/writer/spirv/builder.cc
@@ -265,11 +265,11 @@
bool Builder::Build() {
if (!CheckSupportedExtensions("SPIR-V", builder_.AST(), builder_.Diagnostics(),
utils::Vector{
- ast::Extension::kChromiumDisableUniformityAnalysis,
- ast::Extension::kChromiumExperimentalDp4A,
- ast::Extension::kChromiumExperimentalFullPtrParameters,
- ast::Extension::kChromiumExperimentalPushConstant,
- ast::Extension::kF16,
+ builtin::Extension::kChromiumDisableUniformityAnalysis,
+ builtin::Extension::kChromiumExperimentalDp4A,
+ builtin::Extension::kChromiumExperimentalFullPtrParameters,
+ builtin::Extension::kChromiumExperimentalPushConstant,
+ builtin::Extension::kF16,
})) {
error_ = builder_.Diagnostics().str();
return false;
@@ -394,14 +394,14 @@
extensions_.push_back(Instruction{spv::Op::OpExtension, {Operand(extension)}});
}
-bool Builder::GenerateExtension(ast::Extension extension) {
+bool Builder::GenerateExtension(builtin::Extension extension) {
switch (extension) {
- case ast::Extension::kChromiumExperimentalDp4A:
+ case builtin::Extension::kChromiumExperimentalDp4A:
push_extension("SPV_KHR_integer_dot_product");
push_capability(SpvCapabilityDotProductKHR);
push_capability(SpvCapabilityDotProductInput4x8BitPackedKHR);
break;
- case ast::Extension::kF16:
+ case builtin::Extension::kF16:
push_capability(SpvCapabilityFloat16);
push_capability(SpvCapabilityUniformAndStorageBuffer16BitAccess);
push_capability(SpvCapabilityStorageBuffer16BitAccess);
diff --git a/src/tint/writer/spirv/builder.h b/src/tint/writer/spirv/builder.h
index 9262e15..c56085a 100644
--- a/src/tint/writer/spirv/builder.h
+++ b/src/tint/writer/spirv/builder.h
@@ -228,7 +228,7 @@
/// not supported.
/// @param ext the extension to generate
/// @returns true on success.
- bool GenerateExtension(ast::Extension ext);
+ bool GenerateExtension(builtin::Extension ext);
/// Generates a label for the given id. Emits an error and returns false if
/// we're currently outside a function.
/// @param id the id to use for the label
diff --git a/src/tint/writer/spirv/builder_binary_expression_test.cc b/src/tint/writer/spirv/builder_binary_expression_test.cc
index ed8185d..b6dfb62 100644
--- a/src/tint/writer/spirv/builder_binary_expression_test.cc
+++ b/src/tint/writer/spirv/builder_binary_expression_test.cc
@@ -248,7 +248,7 @@
using BinaryArithF16Test = TestParamHelper<BinaryData>;
TEST_P(BinaryArithF16Test, Scalar) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto param = GetParam();
@@ -273,7 +273,7 @@
}
TEST_P(BinaryArithF16Test, Vector) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto param = GetParam();
@@ -543,7 +543,7 @@
using BinaryCompareF16Test = TestParamHelper<BinaryData>;
TEST_P(BinaryCompareF16Test, Scalar) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto param = GetParam();
@@ -569,7 +569,7 @@
}
TEST_P(BinaryCompareF16Test, Vector) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto param = GetParam();
@@ -629,7 +629,7 @@
}
TEST_F(BuilderTest, Binary_Multiply_VectorScalar_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* lhs = vec3<f16>(1_h, 1_h, 1_h);
auto* rhs = Expr(1_h);
@@ -677,7 +677,7 @@
}
TEST_F(BuilderTest, Binary_Multiply_ScalarVector_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* lhs = Expr(1_h);
auto* rhs = vec3<f16>(1_h, 1_h, 1_h);
@@ -728,7 +728,7 @@
}
TEST_F(BuilderTest, Binary_Multiply_MatrixScalar_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("mat", ty.mat3x3<f16>());
auto* expr = create<ast::BinaryExpression>(ast::BinaryOp::kMultiply, Expr("mat"), Expr(1_h));
@@ -782,7 +782,7 @@
}
TEST_F(BuilderTest, Binary_Multiply_ScalarMatrix_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("mat", ty.mat3x3<f16>());
auto* expr = create<ast::BinaryExpression>(ast::BinaryOp::kMultiply, Expr(1_h), Expr("mat"));
@@ -838,7 +838,7 @@
}
TEST_F(BuilderTest, Binary_Multiply_MatrixVector_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("mat", ty.mat3x3<f16>());
auto* rhs = vec3<f16>(1_h, 1_h, 1_h);
@@ -896,7 +896,7 @@
}
TEST_F(BuilderTest, Binary_Multiply_VectorMatrix_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("mat", ty.mat3x3<f16>());
auto* lhs = vec3<f16>(1_h, 1_h, 1_h);
@@ -953,7 +953,7 @@
}
TEST_F(BuilderTest, Binary_Multiply_MatrixMatrix_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Var("mat", ty.mat3x3<f16>());
auto* expr = create<ast::BinaryExpression>(ast::BinaryOp::kMultiply, Expr("mat"), Expr("mat"));
@@ -1341,7 +1341,7 @@
auto& param = GetParam();
if (param.type == Type::f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
}
const ast::Expression* lhs = MakeVectorExpr(this, param.type);
@@ -1393,7 +1393,7 @@
auto& param = GetParam();
if (param.type == Type::f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
}
const ast::Expression* lhs = MakeScalarExpr(this, param.type);
@@ -1473,7 +1473,7 @@
auto& param = GetParam();
if (param.type == Type::f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
}
const ast::Expression* lhs = MakeVectorExpr(this, param.type);
@@ -1521,7 +1521,7 @@
auto& param = GetParam();
if (param.type == Type::f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
}
const ast::Expression* lhs = MakeScalarExpr(this, param.type);
@@ -1636,7 +1636,7 @@
auto& param = GetParam();
if (param.type == Type::f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
}
const ast::Expression* lhs = MakeMat3x4Expr(this, param.type);
@@ -1699,7 +1699,7 @@
auto& param = GetParam();
if (param.type == Type::f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
}
const ast::Expression* lhs = MakeMat3x4Expr(this, param.type);
diff --git a/src/tint/writer/spirv/builder_builtin_test.cc b/src/tint/writer/spirv/builder_builtin_test.cc
index 0bab161..693fdb1 100644
--- a/src/tint/writer/spirv/builder_builtin_test.cc
+++ b/src/tint/writer/spirv/builder_builtin_test.cc
@@ -132,7 +132,7 @@
}
TEST_F(BuiltinBuilderTest, Call_GLSLMethod_WithLoad_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalVar("ident", ty.f16(), type::AddressSpace::kPrivate);
auto* expr = Call("round", "ident");
@@ -516,7 +516,7 @@
}
TEST_P(Builtin_Builder_SingleParam_Float_Test, Call_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto param = GetParam();
// Use a variable to prevent the function being evaluated as constant.
@@ -599,7 +599,7 @@
}
TEST_P(Builtin_Builder_SingleParam_Float_Test, Call_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto param = GetParam();
@@ -705,7 +705,7 @@
}
TEST_F(BuiltinBuilderTest, Call_Length_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* scalar = Var("a", Expr(1_h));
auto* expr = Call("length", scalar);
@@ -779,7 +779,7 @@
}
TEST_F(BuiltinBuilderTest, Call_Length_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec = Var("a", vec2<f16>(1_h, 1_h));
auto* expr = Call("length", vec);
@@ -855,7 +855,7 @@
}
TEST_F(BuiltinBuilderTest, Call_Normalize_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec = Var("a", vec2<f16>(1_h, 1_h));
auto* expr = Call("normalize", vec);
@@ -934,7 +934,7 @@
}
TEST_P(Builtin_Builder_DualParam_Float_Test, Call_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto param = GetParam();
auto* scalar = Var("scalar", Expr(1_h));
@@ -1016,7 +1016,7 @@
}
TEST_P(Builtin_Builder_DualParam_Float_Test, Call_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto param = GetParam();
auto* vec = Var("vec", vec2<f16>(1_h, 1_h));
@@ -1105,7 +1105,7 @@
}
TEST_F(BuiltinBuilderTest, Call_Reflect_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec = Var("vec", vec2<f16>(1_h, 1_h));
auto* expr = Call("reflect", vec, vec);
@@ -1181,7 +1181,7 @@
}
TEST_F(BuiltinBuilderTest, Call_Distance_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* scalar = Var("scalar", Expr(1_h));
auto* expr = Call("distance", scalar, scalar);
@@ -1257,7 +1257,7 @@
}
TEST_F(BuiltinBuilderTest, Call_Distance_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec = Var("vec", vec2<f16>(1_h, 1_h));
auto* expr = Call("distance", vec, vec);
@@ -1335,7 +1335,7 @@
}
TEST_F(BuiltinBuilderTest, Call_Cross_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec = Var("vec", vec3<f16>(1_h, 1_h, 1_h));
auto* expr = Call("cross", vec, vec);
@@ -1416,7 +1416,7 @@
}
TEST_P(Builtin_Builder_ThreeParam_Float_Test, Call_Scalar_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto param = GetParam();
auto* scalar = Var("scalar", Expr(1_h));
@@ -1500,7 +1500,7 @@
}
TEST_P(Builtin_Builder_ThreeParam_Float_Test, Call_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto param = GetParam();
auto* vec = Var("vec", vec2<f16>(1_h, 1_h));
@@ -1591,7 +1591,7 @@
}
TEST_F(BuiltinBuilderTest, Call_FaceForward_Vector_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec = Var("vec", vec2<f16>(1_h, 1_h));
auto* expr = Call("faceForward", vec, vec, vec);
@@ -1684,7 +1684,7 @@
}
TEST_F(BuiltinBuilderTest, Runtime_Call_Modf_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec = Var("vec", vec2<f16>(1_h, 2_h));
auto* expr = Call("modf", vec);
@@ -1786,7 +1786,7 @@
}
TEST_F(BuiltinBuilderTest, Const_Call_Modf_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* expr = Call("modf", vec2<f16>(1_h, 2_h));
Func("a_func", utils::Empty, ty.void_(),
@@ -1890,7 +1890,7 @@
}
TEST_F(BuiltinBuilderTest, Runtime_Call_Frexp_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* vec = Var("vec", vec2<f16>(1_h, 2_h));
auto* expr = Call("frexp", vec);
@@ -1995,7 +1995,7 @@
}
TEST_F(BuiltinBuilderTest, Const_Call_Frexp_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
Func("a_func", utils::Empty, ty.void_(),
utils::Vector{
@@ -3149,7 +3149,7 @@
}
TEST_F(BuiltinBuilderTest, Call_Determinant_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalVar("var", ty.mat3x3<f16>(), type::AddressSpace::kPrivate);
auto* expr = Call("determinant", "var");
@@ -3222,7 +3222,7 @@
}
TEST_F(BuiltinBuilderTest, Call_Transpose_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalVar("var", ty.mat2x3<f16>(), type::AddressSpace::kPrivate);
auto* expr = Call("transpose", "var");
@@ -3294,7 +3294,7 @@
}
TEST_F(BuiltinBuilderTest, Call_Dot_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalVar("v", ty.vec3<f16>(), type::AddressSpace::kPrivate);
auto* expr = Call("dot", "v", "v");
@@ -4153,7 +4153,7 @@
TEST_F(BuiltinBuilderTest, Call_Dot4I8Packed) {
auto* ext =
create<ast::Enable>(Source{Source::Range{Source::Location{10, 2}, Source::Location{10, 5}}},
- ast::Extension::kChromiumExperimentalDp4A);
+ builtin::Extension::kChromiumExperimentalDp4A);
AST().AddEnable(ext);
auto* val1 = Var("val1", ty.u32());
@@ -4193,7 +4193,7 @@
TEST_F(BuiltinBuilderTest, Call_Dot4U8Packed) {
auto* ext =
create<ast::Enable>(Source{Source::Range{Source::Location{10, 2}, Source::Location{10, 5}}},
- ast::Extension::kChromiumExperimentalDp4A);
+ builtin::Extension::kChromiumExperimentalDp4A);
AST().AddEnable(ext);
auto* val1 = Var("val1", ty.u32());
diff --git a/src/tint/writer/spirv/builder_global_variable_test.cc b/src/tint/writer/spirv/builder_global_variable_test.cc
index 2e58660..ea9c6a8 100644
--- a/src/tint/writer/spirv/builder_global_variable_test.cc
+++ b/src/tint/writer/spirv/builder_global_variable_test.cc
@@ -119,7 +119,7 @@
TEST_F(BuilderTest, GlobalConst_Vec_F16_Initializer) {
// const c = vec3<f16>(1h, 2h, 3h);
// var v = c;
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* c = GlobalConst("c", vec3<f16>(1_h, 2_h, 3_h));
GlobalVar("v", type::AddressSpace::kPrivate, Expr(c));
diff --git a/src/tint/writer/spirv/builder_initializer_expression_test.cc b/src/tint/writer/spirv/builder_initializer_expression_test.cc
index b78bd9d..9fdc4fc 100644
--- a/src/tint/writer/spirv/builder_initializer_expression_test.cc
+++ b/src/tint/writer/spirv/builder_initializer_expression_test.cc
@@ -213,7 +213,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_F16_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = Call<f16>(2_h);
WrapInFunction(cast);
@@ -288,7 +288,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec2_With_F16_Literal) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec2<f16>(2_h);
WrapInFunction(cast);
@@ -332,7 +332,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec2_With_F16_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.f16(), Expr(2_h)));
auto* cast = vec2<f16>("x", "x");
@@ -377,7 +377,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec2_With_F16_F16_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec2<f16>(1_h, 2_h);
WrapInFunction(cast);
@@ -422,7 +422,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec2_F16_With_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.vec2<f16>(), vec2<f16>(1_h, 2_h)));
auto* cast = vec2<f16>("x");
@@ -467,7 +467,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec2_F16_With_Vec2_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec2<f16>(vec2<f16>(1_h, 2_h));
WrapInFunction(cast);
@@ -513,7 +513,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec3_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.f16(), Expr(2_h)));
auto* cast = vec3<f16>("x", "x", "x");
@@ -560,7 +560,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec3_With_F16_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(1_h, 2_h, 3_h);
WrapInFunction(cast);
@@ -651,7 +651,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec3_With_F16_F16_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.f16(), Expr(2_h)));
auto* cast = vec3<f16>("x", "x", "x");
@@ -698,7 +698,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec3_With_F16_F16_F16_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(1_h, 2_h, 3_h);
WrapInFunction(cast);
@@ -749,7 +749,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec3_With_F16_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.vec2<f16>(), vec2<f16>(2_h, 3_h)));
auto* cast = vec3<f16>(1_h, "x");
@@ -800,7 +800,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec3_With_F16_Vec2_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(1_h, vec2<f16>(2_h, 3_h));
WrapInFunction(cast);
@@ -851,7 +851,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec3_With_Vec2_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.vec2<f16>(), vec2<f16>(1_h, 2_h)));
auto* cast = vec3<f16>("x", 3_h);
@@ -902,7 +902,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec3_With_Vec2_F16_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(vec2<f16>(1_h, 2_h), 3_h);
WrapInFunction(cast);
@@ -949,7 +949,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec3_F16_With_Vec3) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.vec3<f16>(), vec3<f16>(1_h, 2_h, 3_h)));
auto* cast = vec3<f16>("x");
@@ -996,7 +996,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec3_F16_With_Vec3_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(vec3<f16>(1_h, 2_h, 3_h));
WrapInFunction(cast);
@@ -1082,7 +1082,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.f16(), Expr(2_h)));
auto* cast = vec4<f16>("x");
@@ -1125,7 +1125,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_F16_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(2_h);
WrapInFunction(cast);
@@ -1171,7 +1171,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_F16_F16_F16_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.f16(), Expr(2_h)));
auto* cast = vec4<f16>("x", "x", "x", "x");
@@ -1220,7 +1220,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_F16_F16_F16_F16_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(1_h, 2_h, 3_h, 4_h);
WrapInFunction(cast);
@@ -1271,7 +1271,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_F16_F16_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.vec2<f16>(), vec2<f16>(1_h, 2_h)));
auto* cast = vec4<f16>(1_h, 2_h, "x");
@@ -1322,7 +1322,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_F16_F16_Vec2_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(1_h, 2_h, vec2<f16>(3_h, 4_h));
WrapInFunction(cast);
@@ -1375,7 +1375,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_F16_Vec2_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.vec2<f16>(), vec2<f16>(2_h, 3_h)));
auto* cast = vec4<f16>(1_h, "x", 4_h);
@@ -1428,7 +1428,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_F16_Vec2_F16_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(1_h, vec2<f16>(2_h, 3_h), 4_h);
WrapInFunction(cast);
@@ -1481,7 +1481,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_Vec2_F16_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.vec2<f16>(), vec2<f16>(1_h, 2_h)));
auto* cast = vec4<f16>("x", 3_h, 4_h);
@@ -1534,7 +1534,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_Vec2_F16_F16_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec2<f16>(1_h, 2_h), 3_h, 4_h);
WrapInFunction(cast);
@@ -1588,7 +1588,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_F16_With_Vec2_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.vec2<f16>(), vec2<f16>(1_h, 2_h)));
auto* cast = vec4<f16>("x", "x");
@@ -1640,7 +1640,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_F16_With_Vec2_Vec2_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec2<f16>(1_h, 2_h), vec2<f16>(1_h, 2_h));
WrapInFunction(cast);
@@ -1689,7 +1689,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_F16_Vec3) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.vec3<f16>(), vec3<f16>(2_h, 2_h, 2_h)));
auto* cast = vec4<f16>(2_h, "x");
@@ -1737,7 +1737,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_F16_Vec3_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(2_h, vec3<f16>(2_h, 2_h, 2_h));
WrapInFunction(cast);
@@ -1785,7 +1785,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_Vec3_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.vec3<f16>(), vec3<f16>(2_h, 2_h, 2_h)));
auto* cast = vec4<f16>("x", 2_h);
@@ -1833,7 +1833,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_With_Vec3_F16_Const) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec3<f16>(2_h, 2_h, 2_h), 2_h);
WrapInFunction(cast);
@@ -1870,7 +1870,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Vec4_F16_With_Vec4) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* value = vec4<f16>(2_h, 2_h, 2_h, 2_h);
auto* cast = vec4<f16>(value);
@@ -1911,7 +1911,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_F16_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* ctor = Call<f16>(2_h);
GlobalConst("g", ty.f16(), ctor);
@@ -1951,7 +1951,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_F16_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* ctor = Call<f16>(2_h);
GlobalVar("g", ty.f16(), type::AddressSpace::kPrivate, ctor);
@@ -1991,7 +1991,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_U32_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* ctor = Call<u32>(1.5_h);
GlobalConst("g", ty.u32(), ctor);
@@ -2031,7 +2031,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_U32_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* ctor = Call<u32>(1.5_h);
GlobalVar("g", ty.u32(), type::AddressSpace::kPrivate, ctor);
@@ -2073,7 +2073,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec2_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec2<f16>(2_h);
GlobalConst("g", ty.vec2<f16>(), cast);
@@ -2114,7 +2114,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec2_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec2<f16>(2_h);
auto* g = GlobalVar("g", ty.vec2<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2155,7 +2155,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec2_F16_With_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec2<f16>(vec2<f16>(2_h, 2_h));
GlobalConst("g", ty.vec2<f16>(), cast);
@@ -2200,7 +2200,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec2_F16_With_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec2<f16>(vec2<f16>(2_h, 2_h));
GlobalVar("a", ty.vec2<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2245,7 +2245,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec3_F16_With_Vec3) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(vec3<f16>(2_h, 2_h, 2_h));
GlobalConst("g", ty.vec3<f16>(), cast);
@@ -2290,7 +2290,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec3_F16_With_Vec3) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(vec3<f16>(2_h, 2_h, 2_h));
GlobalVar("a", ty.vec3<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2335,7 +2335,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec4_F16_With_Vec4) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec4<f16>(2_h, 2_h, 2_h, 2_h));
GlobalConst("g", ty.vec4<f16>(), cast);
@@ -2380,7 +2380,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec4_F16_With_Vec4) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec4<f16>(2_h, 2_h, 2_h, 2_h));
GlobalVar("a", ty.vec4<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2425,7 +2425,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec3_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(2_h);
GlobalConst("g", ty.vec3<f16>(), cast);
@@ -2466,7 +2466,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec3_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(2_h);
auto* g = GlobalVar("g", ty.vec3<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2507,7 +2507,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec3_With_F16_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(2_h, vec2<f16>(2_h, 2_h));
GlobalConst("g", ty.vec3<f16>(), cast);
@@ -2548,7 +2548,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec3_With_F16_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(2_h, vec2<f16>(2_h, 2_h));
auto* g = GlobalVar("g", ty.vec3<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2589,7 +2589,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec3_With_Vec2_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(vec2<f16>(2_h, 2_h), 2_h);
GlobalConst("g", ty.vec3<f16>(), cast);
@@ -2630,7 +2630,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec3_With_Vec2_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(vec2<f16>(2_h, 2_h), 2_h);
auto* g = GlobalVar("g", ty.vec3<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2671,7 +2671,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec4_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(2_h);
GlobalConst("g", ty.vec4<f16>(), cast);
@@ -2712,7 +2712,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec4_With_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(2_h);
auto* g = GlobalVar("g", ty.vec4<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2753,7 +2753,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec4_With_F16_F16_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(2_h, 2_h, vec2<f16>(2_h, 2_h));
GlobalConst("g", ty.vec4<f16>(), cast);
@@ -2794,7 +2794,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec4_With_F16_F16_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(2_h, 2_h, vec2<f16>(2_h, 2_h));
auto* g = GlobalVar("g", ty.vec4<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2835,7 +2835,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec4_With_F16_Vec2_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(2_h, vec2<f16>(2_h, 2_h), 2_h);
GlobalConst("g", ty.vec4<f16>(), cast);
@@ -2876,7 +2876,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec4_With_F16_Vec2_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(2_h, vec2<f16>(2_h, 2_h), 2_h);
auto* g = GlobalVar("g", ty.vec4<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2917,7 +2917,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec4_With_Vec2_F16_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec2<f16>(2_h, 2_h), 2_h, 2_h);
GlobalConst("g", ty.vec4<f16>(), cast);
@@ -2958,7 +2958,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec4_With_Vec2_F16_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec2<f16>(2_h, 2_h), 2_h, 2_h);
auto* g = GlobalVar("g", ty.vec4<f16>(), type::AddressSpace::kPrivate, cast);
@@ -2999,7 +2999,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec4_F16_With_Vec2_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec2<f16>(2_h, 2_h), vec2<f16>(2_h, 2_h));
GlobalConst("g", ty.vec4<f16>(), cast);
@@ -3040,7 +3040,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec4_F16_With_Vec2_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec2<f16>(2_h, 2_h), vec2<f16>(2_h, 2_h));
auto* g = GlobalVar("g", ty.vec4<f16>(), type::AddressSpace::kPrivate, cast);
@@ -3097,7 +3097,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec4_With_F16_Vec3) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(2_h, vec3<f16>(2_h, 2_h, 2_h));
auto* g = GlobalVar("g", ty.vec4<f16>(), type::AddressSpace::kPrivate, cast);
@@ -3138,7 +3138,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalConst_Vec4_With_Vec3_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec3<f16>(2_h, 2_h, 2_h), 2_h);
GlobalConst("g", ty.vec4<f16>(), cast);
@@ -3179,7 +3179,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_GlobalVar_Vec4_With_Vec3_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec4<f16>(vec3<f16>(2_h, 2_h, 2_h), 2_h);
auto* g = GlobalVar("g", ty.vec4<f16>(), type::AddressSpace::kPrivate, cast);
@@ -3215,7 +3215,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Mat2x2_F16_With_Vec2_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = mat2x2<f16>(vec2<f16>(2_h, 2_h), vec2<f16>(2_h, 2_h));
WrapInFunction(cast);
@@ -3253,7 +3253,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Mat3x2_F16_With_Vec2_Vec2_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = mat3x2<f16>(vec2<f16>(2_h, 2_h), vec2<f16>(2_h, 2_h), vec2<f16>(2_h, 2_h));
WrapInFunction(cast);
@@ -3292,7 +3292,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Mat4x2_F16_With_Vec2_Vec2_Vec2_Vec2) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = mat4x2<f16>(vec2<f16>(2_h, 2_h), vec2<f16>(2_h, 2_h), vec2<f16>(2_h, 2_h),
vec2<f16>(2_h, 2_h));
@@ -3331,7 +3331,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Mat2x3_F16_With_Vec3_Vec3) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = mat2x3<f16>(vec3<f16>(2_h, 2_h, 2_h), vec3<f16>(2_h, 2_h, 2_h));
WrapInFunction(cast);
@@ -3370,7 +3370,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Mat3x3_F16_With_Vec3_Vec3_Vec3) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast =
mat3x3<f16>(vec3<f16>(2_h, 2_h, 2_h), vec3<f16>(2_h, 2_h, 2_h), vec3<f16>(2_h, 2_h, 2_h));
@@ -3410,7 +3410,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Mat4x3_F16_With_Vec3_Vec3_Vec3_Vec3) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = mat4x3<f16>(vec3<f16>(2_h, 2_h, 2_h), vec3<f16>(2_h, 2_h, 2_h),
vec3<f16>(2_h, 2_h, 2_h), vec3<f16>(2_h, 2_h, 2_h));
@@ -3449,7 +3449,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Mat2x4_F16_With_Vec4_Vec4) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = mat2x4<f16>(vec4<f16>(2_h, 2_h, 2_h, 2_h), vec4<f16>(2_h, 2_h, 2_h, 2_h));
WrapInFunction(cast);
@@ -3488,7 +3488,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Mat3x4_F16_With_Vec4_Vec4_Vec4) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = mat3x4<f16>(vec4<f16>(2_h, 2_h, 2_h, 2_h), vec4<f16>(2_h, 2_h, 2_h, 2_h),
vec4<f16>(2_h, 2_h, 2_h, 2_h));
@@ -3528,7 +3528,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Mat4x4_F16_With_Vec4_Vec4_Vec4_Vec4) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = mat4x4<f16>(vec4<f16>(2_h, 2_h, 2_h, 2_h), vec4<f16>(2_h, 2_h, 2_h, 2_h),
vec4<f16>(2_h, 2_h, 2_h, 2_h), vec4<f16>(2_h, 2_h, 2_h, 2_h));
@@ -3567,7 +3567,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Array_5_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = array<f16, 5>(2_h, 2_h, 2_h, 2_h, 2_h);
WrapInFunction(cast);
@@ -3609,7 +3609,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Array_2_Vec3_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* first = vec3<f16>(1_h, 2_h, 3_h);
auto* second = vec3<f16>(1_h, 2_h, 3_h);
@@ -3738,7 +3738,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_ZeroInit_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* t = Call<f16>();
@@ -3845,7 +3845,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_ZeroInit_Matrix_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* t = mat4x2<f16>();
@@ -3952,7 +3952,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_F16_To_I32) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.f16(), Expr(2.4_h)));
auto* cast = Call<i32>("x");
@@ -4026,7 +4026,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_F16_To_U32) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.f16(), Expr(2.4_h)));
auto* cast = Call<u32>("x");
@@ -4100,7 +4100,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_F16_To_F32) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.f16(), Expr(2_h)));
auto* cast = Call<f32>("x");
@@ -4126,7 +4126,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_I32_To_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.i32(), Expr(2_i)));
auto* cast = Call<f16>("x");
@@ -4152,7 +4152,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_U32_To_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.u32(), Expr(2_u)));
auto* cast = Call<f16>("x");
@@ -4178,7 +4178,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_F32_To_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = Decl(Var("x", ty.f32(), Expr(2_f)));
auto* cast = Call<f16>("x");
@@ -4256,7 +4256,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_Vectors_F16_to_I32) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalVar("i", ty.vec3<f16>(), type::AddressSpace::kPrivate);
@@ -4336,7 +4336,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_Vectors_F16_to_U32) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalVar("i", ty.vec3<f16>(), type::AddressSpace::kPrivate);
@@ -4416,7 +4416,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_Vectors_F16_to_F32) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalVar("i", ty.vec3<f16>(), type::AddressSpace::kPrivate);
@@ -4444,7 +4444,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_Vectors_I32_to_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalVar("i", ty.vec3<i32>(), type::AddressSpace::kPrivate);
@@ -4472,7 +4472,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_Vectors_U32_to_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalVar("i", ty.vec3<u32>(), type::AddressSpace::kPrivate);
@@ -4500,7 +4500,7 @@
}
TEST_F(SpvBuilderInitializerTest, Type_Convert_Vectors_F32_to_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* var = GlobalVar("i", ty.vec3<f32>(), type::AddressSpace::kPrivate);
diff --git a/src/tint/writer/spirv/builder_literal_test.cc b/src/tint/writer/spirv/builder_literal_test.cc
index 0d53237..3a9ec29 100644
--- a/src/tint/writer/spirv/builder_literal_test.cc
+++ b/src/tint/writer/spirv/builder_literal_test.cc
@@ -164,7 +164,7 @@
}
TEST_F(BuilderTest, Literal_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* i = create<ast::FloatLiteralExpression>(23.245, ast::FloatLiteralExpression::Suffix::kH);
WrapInFunction(i);
@@ -181,7 +181,7 @@
}
TEST_F(BuilderTest, Literal_F16_Dedup) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* i1 = create<ast::FloatLiteralExpression>(23.245, ast::FloatLiteralExpression::Suffix::kH);
auto* i2 = create<ast::FloatLiteralExpression>(23.245, ast::FloatLiteralExpression::Suffix::kH);
diff --git a/src/tint/writer/spirv/builder_test.cc b/src/tint/writer/spirv/builder_test.cc
index b3dce7e..1c79988 100644
--- a/src/tint/writer/spirv/builder_test.cc
+++ b/src/tint/writer/spirv/builder_test.cc
@@ -30,7 +30,7 @@
}
TEST_F(BuilderTest, UnsupportedExtension) {
- Enable(Source{{12, 34}}, ast::Extension::kUndefined);
+ Enable(Source{{12, 34}}, builtin::Extension::kUndefined);
auto program = std::make_unique<Program>(std::move(*this));
auto result = Generate(program.get(), Options{});
diff --git a/src/tint/writer/spirv/builder_type_test.cc b/src/tint/writer/spirv/builder_type_test.cc
index ad13e96..cf35662 100644
--- a/src/tint/writer/spirv/builder_type_test.cc
+++ b/src/tint/writer/spirv/builder_type_test.cc
@@ -320,7 +320,7 @@
}
TEST_F(BuilderTest_Type, GenerateStruct) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* s = Structure("my_struct", utils::Vector{Member("a", ty.f32()), Member("b", ty.f16())});
@@ -341,7 +341,7 @@
}
TEST_F(BuilderTest_Type, GenerateStruct_DecoratedMembers) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* s = Structure("S", utils::Vector{
Member("a", ty.f32()),
@@ -374,7 +374,7 @@
}
TEST_F(BuilderTest_Type, GenerateStruct_DecoratedMembers_Matrix) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* s =
Structure("S", utils::Vector{
@@ -438,7 +438,7 @@
}
TEST_F(BuilderTest_Type, GenerateStruct_DecoratedMembers_ArraysOfMatrix) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto arr_mat2x2_f32 = ty.array(ty.mat2x2<f32>(), 1_u); // Singly nested array
auto arr_mat2x2_f16 = ty.array(ty.mat2x2<f16>(), 1_u); // Singly nested array
diff --git a/src/tint/writer/wgsl/generator_impl_cast_test.cc b/src/tint/writer/wgsl/generator_impl_cast_test.cc
index b10fd8f..66b7a2e 100644
--- a/src/tint/writer/wgsl/generator_impl_cast_test.cc
+++ b/src/tint/writer/wgsl/generator_impl_cast_test.cc
@@ -33,7 +33,7 @@
}
TEST_F(WgslGeneratorImplTest, EmitExpression_Cast_Scalar_F16_From_I32) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = Call<f16>(1_i);
WrapInFunction(cast);
@@ -57,7 +57,7 @@
}
TEST_F(WgslGeneratorImplTest, EmitExpression_Cast_Vector_F16_From_I32) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* cast = vec3<f16>(vec3<i32>(1_i, 2_i, 3_i));
WrapInFunction(cast);
diff --git a/src/tint/writer/wgsl/generator_impl_enable_test.cc b/src/tint/writer/wgsl/generator_impl_enable_test.cc
index 503a9a0..739d893 100644
--- a/src/tint/writer/wgsl/generator_impl_enable_test.cc
+++ b/src/tint/writer/wgsl/generator_impl_enable_test.cc
@@ -20,7 +20,7 @@
using WgslGeneratorImplTest = TestHelper;
TEST_F(WgslGeneratorImplTest, Emit_Enable) {
- auto* enable = Enable(ast::Extension::kF16);
+ auto* enable = Enable(builtin::Extension::kF16);
GeneratorImpl& gen = Build();
diff --git a/src/tint/writer/wgsl/generator_impl_initializer_test.cc b/src/tint/writer/wgsl/generator_impl_initializer_test.cc
index 87dddca..0d5686e 100644
--- a/src/tint/writer/wgsl/generator_impl_initializer_test.cc
+++ b/src/tint/writer/wgsl/generator_impl_initializer_test.cc
@@ -62,7 +62,7 @@
}
TEST_F(WgslGeneratorImplTest, EmitInitializer_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
// Use a number close to 1<<16 but whose decimal representation ends in 0.
WrapInFunction(Expr(f16((1 << 15) - 8)));
@@ -83,7 +83,7 @@
}
TEST_F(WgslGeneratorImplTest, EmitInitializer_Type_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(Call<f16>(Expr(-1.2e-5_h)));
@@ -130,7 +130,7 @@
}
TEST_F(WgslGeneratorImplTest, EmitInitializer_Type_Vec_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(vec3<f16>(1_h, 2_h, 3_h));
@@ -151,7 +151,7 @@
}
TEST_F(WgslGeneratorImplTest, EmitInitializer_Type_Mat_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
WrapInFunction(mat2x3<f16>(vec3<f16>(1_h, 2_h, 3_h), vec3<f16>(3_h, 4_h, 5_h)));
diff --git a/src/tint/writer/wgsl/generator_impl_literal_test.cc b/src/tint/writer/wgsl/generator_impl_literal_test.cc
index f96b09e..c660198 100644
--- a/src/tint/writer/wgsl/generator_impl_literal_test.cc
+++ b/src/tint/writer/wgsl/generator_impl_literal_test.cc
@@ -155,7 +155,7 @@
using WgslGenerator_F16LiteralTest = TestParamHelper<F16Data>;
TEST_P(WgslGenerator_F16LiteralTest, Emit) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* v = Expr(GetParam().value);
diff --git a/src/tint/writer/wgsl/generator_impl_type_test.cc b/src/tint/writer/wgsl/generator_impl_type_test.cc
index 39322f2..4f8740c 100644
--- a/src/tint/writer/wgsl/generator_impl_type_test.cc
+++ b/src/tint/writer/wgsl/generator_impl_type_test.cc
@@ -88,7 +88,7 @@
}
TEST_F(WgslGeneratorImplTest, EmitType_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto type = Alias("make_type_reachable", ty.f16())->type;
@@ -120,7 +120,7 @@
}
TEST_F(WgslGeneratorImplTest, EmitType_Matrix_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto type = Alias("make_type_reachable", ty.mat2x3<f16>())->type;
@@ -305,7 +305,7 @@
}
TEST_F(WgslGeneratorImplTest, EmitType_Vector_F16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto type = Alias("make_type_reachable", ty.vec3<f16>())->type;
diff --git a/src/tint/writer/wgsl/generator_impl_variable_decl_statement_test.cc b/src/tint/writer/wgsl/generator_impl_variable_decl_statement_test.cc
index bf68420..f31aa65 100644
--- a/src/tint/writer/wgsl/generator_impl_variable_decl_statement_test.cc
+++ b/src/tint/writer/wgsl/generator_impl_variable_decl_statement_test.cc
@@ -146,7 +146,7 @@
}
TEST_F(WgslGeneratorImplTest, Emit_VariableDeclStatement_Const_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", Expr(1_h));
Func("f", utils::Empty, ty.void_(),
@@ -226,7 +226,7 @@
}
TEST_F(WgslGeneratorImplTest, Emit_VariableDeclStatement_Const_vec3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", vec3<f16>(1_h, 2_h, 3_h));
Func("f", utils::Empty, ty.void_(),
@@ -287,7 +287,7 @@
}
TEST_F(WgslGeneratorImplTest, Emit_VariableDeclStatement_Const_mat2x3_f16) {
- Enable(ast::Extension::kF16);
+ Enable(builtin::Extension::kF16);
auto* C = Const("C", mat2x3<f16>(1_h, 2_h, 3_h, 4_h, 5_h, 6_h));
Func("f", utils::Empty, ty.void_(),
