public inbox for gcc-bugs@sourceware.org
help / color / mirror / Atom feed
* [Bug c/61878] New: Missing intrinsic functions in avx512intrin.h
@ 2014-07-22 13:32 agner at agner dot org
  2014-07-22 18:35 ` [Bug target/61878] " ubizjak at gmail dot com
                   ` (3 more replies)
  0 siblings, 4 replies; 5+ messages in thread
From: agner at agner dot org @ 2014-07-22 13:32 UTC (permalink / raw)
  To: gcc-bugs

https://gcc.gnu.org/bugzilla/show_bug.cgi?id=61878

            Bug ID: 61878
           Summary: Missing intrinsic functions in avx512intrin.h
           Product: gcc
           Version: 4.10.0
            Status: UNCONFIRMED
          Severity: normal
          Priority: P3
         Component: c
          Assignee: unassigned at gcc dot gnu.org
          Reporter: agner at agner dot org

A few compare functions are missing in avx512intrin.h, e.g.
_mm512_cmpgt_epu32_mask and _mm512_cmpgt_epu64_mask

All intrinsic functions for typecasting are also missing. Please add these
functions, as they are indispensable.

See https://software.intel.com/en-us/node/513903 and
https://software.intel.com/sites/landingpage/IntrinsicsGuide/ for documentation
of these functions.

Definitions copied from Intel's zmmintrin.h:

/* Conversion from one type to another, no change in value. */

extern __m512  __ICL_INTRINCC _mm512_castpd_ps(__m512d);
extern __m512i __ICL_INTRINCC _mm512_castpd_si512(__m512d);
extern __m512d __ICL_INTRINCC _mm512_castps_pd(__m512);
extern __m512i __ICL_INTRINCC _mm512_castps_si512(__m512);
extern __m512  __ICL_INTRINCC _mm512_castsi512_ps(__m512i);
extern __m512d __ICL_INTRINCC _mm512_castsi512_pd(__m512i);

* Casts from a larger type to a smaller type.
 */
extern __m128d __ICL_INTRINCC _mm512_castpd512_pd128(__m512d);
extern __m128  __ICL_INTRINCC _mm512_castps512_ps128(__m512);
extern __m128i __ICL_INTRINCC _mm512_castsi512_si128(__m512i);
extern __m256d __ICL_INTRINCC _mm512_castpd512_pd256(__m512d);
extern __m256  __ICL_INTRINCC _mm512_castps512_ps256(__m512);
extern __m256i __ICL_INTRINCC _mm512_castsi512_si256(__m512i);

/*
 * Casts from a smaller type to a larger type.
 * Upper elements of the result are undefined.
 */
extern __m512d __ICL_INTRINCC _mm512_castpd128_pd512(__m128d);
extern __m512  __ICL_INTRINCC _mm512_castps128_ps512(__m128);
extern __m512i __ICL_INTRINCC _mm512_castsi128_si512(__m128i);
extern __m512d __ICL_INTRINCC _mm512_castpd256_pd512(__m256d);
extern __m512  __ICL_INTRINCC _mm512_castps256_ps512(__m256);
extern __m512i __ICL_INTRINCC _mm512_castsi256_si512(__m256i);


^ permalink raw reply	[flat|nested] 5+ messages in thread

* [Bug target/61878] Missing intrinsic functions in avx512intrin.h
  2014-07-22 13:32 [Bug c/61878] New: Missing intrinsic functions in avx512intrin.h agner at agner dot org
