Bug 104239 - [12 Regression] immintrin.h or x86gprintrin.h headers can't be included
Summary: [12 Regression] immintrin.h or x86gprintrin.h headers can't be included
Status: RESOLVED FIXED
Alias: None
Product: gcc
Classification: Unclassified
Component: target (show other bugs)
Version: 12.0
: P1 normal
Target Milestone: 12.0
Assignee: Jakub Jelinek
URL:
Keywords:
Depends on:
Blocks:
 
Reported: 2022-01-26 12:40 UTC by Jakub Jelinek
Modified: 2022-01-27 11:00 UTC (History)
4 users (show)

See Also:
Host:
Target: powerpc*-*-*
Build:
Known to work:
Known to fail:
Last reconfirmed: 2022-01-26 00:00:00


Attachments
gcc12-pr104239.patch (629 bytes, patch)
2022-01-26 12:45 UTC, Jakub Jelinek
Details | Diff

Note You need to log in before you can comment on or make changes to this bug.
Description Jakub Jelinek 2022-01-26 12:40:17 UTC
Code like:
#if __has_include(<immintrin.h>)
#include <immintrin.h>
#endif
regressed in GCC 12 on powerpc*,
# error "Never use <bmiintrin.h> directly; include <x86intrin.h> instead."
Comment 1 Jakub Jelinek 2022-01-26 12:45:35 UTC
Created attachment 52291 [details]
gcc12-pr104239.patch

Untested fix.
Comment 2 Marc Glisse 2022-01-26 20:48:54 UTC
Thanks for fixing that bug, but don't you still have issues with NO_WARN_X86_INTRINSICS if you rely on __has_include for immintrin.h?
Comment 3 GCC Commits 2022-01-26 21:08:12 UTC
The master branch has been updated by Jakub Jelinek <jakub@gcc.gnu.org>:

https://gcc.gnu.org/g:2bf8da684b712a16c67f3defc0dd97f175f8f4ad

commit r12-6884-g2bf8da684b712a16c67f3defc0dd97f175f8f4ad
Author: Jakub Jelinek <jakub@redhat.com>
Date:   Wed Jan 26 22:07:29 2022 +0100

    rs6000: Fix up #include <immintrin.h> or <x86gprintrin.h> [PR104239]
    
    r12-4717-g7d37abedf58d66 added immintrin.h and x86gprintrin.h headers
    to rs6000, these headers are on x86 standalone headers that various
    programs include directly rather than including them through
    <x86intrin.h>.
    Unfortunately, for that change the bmiintrin.h and bmi2intrin.h
    headers haven't been adjusted, so the effect is that if one includes them
    (without including also x86intrin.h first) #error will trigger.
    Furthermore, when including such headers conditionally as some real-world
    packages do, this means a regression.
    
    The following patch fixes it and matches what the x86 bmi{,2}intrin.h
    headers do.
    
    2022-01-26  Jakub Jelinek  <jakub@redhat.com>
    
            PR target/104239
            * config/rs6000/bmiintrin.h: Test _X86GPRINTRIN_H_INCLUDED instead of
            _X86INTRIN_H_INCLUDED and adjust #error wording.
            * config/rs6000/bmi2intrin.h: Likewise.
    
            * gcc.target/powerpc/pr104239-1.c: New test.
            * gcc.target/powerpc/pr104239-2.c: New test.
Comment 4 GCC Commits 2022-01-26 21:56:25 UTC
The master branch has been updated by Jakub Jelinek <jakub@gcc.gnu.org>:

https://gcc.gnu.org/g:fd5b0488ad5e4f29b65238e06a2d65b7de120235

commit r12-6885-gfd5b0488ad5e4f29b65238e06a2d65b7de120235
Author: Jakub Jelinek <jakub@redhat.com>
Date:   Wed Jan 26 22:55:11 2022 +0100

    rs6000: Fix up *intrin.h for C89 [PR104239]
    
    When writing testcases for the previously posted patch, I have noticed
    that 3 of the headers aren't valid C89 (I didn't have any dg-options
    so -ansi -pedantic-errors was implied and these errors were reported).
    
    The following patch fixes those, ok for trunk?
    
    Note, as can be seen even in this patch, seems older rs6000/*intrin.h
    headers uglify not just argument names (__A instead of A etc.), but also
    automatic variable names and other local identifiers, while e.g. emmintrin.h
    or bmi2intrin.h clearly uglify only the argument names and not local
    variables.  I think that should be fixed but don't have time for that myself
    (libstdc++ or e.g. the x86 headers uglify everything; this is so that one
    can
     #define result a + b
     #include <x86intrin.h>
    etc.).
    
    2022-01-26  Jakub Jelinek  <jakub@redhat.com>
    
            PR target/104239
            * config/rs6000/emmintrin.h (_mm_sad_epu8): Use __asm__ instead of
            asm.
            * config/rs6000/smmintrin.h (_mm_minpos_epu16): Declare iterator
            before for loop instead of for init clause.
            * config/rs6000/bmi2intrin.h (_pext_u64): Likewise.
    
            * gcc.target/powerpc/pr104239-3.c: New test.
Comment 5 Jakub Jelinek 2022-01-27 11:00:10 UTC
Fixed.