2015-11-03 Evgeny Stupachenko <evstupac@gmail.com>

gcc/
	* multiple_target.c (create_dispatcher_calls): Add target check
	on ifunc.
	(create_target_clone): Change assembler name for versioned declarations.
gcc/testsuite/
	* g++.dg/ext/mvc4.C: Add dg-require-ifunc condition.
	* gcc.target/i386/mvc5.c: Ditto.
	* gcc.target/i386/mvc7.c: Add dg-require-ifunc condition and checks on
	resolver.

git-svn-id: svn+ssh://gcc.gnu.org/svn/gcc/trunk@229706 138bc75d-0d04-0410-961f-82ee72b054a4

diff --git a/gcc/ChangeLog b/gcc/ChangeLog
index 947b9a7..97a1101 100644 (file)
--- a/gcc/ChangeLog
+++ b/gcc/ChangeLog
@@ -1,3 +1,9 @@
+2015-11-03  Evgeny Stupachenko  <evstupac@gmail.com>
+
+       * multiple_target.c (create_dispatcher_calls): Add target check
+       on ifunc.
+       (create_target_clone): Change assembler name for versioned declarations.
+
 2015-11-03  Thomas Schwinge  <thomas@codesourcery.com>
            Chung-Lin Tang  <cltang@codesourcery.com>
 

diff --git a/gcc/multiple_target.c b/gcc/multiple_target.c
index 54618d8..8cca281 100644 (file)
--- a/gcc/multiple_target.c
+++ b/gcc/multiple_target.c
@@ -61,12 +61,20 @@ create_dispatcher_calls (struct cgraph_node *node)
          || !DECL_FUNCTION_VERSIONED (decl))
        continue;
 
+      if (!targetm.has_ifunc_p ())
+       {
+         error_at (gimple_location (call),
+                   "the call requires ifunc, which is not"
+                   " supported by this target");
+         break;
+       }
       e_next = e->next_caller;
       idecl = targetm.get_function_versions_dispatcher (decl);
       if (!idecl)
        {
          error_at (gimple_location (call),
                    "default target_clones attribute was not set");
+         break;
        }
       inode = cgraph_node::get (idecl);
       gcc_assert (inode);
@@ -215,6 +223,10 @@ create_target_clone (cgraph_node *node, bool definition, char *name)
     {
       tree new_decl = copy_node (node->decl);
       new_node = cgraph_node::get_create (new_decl);
+      /* Generate a new name for the new version.  */
+      symtab->change_decl_assembler_name (new_node->decl,
+                                         clone_function_name (node->decl,
+                                                              name));
     }
   return new_node;
 }

diff --git a/gcc/testsuite/ChangeLog b/gcc/testsuite/ChangeLog
index c1ac2b0..8b9bf4c 100644 (file)
--- a/gcc/testsuite/ChangeLog
+++ b/gcc/testsuite/ChangeLog
@@ -1,3 +1,10 @@
+2015-11-03  Evgeny Stupachenko  <evstupac@gmail.com>
+
+       * g++.dg/ext/mvc4.C: Add dg-require-ifunc condition.
+       * gcc.target/i386/mvc5.c: Ditto.
+       * gcc.target/i386/mvc7.c: Add dg-require-ifunc condition and checks on
+       resolver.
+
 2015-11-03  Thomas Schwinge  <thomas@codesourcery.com>
 
        * c-c++-common/goacc-gomp/nesting-fail-1.c: Move "atomic" tests

diff --git a/gcc/testsuite/g++.dg/ext/mvc4.C b/gcc/testsuite/g++.dg/ext/mvc4.C
index 98e3502..6e18e56 100644 (file)
--- a/gcc/testsuite/g++.dg/ext/mvc4.C
+++ b/gcc/testsuite/g++.dg/ext/mvc4.C
@@ -1,4 +1,5 @@
 /* { dg-do compile { target i?86-*-* x86_64-*-* } } */
+/* { dg-require-ifunc "" } */
 /* { dg-options "-mavx" } */
 
 #include <immintrin.h>

diff --git a/gcc/testsuite/gcc.target/i386/mvc5.c b/gcc/testsuite/gcc.target/i386/mvc5.c
index 0b1981d..8fea04c 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/mvc5.c
+++ b/gcc/testsuite/gcc.target/i386/mvc5.c
@@ -1,4 +1,5 @@
 /* { dg-do compile } */
+/* { dg-require-ifunc "" } */
 /* { dg-options "-fno-inline" } */
 /* { dg-final { scan-assembler-times "foo.ifunc" 6 } } */
 

diff --git a/gcc/testsuite/gcc.target/i386/mvc7.c b/gcc/testsuite/gcc.target/i386/mvc7.c
index efc4b69..9a9d7a3 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/mvc7.c
+++ b/gcc/testsuite/gcc.target/i386/mvc7.c
@@ -1,4 +1,8 @@
 /* { dg-do compile } */
+/* { dg-require-ifunc "" } */
+/* { dg-final { scan-assembler "foo.resolver" } } */
+/* { dg-final { scan-assembler "avx" } } */
+/* { dg-final { scan-assembler "slm" } } */
 /* { dg-final { scan-assembler-times "foo.ifunc" 4 } } */
 
 __attribute__((target_clones("avx","default","arch=slm","arch=core-avx2")))