aboutsummaryrefslogtreecommitdiff
path: root/gcc
diff options
context:
space:
mode:
authorJakub Jelinek <jakub@redhat.com>2020-12-08 10:45:30 +0100
committerJakub Jelinek <jakub@redhat.com>2020-12-08 10:45:30 +0100
commit31007091b10944c358e5038a6271d7e2744cde37 (patch)
treebeb5b083c035dd644ad764ab68d9ab8f6c240a4c /gcc
parentc2c198bfd1e747b761c6b9b13417685bd4378d57 (diff)
downloadgcc-31007091b10944c358e5038a6271d7e2744cde37.zip
gcc-31007091b10944c358e5038a6271d7e2744cde37.tar.gz
gcc-31007091b10944c358e5038a6271d7e2744cde37.tar.bz2
openmp: -fopenmp-simd fixes [PR98187]
This patch fixes two bugs in the -fopenmp-simd support. One is that in C++ #pragma omp parallel master would actually create OMP_PARALLEL in the IL, which is a big no-no for -fopenmp-simd, we should be creating only the constructs -fopenmp-simd handles (mainly OMP_SIMD, OMP_LOOP which is gimplified as simd in that case, declare simd/reduction and ordered simd). The other bug was that #pragma omp master taskloop simd combined construct contains simd and thus should be recognized as #pragma omp simd (with only the simd applicable clauses), but as master wasn't included in omp_pragmas_simd, we'd ignore it completely instead. 2020-12-08 Jakub Jelinek <jakub@redhat.com> PR c++/98187 * c-pragma.c (omp_pragmas): Remove "master". (omp_pragmas_simd): Add "master". * parser.c (cp_parser_omp_parallel): For parallel master with -fopenmp-simd only, just call cp_parser_omp_master instead of wrapping it in OMP_PARALLEL. * c-c++-common/gomp/pr98187.c: New test.
Diffstat (limited to 'gcc')
-rw-r--r--gcc/c-family/c-pragma.c2
-rw-r--r--gcc/cp/parser.c3
-rw-r--r--gcc/testsuite/c-c++-common/gomp/pr98187.c109
3 files changed, 113 insertions, 1 deletions
diff --git a/gcc/c-family/c-pragma.c b/gcc/c-family/c-pragma.c
index d68985c..14d77e0 100644
--- a/gcc/c-family/c-pragma.c
+++ b/gcc/c-family/c-pragma.c
@@ -1317,7 +1317,6 @@ static const struct omp_pragma_def omp_pragmas[] = {
{ "depobj", PRAGMA_OMP_DEPOBJ },
{ "end", PRAGMA_OMP_END_DECLARE_TARGET },
{ "flush", PRAGMA_OMP_FLUSH },
- { "master", PRAGMA_OMP_MASTER },
{ "requires", PRAGMA_OMP_REQUIRES },
{ "section", PRAGMA_OMP_SECTION },
{ "sections", PRAGMA_OMP_SECTIONS },
@@ -1333,6 +1332,7 @@ static const struct omp_pragma_def omp_pragmas_simd[] = {
{ "distribute", PRAGMA_OMP_DISTRIBUTE },
{ "for", PRAGMA_OMP_FOR },
{ "loop", PRAGMA_OMP_LOOP },
+ { "master", PRAGMA_OMP_MASTER },
{ "ordered", PRAGMA_OMP_ORDERED },
{ "parallel", PRAGMA_OMP_PARALLEL },
{ "scan", PRAGMA_OMP_SCAN },
diff --git a/gcc/cp/parser.c b/gcc/cp/parser.c
index cc3da15..6aa42ef 100644
--- a/gcc/cp/parser.c
+++ b/gcc/cp/parser.c
@@ -40491,6 +40491,9 @@ cp_parser_omp_parallel (cp_parser *parser, cp_token *pragma_tok,
cclauses = cclauses_buf;
cp_lexer_consume_token (parser->lexer);
+ if (!flag_openmp) /* flag_openmp_simd */
+ return cp_parser_omp_master (parser, pragma_tok, p_name, mask,
+ cclauses, if_p);
block = begin_omp_parallel ();
save = cp_parser_begin_omp_structured_block (parser);
tree ret = cp_parser_omp_master (parser, pragma_tok, p_name, mask,
diff --git a/gcc/testsuite/c-c++-common/gomp/pr98187.c b/gcc/testsuite/c-c++-common/gomp/pr98187.c
new file mode 100644
index 0000000..fc252fd
--- /dev/null
+++ b/gcc/testsuite/c-c++-common/gomp/pr98187.c
@@ -0,0 +1,109 @@
+/* PR c++/98187 */
+/* { dg-do compile } */
+/* { dg-options "-fopenmp-simd -O2 -fdump-tree-gimple" } */
+/* { dg-final { scan-tree-dump-times "#pragma omp simd" 17 "gimple" } } */
+
+void
+foo (int *p)
+{
+ int i;
+ #pragma omp distribute parallel for
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp distribute parallel for simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp distribute simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+}
+
+void
+bar (int *p)
+{
+ int i;
+ #pragma omp for simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp master taskloop
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp master taskloop simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp parallel for
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp parallel for simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp parallel loop
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp parallel master
+ p[0]++;
+ #pragma omp parallel master taskloop
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp parallel master taskloop simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp parallel sections
+ {
+ p[0]++;
+ #pragma omp section
+ p[1]++;
+ #pragma omp section
+ p[2]++;
+ }
+ #pragma omp target parallel
+ #pragma omp master
+ p[0]++;
+ #pragma omp target parallel for
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp target parallel for simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp target parallel loop
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp target teams private (i)
+ i = 0;
+ #pragma omp target teams distribute
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp target teams distribute parallel for
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp target teams distribute parallel for simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp target teams distribute simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp target teams loop
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp target simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp taskloop simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp teams distribute
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp teams distribute parallel for
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp teams distribute parallel for simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp teams distribute simd
+ for (i = 0; i < 64; i++)
+ p[i]++;
+ #pragma omp teams loop
+ for (i = 0; i < 64; i++)
+ p[i]++;
+}