[OpenMP] Fix handling of clause on wrong directive, by Joel. E. Denny

Summary:
First, this patch fixes an assert failure when, for example, "omp for"
has num_teams.

Second, this patch prevents duplicate diagnostics when, for example,
"omp for" has uniform.

This patch makes the general assumption (even where it doesn't
necessarily fix an existing bug) that it is worthless to perform sema
for a clause that appears on a directive on which OpenMP does not
permit that clause.  However, due to this assumption, this patch
suppresses some diagnostics that were expected in the test suite.  I
assert that those diagnostics were likely just distracting to the
user.

Reviewers: ABataev

Reviewed By: ABataev

Subscribers: cfe-commits

Differential Revision: https://reviews.llvm.org/D41841

git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@322107 91177308-0d34-0410-b5e6-96231b3b80d8
This commit is contained in:
Alexey Bataev 2018-01-09 19:21:04 +00:00
parent 32a5ecc720
commit 0ec25ccce5
8 changed files with 67 additions and 28 deletions

View File

@ -2675,30 +2675,42 @@ private:
/// \brief Parses clause with a single expression of a kind \a Kind. /// \brief Parses clause with a single expression of a kind \a Kind.
/// ///
/// \param Kind Kind of current clause. /// \param Kind Kind of current clause.
/// \param ParseOnly true to skip the clause's semantic actions and return
/// nullptr.
/// ///
OMPClause *ParseOpenMPSingleExprClause(OpenMPClauseKind Kind); OMPClause *ParseOpenMPSingleExprClause(OpenMPClauseKind Kind,
bool ParseOnly);
/// \brief Parses simple clause of a kind \a Kind. /// \brief Parses simple clause of a kind \a Kind.
/// ///
/// \param Kind Kind of current clause. /// \param Kind Kind of current clause.
/// \param ParseOnly true to skip the clause's semantic actions and return
/// nullptr.
/// ///
OMPClause *ParseOpenMPSimpleClause(OpenMPClauseKind Kind); OMPClause *ParseOpenMPSimpleClause(OpenMPClauseKind Kind, bool ParseOnly);
/// \brief Parses clause with a single expression and an additional argument /// \brief Parses clause with a single expression and an additional argument
/// of a kind \a Kind. /// of a kind \a Kind.
/// ///
/// \param Kind Kind of current clause. /// \param Kind Kind of current clause.
/// \param ParseOnly true to skip the clause's semantic actions and return
/// nullptr.
/// ///
OMPClause *ParseOpenMPSingleExprWithArgClause(OpenMPClauseKind Kind); OMPClause *ParseOpenMPSingleExprWithArgClause(OpenMPClauseKind Kind,
bool ParseOnly);
/// \brief Parses clause without any additional arguments. /// \brief Parses clause without any additional arguments.
/// ///
/// \param Kind Kind of current clause. /// \param Kind Kind of current clause.
/// \param ParseOnly true to skip the clause's semantic actions and return
/// nullptr.
/// ///
OMPClause *ParseOpenMPClause(OpenMPClauseKind Kind); OMPClause *ParseOpenMPClause(OpenMPClauseKind Kind, bool ParseOnly = false);
/// \brief Parses clause with the list of variables of a kind \a Kind. /// \brief Parses clause with the list of variables of a kind \a Kind.
/// ///
/// \param Kind Kind of current clause. /// \param Kind Kind of current clause.
/// \param ParseOnly true to skip the clause's semantic actions and return
/// nullptr.
/// ///
OMPClause *ParseOpenMPVarListClause(OpenMPDirectiveKind DKind, OMPClause *ParseOpenMPVarListClause(OpenMPDirectiveKind DKind,
OpenMPClauseKind Kind); OpenMPClauseKind Kind, bool ParseOnly);
public: public:
/// Parses simple expression in parens for single-expression clauses of OpenMP /// Parses simple expression in parens for single-expression clauses of OpenMP

View File