@ 2014-07-22 18:35 ` ubizjak at gmail dot com
  2014-08-15 12:48 ` tocarip at gcc dot gnu.org
                   ` (2 subsequent siblings)
  3 siblings, 0 replies; 5+ messages in thread
From: ubizjak at gmail dot com @ 2014-07-22 18:35 UTC (permalink / raw)
  To: gcc-bugs

https://gcc.gnu.org/bugzilla/show_bug.cgi?id=61878

Uroš Bizjak <ubizjak at gmail dot com> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
             Status|UNCONFIRMED                 |NEW
   Last reconfirmed|                            |2014-07-22
                 CC|                            |kyukhin at gcc dot gnu.org
   Target Milestone|---                         |4.9.2
     Ever confirmed|0                           |1

--- Comment #1 from Uroš Bizjak <ubizjak at gmail dot com> ---
Confirmed.
>From gcc-bugs-return-456936-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org Tue Jul 22 18:40:08 2014
Return-Path: <gcc-bugs-return-456936-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org>
Delivered-To: listarch-gcc-bugs@gcc.gnu.org
Received: (qmail 12696 invoked by alias); 22 Jul 2014 18:40:08 -0000
Mailing-List: contact gcc-bugs-help@gcc.gnu.org; run by ezmlm
Precedence: bulk
List-Id: <gcc-bugs.gcc.gnu.org>
List-Archive: <http://gcc.gnu.org/ml/gcc-bugs/>
List-Post: <mailto:gcc-bugs@gcc.gnu.org>
List-Help: <mailto:gcc-bugs-help@gcc.gnu.org>
Sender: gcc-bugs-owner@gcc.gnu.org
Delivered-To: mailing list gcc-bugs@gcc.gnu.org
Received: (qmail 12654 invoked by uid 48); 22 Jul 2014 18:40:04 -0000
From: "mpolacek at gcc dot gnu.org" <gcc-bugzilla@gcc.gnu.org>
To: gcc-bugs@gcc.gnu.org
Subject: [Bug c/61861] Incorrect column number for -Wdiscarded-qualifiers
Date: Tue, 22 Jul 2014 18:40:00 -0000
X-Bugzilla-Reason: CC
X-Bugzilla-Type: changed
X-Bugzilla-Watch-Reason: None
X-Bugzilla-Product: gcc
X-Bugzilla-Component: c
X-Bugzilla-Version: 4.10.0
X-Bugzilla-Keywords:
X-Bugzilla-Severity: normal
X-Bugzilla-Who: mpolacek at gcc dot gnu.org
X-Bugzilla-Status: ASSIGNED
X-Bugzilla-Priority: P3
X-Bugzilla-Assigned-To: mpolacek at gcc dot gnu.org
X-Bugzilla-Target-Milestone: 4.10.0
X-Bugzilla-Flags:
X-Bugzilla-Changed-Fields:
Message-ID: <bug-61861-4-i9HaXP7SdM@http.gcc.gnu.org/bugzilla/>
In-Reply-To: <bug-61861-4@http.gcc.gnu.org/bugzilla/>
References: <bug-61861-4@http.gcc.gnu.org/bugzilla/>
Content-Type: text/plain; charset="UTF-8"
Content-Transfer-Encoding: 7bit
X-Bugzilla-URL: http://gcc.gnu.org/bugzilla/
Auto-Submitted: auto-generated
MIME-Version: 1.0
X-SW-Source: 2014-07/txt/msg01527.txt.bz2
Content-length: 164

https://gcc.gnu.org/bugzilla/show_bug.cgi?ida861

--- Comment #3 from Marek Polacek <mpolacek at gcc dot gnu.org> ---
The same for __DATE__, __TIME__, __LINE__.


^ permalink raw reply	[flat|nested] 5+ messages in thread

* [Bug target/61878] Missing intrinsic functions in avx512intrin.h
  2014-07-22 13:32 [Bug c/61878] New: Missing intrinsic functions in avx512intrin.h agner at agner dot org
  2014-07-22 18:35 ` [Bug target/61878] " ubizjak at gmail dot com
