diff mbox

[committed] Fix simd clone creation for C++ inlines etc. (PR middle-end/68762)

Message ID 20160808195313.GP14857@tucnak.redhat.com
State New
Headers show

Commit Message

Jakub Jelinek Aug. 8, 2016, 7:53 p.m. UTC 
Hi!

When a cgraph clone is created for simd clones, it is forced
make_decl_local, but for the simd clones we actually want to preserve their
visibility, weak, comdat etc. (except that we want to use a separate comdat
group).

Fixed thusly, bootstrapped/regtested on x86_64-linux and i686-linux,
committed to trunk, queued for 6.2.

2016-08-08  Jakub Jelinek  <jakub@redhat.com>

	PR middle-end/68762
	* omp-simd-clone.c: Include varasm.h.
	(simd_clone_create): Copy over DECL_COMDAT, DECL_WEAK, DECL_EXTERNAL,
	DECL_VISIBILITY, DECL_VISIBILITY_SPECIFIED, DECL_DLLIMPORT_P and for
	DECL_ONE_ONLY call make_decl_one_only.  Fix up spelling in comment and
	update function name.

	* g++.dg/vect/pr68762-1.cc: New test.
	* g++.dg/vect/pr68762-2.cc: New test.
	* g++.dg/vect/pr68762.h: New file.


	Jakub
diff mbox

Patch

--- gcc/omp-simd-clone.c.jj	2016-05-20 09:05:08.000000000 +0200
+++ gcc/omp-simd-clone.c	2016-08-08 11:44:51.081423066 +0200
@@ -47,6 +47,7 @@  along with GCC; see the file COPYING3.
 #include "symbol-summary.h"
 #include "ipa-prop.h"
 #include "tree-eh.h"
+#include "varasm.h"
 
 
 /* Allocate a fresh `simd_clone' and return it.  NARGS is the number
@@ -435,9 +436,18 @@  simd_clone_create (struct cgraph_node *o
     return new_node;
 
   TREE_PUBLIC (new_node->decl) = TREE_PUBLIC (old_node->decl);
+  DECL_COMDAT (new_node->decl) = DECL_COMDAT (old_node->decl);
+  DECL_WEAK (new_node->decl) = DECL_WEAK (old_node->decl);
+  DECL_EXTERNAL (new_node->decl) = DECL_EXTERNAL (old_node->decl);
+  DECL_VISIBILITY_SPECIFIED (new_node->decl)
+    = DECL_VISIBILITY_SPECIFIED (old_node->decl);
+  DECL_VISIBILITY (new_node->decl) = DECL_VISIBILITY (old_node->decl);
+  DECL_DLLIMPORT_P (new_node->decl) = DECL_DLLIMPORT_P (old_node->decl);
+  if (DECL_ONE_ONLY (old_node->decl))
+    make_decl_one_only (new_node->decl, DECL_ASSEMBLER_NAME (new_node->decl));
 
-  /* The function cgraph_function_versioning () will force the new
-     symbol local.  Undo this, and inherit external visability from
+  /* The method cgraph_version_clone_with_body () will force the new
+     symbol local.  Undo this, and inherit external visibility from
      the old node.  */
   new_node->local.local = old_node->local.local;
   new_node->externally_visible = old_node->externally_visible;
--- gcc/testsuite/g++.dg/vect/pr68762-1.cc.jj	2016-08-08 11:35:32.767418789 +0200
+++ gcc/testsuite/g++.dg/vect/pr68762-1.cc	2016-08-08 11:33:49.590711603 +0200
@@ -0,0 +1,26 @@ 
+// PR middle-end/68762
+// { dg-require-effective-target vect_simd_clones }
+// { dg-additional-options "-fopenmp-simd -fno-inline" }
+// { dg-additional-options "-mavx" { target avx_runtime } }
+// { dg-additional-sources "pr68762-2.cc" }
+
+#include "pr68762.h"
+
+double v[64];
+
+double
+bar ()
+{
+  double sum = 0.0;
+  #pragma omp simd reduction (+: sum)
+  for (int i = 0; i < 64; i++)
+    sum += foo (v[i]);
+  return sum;
+}
+
+int
+main ()
+{
+  if (bar () != 0.0)
+    __builtin_abort ();
+}
--- gcc/testsuite/g++.dg/vect/pr68762-2.cc.jj	2016-08-08 11:35:35.815380598 +0200
+++ gcc/testsuite/g++.dg/vect/pr68762-2.cc	2016-08-08 11:35:07.589734268 +0200
@@ -0,0 +1,17 @@ 
+// PR middle-end/68762
+// { dg-do compile }
+
+#include "pr68762.h"
+
+#pragma omp declare simd
+double
+baz (double x)
+{
+  return x;
+}
+
+double
+fn (double x)
+{
+  return foo (x);
+}
--- gcc/testsuite/g++.dg/vect/pr68762.h.jj	2016-08-08 11:35:38.827342858 +0200
+++ gcc/testsuite/g++.dg/vect/pr68762.h	2016-08-08 11:33:00.381328200 +0200
@@ -0,0 +1,11 @@ 
+// PR middle-end/68762
+
+#pragma omp declare simd
+double baz (double x);
+
+#pragma omp declare simd
+inline double
+foo (double d)
+{
+  return baz (d);
+}