@ -1205,11 +1205,13 @@ OMPClause *Parser::ParseOpenMPClause(OpenMPDirectiveKind DKind,
OpenMPClauseKind CKind, bool FirstClause) { OpenMPClauseKind CKind, bool FirstClause) {
OMPClause *Clause = nullptr; OMPClause *Clause = nullptr;
bool ErrorFound = false; bool ErrorFound = false;
bool WrongDirective = false;
// Check if clause is allowed for the given directive. // Check if clause is allowed for the given directive.
if (CKind != OMPC_unknown && !isAllowedClauseForDirective(DKind, CKind)) { if (CKind != OMPC_unknown && !isAllowedClauseForDirective(DKind, CKind)) {
Diag(Tok, diag::err_omp_unexpected_clause) << getOpenMPClauseName(CKind) Diag(Tok, diag::err_omp_unexpected_clause) << getOpenMPClauseName(CKind)
<< getOpenMPDirectiveName(DKind); << getOpenMPDirectiveName(DKind);
ErrorFound = true; ErrorFound = true;
WrongDirective = true;
} }
switch (CKind) { switch (CKind) {
@ -1253,9 +1255,9 @@ OMPClause *Parser::ParseOpenMPClause(OpenMPDirectiveKind DKind,
} }
if (CKind == OMPC_ordered && PP.LookAhead(/*N=*/0).isNot(tok::l_paren)) if (CKind == OMPC_ordered && PP.LookAhead(/*N=*/0).isNot(tok::l_paren))
Clause = ParseOpenMPClause(CKind); Clause = ParseOpenMPClause(CKind, WrongDirective);
else else
Clause = ParseOpenMPSingleExprClause(CKind); Clause = ParseOpenMPSingleExprClause(CKind, WrongDirective);
break; break;
case OMPC_default: case OMPC_default:
case OMPC_proc_bind: case OMPC_proc_bind:
@ -1270,7 +1272,7 @@ OMPClause *Parser::ParseOpenMPClause(OpenMPDirectiveKind DKind,
ErrorFound = true; ErrorFound = true;
} }
Clause = ParseOpenMPSimpleClause(CKind); Clause = ParseOpenMPSimpleClause(CKind, WrongDirective);
break; break;
case OMPC_schedule: case OMPC_schedule:
case OMPC_dist_schedule: case OMPC_dist_schedule:
@ -1287,7 +1289,7 @@ OMPClause *Parser::ParseOpenMPClause(OpenMPDirectiveKind DKind,
LLVM_FALLTHROUGH; LLVM_FALLTHROUGH;
case OMPC_if: case OMPC_if:
Clause = ParseOpenMPSingleExprWithArgClause(CKind); Clause = ParseOpenMPSingleExprWithArgClause(CKind, WrongDirective);
break; break;
case OMPC_nowait: case OMPC_nowait:
case OMPC_untied: case OMPC_untied:
@ -1310,7 +1312,7 @@ OMPClause *Parser::ParseOpenMPClause(OpenMPDirectiveKind DKind,
ErrorFound = true; ErrorFound = true;
} }
Clause = ParseOpenMPClause(CKind); Clause = ParseOpenMPClause(CKind, WrongDirective);
break; break;
case OMPC_private: case OMPC_private:
case OMPC_firstprivate: case OMPC_firstprivate:
@ -1330,7 +1332,7 @@ OMPClause *Parser::ParseOpenMPClause(OpenMPDirectiveKind DKind,
case OMPC_from: case OMPC_from:
case OMPC_use_device_ptr: case OMPC_use_device_ptr:
case OMPC_is_device_ptr: case OMPC_is_device_ptr:
Clause = ParseOpenMPVarListClause(DKind, CKind); Clause = ParseOpenMPVarListClause(DKind, CKind, WrongDirective);
break; break;
case OMPC_unknown: case OMPC_unknown:
Diag(Tok, diag::warn_omp_extra_tokens_at_eol) Diag(Tok, diag::warn_omp_extra_tokens_at_eol)
@ -1339,8 +1341,9 @@ OMPClause *Parser::ParseOpenMPClause(OpenMPDirectiveKind DKind,
break; break;
case OMPC_threadprivate: case OMPC_threadprivate:
case OMPC_uniform: case OMPC_uniform:
Diag(Tok, diag::err_omp_unexpected_clause) << getOpenMPClauseName(CKind) if (!WrongDirective)
<< getOpenMPDirectiveName(DKind); Diag(Tok, diag::err_omp_unexpected_clause)
<< getOpenMPClauseName(CKind) << getOpenMPDirectiveName(DKind);
SkipUntil(tok::comma, tok::annot_pragma_openmp_end, StopBeforeMatch); SkipUntil(tok::comma, tok::annot_pragma_openmp_end, StopBeforeMatch);
break; break;
} }
@ -1400,7 +1403,8 @@ ExprResult Parser::ParseOpenMPParensExpr(StringRef ClauseName,
/// hint-clause: /// hint-clause:
/// 'hint' '(' expression ')' /// 'hint' '(' expression ')'
/// ///
OMPClause *Parser::ParseOpenMPSingleExprClause(OpenMPClauseKind Kind) { OMPClause *Parser::ParseOpenMPSingleExprClause(OpenMPClauseKind Kind,
bool ParseOnly) {
SourceLocation Loc = ConsumeToken(); SourceLocation Loc = ConsumeToken();
SourceLocation LLoc = Tok.getLocation(); SourceLocation LLoc = Tok.getLocation();
SourceLocation RLoc; SourceLocation RLoc;
@ -1410,6 +1414,8 @@ OMPClause *Parser::ParseOpenMPSingleExprClause(OpenMPClauseKind Kind) {
if (Val.isInvalid()) if (Val.isInvalid())
return nullptr; return nullptr;
if (ParseOnly)
return nullptr;
return Actions.ActOnOpenMPSingleExprClause(Kind, Val.get(), Loc, LLoc, RLoc); return Actions.ActOnOpenMPSingleExprClause(Kind, Val.get(), Loc, LLoc, RLoc);
} }
@ -1421,7 +1427,8 @@ OMPClause *Parser::ParseOpenMPSingleExprClause(OpenMPClauseKind Kind) {
/// proc_bind-clause: /// proc_bind-clause:
/// 'proc_bind' '(' 'master' | 'close' | 'spread' ') /// 'proc_bind' '(' 'master' | 'close' | 'spread' ')
/// ///
OMPClause *Parser::ParseOpenMPSimpleClause(OpenMPClauseKind Kind) { OMPClause *Parser::ParseOpenMPSimpleClause(OpenMPClauseKind Kind,
bool ParseOnly) {
SourceLocation Loc = Tok.getLocation(); SourceLocation Loc = Tok.getLocation();
SourceLocation LOpen = ConsumeToken(); SourceLocation LOpen = ConsumeToken();
// Parse '('. // Parse '('.
@ -1440,6 +1447,8 @@ OMPClause *Parser::ParseOpenMPSimpleClause(OpenMPClauseKind Kind) {
// Parse ')'. // Parse ')'.
T.consumeClose(); T.consumeClose();
if (ParseOnly)
return nullptr;
return Actions.ActOnOpenMPSimpleClause(Kind, Type, TypeLoc, LOpen, Loc, return Actions.ActOnOpenMPSimpleClause(Kind, Type, TypeLoc, LOpen, Loc,
Tok.getLocation()); Tok.getLocation());
} }
@ -1470,10 +1479,12 @@ OMPClause *Parser::ParseOpenMPSimpleClause(OpenMPClauseKind Kind) {
/// nogroup-clause: /// nogroup-clause:
/// 'nogroup' /// 'nogroup'
/// ///
OMPClause *Parser::ParseOpenMPClause(OpenMPClauseKind Kind) { OMPClause *Parser::ParseOpenMPClause(OpenMPClauseKind Kind, bool ParseOnly) {
SourceLocation Loc = Tok.getLocation(); SourceLocation Loc = Tok.getLocation();
ConsumeAnyToken(); ConsumeAnyToken();
if (ParseOnly)
return nullptr;
return Actions.ActOnOpenMPClause(Kind, Loc, Tok.getLocation()); return Actions.ActOnOpenMPClause(Kind, Loc, Tok.getLocation());
} }
@ -1491,7 +1502,8 @@ OMPClause *Parser::ParseOpenMPClause(OpenMPClauseKind Kind) {
/// defaultmap: /// defaultmap:
/// 'defaultmap' '(' modifier ':' kind ')' /// 'defaultmap' '(' modifier ':' kind ')'
/// ///
OMPClause *Parser::ParseOpenMPSingleExprWithArgClause(OpenMPClauseKind Kind) { OMPClause *Parser::ParseOpenMPSingleExprWithArgClause(OpenMPClauseKind Kind,
bool ParseOnly) {
SourceLocation Loc = ConsumeToken(); SourceLocation Loc = ConsumeToken();
SourceLocation DelimLoc; SourceLocation DelimLoc;
// Parse '('. // Parse '('.
@ -1613,6 +1625,8 @@ OMPClause *Parser::ParseOpenMPSingleExprWithArgClause(OpenMPClauseKind Kind) {
if (NeedAnExpression && Val.isInvalid()) if (NeedAnExpression && Val.isInvalid())
return nullptr; return nullptr;
if (ParseOnly)
return nullptr;
return Actions.ActOnOpenMPSingleExprWithArgClause( return Actions.ActOnOpenMPSingleExprWithArgClause(
Kind, Arg, Val.get(), Loc, T.getOpenLocation(), KLoc, DelimLoc, Kind, Arg, Val.get(), Loc, T.getOpenLocation(), KLoc, DelimLoc,
T.getCloseLocation()); T.getCloseLocation());
@ -1940,7 +1954,8 @@ bool Parser::ParseOpenMPVarList(OpenMPDirectiveKind DKind,
/// modifier(list) /// modifier(list)
/// where modifier is 'val' (C) or 'ref', 'val' or 'uval'(C++). /// where modifier is 'val' (C) or 'ref', 'val' or 'uval'(C++).
OMPClause *Parser::ParseOpenMPVarListClause(OpenMPDirectiveKind DKind, OMPClause *Parser::ParseOpenMPVarListClause(OpenMPDirectiveKind DKind,
OpenMPClauseKind Kind) { OpenMPClauseKind Kind,
bool ParseOnly) {
SourceLocation Loc = Tok.getLocation(); SourceLocation Loc = Tok.getLocation();
SourceLocation LOpen = ConsumeToken(); SourceLocation LOpen = ConsumeToken();
SmallVector<Expr *, 4> Vars; SmallVector<Expr *, 4> Vars;
@ -1949,6 +1964,8 @@ OMPClause *Parser::ParseOpenMPVarListClause(OpenMPDirectiveKind DKind,
if (ParseOpenMPVarList(DKind, Kind, Vars, Data)) if (ParseOpenMPVarList(DKind, Kind, Vars, Data))
return nullptr; return nullptr;
if (ParseOnly)
return nullptr;
return Actions.ActOnOpenMPVarListClause( return Actions.ActOnOpenMPVarListClause(
Kind, Vars, Data.TailExpr, Loc, LOpen, Data.ColonLoc, Tok.getLocation(), Kind, Vars, Data.TailExpr, Loc, LOpen, Data.ColonLoc, Tok.getLocation(),
Data.ReductionIdScopeSpec, Data.ReductionId, Data.DepKind, Data.LinKind, Data.ReductionIdScopeSpec, Data.ReductionId, Data.DepKind, Data.LinKind,

View File

@ -324,9 +324,7 @@ int test_iteration_spaces() {
#pragma omp target #pragma omp target
#pragma omp teams #pragma omp teams
// expected-error@+3 {{unexpected OpenMP clause 'shared' in directive '#pragma omp distribute simd'}} // expected-error@+1 {{unexpected OpenMP clause 'shared' in directive '#pragma omp distribute simd'}}
// expected-note@+2 {{defined as shared}}
// expected-error@+2 {{loop iteration variable in the associated loop of 'omp distribute simd' directive may not be shared, predetermined as linear}}
#pragma omp distribute simd shared(ii) #pragma omp distribute simd shared(ii)
for (ii = 0; ii < 10; ii++) for (ii = 0; ii < 10; ii++)
c[ii] = a[ii]; c[ii] = a[ii];

View File

@ -54,6 +54,20 @@ void test_invalid_clause() {
#pragma omp for foo bar #pragma omp for foo bar
for (i = 0; i < 16; ++i) for (i = 0; i < 16; ++i)
; ;
// At one time, this failed an assert.
// expected-error@+1 {{unexpected OpenMP clause 'num_teams' in directive '#pragma omp for'}}
#pragma omp for num_teams(3)
for (i = 0; i < 16; ++i)
;
// At one time, this error was reported twice.
// expected-error@+1 {{unexpected OpenMP clause 'uniform' in directive '#pragma omp for'}}
#pragma omp for uniform
for (i = 0; i < 16; ++i)
;
// expected-error@+1 {{unexpected OpenMP clause 'if' in directive '#pragma omp for'}}
#pragma omp for if(0)
for (i = 0; i < 16; ++i)
;
} }
void test_non_identifiers() { void test_non_identifiers() {

View File

@ -31,6 +31,8 @@ int main(int argc, char **argv) {
foo(); foo();
L1: L1:
foo(); foo();
#pragma omp parallel ordered // expected-error {{unexpected OpenMP clause 'ordered' in directive '#pragma omp parallel'}}
;
#pragma omp parallel #pragma omp parallel
; ;
#pragma omp parallel #pragma omp parallel

View File

@ -236,9 +236,7 @@ int test_iteration_spaces() {
for (ii = 0; ii < 10; ii++) for (ii = 0; ii < 10; ii++)
c[ii] = a[ii]; c[ii] = a[ii];
// expected-error@+3 {{unexpected OpenMP clause 'shared' in directive '#pragma omp simd'}} // expected-error@+1 {{unexpected OpenMP clause 'shared' in directive '#pragma omp simd'}}
// expected-note@+2 {{defined as shared}}
// expected-error@+2 {{loop iteration variable in the associated loop of 'omp simd' directive may not be shared, predetermined as linear}}
#pragma omp simd shared(ii) #pragma omp simd shared(ii)
for (ii = 0; ii < 10; ii++) for (ii = 0; ii < 10; ii++)
c[ii] = a[ii]; c[ii] = a[ii];

View File

@ -64,7 +64,7 @@ L1:
// expected-error@+1 {{unexpected OpenMP clause 'default' in directive '#pragma omp target teams distribute simd'}} // expected-error@+1 {{unexpected OpenMP clause 'default' in directive '#pragma omp target teams distribute simd'}}
#pragma omp target teams distribute simd default(none) #pragma omp target teams distribute simd default(none)
for (int i = 0; i < 10; ++i) for (int i = 0; i < 10; ++i)
++argc; // expected-error {{ariable 'argc' must have explicitly specified data sharing attributes}} ++argc;
goto L2; // expected-error {{use of undeclared label 'L2'}} goto L2; // expected-error {{use of undeclared label 'L2'}}
#pragma omp target teams distribute simd #pragma omp target teams distribute simd

View File

@ -294,10 +294,8 @@ int test_iteration_spaces() {
c[ii] = a[ii]; c[ii] = a[ii];
#pragma omp parallel #pragma omp parallel
// expected-error@+2 {{unexpected OpenMP clause 'linear' in directive '#pragma omp taskloop'}} // expected-error@+1 {{unexpected OpenMP clause 'linear' in directive '#pragma omp taskloop'}}
// expected-note@+1 {{defined as linear}}
#pragma omp taskloop linear(ii) #pragma omp taskloop linear(ii)
// expected-error@+1 {{loop iteration variable in the associated loop of 'omp taskloop' directive may not be linear, predetermined as private}}
for (ii = 0; ii < 10; ii++) for (ii = 0; ii < 10; ii++)
c[ii] = a[ii]; c[ii] = a[ii];