@ 2014-08-15 12:48 ` tocarip at gcc dot gnu.org
  2014-10-30 10:39 ` jakub at gcc dot gnu.org
  2014-12-01 12:30 ` rguenth at gcc dot gnu.org
  3 siblings, 0 replies; 5+ messages in thread
From: tocarip at gcc dot gnu.org @ 2014-08-15 12:48 UTC (permalink / raw)
  To: gcc-bugs

https://gcc.gnu.org/bugzilla/show_bug.cgi?id=61878

--- Comment #2 from tocarip at gcc dot gnu.org ---
Author: tocarip
Date: Fri Aug 15 12:47:41 2014
New Revision: 214019

URL: https://gcc.gnu.org/viewcvs?rev=214019&root=gcc&view=rev
Log:
    gcc/

    PR target/61878
    * config/i386/avx512fintrin.h (_mm512_mask_cmpge_epi32_mask): New.
    (_mm512_mask_cmpge_epu32_mask): Ditto.
    (_mm512_cmpge_epu32_mask): Ditto.
    (_mm512_mask_cmpge_epi64_mask): Ditto.
    (_mm512_cmpge_epi64_mask): Ditto.
    (_mm512_mask_cmpge_epu64_mask): Ditto.
    (_mm512_cmpge_epu64_mask): Ditto.
    (_mm512_mask_cmple_epi32_mask): Ditto.
    (_mm512_cmple_epi32_mask): Ditto.
    (_mm512_mask_cmple_epu32_mask): Ditto.
    (_mm512_cmple_epu32_mask): Ditto.
    (_mm512_mask_cmple_epi64_mask): Ditto.
    (_mm512_cmple_epi64_mask): Ditto.
    (_mm512_mask_cmple_epu64_mask): Ditto.
    (_mm512_cmple_epu64_mask): Ditto.
    (_mm512_mask_cmplt_epi32_mask): Ditto.
    (_mm512_cmplt_epi32_mask): Ditto.
    (_mm512_mask_cmplt_epu32_mask): Ditto.
    (_mm512_cmplt_epu32_mask): Ditto.
    (_mm512_mask_cmplt_epi64_mask): Ditto.
    (_mm512_cmplt_epi64_mask): Ditto.
    (_mm512_mask_cmplt_epu64_mask): Ditto.
    (_mm512_cmplt_epu64_mask): Ditto.
    (_mm512_mask_cmpneq_epi32_mask): Ditto.
    (_mm512_mask_cmpneq_epu32_mask): Ditto.
    (_mm512_cmpneq_epu32_mask): Ditto.
    (_mm512_mask_cmpneq_epi64_mask): Ditto.
    (_mm512_cmpneq_epi64_mask): Ditto.
    (_mm512_mask_cmpneq_epu64_mask): Ditto.
    (_mm512_cmpneq_epu64_mask): Ditto.
    (_mm512_castpd_ps): Ditto.
    (_mm512_castpd_si512): Ditto.
    (_mm512_castps_pd): Ditto.
    (_mm512_castps_si512): Ditto.
    (_mm512_castsi512_ps): Ditto.
    (_mm512_castsi512_pd): Ditto.
    (_mm512_castpd512_pd128): Ditto.
    (_mm512_castps512_ps128): Ditto.
    (_mm512_castsi512_si128): Ditto.
    (_mm512_castpd512_pd256): Ditto.
    (_mm512_castps512_ps256): Ditto.
    (_mm512_castsi512_si256): Ditto.
    (_mm512_castpd128_pd512): Ditto.
    (_mm512_castps128_ps512): Ditto.
    (_mm512_castsi128_si512): Ditto.
    (_mm512_castpd256_pd512): Ditto.
    (_mm512_castps256_ps512): Ditto.
    (_mm512_castsi256_si512): Ditto.
    (_mm512_cmpeq_epu32_mask): Ditto.
    (_mm512_mask_cmpeq_epu32_mask): Ditto.
    (_mm512_mask_cmpeq_epu64_mask): Ditto.
    (_mm512_cmpeq_epu64_mask): Ditto.
    (_mm512_cmpgt_epu32_mask): Ditto.
    (_mm512_mask_cmpgt_epu32_mask): Ditto.
    (_mm512_mask_cmpgt_epu64_mask): Ditto.
    (_mm512_cmpgt_epu64_mask): Ditto.
    * config/i386/i386-builtin-types.def: Add V16SF_FTYPE_V8SF,
    V16SI_FTYPE_V8SI, V16SI_FTYPE_V4SI, V8DF_FTYPE_V2DF.
    * config/i386/i386.c (enum ix86_builtins): Add
    IX86_BUILTIN_SI512_SI256, IX86_BUILTIN_PD512_PD256,
    IX86_BUILTIN_PS512_PS256, IX86_BUILTIN_SI512_SI,
    IX86_BUILTIN_PD512_PD, IX86_BUILTIN_PS512_PS.
    (bdesc_args): Add __builtin_ia32_si512_256si,
    __builtin_ia32_ps512_256ps, __builtin_ia32_pd512_256pd,
    __builtin_ia32_si512_si, __builtin_ia32_ps512_ps,
    __builtin_ia32_pd512_pd.
    (ix86_expand_args_builtin): Handle new FTYPEs.
    * config/i386/sse.md (castmode): Add 512-bit modes.
    (AVX512MODE2P): New.
    (avx512f_<castmode><avxsizesuffix>_<castmode): New.
    (avx512f_<castmode><avxsizesuffix>_256<castmode): Ditto.


    gcc/testsuite/

    PR target/61878
    * gcc.target/i386/avx512f-typecast-1.c: New test.
    * gcc.target/i386/avx512f-vpcmpequd-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpequd-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpequq-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpequq-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpged-1.c: Add new intrinsic.
    * gcc.target/i386/avx512f-vpcmpged-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpgeq-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpgeq-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpgeud-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpgeud-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpgeuq-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpgeuq-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpgtud-1.c: New test.
    * gcc.target/i386/avx512f-vpcmpgtud-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpgtuq-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpgtuq-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpled-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpled-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpleq-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpleq-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpleud-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpleud-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpleuq-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpleuq-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpltd-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpltd-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpltq-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpltq-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpltud-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpltud-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpltuq-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpltuq-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpneqd-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpneqd-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpneqq-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpneqq-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpnequd-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpnequd-2.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpnequq-1.c: Ditto.
    * gcc.target/i386/avx512f-vpcmpnequq-2.c: Ditto.

Added:
    trunk/gcc/testsuite/gcc.target/i386/avx512f-typecast-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpequd-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpequd-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpequq-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpequq-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpgtud-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpgtud-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpgtuq-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpgtuq-2.c
Modified:
    trunk/gcc/ChangeLog
    trunk/gcc/config/i386/avx512fintrin.h
    trunk/gcc/config/i386/i386-builtin-types.def
    trunk/gcc/config/i386/i386.c
    trunk/gcc/config/i386/sse.md
    trunk/gcc/testsuite/ChangeLog
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpged-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpged-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpgeq-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpgeq-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpgeud-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpgeud-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpgeuq-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpgeuq-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpled-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpled-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpleq-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpleq-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpleud-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpleud-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpleuq-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpleuq-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpltd-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpltd-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpltq-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpltq-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpltud-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpltud-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpltuq-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpltuq-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpneqd-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpneqd-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpneqq-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpneqq-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpnequd-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpnequd-2.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpnequq-1.c
    trunk/gcc/testsuite/gcc.target/i386/avx512f-vpcmpnequq-2.c


^ permalink raw reply	[flat|nested] 5+ messages in thread

* [Bug target/61878] Missing intrinsic functions in avx512intrin.h
  2014-07-22 13:32 [Bug c/61878] New: Missing intrinsic functions in avx512intrin.h agner at agner dot org
  2014-07-22 18:35 ` [Bug target/61878] " ubizjak at gmail dot com
  2014-08-15 12:48 ` tocarip at gcc dot gnu.org
@ 2014-10-30 10:39 ` jakub at gcc dot gnu.org
  2014-12-01 12:30 ` rguenth at gcc dot gnu.org
  3 siblings, 0 replies; 5+ messages in thread
From: jakub at gcc dot gnu.org @ 2014-10-30 10:39 UTC (permalink / raw)
  To: gcc-bugs

https://gcc.gnu.org/bugzilla/show_bug.cgi?id=61878

Jakub Jelinek <jakub at gcc dot gnu.org> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
   Target Milestone|4.9.2                       |4.9.3

--- Comment #3 from Jakub Jelinek <jakub at gcc dot gnu.org> ---
GCC 4.9.2 has been released.


^ permalink raw reply	[flat|nested] 5+ messages in thread

* [Bug target/61878] Missing intrinsic functions in avx512intrin.h
  2014-07-22 13:32 [Bug c/61878] New: Missing intrinsic functions in avx512intrin.h agner at agner dot org
                   ` (2 preceding siblings ...)
  2014-10-30 10:39 ` jakub at gcc dot gnu.org
@ 2014-12-01 12:30 ` rguenth at gcc dot gnu.org
  3 siblings, 0 replies; 5+ messages in thread
