aboutsummaryrefslogtreecommitdiff
diff options
context:
space:
mode:
authorJakub Jelinek <jakub@redhat.com>2017-05-22 20:51:54 +0200
committerJakub Jelinek <jakub@gcc.gnu.org>2017-05-22 20:51:54 +0200
commitc24783c49924474f54feb0c6038cba4719125634 (patch)
treeac190183444200175ba69ab2d6aaf216d6806398
parent051e40e0cb151d3fd7a773213ee00f84043e2a25 (diff)
downloadgcc-c24783c49924474f54feb0c6038cba4719125634.zip
gcc-c24783c49924474f54feb0c6038cba4719125634.tar.gz
gcc-c24783c49924474f54feb0c6038cba4719125634.tar.bz2
re PR middle-end/80853 (OpenMP ICE in build_outer_var_ref with array reduction)
PR middle-end/80853 * omp-low.c (lower_reduction_clauses): Pass OMP_CLAUSE_PRIVATE as last argument to build_outer_var_ref for pointer bases of array section reductions. * testsuite/libgomp.c/pr80853.c: New test. From-SVN: r248344
-rw-r--r--gcc/ChangeLog7
-rw-r--r--gcc/omp-low.c16
-rw-r--r--libgomp/ChangeLog5
-rw-r--r--libgomp/testsuite/libgomp.c/pr80853.c29
4 files changed, 54 insertions, 3 deletions
diff --git a/gcc/ChangeLog b/gcc/ChangeLog
index 3dac225..b69ffc0 100644
--- a/gcc/ChangeLog
+++ b/gcc/ChangeLog
@@ -1,3 +1,10 @@
+2017-05-22 Jakub Jelinek <jakub@redhat.com>
+
+ PR middle-end/80853
+ * omp-low.c (lower_reduction_clauses): Pass OMP_CLAUSE_PRIVATE
+ as last argument to build_outer_var_ref for pointer bases of array
+ section reductions.
+
2017-05-19 Martin Sebor <msebor@redhat.com>
* print-tree.c (print_node): Print DECL_READ_P flag.
diff --git a/gcc/omp-low.c b/gcc/omp-low.c
index 9cc2996..26e6586 100644
--- a/gcc/omp-low.c
+++ b/gcc/omp-low.c
@@ -5140,15 +5140,25 @@ lower_reduction_clauses (tree clauses, gimple_seq *stmt_seqp, omp_context *ctx)
if (OMP_CLAUSE_CODE (c) != OMP_CLAUSE_REDUCTION)
continue;
+ enum omp_clause_code ccode = OMP_CLAUSE_REDUCTION;
orig_var = var = OMP_CLAUSE_DECL (c);
if (TREE_CODE (var) == MEM_REF)
{
var = TREE_OPERAND (var, 0);
if (TREE_CODE (var) == POINTER_PLUS_EXPR)
var = TREE_OPERAND (var, 0);
- if (TREE_CODE (var) == INDIRECT_REF
- || TREE_CODE (var) == ADDR_EXPR)
+ if (TREE_CODE (var) == ADDR_EXPR)
var = TREE_OPERAND (var, 0);
+ else
+ {
+ /* If this is a pointer or referenced based array
+ section, the var could be private in the outer
+ context e.g. on orphaned loop construct. Pretend this
+ is private variable's outer reference. */
+ ccode = OMP_CLAUSE_PRIVATE;
+ if (TREE_CODE (var) == INDIRECT_REF)
+ var = TREE_OPERAND (var, 0);
+ }
orig_var = var;
if (is_variable_sized (var))
{
@@ -5162,7 +5172,7 @@ lower_reduction_clauses (tree clauses, gimple_seq *stmt_seqp, omp_context *ctx)
new_var = lookup_decl (var, ctx);
if (var == OMP_CLAUSE_DECL (c) && omp_is_reference (var))
new_var = build_simple_mem_ref_loc (clause_loc, new_var);
- ref = build_outer_var_ref (var, ctx);
+ ref = build_outer_var_ref (var, ctx, ccode);
code = OMP_CLAUSE_REDUCTION_CODE (c);
/* reduction(-:var) sums up the partial results, so it acts
diff --git a/libgomp/ChangeLog b/libgomp/ChangeLog
index 460605b..d49420a 100644
--- a/libgomp/ChangeLog
+++ b/libgomp/ChangeLog
@@ -1,3 +1,8 @@
+2017-05-22 Jakub Jelinek <jakub@redhat.com>
+
+ PR middle-end/80853
+ * testsuite/libgomp.c/pr80853.c: New test.
+
2017-05-19 Thomas Schwinge <thomas@codesourcery.com>
* testsuite/libgomp.oacc-c++/template-reduction.C: Update.
diff --git a/libgomp/testsuite/libgomp.c/pr80853.c b/libgomp/testsuite/libgomp.c/pr80853.c
new file mode 100644
index 0000000..3c0ff10
--- /dev/null
+++ b/libgomp/testsuite/libgomp.c/pr80853.c
@@ -0,0 +1,29 @@
+/* PR middle-end/80853 */
+/* { dg-do run } */
+
+__attribute__((noinline, noclone)) void
+foo (int *p)
+{
+ #pragma omp for reduction(+:p[:4])
+ for (int i = 0; i < 64; i++)
+ {
+ p[0] += i;
+ p[1] += i / 2;
+ p[2] += 2 * i;
+ p[3] += 3 * i;
+ }
+}
+
+int
+main ()
+{
+ int p[4] = { 0, 0, 0, 0 };
+ #pragma omp parallel
+ foo (p);
+ if (p[0] != 63 * 64 / 2
+ || p[1] != 31 * 32
+ || p[2] != 63 * 64
+ || p[3] != 3 * 63 * 64 / 2)
+ __builtin_abort ();
+ return 0;
+}