[Date Prev][Date Next][Thread Prev][Thread Next][Date Index][Thread Index]
Re: [Qemu-devel] [PULL 00/11] Misc changes for 2016-06-06
From: |
Dr. David Alan Gilbert |
Subject: |
Re: [Qemu-devel] [PULL 00/11] Misc changes for 2016-06-06 |
Date: |
Tue, 7 Jun 2016 10:51:02 +0100 |
User-agent: |
Mutt/1.6.1 (2016-04-27) |
* Peter Maydell (address@hidden) wrote:
> On 6 June 2016 at 20:22, Dr. David Alan Gilbert <address@hidden> wrote:
> > Sigh I see; so the configure test is run with a different set of compiler
> > options than the main compiles? How is any configure test supposed to
> > check that it's got a sane configuration?
>
> I wasn't quite right -- we do run configure tests with ccache, we just
> force it to not read the cache. So I think your problem is just that
> your configure test doesn't fail when run under ccache, even though the
> main cutils.c compile does:
>
> $ cat /tmp/zz9.c
> #pragma GCC push_options
> #pragma GCC target("avx2")
> #include <cpuid.h>
> #include <immintrin.h>
>
> static int bar(void *a) {
> return _mm256_movemask_epi8(_mm256_cmpeq_epi8(*(__m256i *)a,
> (__m256i){0}));
> }
> static void *bar_ifunc(void) {return (void*) bar;}
> int foo(void *a) __attribute__((ifunc("bar_ifunc")));
> int main(int argc, char *argv[]) { return foo(argv[0]);}
> $ ccache gcc -g -Wall -o /tmp/zz9 /tmp/zz9.c
>
> This seems to be because to get the compile failure you have
> to be doing a .c to .o compile:
<snip>
> The difference is because ccache doesn't intercept .c-to-executable
> compiles, so they go straight to real gcc and don't have -save-temps,
> but it does intercept a .c-to-.o compile, which thus does get -save-temps
> and so hits the gcc bug.
>
> TLDR: if you make your configure test use compile_object it ought to
> correctly detect that AVX2 doesn't work for this gcc+ccache combo.
Does the following (on top of the existing patch) fix it for you:
diff --git a/configure b/configure
index 6449e65..65e603c 100755
--- a/configure
+++ b/configure
@@ -1793,8 +1793,8 @@ static void *bar_ifunc(void) {return (void*) bar;}
int foo(void *a) __attribute__((ifunc("bar_ifunc")));
int main(int argc, char *argv[]) { return foo(argv[0]);}
EOF
-if compile_prog "" ; then
- if readelf --syms $TMPE |grep "IFUNC.*foo" >/dev/null 2>&1; then
+if compile_object "" ; then
+ if readelf --syms $TMPO |grep "IFUNC.*foo" >/dev/null 2>&1; then
avx2_opt="yes"
fi
fi
Dave
>
> thanks
> -- PMM
--
Dr. David Alan Gilbert / address@hidden / Manchester, UK
- [Qemu-devel] [PULL 01/11] tests: Rename tests/Makefile to tests/Makefile.include, (continued)
- [Qemu-devel] [PULL 01/11] tests: Rename tests/Makefile to tests/Makefile.include, Paolo Bonzini, 2016/06/06
- [Qemu-devel] [PULL 09/11] vnc: list the 'to' parameter of '-vnc' in the qemu man page, Paolo Bonzini, 2016/06/06
- [Qemu-devel] [PULL 10/11] Make avx2 configure test work with -O2, Paolo Bonzini, 2016/06/06
- [Qemu-devel] [PULL 07/11] Makefile: Derive "PKGVERSION" from "git describe" by default, Paolo Bonzini, 2016/06/06
- [Qemu-devel] [PULL 06/11] Makefile: Add a "FORCE" target, Paolo Bonzini, 2016/06/06
- [Qemu-devel] [PULL 11/11] avx2 configure: Use primitives in test, Paolo Bonzini, 2016/06/06
- [Qemu-devel] [PULL 08/11] scsi-disk: add missing break, Paolo Bonzini, 2016/06/06
- Re: [Qemu-devel] [PULL 00/11] Misc changes for 2016-06-06, Peter Maydell, 2016/06/06