From: rguenth at gcc dot gnu.org @ 2014-12-01 12:30 UTC (permalink / raw)
  To: gcc-bugs

https://gcc.gnu.org/bugzilla/show_bug.cgi?id=61878

Richard Biener <rguenth at gcc dot gnu.org> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
             Status|NEW                         |RESOLVED
         Resolution|---                         |FIXED

--- Comment #4 from Richard Biener <rguenth at gcc dot gnu.org> ---
Fixed.


^ permalink raw reply	[flat|nested] 5+ messages in thread

end of thread, other threads:[~2014-12-01 12:30 UTC | newest]

Thread overview: 5+ messages (download: mbox.gz / follow: Atom feed)
-- links below jump to the message on this page --
2014-07-22 13:32 [Bug c/61878] New: Missing intrinsic functions in avx512intrin.h agner at agner dot org
2014-07-22 18:35 ` [Bug target/61878] " ubizjak at gmail dot com
2014-08-15 12:48 ` tocarip at gcc dot gnu.org
2014-10-30 10:39 ` jakub at gcc dot gnu.org
2014-12-01 12:30 ` rguenth at gcc dot gnu.org

This is a public inbox, see mirroring instructions
for how to clone and mirror all data and code used for this inbox;
as well as URLs for read-only IMAP folder(s) and NNTP newsgroup(s).