mirror of
https://github.com/encounter/dawn-cmake.git
synced 2025-05-14 19:31:25 +00:00
This CL adds a Symbol to the struct type along side the name. The name will be removed in a future CL when the symbol is used everywhere. Change-Id: I6c355908651ba0a155a1e0c9ed1192313a405568 Reviewed-on: https://dawn-review.googlesource.com/c/tint/+/35620 Commit-Queue: dan sinclair <dsinclair@chromium.org> Commit-Queue: Ben Clayton <bclayton@google.com> Auto-Submit: dan sinclair <dsinclair@chromium.org> Reviewed-by: Ben Clayton <bclayton@google.com>
3203 lines
89 KiB
C++
3203 lines
89 KiB
C++
// Copyright 2020 The Tint Authors.
|
|
//
|
|
// Licensed under the Apache License, Version 2.0 (the "License");
|
|
// you may not use this file except in compliance with the License.
|
|
// You may obtain a copy of the License at
|
|
//
|
|
// http://www.apache.org/licenses/LICENSE-2.0
|
|
//
|
|
// Unless required by applicable law or agreed to in writing, software
|
|
// distributed under the License is distributed on an "AS IS" BASIS,
|
|
// WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
|
|
// See the License for the specific language governing permissions and
|
|
// limitations under the License.
|
|
|
|
#include "src/reader/wgsl/parser_impl.h"
|
|
|
|
#include <memory>
|
|
#include <vector>
|
|
|
|
#include "src/ast/access_decoration.h"
|
|
#include "src/ast/array_accessor_expression.h"
|
|
#include "src/ast/binary_expression.h"
|
|
#include "src/ast/binding_decoration.h"
|
|
#include "src/ast/bitcast_expression.h"
|
|
#include "src/ast/bool_literal.h"
|
|
#include "src/ast/break_statement.h"
|
|
#include "src/ast/builtin_decoration.h"
|
|
#include "src/ast/call_expression.h"
|
|
#include "src/ast/case_statement.h"
|
|
#include "src/ast/continue_statement.h"
|
|
#include "src/ast/discard_statement.h"
|
|
#include "src/ast/else_statement.h"
|
|
#include "src/ast/fallthrough_statement.h"
|
|
#include "src/ast/float_literal.h"
|
|
#include "src/ast/identifier_expression.h"
|
|
#include "src/ast/if_statement.h"
|
|
#include "src/ast/location_decoration.h"
|
|
#include "src/ast/member_accessor_expression.h"
|
|
#include "src/ast/return_statement.h"
|
|
#include "src/ast/scalar_constructor_expression.h"
|
|
#include "src/ast/set_decoration.h"
|
|
#include "src/ast/sint_literal.h"
|
|
#include "src/ast/stage_decoration.h"
|
|
#include "src/ast/stride_decoration.h"
|
|
#include "src/ast/struct_block_decoration.h"
|
|
#include "src/ast/struct_member_offset_decoration.h"
|
|
#include "src/ast/switch_statement.h"
|
|
#include "src/ast/type/access_control_type.h"
|
|
#include "src/ast/type/alias_type.h"
|
|
#include "src/ast/type/array_type.h"
|
|
#include "src/ast/type/bool_type.h"
|
|
#include "src/ast/type/depth_texture_type.h"
|
|
#include "src/ast/type/f32_type.h"
|
|
#include "src/ast/type/i32_type.h"
|
|
#include "src/ast/type/matrix_type.h"
|
|
#include "src/ast/type/multisampled_texture_type.h"
|
|
#include "src/ast/type/pointer_type.h"
|
|
#include "src/ast/type/sampled_texture_type.h"
|
|
#include "src/ast/type/sampler_type.h"
|
|
#include "src/ast/type/struct_type.h"
|
|
#include "src/ast/type/u32_type.h"
|
|
#include "src/ast/type/vector_type.h"
|
|
#include "src/ast/type/void_type.h"
|
|
#include "src/ast/type_constructor_expression.h"
|
|
#include "src/ast/type_decoration.h"
|
|
#include "src/ast/uint_literal.h"
|
|
#include "src/ast/unary_op.h"
|
|
#include "src/ast/unary_op_expression.h"
|
|
#include "src/ast/variable.h"
|
|
#include "src/ast/variable_decl_statement.h"
|
|
#include "src/ast/workgroup_decoration.h"
|
|
#include "src/reader/wgsl/lexer.h"
|
|
|
|
namespace tint {
|
|
namespace reader {
|
|
namespace wgsl {
|
|
namespace {
|
|
|
|
template <typename T>
|
|
using Expect = ParserImpl::Expect<T>;
|
|
|
|
template <typename T>
|
|
using Maybe = ParserImpl::Maybe<T>;
|
|
|
|
/// Controls the maximum number of times we'll call into the const_expr function
|
|
/// from itself. This is to guard against stack overflow when there is an
|
|
/// excessive number of type constructors inside the const_expr.
|
|
constexpr uint32_t kMaxConstExprDepth = 128;
|
|
|
|
/// The maximum number of tokens to look ahead to try and sync the
|
|
/// parser on error.
|
|
constexpr size_t const kMaxResynchronizeLookahead = 32;
|
|
|
|
const char kVertexStage[] = "vertex";
|
|
const char kFragmentStage[] = "fragment";
|
|
const char kComputeStage[] = "compute";
|
|
|
|
const char kReadAccessControl[] = "read";
|
|
const char kReadWriteAccessControl[] = "read_write";
|
|
|
|
ast::Builtin ident_to_builtin(const std::string& str) {
|
|
if (str == "position") {
|
|
return ast::Builtin::kPosition;
|
|
}
|
|
if (str == "vertex_idx") {
|
|
return ast::Builtin::kVertexIdx;
|
|
}
|
|
if (str == "instance_idx") {
|
|
return ast::Builtin::kInstanceIdx;
|
|
}
|
|
if (str == "front_facing") {
|
|
return ast::Builtin::kFrontFacing;
|
|
}
|
|
if (str == "frag_coord") {
|
|
return ast::Builtin::kFragCoord;
|
|
}
|
|
if (str == "frag_depth") {
|
|
return ast::Builtin::kFragDepth;
|
|
}
|
|
if (str == "local_invocation_id") {
|
|
return ast::Builtin::kLocalInvocationId;
|
|
}
|
|
if (str == "local_invocation_idx") {
|
|
return ast::Builtin::kLocalInvocationIdx;
|
|
}
|
|
if (str == "global_invocation_id") {
|
|
return ast::Builtin::kGlobalInvocationId;
|
|
}
|
|
return ast::Builtin::kNone;
|
|
}
|
|
|
|
const char kAccessDecoration[] = "access";
|
|
const char kBindingDecoration[] = "binding";
|
|
const char kBlockDecoration[] = "block";
|
|
const char kBuiltinDecoration[] = "builtin";
|
|
const char kLocationDecoration[] = "location";
|
|
const char kOffsetDecoration[] = "offset";
|
|
const char kSetDecoration[] = "set";
|
|
const char kStageDecoration[] = "stage";
|
|
const char kStrideDecoration[] = "stride";
|
|
const char kWorkgroupSizeDecoration[] = "workgroup_size";
|
|
|
|
bool is_decoration(Token t) {
|
|
if (!t.IsIdentifier())
|
|
return false;
|
|
|
|
auto s = t.to_str();
|
|
return s == kAccessDecoration || s == kBindingDecoration ||
|
|
s == kBlockDecoration || s == kBuiltinDecoration ||
|
|
s == kLocationDecoration || s == kOffsetDecoration ||
|
|
s == kSetDecoration || s == kStageDecoration ||
|
|
s == kStrideDecoration || s == kWorkgroupSizeDecoration;
|
|
}
|
|
|
|
/// Enter-exit counters for block token types.
|
|
/// Used by sync_to() to skip over closing block tokens that were opened during
|
|
/// the forward scan.
|
|
struct BlockCounters {
|
|
int attrs = 0; // [[ ]]
|
|
int brace = 0; // { }
|
|
int bracket = 0; // [ ]
|
|
int paren = 0; // ( )
|
|
|
|
/// @return the current enter-exit depth for the given block token type. If
|
|
/// `t` is not a block token type, then 0 is always returned.
|
|
int consume(const Token& t) {
|
|
if (t.Is(Token::Type::kAttrLeft))
|
|
return attrs++;
|
|
if (t.Is(Token::Type::kAttrRight))
|
|
return attrs--;
|
|
if (t.Is(Token::Type::kBraceLeft))
|
|
return brace++;
|
|
if (t.Is(Token::Type::kBraceRight))
|
|
return brace--;
|
|
if (t.Is(Token::Type::kBracketLeft))
|
|
return bracket++;
|
|
if (t.Is(Token::Type::kBracketRight))
|
|
return bracket--;
|
|
if (t.Is(Token::Type::kParenLeft))
|
|
return paren++;
|
|
if (t.Is(Token::Type::kParenRight))
|
|
return paren--;
|
|
return 0;
|
|
}
|
|
};
|
|
|
|
} // namespace
|
|
|
|
ParserImpl::FunctionHeader::FunctionHeader() = default;
|
|
|
|
ParserImpl::FunctionHeader::FunctionHeader(const FunctionHeader&) = default;
|
|
|
|
ParserImpl::FunctionHeader::FunctionHeader(Source src,
|
|
std::string n,
|
|
ast::VariableList p,
|
|
ast::type::Type* ret_ty)
|
|
: source(src), name(n), params(p), return_type(ret_ty) {}
|
|
|
|
ParserImpl::FunctionHeader::~FunctionHeader() = default;
|
|
|
|
ParserImpl::FunctionHeader& ParserImpl::FunctionHeader::operator=(
|
|
const FunctionHeader& rhs) = default;
|
|
|
|
ParserImpl::ParserImpl(Source::File const* file)
|
|
: lexer_(std::make_unique<Lexer>(file)) {}
|
|
|
|
ParserImpl::~ParserImpl() = default;
|
|
|
|
ParserImpl::Failure::Errored ParserImpl::add_error(const Source& source,
|
|
const std::string& err,
|
|
const std::string& use) {
|
|
std::stringstream msg;
|
|
msg << err;
|
|
if (!use.empty()) {
|
|
msg << " for " << use;
|
|
}
|
|
add_error(source, msg.str());
|
|
return Failure::kErrored;
|
|
}
|
|
|
|
ParserImpl::Failure::Errored ParserImpl::add_error(const Token& t,
|
|
const std::string& err) {
|
|
add_error(t.source(), err);
|
|
return Failure::kErrored;
|
|
}
|
|
|
|
ParserImpl::Failure::Errored ParserImpl::add_error(const Source& source,
|
|
const std::string& err) {
|
|
if (silence_errors_ == 0) {
|
|
diag::Diagnostic diagnostic;
|
|
diagnostic.severity = diag::Severity::Error;
|
|
diagnostic.message = err;
|
|
diagnostic.source = source;
|
|
diags_.add(std::move(diagnostic));
|
|
}
|
|
return Failure::kErrored;
|
|
}
|
|
|
|
Token ParserImpl::next() {
|
|
if (!token_queue_.empty()) {
|
|
auto t = token_queue_.front();
|
|
token_queue_.pop_front();
|
|
return t;
|
|
}
|
|
return lexer_->next();
|
|
}
|
|
|
|
Token ParserImpl::peek(size_t idx) {
|
|
while (token_queue_.size() < (idx + 1))
|
|
token_queue_.push_back(lexer_->next());
|
|
|
|
return token_queue_[idx];
|
|
}
|
|
|
|
Token ParserImpl::peek() {
|
|
return peek(0);
|
|
}
|
|
|
|
void ParserImpl::register_constructed(const std::string& name,
|
|
ast::type::Type* type) {
|
|
assert(type);
|
|
registered_constructs_[name] = type;
|
|
}
|
|
|
|
ast::type::Type* ParserImpl::get_constructed(const std::string& name) {
|
|
if (registered_constructs_.find(name) == registered_constructs_.end()) {
|
|
return nullptr;
|
|
}
|
|
return registered_constructs_[name];
|
|
}
|
|
|
|
bool ParserImpl::Parse() {
|
|
translation_unit();
|
|
return !has_error();
|
|
}
|
|
|
|
// translation_unit
|
|
// : global_decl* EOF
|
|
void ParserImpl::translation_unit() {
|
|
while (synchronized_) {
|
|
auto p = peek();
|
|
if (p.IsEof()) {
|
|
break;
|
|
}
|
|
expect_global_decl();
|
|
if (diags_.error_count() >= max_errors_) {
|
|
add_error(Source{{}, p.source().file},
|
|
"stopping after " + std::to_string(max_errors_) + " errors");
|
|
break;
|
|
}
|
|
}
|
|
|
|
assert(module_.IsValid());
|
|
}
|
|
|
|
// global_decl
|
|
// : SEMICOLON
|
|
// | global_variable_decl SEMICLON
|
|
// | global_constant_decl SEMICOLON
|
|
// | type_alias SEMICOLON
|
|
// | struct_decl SEMICOLON
|
|
// | function_decl
|
|
Expect<bool> ParserImpl::expect_global_decl() {
|
|
if (match(Token::Type::kSemicolon) || match(Token::Type::kEOF))
|
|
return true;
|
|
|
|
bool errored = false;
|
|
|
|
auto decos = decoration_list();
|
|
if (decos.errored)
|
|
errored = true;
|
|
if (!synchronized_)
|
|
return Failure::kErrored;
|
|
|
|
auto decl = sync(Token::Type::kSemicolon, [&]() -> Maybe<bool> {
|
|
auto gv = global_variable_decl(decos.value);
|
|
if (gv.errored)
|
|
return Failure::kErrored;
|
|
if (gv.matched) {
|
|
if (!expect("variable declaration", Token::Type::kSemicolon))
|
|
return Failure::kErrored;
|
|
|
|
module_.AddGlobalVariable(gv.value);
|
|
return true;
|
|
}
|
|
|
|
auto gc = global_constant_decl();
|
|
if (gc.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (gc.matched) {
|
|
if (!expect("constant declaration", Token::Type::kSemicolon))
|
|
return Failure::kErrored;
|
|
|
|
module_.AddGlobalVariable(gc.value);
|
|
return true;
|
|
}
|
|
|
|
auto ta = type_alias();
|
|
if (ta.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (ta.matched) {
|
|
if (!expect("type alias", Token::Type::kSemicolon))
|
|
return Failure::kErrored;
|
|
|
|
module_.AddConstructedType(ta.value);
|
|
return true;
|
|
}
|
|
|
|
auto str = struct_decl(decos.value);
|
|
if (str.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (str.matched) {
|
|
if (!expect("struct declaration", Token::Type::kSemicolon))
|
|
return Failure::kErrored;
|
|
|
|
auto* type = module_.unique_type(std::move(str.value));
|
|
register_constructed(type->As<ast::type::Struct>()->name(), type);
|
|
module_.AddConstructedType(type);
|
|
return true;
|
|
}
|
|
|
|
return Failure::kNoMatch;
|
|
});
|
|
|
|
if (decl.errored)
|
|
errored = true;
|
|
if (decl.matched)
|
|
return true;
|
|
|
|
auto func = function_decl(decos.value);
|
|
if (func.errored)
|
|
errored = true;
|
|
if (func.matched) {
|
|
module_.AddFunction(func.value);
|
|
return true;
|
|
}
|
|
|
|
if (errored)
|
|
return Failure::kErrored;
|
|
|
|
// Invalid syntax found - try and determine the best error message
|
|
|
|
// We have decorations parsed, but nothing to consume them?
|
|
if (decos.value.size() > 0)
|
|
return add_error(next(), "expected declaration after decorations");
|
|
|
|
// We have a statement outside of a function?
|
|
auto t = peek();
|
|
auto stat = without_error([&] { return statement(); });
|
|
if (stat.matched) {
|
|
// Attempt to jump to the next '}' - the function might have just been
|
|
// missing an opening line.
|
|
sync_to(Token::Type::kBraceRight, true);
|
|
return add_error(t, "statement found outside of function body");
|
|
}
|
|
if (!stat.errored) {
|
|
// No match, no error - the parser might not have progressed.
|
|
// Ensure we always make _some_ forward progress.
|
|
next();
|
|
}
|
|
|
|
// Exhausted all attempts to make sense of where we're at.
|
|
// Spew a generic error.
|
|
|
|
return add_error(t, "unexpected token");
|
|
}
|
|
|
|
// global_variable_decl
|
|
// : variable_decoration_list* variable_decl
|
|
// | variable_decoration_list* variable_decl EQUAL const_expr
|
|
Maybe<ast::Variable*> ParserImpl::global_variable_decl(
|
|
ast::DecorationList& decos) {
|
|
auto decl = variable_decl();
|
|
if (decl.errored)
|
|
return Failure::kErrored;
|
|
if (!decl.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
auto var_decos = cast_decorations<ast::VariableDecoration>(decos);
|
|
if (var_decos.errored)
|
|
return Failure::kErrored;
|
|
|
|
ast::Expression* constructor = nullptr;
|
|
if (match(Token::Type::kEqual)) {
|
|
auto expr = expect_const_expr();
|
|
if (expr.errored)
|
|
return Failure::kErrored;
|
|
constructor = expr.value;
|
|
}
|
|
|
|
return create<ast::Variable>(decl->source, // source
|
|
decl->name, // name
|
|
decl->storage_class, // storage_class
|
|
decl->type, // type
|
|
false, // is_const
|
|
constructor, // constructor
|
|
std::move(var_decos.value)); // decorations
|
|
}
|
|
|
|
// global_constant_decl
|
|
// : CONST variable_ident_decl EQUAL const_expr
|
|
Maybe<ast::Variable*> ParserImpl::global_constant_decl() {
|
|
if (!match(Token::Type::kConst))
|
|
return Failure::kNoMatch;
|
|
|
|
const char* use = "constant declaration";
|
|
|
|
auto decl = expect_variable_ident_decl(use);
|
|
if (decl.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!expect(use, Token::Type::kEqual))
|
|
return Failure::kErrored;
|
|
|
|
auto init = expect_const_expr();
|
|
if (init.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::Variable>(decl->source, // source
|
|
decl->name, // name
|
|
ast::StorageClass::kNone, // storage_class
|
|
decl->type, // type
|
|
true, // is_const
|
|
init.value, // constructor
|
|
ast::VariableDecorationList{}); // decorations
|
|
}
|
|
|
|
// variable_decl
|
|
// : VAR variable_storage_decoration? variable_ident_decl
|
|
Maybe<ParserImpl::VarDeclInfo> ParserImpl::variable_decl() {
|
|
if (!match(Token::Type::kVar))
|
|
return Failure::kNoMatch;
|
|
|
|
auto sc = variable_storage_decoration();
|
|
if (sc.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto decl = expect_variable_ident_decl("variable declaration");
|
|
if (decl.errored)
|
|
return Failure::kErrored;
|
|
|
|
return VarDeclInfo{decl->source, decl->name,
|
|
sc.matched ? sc.value : ast::StorageClass::kNone,
|
|
decl->type};
|
|
}
|
|
|
|
// texture_sampler_types
|
|
// : sampler_type
|
|
// | depth_texture_type
|
|
// | sampled_texture_type LESS_THAN type_decl GREATER_THAN
|
|
// | multisampled_texture_type LESS_THAN type_decl GREATER_THAN
|
|
// | storage_texture_type LESS_THAN image_storage_type GREATER_THAN
|
|
Maybe<ast::type::Type*> ParserImpl::texture_sampler_types() {
|
|
auto type = sampler_type();
|
|
if (type.matched)
|
|
return type;
|
|
|
|
type = depth_texture_type();
|
|
if (type.matched)
|
|
return type.value;
|
|
|
|
auto dim = sampled_texture_type();
|
|
if (dim.matched) {
|
|
const char* use = "sampled texture type";
|
|
|
|
auto subtype = expect_lt_gt_block(use, [&] { return expect_type(use); });
|
|
if (subtype.errored)
|
|
return Failure::kErrored;
|
|
|
|
return module_.create<ast::type::SampledTexture>(dim.value, subtype.value);
|
|
}
|
|
|
|
auto ms_dim = multisampled_texture_type();
|
|
if (ms_dim.matched) {
|
|
const char* use = "multisampled texture type";
|
|
|
|
auto subtype = expect_lt_gt_block(use, [&] { return expect_type(use); });
|
|
if (subtype.errored)
|
|
return Failure::kErrored;
|
|
|
|
return module_.create<ast::type::MultisampledTexture>(ms_dim.value,
|
|
subtype.value);
|
|
}
|
|
|
|
auto storage = storage_texture_type();
|
|
if (storage.matched) {
|
|
const char* use = "storage texture type";
|
|
|
|
auto format =
|
|
expect_lt_gt_block(use, [&] { return expect_image_storage_type(use); });
|
|
|
|
if (format.errored)
|
|
return Failure::kErrored;
|
|
|
|
return module_.create<ast::type::StorageTexture>(
|
|
storage->first, storage->second, format.value);
|
|
}
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// sampler_type
|
|
// : SAMPLER
|
|
// | SAMPLER_COMPARISON
|
|
Maybe<ast::type::Type*> ParserImpl::sampler_type() {
|
|
if (match(Token::Type::kSampler))
|
|
return module_.create<ast::type::Sampler>(ast::type::SamplerKind::kSampler);
|
|
|
|
if (match(Token::Type::kComparisonSampler))
|
|
return module_.create<ast::type::Sampler>(
|
|
ast::type::SamplerKind::kComparisonSampler);
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// sampled_texture_type
|
|
// : TEXTURE_SAMPLED_1D
|
|
// | TEXTURE_SAMPLED_1D_ARRAY
|
|
// | TEXTURE_SAMPLED_2D
|
|
// | TEXTURE_SAMPLED_2D_ARRAY
|
|
// | TEXTURE_SAMPLED_3D
|
|
// | TEXTURE_SAMPLED_CUBE
|
|
// | TEXTURE_SAMPLED_CUBE_ARRAY
|
|
Maybe<ast::type::TextureDimension> ParserImpl::sampled_texture_type() {
|
|
if (match(Token::Type::kTextureSampled1d))
|
|
return ast::type::TextureDimension::k1d;
|
|
|
|
if (match(Token::Type::kTextureSampled1dArray))
|
|
return ast::type::TextureDimension::k1dArray;
|
|
|
|
if (match(Token::Type::kTextureSampled2d))
|
|
return ast::type::TextureDimension::k2d;
|
|
|
|
if (match(Token::Type::kTextureSampled2dArray))
|
|
return ast::type::TextureDimension::k2dArray;
|
|
|
|
if (match(Token::Type::kTextureSampled3d))
|
|
return ast::type::TextureDimension::k3d;
|
|
|
|
if (match(Token::Type::kTextureSampledCube))
|
|
return ast::type::TextureDimension::kCube;
|
|
|
|
if (match(Token::Type::kTextureSampledCubeArray))
|
|
return ast::type::TextureDimension::kCubeArray;
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// multisampled_texture_type
|
|
// : TEXTURE_MULTISAMPLED_2D
|
|
Maybe<ast::type::TextureDimension> ParserImpl::multisampled_texture_type() {
|
|
if (match(Token::Type::kTextureMultisampled2d))
|
|
return ast::type::TextureDimension::k2d;
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// storage_texture_type
|
|
// : TEXTURE_RO_1D
|
|
// | TEXTURE_RO_1D_ARRAY
|
|
// | TEXTURE_RO_2D
|
|
// | TEXTURE_RO_2D_ARRAY
|
|
// | TEXTURE_RO_3D
|
|
// | TEXTURE_WO_1D
|
|
// | TEXTURE_WO_1D_ARRAY
|
|
// | TEXTURE_WO_2D
|
|
// | TEXTURE_WO_2D_ARRAY
|
|
// | TEXTURE_WO_3D
|
|
// | TEXTURE_STORAGE_RO_1D
|
|
// | TEXTURE_STORAGE_RO_1D_ARRAY
|
|
// | TEXTURE_STORAGE_RO_2D
|
|
// | TEXTURE_STORAGE_RO_2D_ARRAY
|
|
// | TEXTURE_STORAGE_RO_3D
|
|
// | TEXTURE_STORAGE_WO_1D
|
|
// | TEXTURE_STORAGE_WO_1D_ARRAY
|
|
// | TEXTURE_STORAGE_WO_2D
|
|
// | TEXTURE_STORAGE_WO_2D_ARRAY
|
|
// | TEXTURE_STORAGE_WO_3D
|
|
Maybe<std::pair<ast::type::TextureDimension, ast::AccessControl>>
|
|
ParserImpl::storage_texture_type() {
|
|
using Ret = std::pair<ast::type::TextureDimension, ast::AccessControl>;
|
|
if (match(Token::Type::kTextureStorageReadonly1d)) {
|
|
return Ret{ast::type::TextureDimension::k1d, ast::AccessControl::kReadOnly};
|
|
}
|
|
|
|
if (match(Token::Type::kTextureStorageReadonly1dArray)) {
|
|
return Ret{ast::type::TextureDimension::k1dArray,
|
|
ast::AccessControl::kReadOnly};
|
|
}
|
|
|
|
if (match(Token::Type::kTextureStorageReadonly2d)) {
|
|
return Ret{ast::type::TextureDimension::k2d, ast::AccessControl::kReadOnly};
|
|
}
|
|
|
|
if (match(Token::Type::kTextureStorageReadonly2dArray)) {
|
|
return Ret{ast::type::TextureDimension::k2dArray,
|
|
ast::AccessControl::kReadOnly};
|
|
}
|
|
|
|
if (match(Token::Type::kTextureStorageReadonly3d)) {
|
|
return Ret{ast::type::TextureDimension::k3d, ast::AccessControl::kReadOnly};
|
|
}
|
|
|
|
if (match(Token::Type::kTextureStorageWriteonly1d)) {
|
|
return Ret{ast::type::TextureDimension::k1d,
|
|
ast::AccessControl::kWriteOnly};
|
|
}
|
|
|
|
if (match(Token::Type::kTextureStorageWriteonly1dArray)) {
|
|
return Ret{ast::type::TextureDimension::k1dArray,
|
|
ast::AccessControl::kWriteOnly};
|
|
}
|
|
|
|
if (match(Token::Type::kTextureStorageWriteonly2d)) {
|
|
return Ret{ast::type::TextureDimension::k2d,
|
|
ast::AccessControl::kWriteOnly};
|
|
}
|
|
|
|
if (match(Token::Type::kTextureStorageWriteonly2dArray)) {
|
|
return Ret{ast::type::TextureDimension::k2dArray,
|
|
ast::AccessControl::kWriteOnly};
|
|
}
|
|
|
|
if (match(Token::Type::kTextureStorageWriteonly3d)) {
|
|
return Ret{ast::type::TextureDimension::k3d,
|
|
ast::AccessControl::kWriteOnly};
|
|
}
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// depth_texture_type
|
|
// : TEXTURE_DEPTH_2D
|
|
// | TEXTURE_DEPTH_2D_ARRAY
|
|
// | TEXTURE_DEPTH_CUBE
|
|
// | TEXTURE_DEPTH_CUBE_ARRAY
|
|
Maybe<ast::type::Type*> ParserImpl::depth_texture_type() {
|
|
if (match(Token::Type::kTextureDepth2d))
|
|
return module_.create<ast::type::DepthTexture>(
|
|
ast::type::TextureDimension::k2d);
|
|
|
|
if (match(Token::Type::kTextureDepth2dArray))
|
|
return module_.create<ast::type::DepthTexture>(
|
|
ast::type::TextureDimension::k2dArray);
|
|
|
|
if (match(Token::Type::kTextureDepthCube))
|
|
return module_.create<ast::type::DepthTexture>(
|
|
ast::type::TextureDimension::kCube);
|
|
|
|
if (match(Token::Type::kTextureDepthCubeArray))
|
|
return module_.create<ast::type::DepthTexture>(
|
|
ast::type::TextureDimension::kCubeArray);
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// image_storage_type
|
|
// : R8UNORM
|
|
// | R8SNORM
|
|
// | R8UINT
|
|
// | R8SINT
|
|
// | R16UINT
|
|
// | R16SINT
|
|
// | R16FLOAT
|
|
// | RG8UNORM
|
|
// | RG8SNORM
|
|
// | RG8UINT
|
|
// | RG8SINT
|
|
// | R32UINT
|
|
// | R32SINT
|
|
// | R32FLOAT
|
|
// | RG16UINT
|
|
// | RG16SINT
|
|
// | RG16FLOAT
|
|
// | RGBA8UNORM
|
|
/// | RGBA8UNORM-SRGB
|
|
// | RGBA8SNORM
|
|
// | RGBA8UINT
|
|
// | RGBA8SINT
|
|
// | BGRA8UNORM
|
|
// | BGRA8UNORM-SRGB
|
|
// | RGB10A2UNORM
|
|
// | RG11B10FLOAT
|
|
// | RG32UINT
|
|
// | RG32SINT
|
|
// | RG32FLOAT
|
|
// | RGBA16UINT
|
|
// | RGBA16SINT
|
|
// | RGBA16FLOAT
|
|
// | RGBA32UINT
|
|
// | RGBA32SINT
|
|
// | RGBA32FLOAT
|
|
Expect<ast::type::ImageFormat> ParserImpl::expect_image_storage_type(
|
|
const std::string& use) {
|
|
if (match(Token::Type::kFormatR8Unorm))
|
|
return ast::type::ImageFormat::kR8Unorm;
|
|
|
|
if (match(Token::Type::kFormatR8Snorm))
|
|
return ast::type::ImageFormat::kR8Snorm;
|
|
|
|
if (match(Token::Type::kFormatR8Uint))
|
|
return ast::type::ImageFormat::kR8Uint;
|
|
|
|
if (match(Token::Type::kFormatR8Sint))
|
|
return ast::type::ImageFormat::kR8Sint;
|
|
|
|
if (match(Token::Type::kFormatR16Uint))
|
|
return ast::type::ImageFormat::kR16Uint;
|
|
|
|
if (match(Token::Type::kFormatR16Sint))
|
|
return ast::type::ImageFormat::kR16Sint;
|
|
|
|
if (match(Token::Type::kFormatR16Float))
|
|
return ast::type::ImageFormat::kR16Float;
|
|
|
|
if (match(Token::Type::kFormatRg8Unorm))
|
|
return ast::type::ImageFormat::kRg8Unorm;
|
|
|
|
if (match(Token::Type::kFormatRg8Snorm))
|
|
return ast::type::ImageFormat::kRg8Snorm;
|
|
|
|
if (match(Token::Type::kFormatRg8Uint))
|
|
return ast::type::ImageFormat::kRg8Uint;
|
|
|
|
if (match(Token::Type::kFormatRg8Sint))
|
|
return ast::type::ImageFormat::kRg8Sint;
|
|
|
|
if (match(Token::Type::kFormatR32Uint))
|
|
return ast::type::ImageFormat::kR32Uint;
|
|
|
|
if (match(Token::Type::kFormatR32Sint))
|
|
return ast::type::ImageFormat::kR32Sint;
|
|
|
|
if (match(Token::Type::kFormatR32Float))
|
|
return ast::type::ImageFormat::kR32Float;
|
|
|
|
if (match(Token::Type::kFormatRg16Uint))
|
|
return ast::type::ImageFormat::kRg16Uint;
|
|
|
|
if (match(Token::Type::kFormatRg16Sint))
|
|
return ast::type::ImageFormat::kRg16Sint;
|
|
|
|
if (match(Token::Type::kFormatRg16Float))
|
|
return ast::type::ImageFormat::kRg16Float;
|
|
|
|
if (match(Token::Type::kFormatRgba8Unorm))
|
|
return ast::type::ImageFormat::kRgba8Unorm;
|
|
|
|
if (match(Token::Type::kFormatRgba8UnormSrgb))
|
|
return ast::type::ImageFormat::kRgba8UnormSrgb;
|
|
|
|
if (match(Token::Type::kFormatRgba8Snorm))
|
|
return ast::type::ImageFormat::kRgba8Snorm;
|
|
|
|
if (match(Token::Type::kFormatRgba8Uint))
|
|
return ast::type::ImageFormat::kRgba8Uint;
|
|
|
|
if (match(Token::Type::kFormatRgba8Sint))
|
|
return ast::type::ImageFormat::kRgba8Sint;
|
|
|
|
if (match(Token::Type::kFormatBgra8Unorm))
|
|
return ast::type::ImageFormat::kBgra8Unorm;
|
|
|
|
if (match(Token::Type::kFormatBgra8UnormSrgb))
|
|
return ast::type::ImageFormat::kBgra8UnormSrgb;
|
|
|
|
if (match(Token::Type::kFormatRgb10A2Unorm))
|
|
return ast::type::ImageFormat::kRgb10A2Unorm;
|
|
|
|
if (match(Token::Type::kFormatRg11B10Float))
|
|
return ast::type::ImageFormat::kRg11B10Float;
|
|
|
|
if (match(Token::Type::kFormatRg32Uint))
|
|
return ast::type::ImageFormat::kRg32Uint;
|
|
|
|
if (match(Token::Type::kFormatRg32Sint))
|
|
return ast::type::ImageFormat::kRg32Sint;
|
|
|
|
if (match(Token::Type::kFormatRg32Float))
|
|
return ast::type::ImageFormat::kRg32Float;
|
|
|
|
if (match(Token::Type::kFormatRgba16Uint))
|
|
return ast::type::ImageFormat::kRgba16Uint;
|
|
|
|
if (match(Token::Type::kFormatRgba16Sint))
|
|
return ast::type::ImageFormat::kRgba16Sint;
|
|
|
|
if (match(Token::Type::kFormatRgba16Float))
|
|
return ast::type::ImageFormat::kRgba16Float;
|
|
|
|
if (match(Token::Type::kFormatRgba32Uint))
|
|
return ast::type::ImageFormat::kRgba32Uint;
|
|
|
|
if (match(Token::Type::kFormatRgba32Sint))
|
|
return ast::type::ImageFormat::kRgba32Sint;
|
|
|
|
if (match(Token::Type::kFormatRgba32Float))
|
|
return ast::type::ImageFormat::kRgba32Float;
|
|
|
|
return add_error(peek().source(), "invalid format", use);
|
|
}
|
|
|
|
// variable_ident_decl
|
|
// : IDENT COLON variable_decoration_list* type_decl
|
|
Expect<ParserImpl::TypedIdentifier> ParserImpl::expect_variable_ident_decl(
|
|
const std::string& use) {
|
|
auto ident = expect_ident(use);
|
|
if (ident.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!expect(use, Token::Type::kColon))
|
|
return Failure::kErrored;
|
|
|
|
auto decos = decoration_list();
|
|
if (decos.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto access_decos = take_decorations<ast::AccessDecoration>(decos.value);
|
|
|
|
auto t = peek();
|
|
auto type = type_decl(decos.value);
|
|
if (type.errored)
|
|
return Failure::kErrored;
|
|
if (!type.matched)
|
|
return add_error(t.source(), "invalid type", use);
|
|
|
|
if (!expect_decorations_consumed(decos.value))
|
|
return Failure::kErrored;
|
|
|
|
if (access_decos.size() > 1)
|
|
return add_error(ident.source, "multiple access decorations not allowed");
|
|
|
|
auto* ty = type.value;
|
|
for (auto* deco : access_decos) {
|
|
// If we have an access control decoration then we take it and wrap our
|
|
// type up with that decoration
|
|
ty = module_.create<ast::type::AccessControl>(
|
|
deco->As<ast::AccessDecoration>()->value(), ty);
|
|
}
|
|
|
|
return TypedIdentifier{ty, ident.value, ident.source};
|
|
}
|
|
|
|
Expect<ast::AccessControl> ParserImpl::expect_access_type() {
|
|
auto ident = expect_ident("access_type");
|
|
if (ident.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (ident.value == kReadAccessControl)
|
|
return {ast::AccessControl::kReadOnly, ident.source};
|
|
if (ident.value == kReadWriteAccessControl)
|
|
return {ast::AccessControl::kReadWrite, ident.source};
|
|
|
|
return add_error(ident.source, "invalid value for access decoration");
|
|
}
|
|
|
|
// variable_storage_decoration
|
|
// : LESS_THAN storage_class GREATER_THAN
|
|
Maybe<ast::StorageClass> ParserImpl::variable_storage_decoration() {
|
|
if (!peek().IsLessThan())
|
|
return Failure::kNoMatch;
|
|
|
|
const char* use = "variable decoration";
|
|
|
|
auto sc = expect_lt_gt_block(use, [&] { return expect_storage_class(use); });
|
|
|
|
if (sc.errored)
|
|
return Failure::kErrored;
|
|
|
|
return sc.value;
|
|
}
|
|
|
|
// type_alias
|
|
// : TYPE IDENT EQUAL type_decl
|
|
Maybe<ast::type::Type*> ParserImpl::type_alias() {
|
|
auto t = peek();
|
|
if (!t.IsType())
|
|
return Failure::kNoMatch;
|
|
|
|
next(); // Consume the peek
|
|
|
|
const char* use = "type alias";
|
|
|
|
auto name = expect_ident(use);
|
|
if (name.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!expect(use, Token::Type::kEqual))
|
|
return Failure::kErrored;
|
|
|
|
auto type = type_decl();
|
|
if (type.errored)
|
|
return Failure::kErrored;
|
|
if (!type.matched)
|
|
return add_error(peek(), "invalid type alias");
|
|
|
|
auto* alias = module_.create<ast::type::Alias>(
|
|
module_.RegisterSymbol(name.value), name.value, type.value);
|
|
register_constructed(name.value, alias);
|
|
|
|
return alias;
|
|
}
|
|
|
|
// type_decl
|
|
// : IDENTIFIER
|
|
// | BOOL
|
|
// | FLOAT32
|
|
// | INT32
|
|
// | UINT32
|
|
// | VEC2 LESS_THAN type_decl GREATER_THAN
|
|
// | VEC3 LESS_THAN type_decl GREATER_THAN
|
|
// | VEC4 LESS_THAN type_decl GREATER_THAN
|
|
// | PTR LESS_THAN storage_class, type_decl GREATER_THAN
|
|
// | array_decoration_list* ARRAY LESS_THAN type_decl COMMA
|
|
// INT_LITERAL GREATER_THAN
|
|
// | array_decoration_list* ARRAY LESS_THAN type_decl
|
|
// GREATER_THAN
|
|
// | MAT2x2 LESS_THAN type_decl GREATER_THAN
|
|
// | MAT2x3 LESS_THAN type_decl GREATER_THAN
|
|
// | MAT2x4 LESS_THAN type_decl GREATER_THAN
|
|
// | MAT3x2 LESS_THAN type_decl GREATER_THAN
|
|
// | MAT3x3 LESS_THAN type_decl GREATER_THAN
|
|
// | MAT3x4 LESS_THAN type_decl GREATER_THAN
|
|
// | MAT4x2 LESS_THAN type_decl GREATER_THAN
|
|
// | MAT4x3 LESS_THAN type_decl GREATER_THAN
|
|
// | MAT4x4 LESS_THAN type_decl GREATER_THAN
|
|
// | texture_sampler_types
|
|
Maybe<ast::type::Type*> ParserImpl::type_decl() {
|
|
auto decos = decoration_list();
|
|
if (decos.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto type = type_decl(decos.value);
|
|
if (type.errored)
|
|
return Failure::kErrored;
|
|
if (!type.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
if (!expect_decorations_consumed(decos.value))
|
|
return Failure::kErrored;
|
|
|
|
return type.value;
|
|
}
|
|
|
|
Maybe<ast::type::Type*> ParserImpl::type_decl(ast::DecorationList& decos) {
|
|
auto t = peek();
|
|
if (match(Token::Type::kIdentifier)) {
|
|
auto* ty = get_constructed(t.to_str());
|
|
if (ty == nullptr)
|
|
return add_error(t, "unknown constructed type '" + t.to_str() + "'");
|
|
|
|
return ty;
|
|
}
|
|
|
|
if (match(Token::Type::kBool))
|
|
return module_.create<ast::type::Bool>();
|
|
|
|
if (match(Token::Type::kF32))
|
|
return module_.create<ast::type::F32>();
|
|
|
|
if (match(Token::Type::kI32))
|
|
return module_.create<ast::type::I32>();
|
|
|
|
if (match(Token::Type::kU32))
|
|
return module_.create<ast::type::U32>();
|
|
|
|
if (t.IsVec2() || t.IsVec3() || t.IsVec4()) {
|
|
next(); // Consume the peek
|
|
return expect_type_decl_vector(t);
|
|
}
|
|
|
|
if (match(Token::Type::kPtr))
|
|
return expect_type_decl_pointer();
|
|
|
|
if (match(Token::Type::kArray)) {
|
|
auto array_decos = cast_decorations<ast::ArrayDecoration>(decos);
|
|
if (array_decos.errored)
|
|
return Failure::kErrored;
|
|
|
|
return expect_type_decl_array(std::move(array_decos.value));
|
|
}
|
|
|
|
if (t.IsMat2x2() || t.IsMat2x3() || t.IsMat2x4() || t.IsMat3x2() ||
|
|
t.IsMat3x3() || t.IsMat3x4() || t.IsMat4x2() || t.IsMat4x3() ||
|
|
t.IsMat4x4()) {
|
|
next(); // Consume the peek
|
|
return expect_type_decl_matrix(t);
|
|
}
|
|
|
|
auto texture_or_sampler = texture_sampler_types();
|
|
if (texture_or_sampler.errored)
|
|
return Failure::kErrored;
|
|
if (texture_or_sampler.matched)
|
|
return texture_or_sampler.value;
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
Expect<ast::type::Type*> ParserImpl::expect_type(const std::string& use) {
|
|
auto type = type_decl();
|
|
if (type.errored)
|
|
return Failure::kErrored;
|
|
if (!type.matched)
|
|
return add_error(peek().source(), "invalid type", use);
|
|
return type.value;
|
|
}
|
|
|
|
Expect<ast::type::Type*> ParserImpl::expect_type_decl_pointer() {
|
|
const char* use = "ptr declaration";
|
|
|
|
return expect_lt_gt_block(use, [&]() -> Expect<ast::type::Type*> {
|
|
auto sc = expect_storage_class(use);
|
|
if (sc.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!expect(use, Token::Type::kComma))
|
|
return Failure::kErrored;
|
|
|
|
auto subtype = expect_type(use);
|
|
if (subtype.errored)
|
|
return Failure::kErrored;
|
|
|
|
return module_.create<ast::type::Pointer>(subtype.value, sc.value);
|
|
});
|
|
}
|
|
|
|
Expect<ast::type::Type*> ParserImpl::expect_type_decl_vector(Token t) {
|
|
uint32_t count = 2;
|
|
if (t.IsVec3())
|
|
count = 3;
|
|
else if (t.IsVec4())
|
|
count = 4;
|
|
|
|
const char* use = "vector";
|
|
|
|
auto subtype = expect_lt_gt_block(use, [&] { return expect_type(use); });
|
|
if (subtype.errored)
|
|
return Failure::kErrored;
|
|
|
|
return module_.create<ast::type::Vector>(subtype.value, count);
|
|
}
|
|
|
|
Expect<ast::type::Type*> ParserImpl::expect_type_decl_array(
|
|
ast::ArrayDecorationList decos) {
|
|
const char* use = "array declaration";
|
|
|
|
return expect_lt_gt_block(use, [&]() -> Expect<ast::type::Type*> {
|
|
auto subtype = expect_type(use);
|
|
if (subtype.errored)
|
|
return Failure::kErrored;
|
|
|
|
uint32_t size = 0;
|
|
if (match(Token::Type::kComma)) {
|
|
auto val = expect_nonzero_positive_sint("array size");
|
|
if (val.errored)
|
|
return Failure::kErrored;
|
|
size = val.value;
|
|
}
|
|
|
|
return create<ast::type::Array>(subtype.value, size, std::move(decos));
|
|
});
|
|
}
|
|
|
|
Expect<ast::type::Type*> ParserImpl::expect_type_decl_matrix(Token t) {
|
|
uint32_t rows = 2;
|
|
uint32_t columns = 2;
|
|
if (t.IsMat3x2() || t.IsMat3x3() || t.IsMat3x4()) {
|
|
rows = 3;
|
|
} else if (t.IsMat4x2() || t.IsMat4x3() || t.IsMat4x4()) {
|
|
rows = 4;
|
|
}
|
|
if (t.IsMat2x3() || t.IsMat3x3() || t.IsMat4x3()) {
|
|
columns = 3;
|
|
} else if (t.IsMat2x4() || t.IsMat3x4() || t.IsMat4x4()) {
|
|
columns = 4;
|
|
}
|
|
|
|
const char* use = "matrix";
|
|
|
|
auto subtype = expect_lt_gt_block(use, [&] { return expect_type(use); });
|
|
if (subtype.errored)
|
|
return Failure::kErrored;
|
|
|
|
return module_.create<ast::type::Matrix>(subtype.value, rows, columns);
|
|
}
|
|
|
|
// storage_class
|
|
// : INPUT
|
|
// | OUTPUT
|
|
// | UNIFORM
|
|
// | WORKGROUP
|
|
// | UNIFORM_CONSTANT
|
|
// | STORAGE_BUFFER
|
|
// | IMAGE
|
|
// | PRIVATE
|
|
// | FUNCTION
|
|
Expect<ast::StorageClass> ParserImpl::expect_storage_class(
|
|
const std::string& use) {
|
|
if (match(Token::Type::kIn))
|
|
return ast::StorageClass::kInput;
|
|
|
|
if (match(Token::Type::kOut))
|
|
return ast::StorageClass::kOutput;
|
|
|
|
if (match(Token::Type::kUniform))
|
|
return ast::StorageClass::kUniform;
|
|
|
|
if (match(Token::Type::kWorkgroup))
|
|
return ast::StorageClass::kWorkgroup;
|
|
|
|
if (match(Token::Type::kUniformConstant))
|
|
return ast::StorageClass::kUniformConstant;
|
|
|
|
if (match(Token::Type::kStorageBuffer))
|
|
return ast::StorageClass::kStorageBuffer;
|
|
|
|
if (match(Token::Type::kImage))
|
|
return ast::StorageClass::kImage;
|
|
|
|
if (match(Token::Type::kPrivate))
|
|
return ast::StorageClass::kPrivate;
|
|
|
|
if (match(Token::Type::kFunction))
|
|
return ast::StorageClass::kFunction;
|
|
|
|
return add_error(peek().source(), "invalid storage class", use);
|
|
}
|
|
|
|
// struct_decl
|
|
// : struct_decoration_decl* STRUCT IDENT struct_body_decl
|
|
Maybe<std::unique_ptr<ast::type::Struct>> ParserImpl::struct_decl(
|
|
ast::DecorationList& decos) {
|
|
auto t = peek();
|
|
auto source = t.source();
|
|
|
|
if (!match(Token::Type::kStruct))
|
|
return Failure::kNoMatch;
|
|
|
|
auto name = expect_ident("struct declaration");
|
|
if (name.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto body = expect_struct_body_decl();
|
|
if (body.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto struct_decos = cast_decorations<ast::StructDecoration>(decos);
|
|
if (struct_decos.errored)
|
|
return Failure::kErrored;
|
|
|
|
return std::make_unique<ast::type::Struct>(
|
|
module_.RegisterSymbol(name.value), name.value,
|
|
create<ast::Struct>(source, std::move(body.value),
|
|
std::move(struct_decos.value)));
|
|
}
|
|
|
|
// struct_body_decl
|
|
// : BRACKET_LEFT struct_member* BRACKET_RIGHT
|
|
Expect<ast::StructMemberList> ParserImpl::expect_struct_body_decl() {
|
|
return expect_brace_block(
|
|
"struct declaration", [&]() -> Expect<ast::StructMemberList> {
|
|
bool errored = false;
|
|
|
|
ast::StructMemberList members;
|
|
|
|
while (synchronized_ && !peek().IsBraceRight() && !peek().IsEof()) {
|
|
auto member = sync(Token::Type::kSemicolon,
|
|
[&]() -> Expect<ast::StructMember*> {
|
|
auto decos = decoration_list();
|
|
if (decos.errored)
|
|
errored = true;
|
|
if (!synchronized_)
|
|
return Failure::kErrored;
|
|
return expect_struct_member(decos.value);
|
|
});
|
|
|
|
if (member.errored) {
|
|
errored = true;
|
|
} else {
|
|
members.push_back(member.value);
|
|
}
|
|
}
|
|
|
|
if (errored)
|
|
return Failure::kErrored;
|
|
|
|
return members;
|
|
});
|
|
}
|
|
|
|
// struct_member
|
|
// : struct_member_decoration_decl+ variable_ident_decl SEMICOLON
|
|
Expect<ast::StructMember*> ParserImpl::expect_struct_member(
|
|
ast::DecorationList& decos) {
|
|
auto decl = expect_variable_ident_decl("struct member");
|
|
if (decl.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto member_decos = cast_decorations<ast::StructMemberDecoration>(decos);
|
|
if (member_decos.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!expect("struct member", Token::Type::kSemicolon))
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::StructMember>(decl->source, decl->name, decl->type,
|
|
std::move(member_decos.value));
|
|
}
|
|
|
|
// function_decl
|
|
// : function_header body_stmt
|
|
Maybe<ast::Function*> ParserImpl::function_decl(ast::DecorationList& decos) {
|
|
auto header = function_header();
|
|
if (header.errored) {
|
|
if (sync_to(Token::Type::kBraceLeft, /* consume: */ false)) {
|
|
// There were errors in the function header, but the parser has managed to
|
|
// resynchronize with the opening brace. As there's no outer
|
|
// synchronization token for function declarations, attempt to parse the
|
|
// function body. The AST isn't used as we've already errored, but this
|
|
// catches any errors inside the body, and can help keep the parser in
|
|
// sync.
|
|
expect_body_stmt();
|
|
}
|
|
return Failure::kErrored;
|
|
}
|
|
if (!header.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
bool errored = false;
|
|
|
|
auto func_decos = cast_decorations<ast::FunctionDecoration>(decos);
|
|
if (func_decos.errored)
|
|
errored = true;
|
|
|
|
auto body = expect_body_stmt();
|
|
if (body.errored)
|
|
errored = true;
|
|
|
|
if (errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::Function>(
|
|
header->source, module_.RegisterSymbol(header->name), header->name,
|
|
header->params, header->return_type, body.value, func_decos.value);
|
|
}
|
|
|
|
// function_type_decl
|
|
// : type_decl
|
|
// | VOID
|
|
Maybe<ast::type::Type*> ParserImpl::function_type_decl() {
|
|
if (match(Token::Type::kVoid))
|
|
return module_.create<ast::type::Void>();
|
|
|
|
return type_decl();
|
|
}
|
|
|
|
// function_header
|
|
// : FN IDENT PAREN_LEFT param_list PAREN_RIGHT ARROW function_type_decl
|
|
Maybe<ParserImpl::FunctionHeader> ParserImpl::function_header() {
|
|
Source source;
|
|
if (!match(Token::Type::kFn, &source))
|
|
return Failure::kNoMatch;
|
|
|
|
const char* use = "function declaration";
|
|
bool errored = false;
|
|
|
|
auto name = expect_ident(use);
|
|
if (name.errored) {
|
|
errored = true;
|
|
if (!sync_to(Token::Type::kParenLeft, /* consume: */ false))
|
|
return Failure::kErrored;
|
|
}
|
|
|
|
auto params = expect_paren_block(use, [&] { return expect_param_list(); });
|
|
if (params.errored) {
|
|
errored = true;
|
|
if (!synchronized_)
|
|
return Failure::kErrored;
|
|
}
|
|
|
|
if (!expect(use, Token::Type::kArrow))
|
|
return Failure::kErrored;
|
|
|
|
auto type = function_type_decl();
|
|
if (type.errored) {
|
|
errored = true;
|
|
} else if (!type.matched) {
|
|
return add_error(peek(), "unable to determine function return type");
|
|
}
|
|
|
|
if (errored)
|
|
return Failure::kErrored;
|
|
|
|
return FunctionHeader{source, name.value, std::move(params.value),
|
|
type.value};
|
|
}
|
|
|
|
// param_list
|
|
// :
|
|
// | (variable_ident_decl COMMA)* variable_ident_decl
|
|
Expect<ast::VariableList> ParserImpl::expect_param_list() {
|
|
if (!peek().IsIdentifier()) // Empty list
|
|
return ast::VariableList{};
|
|
|
|
auto decl = expect_variable_ident_decl("parameter");
|
|
if (decl.errored)
|
|
return Failure::kErrored;
|
|
|
|
ast::VariableList ret;
|
|
for (;;) {
|
|
auto* var =
|
|
create<ast::Variable>(decl->source, // source
|
|
decl->name, // name
|
|
ast::StorageClass::kNone, // storage_class
|
|
decl->type, // type
|
|
true, // is_const
|
|
nullptr, // constructor
|
|
ast::VariableDecorationList{}); // decorations
|
|
// Formal parameters are treated like a const declaration where the
|
|
// initializer value is provided by the call's argument. The key point is
|
|
// that it's not updatable after intially set. This is unlike C or GLSL
|
|
// which treat formal parameters like local variables that can be updated.
|
|
ret.push_back(var);
|
|
|
|
if (!match(Token::Type::kComma))
|
|
break;
|
|
|
|
decl = expect_variable_ident_decl("parameter");
|
|
if (decl.errored)
|
|
return Failure::kErrored;
|
|
}
|
|
|
|
return ret;
|
|
}
|
|
|
|
// pipeline_stage
|
|
// : VERTEX
|
|
// | FRAGMENT
|
|
// | COMPUTE
|
|
Expect<ast::PipelineStage> ParserImpl::expect_pipeline_stage() {
|
|
auto t = peek();
|
|
if (!t.IsIdentifier()) {
|
|
return add_error(t, "invalid value for stage decoration");
|
|
}
|
|
|
|
auto s = t.to_str();
|
|
if (s == kVertexStage) {
|
|
next(); // Consume the peek
|
|
return {ast::PipelineStage::kVertex, t.source()};
|
|
}
|
|
if (s == kFragmentStage) {
|
|
next(); // Consume the peek
|
|
return {ast::PipelineStage::kFragment, t.source()};
|
|
}
|
|
if (s == kComputeStage) {
|
|
next(); // Consume the peek
|
|
return {ast::PipelineStage::kCompute, t.source()};
|
|
}
|
|
|
|
return add_error(peek(), "invalid value for stage decoration");
|
|
}
|
|
|
|
Expect<ast::Builtin> ParserImpl::expect_builtin() {
|
|
auto ident = expect_ident("builtin");
|
|
if (ident.errored)
|
|
return Failure::kErrored;
|
|
|
|
ast::Builtin builtin = ident_to_builtin(ident.value);
|
|
if (builtin == ast::Builtin::kNone)
|
|
return add_error(ident.source, "invalid value for builtin decoration");
|
|
|
|
return {builtin, ident.source};
|
|
}
|
|
|
|
// body_stmt
|
|
// : BRACKET_LEFT statements BRACKET_RIGHT
|
|
Expect<ast::BlockStatement*> ParserImpl::expect_body_stmt() {
|
|
return expect_brace_block("", [&] { return expect_statements(); });
|
|
}
|
|
|
|
// paren_rhs_stmt
|
|
// : PAREN_LEFT logical_or_expression PAREN_RIGHT
|
|
Expect<ast::Expression*> ParserImpl::expect_paren_rhs_stmt() {
|
|
return expect_paren_block("", [&]() -> Expect<ast::Expression*> {
|
|
auto expr = logical_or_expression();
|
|
if (expr.errored)
|
|
return Failure::kErrored;
|
|
if (!expr.matched)
|
|
return add_error(peek(), "unable to parse expression");
|
|
|
|
return expr.value;
|
|
});
|
|
}
|
|
|
|
// statements
|
|
// : statement*
|
|
Expect<ast::BlockStatement*> ParserImpl::expect_statements() {
|
|
bool errored = false;
|
|
auto* ret = create<ast::BlockStatement>(Source{});
|
|
|
|
while (synchronized_) {
|
|
auto stmt = statement();
|
|
if (stmt.errored) {
|
|
errored = true;
|
|
} else if (stmt.matched) {
|
|
ret->append(stmt.value);
|
|
} else {
|
|
break;
|
|
}
|
|
}
|
|
|
|
if (errored)
|
|
return Failure::kErrored;
|
|
|
|
return ret;
|
|
}
|
|
|
|
// statement
|
|
// : SEMICOLON
|
|
// | body_stmt?
|
|
// | if_stmt
|
|
// | switch_stmt
|
|
// | loop_stmt
|
|
// | for_stmt
|
|
// | non_block_statement
|
|
// : return_stmt SEMICOLON
|
|
// | func_call_stmt SEMICOLON
|
|
// | variable_stmt SEMICOLON
|
|
// | break_stmt SEMICOLON
|
|
// | continue_stmt SEMICOLON
|
|
// | DISCARD SEMICOLON
|
|
// | assignment_stmt SEMICOLON
|
|
Maybe<ast::Statement*> ParserImpl::statement() {
|
|
while (match(Token::Type::kSemicolon)) {
|
|
// Skip empty statements
|
|
}
|
|
|
|
// Non-block statments that error can resynchronize on semicolon.
|
|
auto stmt =
|
|
sync(Token::Type::kSemicolon, [&] { return non_block_statement(); });
|
|
|
|
if (stmt.errored)
|
|
return Failure::kErrored;
|
|
if (stmt.matched)
|
|
return stmt;
|
|
|
|
auto stmt_if = if_stmt();
|
|
if (stmt_if.errored)
|
|
return Failure::kErrored;
|
|
if (stmt_if.matched)
|
|
return stmt_if.value;
|
|
|
|
auto sw = switch_stmt();
|
|
if (sw.errored)
|
|
return Failure::kErrored;
|
|
if (sw.matched)
|
|
return sw.value;
|
|
|
|
auto loop = loop_stmt();
|
|
if (loop.errored)
|
|
return Failure::kErrored;
|
|
if (loop.matched)
|
|
return loop.value;
|
|
|
|
auto stmt_for = for_stmt();
|
|
if (stmt_for.errored)
|
|
return Failure::kErrored;
|
|
if (stmt_for.matched)
|
|
return stmt_for.value;
|
|
|
|
if (peek().IsBraceLeft()) {
|
|
auto body = expect_body_stmt();
|
|
if (body.errored)
|
|
return Failure::kErrored;
|
|
return body.value;
|
|
}
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// statement (continued)
|
|
// : return_stmt SEMICOLON
|
|
// | func_call_stmt SEMICOLON
|
|
// | variable_stmt SEMICOLON
|
|
// | break_stmt SEMICOLON
|
|
// | continue_stmt SEMICOLON
|
|
// | DISCARD SEMICOLON
|
|
// | assignment_stmt SEMICOLON
|
|
Maybe<ast::Statement*> ParserImpl::non_block_statement() {
|
|
auto stmt = [&]() -> Maybe<ast::Statement*> {
|
|
auto ret_stmt = return_stmt();
|
|
if (ret_stmt.errored)
|
|
return Failure::kErrored;
|
|
if (ret_stmt.matched)
|
|
return ret_stmt.value;
|
|
|
|
auto func = func_call_stmt();
|
|
if (func.errored)
|
|
return Failure::kErrored;
|
|
if (func.matched)
|
|
return func.value;
|
|
|
|
auto var = variable_stmt();
|
|
if (var.errored)
|
|
return Failure::kErrored;
|
|
if (var.matched)
|
|
return var.value;
|
|
|
|
auto b = break_stmt();
|
|
if (b.errored)
|
|
return Failure::kErrored;
|
|
if (b.matched)
|
|
return b.value;
|
|
|
|
auto cont = continue_stmt();
|
|
if (cont.errored)
|
|
return Failure::kErrored;
|
|
if (cont.matched)
|
|
return cont.value;
|
|
|
|
auto assign = assignment_stmt();
|
|
if (assign.errored)
|
|
return Failure::kErrored;
|
|
if (assign.matched)
|
|
return assign.value;
|
|
|
|
Source source;
|
|
if (match(Token::Type::kDiscard, &source))
|
|
return create<ast::DiscardStatement>(source);
|
|
|
|
return Failure::kNoMatch;
|
|
}();
|
|
|
|
if (stmt.matched && !expect(stmt->Name(), Token::Type::kSemicolon))
|
|
return Failure::kErrored;
|
|
|
|
return stmt;
|
|
}
|
|
|
|
// return_stmt
|
|
// : RETURN logical_or_expression?
|
|
Maybe<ast::ReturnStatement*> ParserImpl::return_stmt() {
|
|
Source source;
|
|
if (!match(Token::Type::kReturn, &source))
|
|
return Failure::kNoMatch;
|
|
|
|
if (peek().IsSemicolon())
|
|
return create<ast::ReturnStatement>(source, nullptr);
|
|
|
|
auto expr = logical_or_expression();
|
|
if (expr.errored)
|
|
return Failure::kErrored;
|
|
|
|
// TODO(bclayton): Check matched?
|
|
return create<ast::ReturnStatement>(source, expr.value);
|
|
}
|
|
|
|
// variable_stmt
|
|
// : variable_decl
|
|
// | variable_decl EQUAL logical_or_expression
|
|
// | CONST variable_ident_decl EQUAL logical_or_expression
|
|
Maybe<ast::VariableDeclStatement*> ParserImpl::variable_stmt() {
|
|
if (match(Token::Type::kConst)) {
|
|
auto decl = expect_variable_ident_decl("constant declaration");
|
|
if (decl.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!expect("constant declaration", Token::Type::kEqual))
|
|
return Failure::kErrored;
|
|
|
|
auto constructor = logical_or_expression();
|
|
if (constructor.errored)
|
|
return Failure::kErrored;
|
|
if (!constructor.matched)
|
|
return add_error(peek(), "missing constructor for const declaration");
|
|
|
|
auto* var =
|
|
create<ast::Variable>(decl->source, // source
|
|
decl->name, // name
|
|
ast::StorageClass::kNone, // storage_class
|
|
decl->type, // type
|
|
true, // is_const
|
|
constructor.value, // constructor
|
|
ast::VariableDecorationList{}); // decorations
|
|
|
|
return create<ast::VariableDeclStatement>(decl->source, var);
|
|
}
|
|
|
|
auto decl = variable_decl();
|
|
if (decl.errored)
|
|
return Failure::kErrored;
|
|
if (!decl.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
ast::Expression* constructor = nullptr;
|
|
if (match(Token::Type::kEqual)) {
|
|
auto constructor_expr = logical_or_expression();
|
|
if (constructor_expr.errored)
|
|
return Failure::kErrored;
|
|
if (!constructor_expr.matched)
|
|
return add_error(peek(), "missing constructor for variable declaration");
|
|
|
|
constructor = constructor_expr.value;
|
|
}
|
|
|
|
auto* var =
|
|
create<ast::Variable>(decl->source, // source
|
|
decl->name, // name
|
|
decl->storage_class, // storage_class
|
|
decl->type, // type
|
|
false, // is_const
|
|
constructor, // constructor
|
|
ast::VariableDecorationList{}); // decorations
|
|
|
|
return create<ast::VariableDeclStatement>(var->source(), var);
|
|
}
|
|
|
|
// if_stmt
|
|
// : IF paren_rhs_stmt body_stmt elseif_stmt? else_stmt?
|
|
Maybe<ast::IfStatement*> ParserImpl::if_stmt() {
|
|
Source source;
|
|
if (!match(Token::Type::kIf, &source))
|
|
return Failure::kNoMatch;
|
|
|
|
auto condition = expect_paren_rhs_stmt();
|
|
if (condition.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto body = expect_body_stmt();
|
|
if (body.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto elseif = elseif_stmt();
|
|
if (elseif.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto el = else_stmt();
|
|
if (el.errored)
|
|
return Failure::kErrored;
|
|
if (el.matched)
|
|
elseif.value.push_back(el.value);
|
|
|
|
return create<ast::IfStatement>(source, condition.value, body.value,
|
|
elseif.value);
|
|
}
|
|
|
|
// elseif_stmt
|
|
// : ELSE_IF paren_rhs_stmt body_stmt elseif_stmt?
|
|
Maybe<ast::ElseStatementList> ParserImpl::elseif_stmt() {
|
|
Source source;
|
|
if (!match(Token::Type::kElseIf, &source))
|
|
return Failure::kNoMatch;
|
|
|
|
ast::ElseStatementList ret;
|
|
for (;;) {
|
|
auto condition = expect_paren_rhs_stmt();
|
|
if (condition.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto body = expect_body_stmt();
|
|
if (body.errored)
|
|
return Failure::kErrored;
|
|
|
|
ret.push_back(
|
|
create<ast::ElseStatement>(source, condition.value, body.value));
|
|
|
|
if (!match(Token::Type::kElseIf, &source))
|
|
break;
|
|
}
|
|
|
|
return ret;
|
|
}
|
|
|
|
// else_stmt
|
|
// : ELSE body_stmt
|
|
Maybe<ast::ElseStatement*> ParserImpl::else_stmt() {
|
|
Source source;
|
|
if (!match(Token::Type::kElse, &source))
|
|
return Failure::kNoMatch;
|
|
|
|
auto body = expect_body_stmt();
|
|
if (body.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::ElseStatement>(source, nullptr, body.value);
|
|
}
|
|
|
|
// switch_stmt
|
|
// : SWITCH paren_rhs_stmt BRACKET_LEFT switch_body+ BRACKET_RIGHT
|
|
Maybe<ast::SwitchStatement*> ParserImpl::switch_stmt() {
|
|
Source source;
|
|
if (!match(Token::Type::kSwitch, &source))
|
|
return Failure::kNoMatch;
|
|
|
|
auto condition = expect_paren_rhs_stmt();
|
|
if (condition.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto body = expect_brace_block("switch statement",
|
|
[&]() -> Expect<ast::CaseStatementList> {
|
|
bool errored = false;
|
|
ast::CaseStatementList list;
|
|
while (synchronized_) {
|
|
auto stmt = switch_body();
|
|
if (stmt.errored) {
|
|
errored = true;
|
|
continue;
|
|
}
|
|
if (!stmt.matched)
|
|
break;
|
|
list.push_back(stmt.value);
|
|
}
|
|
if (errored)
|
|
return Failure::kErrored;
|
|
return list;
|
|
});
|
|
|
|
if (body.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::SwitchStatement>(source, condition.value, body.value);
|
|
}
|
|
|
|
// switch_body
|
|
// : CASE case_selectors COLON BRACKET_LEFT case_body BRACKET_RIGHT
|
|
// | DEFAULT COLON BRACKET_LEFT case_body BRACKET_RIGHT
|
|
Maybe<ast::CaseStatement*> ParserImpl::switch_body() {
|
|
auto t = peek();
|
|
if (!t.IsCase() && !t.IsDefault())
|
|
return Failure::kNoMatch;
|
|
|
|
auto source = t.source();
|
|
next(); // Consume the peek
|
|
|
|
ast::CaseSelectorList selector_list;
|
|
if (t.IsCase()) {
|
|
auto selectors = expect_case_selectors();
|
|
if (selectors.errored)
|
|
return Failure::kErrored;
|
|
|
|
selector_list = std::move(selectors.value);
|
|
}
|
|
|
|
const char* use = "case statement";
|
|
|
|
if (!expect(use, Token::Type::kColon))
|
|
return Failure::kErrored;
|
|
|
|
auto body = expect_brace_block(use, [&] { return case_body(); });
|
|
|
|
if (body.errored)
|
|
return Failure::kErrored;
|
|
if (!body.matched)
|
|
return add_error(body.source, "expected case body");
|
|
|
|
return create<ast::CaseStatement>(source, selector_list, body.value);
|
|
}
|
|
|
|
// case_selectors
|
|
// : const_literal (COMMA const_literal)*
|
|
Expect<ast::CaseSelectorList> ParserImpl::expect_case_selectors() {
|
|
ast::CaseSelectorList selectors;
|
|
|
|
for (;;) {
|
|
auto t = peek();
|
|
auto cond = const_literal();
|
|
if (cond.errored)
|
|
return Failure::kErrored;
|
|
if (!cond.matched)
|
|
break;
|
|
if (!cond->Is<ast::IntLiteral>())
|
|
return add_error(t, "invalid case selector must be an integer value");
|
|
|
|
selectors.push_back(cond.value->As<ast::IntLiteral>());
|
|
}
|
|
|
|
if (selectors.empty())
|
|
return add_error(peek(), "unable to parse case selectors");
|
|
|
|
return selectors;
|
|
}
|
|
|
|
// case_body
|
|
// :
|
|
// | statement case_body
|
|
// | FALLTHROUGH SEMICOLON
|
|
Maybe<ast::BlockStatement*> ParserImpl::case_body() {
|
|
auto* ret = create<ast::BlockStatement>(Source{});
|
|
for (;;) {
|
|
Source source;
|
|
if (match(Token::Type::kFallthrough, &source)) {
|
|
if (!expect("fallthrough statement", Token::Type::kSemicolon))
|
|
return Failure::kErrored;
|
|
|
|
ret->append(create<ast::FallthroughStatement>(source));
|
|
break;
|
|
}
|
|
|
|
auto stmt = statement();
|
|
if (stmt.errored)
|
|
return Failure::kErrored;
|
|
if (!stmt.matched)
|
|
break;
|
|
|
|
ret->append(stmt.value);
|
|
}
|
|
|
|
return ret;
|
|
}
|
|
|
|
// loop_stmt
|
|
// : LOOP BRACKET_LEFT statements continuing_stmt? BRACKET_RIGHT
|
|
Maybe<ast::LoopStatement*> ParserImpl::loop_stmt() {
|
|
Source source;
|
|
if (!match(Token::Type::kLoop, &source))
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_brace_block("loop", [&]() -> Maybe<ast::LoopStatement*> {
|
|
auto body = expect_statements();
|
|
if (body.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto continuing = continuing_stmt();
|
|
if (continuing.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::LoopStatement>(source, body.value, continuing.value);
|
|
});
|
|
}
|
|
|
|
ForHeader::ForHeader(ast::Statement* init,
|
|
ast::Expression* cond,
|
|
ast::Statement* cont)
|
|
: initializer(init), condition(cond), continuing(cont) {}
|
|
|
|
ForHeader::~ForHeader() = default;
|
|
|
|
// (variable_stmt | assignment_stmt | func_call_stmt)?
|
|
Maybe<ast::Statement*> ParserImpl::for_header_initializer() {
|
|
auto call = func_call_stmt();
|
|
if (call.errored)
|
|
return Failure::kErrored;
|
|
if (call.matched)
|
|
return call.value;
|
|
|
|
auto var = variable_stmt();
|
|
if (var.errored)
|
|
return Failure::kErrored;
|
|
if (var.matched)
|
|
return var.value;
|
|
|
|
auto assign = assignment_stmt();
|
|
if (assign.errored)
|
|
return Failure::kErrored;
|
|
if (assign.matched)
|
|
return assign.value;
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// (assignment_stmt | func_call_stmt)?
|
|
Maybe<ast::Statement*> ParserImpl::for_header_continuing() {
|
|
auto call_stmt = func_call_stmt();
|
|
if (call_stmt.errored)
|
|
return Failure::kErrored;
|
|
if (call_stmt.matched)
|
|
return call_stmt.value;
|
|
|
|
auto assign = assignment_stmt();
|
|
if (assign.errored)
|
|
return Failure::kErrored;
|
|
if (assign.matched)
|
|
return assign.value;
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// for_header
|
|
// : (variable_stmt | assignment_stmt | func_call_stmt)?
|
|
// SEMICOLON
|
|
// logical_or_expression? SEMICOLON
|
|
// (assignment_stmt | func_call_stmt)?
|
|
Expect<std::unique_ptr<ForHeader>> ParserImpl::expect_for_header() {
|
|
auto initializer = for_header_initializer();
|
|
if (initializer.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!expect("initializer in for loop", Token::Type::kSemicolon))
|
|
return Failure::kErrored;
|
|
|
|
auto condition = logical_or_expression();
|
|
if (condition.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!expect("condition in for loop", Token::Type::kSemicolon))
|
|
return Failure::kErrored;
|
|
|
|
auto continuing = for_header_continuing();
|
|
if (continuing.errored)
|
|
return Failure::kErrored;
|
|
|
|
return std::make_unique<ForHeader>(initializer.value, condition.value,
|
|
continuing.value);
|
|
}
|
|
|
|
// for_statement
|
|
// : FOR PAREN_LEFT for_header PAREN_RIGHT BRACE_LEFT statements BRACE_RIGHT
|
|
Maybe<ast::Statement*> ParserImpl::for_stmt() {
|
|
Source source;
|
|
if (!match(Token::Type::kFor, &source))
|
|
return Failure::kNoMatch;
|
|
|
|
auto header =
|
|
expect_paren_block("for loop", [&] { return expect_for_header(); });
|
|
if (header.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto body =
|
|
expect_brace_block("for loop", [&] { return expect_statements(); });
|
|
if (body.errored)
|
|
return Failure::kErrored;
|
|
|
|
// The for statement is a syntactic sugar on top of the loop statement.
|
|
// We create corresponding nodes in ast with the exact same behaviour
|
|
// as we would expect from the loop statement.
|
|
if (header->condition != nullptr) {
|
|
// !condition
|
|
auto* not_condition = create<ast::UnaryOpExpression>(
|
|
header->condition->source(), ast::UnaryOp::kNot, header->condition);
|
|
// { break; }
|
|
auto* break_stmt = create<ast::BreakStatement>(not_condition->source());
|
|
auto* break_body = create<ast::BlockStatement>(not_condition->source());
|
|
break_body->append(break_stmt);
|
|
// if (!condition) { break; }
|
|
auto* break_if_not_condition =
|
|
create<ast::IfStatement>(not_condition->source(), not_condition,
|
|
break_body, ast::ElseStatementList{});
|
|
body->insert(0, break_if_not_condition);
|
|
}
|
|
|
|
ast::BlockStatement* continuing_body = nullptr;
|
|
if (header->continuing != nullptr) {
|
|
continuing_body = create<ast::BlockStatement>(header->continuing->source());
|
|
continuing_body->append(header->continuing);
|
|
}
|
|
|
|
auto* loop = create<ast::LoopStatement>(source, body.value, continuing_body);
|
|
|
|
if (header->initializer != nullptr) {
|
|
auto* result = create<ast::BlockStatement>(source);
|
|
result->append(header->initializer);
|
|
result->append(loop);
|
|
return result;
|
|
}
|
|
|
|
return loop;
|
|
}
|
|
|
|
// func_call_stmt
|
|
// : IDENT PAREN_LEFT argument_expression_list* PAREN_RIGHT
|
|
Maybe<ast::CallStatement*> ParserImpl::func_call_stmt() {
|
|
auto t = peek();
|
|
auto t2 = peek(1);
|
|
if (!t.IsIdentifier() || !t2.IsParenLeft())
|
|
return Failure::kNoMatch;
|
|
|
|
auto source = t.source();
|
|
|
|
next(); // Consume the peek
|
|
next(); // Consume the 2nd peek
|
|
|
|
auto name = t.to_str();
|
|
|
|
ast::ExpressionList params;
|
|
|
|
t = peek();
|
|
if (!t.IsParenRight() && !t.IsEof()) {
|
|
auto list = expect_argument_expression_list();
|
|
if (list.errored)
|
|
return Failure::kErrored;
|
|
params = std::move(list.value);
|
|
}
|
|
|
|
if (!expect("call statement", Token::Type::kParenRight))
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::CallStatement>(
|
|
Source{}, create<ast::CallExpression>(
|
|
source,
|
|
create<ast::IdentifierExpression>(
|
|
source, module_.RegisterSymbol(name), name),
|
|
std::move(params)));
|
|
}
|
|
|
|
// break_stmt
|
|
// : BREAK
|
|
Maybe<ast::BreakStatement*> ParserImpl::break_stmt() {
|
|
Source source;
|
|
if (!match(Token::Type::kBreak, &source))
|
|
return Failure::kNoMatch;
|
|
|
|
return create<ast::BreakStatement>(source);
|
|
}
|
|
|
|
// continue_stmt
|
|
// : CONTINUE
|
|
Maybe<ast::ContinueStatement*> ParserImpl::continue_stmt() {
|
|
Source source;
|
|
if (!match(Token::Type::kContinue, &source))
|
|
return Failure::kNoMatch;
|
|
|
|
return create<ast::ContinueStatement>(source);
|
|
}
|
|
|
|
// continuing_stmt
|
|
// : CONTINUING body_stmt
|
|
Maybe<ast::BlockStatement*> ParserImpl::continuing_stmt() {
|
|
if (!match(Token::Type::kContinuing))
|
|
return create<ast::BlockStatement>(Source{});
|
|
|
|
return expect_body_stmt();
|
|
}
|
|
|
|
// primary_expression
|
|
// : IDENT
|
|
// | type_decl PAREN_LEFT argument_expression_list* PAREN_RIGHT
|
|
// | const_literal
|
|
// | paren_rhs_stmt
|
|
// | BITCAST LESS_THAN type_decl GREATER_THAN paren_rhs_stmt
|
|
Maybe<ast::Expression*> ParserImpl::primary_expression() {
|
|
auto t = peek();
|
|
auto source = t.source();
|
|
|
|
auto lit = const_literal();
|
|
if (lit.errored)
|
|
return Failure::kErrored;
|
|
if (lit.matched)
|
|
return create<ast::ScalarConstructorExpression>(source, lit.value);
|
|
|
|
if (t.IsParenLeft()) {
|
|
auto paren = expect_paren_rhs_stmt();
|
|
if (paren.errored)
|
|
return Failure::kErrored;
|
|
|
|
return paren.value;
|
|
}
|
|
|
|
if (match(Token::Type::kBitcast)) {
|
|
const char* use = "bitcast expression";
|
|
|
|
auto type = expect_lt_gt_block(use, [&] { return expect_type(use); });
|
|
if (type.errored)
|
|
return Failure::kErrored;
|
|
|
|
auto params = expect_paren_rhs_stmt();
|
|
if (params.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::BitcastExpression>(source, type.value, params.value);
|
|
}
|
|
|
|
if (match(Token::Type::kIdentifier))
|
|
return create<ast::IdentifierExpression>(
|
|
t.source(), module_.RegisterSymbol(t.to_str()), t.to_str());
|
|
|
|
auto type = type_decl();
|
|
if (type.errored)
|
|
return Failure::kErrored;
|
|
if (type.matched) {
|
|
auto expr = expect_paren_block(
|
|
"type constructor", [&]() -> Expect<ast::TypeConstructorExpression*> {
|
|
t = peek();
|
|
if (t.IsParenRight() || t.IsEof())
|
|
return create<ast::TypeConstructorExpression>(
|
|
source, type.value, ast::ExpressionList{});
|
|
|
|
auto params = expect_argument_expression_list();
|
|
if (params.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::TypeConstructorExpression>(source, type.value,
|
|
params.value);
|
|
});
|
|
|
|
if (expr.errored)
|
|
return Failure::kErrored;
|
|
|
|
return expr.value;
|
|
}
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// postfix_expr
|
|
// :
|
|
// | BRACE_LEFT logical_or_expression BRACE_RIGHT postfix_expr
|
|
// | PAREN_LEFT argument_expression_list* PAREN_RIGHT postfix_expr
|
|
// | PERIOD IDENTIFIER postfix_expr
|
|
Maybe<ast::Expression*> ParserImpl::postfix_expr(ast::Expression* prefix) {
|
|
Source source;
|
|
if (match(Token::Type::kBracketLeft, &source)) {
|
|
auto param = logical_or_expression();
|
|
if (param.errored)
|
|
return Failure::kErrored;
|
|
if (!param.matched)
|
|
return add_error(peek(), "unable to parse expression inside []");
|
|
|
|
if (!expect("array accessor", Token::Type::kBracketRight))
|
|
return Failure::kErrored;
|
|
|
|
return postfix_expr(
|
|
create<ast::ArrayAccessorExpression>(source, prefix, param.value));
|
|
}
|
|
|
|
if (match(Token::Type::kParenLeft, &source)) {
|
|
ast::ExpressionList params;
|
|
|
|
auto t = peek();
|
|
if (!t.IsParenRight() && !t.IsEof()) {
|
|
auto list = expect_argument_expression_list();
|
|
if (list.errored)
|
|
return Failure::kErrored;
|
|
params = list.value;
|
|
}
|
|
|
|
if (!expect("call expression", Token::Type::kParenRight))
|
|
return Failure::kErrored;
|
|
|
|
return postfix_expr(create<ast::CallExpression>(source, prefix, params));
|
|
}
|
|
|
|
if (match(Token::Type::kPeriod)) {
|
|
auto ident = expect_ident("member accessor");
|
|
if (ident.errored)
|
|
return Failure::kErrored;
|
|
|
|
return postfix_expr(create<ast::MemberAccessorExpression>(
|
|
ident.source, prefix,
|
|
create<ast::IdentifierExpression>(
|
|
ident.source, module_.RegisterSymbol(ident.value), ident.value)));
|
|
}
|
|
|
|
return prefix;
|
|
}
|
|
|
|
// postfix_expression
|
|
// : primary_expression postfix_expr
|
|
Maybe<ast::Expression*> ParserImpl::postfix_expression() {
|
|
auto prefix = primary_expression();
|
|
if (prefix.errored)
|
|
return Failure::kErrored;
|
|
if (!prefix.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return postfix_expr(prefix.value);
|
|
}
|
|
|
|
// argument_expression_list
|
|
// : (logical_or_expression COMMA)* logical_or_expression
|
|
Expect<ast::ExpressionList> ParserImpl::expect_argument_expression_list() {
|
|
auto arg = logical_or_expression();
|
|
if (arg.errored)
|
|
return Failure::kErrored;
|
|
if (!arg.matched)
|
|
return add_error(peek(), "unable to parse argument expression");
|
|
|
|
ast::ExpressionList ret;
|
|
ret.push_back(arg.value);
|
|
|
|
while (match(Token::Type::kComma)) {
|
|
arg = logical_or_expression();
|
|
if (arg.errored)
|
|
return Failure::kErrored;
|
|
if (!arg.matched) {
|
|
return add_error(peek(),
|
|
"unable to parse argument expression after comma");
|
|
}
|
|
ret.push_back(arg.value);
|
|
}
|
|
return ret;
|
|
}
|
|
|
|
// unary_expression
|
|
// : postfix_expression
|
|
// | MINUS unary_expression
|
|
// | BANG unary_expression
|
|
Maybe<ast::Expression*> ParserImpl::unary_expression() {
|
|
auto t = peek();
|
|
auto source = t.source();
|
|
if (t.IsMinus() || t.IsBang()) {
|
|
auto name = t.to_name();
|
|
|
|
next(); // Consume the peek
|
|
|
|
auto op = ast::UnaryOp::kNegation;
|
|
if (t.IsBang())
|
|
op = ast::UnaryOp::kNot;
|
|
|
|
auto expr = unary_expression();
|
|
if (expr.errored)
|
|
return Failure::kErrored;
|
|
if (!expr.matched)
|
|
return add_error(peek(),
|
|
"unable to parse right side of " + name + " expression");
|
|
|
|
return create<ast::UnaryOpExpression>(source, op, expr.value);
|
|
}
|
|
return postfix_expression();
|
|
}
|
|
|
|
// multiplicative_expr
|
|
// :
|
|
// | STAR unary_expression multiplicative_expr
|
|
// | FORWARD_SLASH unary_expression multiplicative_expr
|
|
// | MODULO unary_expression multiplicative_expr
|
|
Expect<ast::Expression*> ParserImpl::expect_multiplicative_expr(
|
|
ast::Expression* lhs) {
|
|
auto t = peek();
|
|
|
|
ast::BinaryOp op = ast::BinaryOp::kNone;
|
|
if (t.IsStar())
|
|
op = ast::BinaryOp::kMultiply;
|
|
else if (t.IsForwardSlash())
|
|
op = ast::BinaryOp::kDivide;
|
|
else if (t.IsMod())
|
|
op = ast::BinaryOp::kModulo;
|
|
else
|
|
return lhs;
|
|
|
|
auto source = t.source();
|
|
auto name = t.to_name();
|
|
next(); // Consume the peek
|
|
|
|
auto rhs = unary_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched) {
|
|
return add_error(peek(),
|
|
"unable to parse right side of " + name + " expression");
|
|
}
|
|
|
|
return expect_multiplicative_expr(
|
|
create<ast::BinaryExpression>(source, op, lhs, rhs.value));
|
|
}
|
|
|
|
// multiplicative_expression
|
|
// : unary_expression multiplicative_expr
|
|
Maybe<ast::Expression*> ParserImpl::multiplicative_expression() {
|
|
auto lhs = unary_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_multiplicative_expr(lhs.value);
|
|
}
|
|
|
|
// additive_expr
|
|
// :
|
|
// | PLUS multiplicative_expression additive_expr
|
|
// | MINUS multiplicative_expression additive_expr
|
|
Expect<ast::Expression*> ParserImpl::expect_additive_expr(
|
|
ast::Expression* lhs) {
|
|
auto t = peek();
|
|
|
|
ast::BinaryOp op = ast::BinaryOp::kNone;
|
|
if (t.IsPlus())
|
|
op = ast::BinaryOp::kAdd;
|
|
else if (t.IsMinus())
|
|
op = ast::BinaryOp::kSubtract;
|
|
else
|
|
return lhs;
|
|
|
|
auto source = t.source();
|
|
next(); // Consume the peek
|
|
|
|
auto rhs = multiplicative_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched)
|
|
return add_error(peek(), "unable to parse right side of + expression");
|
|
|
|
return expect_additive_expr(
|
|
create<ast::BinaryExpression>(source, op, lhs, rhs.value));
|
|
}
|
|
|
|
// additive_expression
|
|
// : multiplicative_expression additive_expr
|
|
Maybe<ast::Expression*> ParserImpl::additive_expression() {
|
|
auto lhs = multiplicative_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_additive_expr(lhs.value);
|
|
}
|
|
|
|
// shift_expr
|
|
// :
|
|
// | LESS_THAN LESS_THAN additive_expression shift_expr
|
|
// | GREATER_THAN GREATER_THAN additive_expression shift_expr
|
|
Expect<ast::Expression*> ParserImpl::expect_shift_expr(ast::Expression* lhs) {
|
|
auto t = peek();
|
|
auto source = t.source();
|
|
auto t2 = peek(1);
|
|
|
|
auto* name = "";
|
|
ast::BinaryOp op = ast::BinaryOp::kNone;
|
|
if (t.IsLessThan() && t2.IsLessThan()) {
|
|
next(); // Consume the t peek
|
|
next(); // Consume the t2 peek
|
|
op = ast::BinaryOp::kShiftLeft;
|
|
name = "<<";
|
|
} else if (t.IsGreaterThan() && t2.IsGreaterThan()) {
|
|
next(); // Consume the t peek
|
|
next(); // Consume the t2 peek
|
|
op = ast::BinaryOp::kShiftRight;
|
|
name = ">>";
|
|
} else {
|
|
return lhs;
|
|
}
|
|
|
|
auto rhs = additive_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched) {
|
|
return add_error(peek(), std::string("unable to parse right side of ") +
|
|
name + " expression");
|
|
}
|
|
return expect_shift_expr(
|
|
create<ast::BinaryExpression>(source, op, lhs, rhs.value));
|
|
} // namespace wgsl
|
|
|
|
// shift_expression
|
|
// : additive_expression shift_expr
|
|
Maybe<ast::Expression*> ParserImpl::shift_expression() {
|
|
auto lhs = additive_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_shift_expr(lhs.value);
|
|
}
|
|
|
|
// relational_expr
|
|
// :
|
|
// | LESS_THAN shift_expression relational_expr
|
|
// | GREATER_THAN shift_expression relational_expr
|
|
// | LESS_THAN_EQUAL shift_expression relational_expr
|
|
// | GREATER_THAN_EQUAL shift_expression relational_expr
|
|
Expect<ast::Expression*> ParserImpl::expect_relational_expr(
|
|
ast::Expression* lhs) {
|
|
auto t = peek();
|
|
ast::BinaryOp op = ast::BinaryOp::kNone;
|
|
if (t.IsLessThan())
|
|
op = ast::BinaryOp::kLessThan;
|
|
else if (t.IsGreaterThan())
|
|
op = ast::BinaryOp::kGreaterThan;
|
|
else if (t.IsLessThanEqual())
|
|
op = ast::BinaryOp::kLessThanEqual;
|
|
else if (t.IsGreaterThanEqual())
|
|
op = ast::BinaryOp::kGreaterThanEqual;
|
|
else
|
|
return lhs;
|
|
|
|
auto source = t.source();
|
|
auto name = t.to_name();
|
|
next(); // Consume the peek
|
|
|
|
auto rhs = shift_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched) {
|
|
return add_error(peek(),
|
|
"unable to parse right side of " + name + " expression");
|
|
}
|
|
|
|
return expect_relational_expr(
|
|
create<ast::BinaryExpression>(source, op, lhs, rhs.value));
|
|
}
|
|
|
|
// relational_expression
|
|
// : shift_expression relational_expr
|
|
Maybe<ast::Expression*> ParserImpl::relational_expression() {
|
|
auto lhs = shift_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_relational_expr(lhs.value);
|
|
}
|
|
|
|
// equality_expr
|
|
// :
|
|
// | EQUAL_EQUAL relational_expression equality_expr
|
|
// | NOT_EQUAL relational_expression equality_expr
|
|
Expect<ast::Expression*> ParserImpl::expect_equality_expr(
|
|
ast::Expression* lhs) {
|
|
auto t = peek();
|
|
ast::BinaryOp op = ast::BinaryOp::kNone;
|
|
if (t.IsEqualEqual())
|
|
op = ast::BinaryOp::kEqual;
|
|
else if (t.IsNotEqual())
|
|
op = ast::BinaryOp::kNotEqual;
|
|
else
|
|
return lhs;
|
|
|
|
auto source = t.source();
|
|
auto name = t.to_name();
|
|
next(); // Consume the peek
|
|
|
|
auto rhs = relational_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched) {
|
|
return add_error(peek(),
|
|
"unable to parse right side of " + name + " expression");
|
|
}
|
|
|
|
return expect_equality_expr(
|
|
create<ast::BinaryExpression>(source, op, lhs, rhs.value));
|
|
}
|
|
|
|
// equality_expression
|
|
// : relational_expression equality_expr
|
|
Maybe<ast::Expression*> ParserImpl::equality_expression() {
|
|
auto lhs = relational_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_equality_expr(lhs.value);
|
|
}
|
|
|
|
// and_expr
|
|
// :
|
|
// | AND equality_expression and_expr
|
|
Expect<ast::Expression*> ParserImpl::expect_and_expr(ast::Expression* lhs) {
|
|
auto t = peek();
|
|
if (!t.IsAnd())
|
|
return lhs;
|
|
|
|
auto source = t.source();
|
|
next(); // Consume the peek
|
|
|
|
auto rhs = equality_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched)
|
|
return add_error(peek(), "unable to parse right side of & expression");
|
|
|
|
return expect_and_expr(create<ast::BinaryExpression>(
|
|
source, ast::BinaryOp::kAnd, lhs, rhs.value));
|
|
}
|
|
|
|
// and_expression
|
|
// : equality_expression and_expr
|
|
Maybe<ast::Expression*> ParserImpl::and_expression() {
|
|
auto lhs = equality_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_and_expr(lhs.value);
|
|
}
|
|
|
|
// exclusive_or_expr
|
|
// :
|
|
// | XOR and_expression exclusive_or_expr
|
|
Expect<ast::Expression*> ParserImpl::expect_exclusive_or_expr(
|
|
ast::Expression* lhs) {
|
|
Source source;
|
|
if (!match(Token::Type::kXor, &source))
|
|
return lhs;
|
|
|
|
auto rhs = and_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched)
|
|
return add_error(peek(), "unable to parse right side of ^ expression");
|
|
|
|
return expect_exclusive_or_expr(create<ast::BinaryExpression>(
|
|
source, ast::BinaryOp::kXor, lhs, rhs.value));
|
|
}
|
|
|
|
// exclusive_or_expression
|
|
// : and_expression exclusive_or_expr
|
|
Maybe<ast::Expression*> ParserImpl::exclusive_or_expression() {
|
|
auto lhs = and_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_exclusive_or_expr(lhs.value);
|
|
}
|
|
|
|
// inclusive_or_expr
|
|
// :
|
|
// | OR exclusive_or_expression inclusive_or_expr
|
|
Expect<ast::Expression*> ParserImpl::expect_inclusive_or_expr(
|
|
ast::Expression* lhs) {
|
|
Source source;
|
|
if (!match(Token::Type::kOr))
|
|
return lhs;
|
|
|
|
auto rhs = exclusive_or_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched)
|
|
return add_error(peek(), "unable to parse right side of | expression");
|
|
|
|
return expect_inclusive_or_expr(create<ast::BinaryExpression>(
|
|
source, ast::BinaryOp::kOr, lhs, rhs.value));
|
|
}
|
|
|
|
// inclusive_or_expression
|
|
// : exclusive_or_expression inclusive_or_expr
|
|
Maybe<ast::Expression*> ParserImpl::inclusive_or_expression() {
|
|
auto lhs = exclusive_or_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_inclusive_or_expr(lhs.value);
|
|
}
|
|
|
|
// logical_and_expr
|
|
// :
|
|
// | AND_AND inclusive_or_expression logical_and_expr
|
|
Expect<ast::Expression*> ParserImpl::expect_logical_and_expr(
|
|
ast::Expression* lhs) {
|
|
auto t = peek();
|
|
if (!t.IsAndAnd())
|
|
return lhs;
|
|
|
|
auto source = t.source();
|
|
next(); // Consume the peek
|
|
|
|
auto rhs = inclusive_or_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched)
|
|
return add_error(peek(), "unable to parse right side of && expression");
|
|
|
|
return expect_logical_and_expr(create<ast::BinaryExpression>(
|
|
source, ast::BinaryOp::kLogicalAnd, lhs, rhs.value));
|
|
}
|
|
|
|
// logical_and_expression
|
|
// : inclusive_or_expression logical_and_expr
|
|
Maybe<ast::Expression*> ParserImpl::logical_and_expression() {
|
|
auto lhs = inclusive_or_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_logical_and_expr(lhs.value);
|
|
}
|
|
|
|
// logical_or_expr
|
|
// :
|
|
// | OR_OR logical_and_expression logical_or_expr
|
|
Expect<ast::Expression*> ParserImpl::expect_logical_or_expr(
|
|
ast::Expression* lhs) {
|
|
Source source;
|
|
if (!match(Token::Type::kOrOr))
|
|
return lhs;
|
|
|
|
auto rhs = logical_and_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched)
|
|
return add_error(peek(), "unable to parse right side of || expression");
|
|
|
|
return expect_logical_or_expr(create<ast::BinaryExpression>(
|
|
source, ast::BinaryOp::kLogicalOr, lhs, rhs.value));
|
|
}
|
|
|
|
// logical_or_expression
|
|
// : logical_and_expression logical_or_expr
|
|
Maybe<ast::Expression*> ParserImpl::logical_or_expression() {
|
|
auto lhs = logical_and_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return expect_logical_or_expr(lhs.value);
|
|
}
|
|
|
|
// assignment_stmt
|
|
// : unary_expression EQUAL logical_or_expression
|
|
Maybe<ast::AssignmentStatement*> ParserImpl::assignment_stmt() {
|
|
auto t = peek();
|
|
auto source = t.source();
|
|
|
|
// tint:295 - Test for `ident COLON` - this is invalid grammar, and without
|
|
// special casing will error as "missing = for assignment", which is less
|
|
// helpful than this error message:
|
|
if (peek(0).IsIdentifier() && peek(1).IsColon()) {
|
|
return add_error(peek(0).source(),
|
|
"expected 'var' for variable declaration");
|
|
}
|
|
|
|
auto lhs = unary_expression();
|
|
if (lhs.errored)
|
|
return Failure::kErrored;
|
|
if (!lhs.matched)
|
|
return Failure::kNoMatch;
|
|
|
|
if (!expect("assignment", Token::Type::kEqual))
|
|
return Failure::kErrored;
|
|
|
|
auto rhs = logical_or_expression();
|
|
if (rhs.errored)
|
|
return Failure::kErrored;
|
|
if (!rhs.matched)
|
|
return add_error(peek(), "unable to parse right side of assignment");
|
|
|
|
return create<ast::AssignmentStatement>(source, lhs.value, rhs.value);
|
|
}
|
|
|
|
// const_literal
|
|
// : INT_LITERAL
|
|
// | UINT_LITERAL
|
|
// | FLOAT_LITERAL
|
|
// | TRUE
|
|
// | FALSE
|
|
Maybe<ast::Literal*> ParserImpl::const_literal() {
|
|
auto t = peek();
|
|
if (match(Token::Type::kTrue)) {
|
|
auto* type = module_.create<ast::type::Bool>();
|
|
return create<ast::BoolLiteral>(Source{}, type, true);
|
|
}
|
|
if (match(Token::Type::kFalse)) {
|
|
auto* type = module_.create<ast::type::Bool>();
|
|
return create<ast::BoolLiteral>(Source{}, type, false);
|
|
}
|
|
if (match(Token::Type::kSintLiteral)) {
|
|
auto* type = module_.create<ast::type::I32>();
|
|
return create<ast::SintLiteral>(Source{}, type, t.to_i32());
|
|
}
|
|
if (match(Token::Type::kUintLiteral)) {
|
|
auto* type = module_.create<ast::type::U32>();
|
|
return create<ast::UintLiteral>(Source{}, type, t.to_u32());
|
|
}
|
|
if (match(Token::Type::kFloatLiteral)) {
|
|
auto p = peek();
|
|
if (p.IsIdentifier() && p.to_str() == "f") {
|
|
next(); // Consume 'f'
|
|
add_error(p.source(), "float literals must not be suffixed with 'f'");
|
|
}
|
|
auto* type = module_.create<ast::type::F32>();
|
|
return create<ast::FloatLiteral>(Source{}, type, t.to_f32());
|
|
}
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
// const_expr
|
|
// : type_decl PAREN_LEFT (const_expr COMMA)? const_expr PAREN_RIGHT
|
|
// | const_literal
|
|
Expect<ast::ConstructorExpression*> ParserImpl::expect_const_expr() {
|
|
return expect_const_expr_internal(0);
|
|
}
|
|
|
|
Expect<ast::ConstructorExpression*> ParserImpl::expect_const_expr_internal(
|
|
uint32_t depth) {
|
|
auto t = peek();
|
|
|
|
if (depth > kMaxConstExprDepth) {
|
|
return add_error(t, "max const_expr depth reached");
|
|
}
|
|
|
|
auto source = t.source();
|
|
|
|
auto type = type_decl();
|
|
if (type.errored)
|
|
return Failure::kErrored;
|
|
if (type.matched) {
|
|
auto params = expect_paren_block(
|
|
"type constructor", [&]() -> Expect<ast::ExpressionList> {
|
|
ast::ExpressionList list;
|
|
auto param = expect_const_expr_internal(depth + 1);
|
|
if (param.errored)
|
|
return Failure::kErrored;
|
|
list.emplace_back(param.value);
|
|
while (match(Token::Type::kComma)) {
|
|
param = expect_const_expr_internal(depth + 1);
|
|
if (param.errored)
|
|
return Failure::kErrored;
|
|
list.emplace_back(param.value);
|
|
}
|
|
return list;
|
|
});
|
|
|
|
if (params.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::TypeConstructorExpression>(source, type.value,
|
|
params.value);
|
|
}
|
|
|
|
auto lit = const_literal();
|
|
if (lit.errored)
|
|
return Failure::kErrored;
|
|
if (!lit.matched)
|
|
return add_error(peek(), "unable to parse const literal");
|
|
|
|
return create<ast::ScalarConstructorExpression>(source, lit.value);
|
|
}
|
|
|
|
Maybe<ast::DecorationList> ParserImpl::decoration_list() {
|
|
bool errored = false;
|
|
bool matched = false;
|
|
ast::DecorationList decos;
|
|
|
|
while (synchronized_) {
|
|
auto list = decoration_bracketed_list(decos);
|
|
if (list.errored)
|
|
errored = true;
|
|
if (!list.matched)
|
|
break;
|
|
|
|
matched = true;
|
|
}
|
|
|
|
if (errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!matched)
|
|
return Failure::kNoMatch;
|
|
|
|
return decos;
|
|
}
|
|
|
|
Maybe<bool> ParserImpl::decoration_bracketed_list(ast::DecorationList& decos) {
|
|
const char* use = "decoration list";
|
|
|
|
if (!match(Token::Type::kAttrLeft)) {
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
Source source;
|
|
if (match(Token::Type::kAttrRight, &source))
|
|
return add_error(source, "empty decoration list");
|
|
|
|
return sync(Token::Type::kAttrRight, [&]() -> Expect<bool> {
|
|
bool errored = false;
|
|
|
|
while (synchronized_) {
|
|
auto deco = expect_decoration();
|
|
if (deco.errored)
|
|
errored = true;
|
|
decos.emplace_back(deco.value);
|
|
|
|
if (match(Token::Type::kComma))
|
|
continue;
|
|
|
|
if (is_decoration(peek())) {
|
|
// We have two decorations in a bracket without a separating comma.
|
|
// e.g. [[location(1) set(2)]]
|
|
// ^^^ expected comma
|
|
expect(use, Token::Type::kComma);
|
|
return Failure::kErrored;
|
|
}
|
|
|
|
break;
|
|
}
|
|
|
|
if (errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!expect(use, Token::Type::kAttrRight))
|
|
return Failure::kErrored;
|
|
|
|
return true;
|
|
});
|
|
}
|
|
|
|
Expect<ast::Decoration*> ParserImpl::expect_decoration() {
|
|
auto t = peek();
|
|
auto deco = decoration();
|
|
if (deco.errored)
|
|
return Failure::kErrored;
|
|
if (deco.matched)
|
|
return deco.value;
|
|
return add_error(t, "expected decoration");
|
|
}
|
|
|
|
Maybe<ast::Decoration*> ParserImpl::decoration() {
|
|
using Result = Maybe<ast::Decoration*>;
|
|
auto t = next();
|
|
|
|
if (!t.IsIdentifier()) {
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
auto s = t.to_str();
|
|
if (s == kAccessDecoration) {
|
|
const char* use = "access decoration";
|
|
return expect_paren_block(use, [&]() -> Result {
|
|
auto val = expect_access_type();
|
|
if (val.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::AccessDecoration>(val.value, val.source);
|
|
});
|
|
}
|
|
|
|
if (s == kLocationDecoration) {
|
|
const char* use = "location decoration";
|
|
return expect_paren_block(use, [&]() -> Result {
|
|
auto val = expect_positive_sint(use);
|
|
if (val.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::LocationDecoration>(val.value, val.source);
|
|
});
|
|
}
|
|
|
|
if (s == kBindingDecoration) {
|
|
const char* use = "binding decoration";
|
|
return expect_paren_block(use, [&]() -> Result {
|
|
auto val = expect_positive_sint(use);
|
|
if (val.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::BindingDecoration>(val.value, val.source);
|
|
});
|
|
}
|
|
|
|
if (s == kSetDecoration) {
|
|
const char* use = "set decoration";
|
|
return expect_paren_block(use, [&]() -> Result {
|
|
auto val = expect_positive_sint(use);
|
|
if (val.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::SetDecoration>(val.value, val.source);
|
|
});
|
|
}
|
|
|
|
if (s == kBuiltinDecoration) {
|
|
return expect_paren_block("builtin decoration", [&]() -> Result {
|
|
auto builtin = expect_builtin();
|
|
if (builtin.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::BuiltinDecoration>(builtin.value, builtin.source);
|
|
});
|
|
}
|
|
|
|
if (s == kWorkgroupSizeDecoration) {
|
|
return expect_paren_block("workgroup_size decoration", [&]() -> Result {
|
|
uint32_t x;
|
|
uint32_t y = 1;
|
|
uint32_t z = 1;
|
|
|
|
auto val = expect_nonzero_positive_sint("workgroup_size x parameter");
|
|
if (val.errored)
|
|
return Failure::kErrored;
|
|
x = val.value;
|
|
|
|
if (match(Token::Type::kComma)) {
|
|
val = expect_nonzero_positive_sint("workgroup_size y parameter");
|
|
if (val.errored)
|
|
return Failure::kErrored;
|
|
y = val.value;
|
|
|
|
if (match(Token::Type::kComma)) {
|
|
val = expect_nonzero_positive_sint("workgroup_size z parameter");
|
|
if (val.errored)
|
|
return Failure::kErrored;
|
|
z = val.value;
|
|
}
|
|
}
|
|
|
|
return create<ast::WorkgroupDecoration>(x, y, z, t.source());
|
|
});
|
|
}
|
|
|
|
if (s == kStageDecoration) {
|
|
return expect_paren_block("stage decoration", [&]() -> Result {
|
|
auto stage = expect_pipeline_stage();
|
|
if (stage.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::StageDecoration>(stage.value, stage.source);
|
|
});
|
|
}
|
|
|
|
if (s == kBlockDecoration) {
|
|
return create<ast::StructBlockDecoration>(t.source());
|
|
}
|
|
|
|
if (s == kStrideDecoration) {
|
|
const char* use = "stride decoration";
|
|
return expect_paren_block(use, [&]() -> Result {
|
|
auto val = expect_nonzero_positive_sint(use);
|
|
if (val.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::StrideDecoration>(val.value, t.source());
|
|
});
|
|
}
|
|
|
|
if (s == kOffsetDecoration) {
|
|
const char* use = "offset decoration";
|
|
return expect_paren_block(use, [&]() -> Result {
|
|
auto val = expect_positive_sint(use);
|
|
if (val.errored)
|
|
return Failure::kErrored;
|
|
|
|
return create<ast::StructMemberOffsetDecoration>(val.value, t.source());
|
|
});
|
|
}
|
|
|
|
return Failure::kNoMatch;
|
|
}
|
|
|
|
template <typename T>
|
|
std::vector<T*> ParserImpl::take_decorations(ast::DecorationList& in) {
|
|
ast::DecorationList remaining;
|
|
std::vector<T*> out;
|
|
out.reserve(in.size());
|
|
for (auto* deco : in) {
|
|
if (auto* t = deco->As<T>()) {
|
|
out.emplace_back(t);
|
|
} else {
|
|
remaining.emplace_back(deco);
|
|
}
|
|
}
|
|
|
|
in = std::move(remaining);
|
|
return out;
|
|
}
|
|
|
|
template <typename T>
|
|
Expect<std::vector<T*>> ParserImpl::cast_decorations(ast::DecorationList& in) {
|
|
auto out = take_decorations<T>(in);
|
|
|
|
bool ok = true;
|
|
|
|
for (auto* deco : in) {
|
|
std::stringstream msg;
|
|
msg << deco->GetKind() << " decoration type cannot be used for " << T::Kind;
|
|
add_error(deco->source(), msg.str());
|
|
ok = false;
|
|
}
|
|
|
|
// clear in so that expect_decorations_consumed() doesn't error again on the
|
|
// decorations we've already errored on.
|
|
in.clear();
|
|
|
|
if (!ok)
|
|
return Failure::kErrored;
|
|
|
|
return out;
|
|
}
|
|
|
|
bool ParserImpl::expect_decorations_consumed(const ast::DecorationList& in) {
|
|
if (in.empty()) {
|
|
return true;
|
|
}
|
|
add_error(in[0]->source(), "unexpected decorations");
|
|
return false;
|
|
}
|
|
|
|
bool ParserImpl::match(Token::Type tok, Source* source /*= nullptr*/) {
|
|
auto t = peek();
|
|
|
|
if (source != nullptr)
|
|
*source = t.source();
|
|
|
|
if (t.Is(tok)) {
|
|
next();
|
|
return true;
|
|
}
|
|
return false;
|
|
}
|
|
|
|
bool ParserImpl::expect(const std::string& use, Token::Type tok) {
|
|
auto t = peek();
|
|
if (t.Is(tok)) {
|
|
next();
|
|
synchronized_ = true;
|
|
return true;
|
|
}
|
|
|
|
std::stringstream err;
|
|
err << "expected '" << Token::TypeToName(tok) << "'";
|
|
if (!use.empty()) {
|
|
err << " for " << use;
|
|
}
|
|
add_error(t, err.str());
|
|
synchronized_ = false;
|
|
return false;
|
|
}
|
|
|
|
Expect<int32_t> ParserImpl::expect_sint(const std::string& use) {
|
|
auto t = peek();
|
|
if (!t.IsSintLiteral())
|
|
return add_error(t.source(), "expected signed integer literal", use);
|
|
|
|
next();
|
|
return {t.to_i32(), t.source()};
|
|
}
|
|
|
|
Expect<uint32_t> ParserImpl::expect_positive_sint(const std::string& use) {
|
|
auto sint = expect_sint(use);
|
|
if (sint.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (sint.value < 0)
|
|
return add_error(sint.source, use + " must be positive");
|
|
|
|
return {static_cast<uint32_t>(sint.value), sint.source};
|
|
}
|
|
|
|
Expect<uint32_t> ParserImpl::expect_nonzero_positive_sint(
|
|
const std::string& use) {
|
|
auto sint = expect_sint(use);
|
|
if (sint.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (sint.value <= 0)
|
|
return add_error(sint.source, use + " must be greater than 0");
|
|
|
|
return {static_cast<uint32_t>(sint.value), sint.source};
|
|
}
|
|
|
|
Expect<std::string> ParserImpl::expect_ident(const std::string& use) {
|
|
auto t = peek();
|
|
if (t.IsIdentifier()) {
|
|
synchronized_ = true;
|
|
next();
|
|
return {t.to_str(), t.source()};
|
|
}
|
|
synchronized_ = false;
|
|
return add_error(t.source(), "expected identifier", use);
|
|
}
|
|
|
|
template <typename F, typename T>
|
|
T ParserImpl::expect_block(Token::Type start,
|
|
Token::Type end,
|
|
const std::string& use,
|
|
F&& body) {
|
|
if (!expect(use, start)) {
|
|
return Failure::kErrored;
|
|
}
|
|
|
|
return sync(end, [&]() -> T {
|
|
auto res = body();
|
|
|
|
if (res.errored)
|
|
return Failure::kErrored;
|
|
|
|
if (!expect(use, end))
|
|
return Failure::kErrored;
|
|
|
|
return res;
|
|
});
|
|
}
|
|
|
|
template <typename F, typename T>
|
|
T ParserImpl::expect_paren_block(const std::string& use, F&& body) {
|
|
return expect_block(Token::Type::kParenLeft, Token::Type::kParenRight, use,
|
|
std::forward<F>(body));
|
|
}
|
|
|
|
template <typename F, typename T>
|
|
T ParserImpl::expect_brace_block(const std::string& use, F&& body) {
|
|
return expect_block(Token::Type::kBraceLeft, Token::Type::kBraceRight, use,
|
|
std::forward<F>(body));
|
|
}
|
|
|
|
template <typename F, typename T>
|
|
T ParserImpl::expect_lt_gt_block(const std::string& use, F&& body) {
|
|
return expect_block(Token::Type::kLessThan, Token::Type::kGreaterThan, use,
|
|
std::forward<F>(body));
|
|
}
|
|
|
|
template <typename F, typename T>
|
|
T ParserImpl::sync(Token::Type tok, F&& body) {
|
|
sync_tokens_.push_back(tok);
|
|
|
|
auto result = body();
|
|
|
|
assert(sync_tokens_.back() == tok);
|
|
sync_tokens_.pop_back();
|
|
|
|
if (result.errored) {
|
|
sync_to(tok, /* consume: */ true);
|
|
}
|
|
|
|
return result;
|
|
}
|
|
|
|
bool ParserImpl::sync_to(Token::Type tok, bool consume) {
|
|
// Clear the synchronized state - gets set to true again on success.
|
|
synchronized_ = false;
|
|
|
|
BlockCounters counters;
|
|
|
|
for (size_t i = 0; i < kMaxResynchronizeLookahead; i++) {
|
|
auto t = peek(i);
|
|
if (counters.consume(t) > 0)
|
|
continue; // Nested block
|
|
if (!t.Is(tok) && !is_sync_token(t))
|
|
continue; // Not a synchronization point
|
|
|
|
// Synchronization point found.
|
|
|
|
// Skip any tokens we don't understand, bringing us to just before the
|
|
// resync point.
|
|
while (i-- > 0) {
|
|
next();
|
|
}
|
|
|
|
// Is this synchronization token |tok|?
|
|
if (t.Is(tok)) {
|
|
if (consume)
|
|
next();
|
|
synchronized_ = true;
|
|
return true;
|
|
}
|
|
break;
|
|
}
|
|
|
|
return false;
|
|
}
|
|
|
|
bool ParserImpl::is_sync_token(const Token& t) const {
|
|
for (auto r : sync_tokens_) {
|
|
if (t.Is(r))
|
|
return true;
|
|
}
|
|
return false;
|
|
}
|
|
|
|
template <typename F, typename T>
|
|
T ParserImpl::without_error(F&& body) {
|
|
silence_errors_++;
|
|
auto result = body();
|
|
silence_errors_--;
|
|
return result;
|
|
}
|
|
|
|
} // namespace wgsl
|
|
} // namespace reader
|
|
} // namespace tint
|