Home | History | Annotate | Line # | Download | only in i386
fma4intrin.h revision 1.1.1.1.4.2 
      1  1.1.1.1.4.2  yamt /* Copyright (C) 2007, 2008, 2009 Free Software Foundation, Inc.
      2  1.1.1.1.4.2  yamt 
      3  1.1.1.1.4.2  yamt    This file is part of GCC.
      4  1.1.1.1.4.2  yamt 
      5  1.1.1.1.4.2  yamt    GCC is free software; you can redistribute it and/or modify
      6  1.1.1.1.4.2  yamt    it under the terms of the GNU General Public License as published by
      7  1.1.1.1.4.2  yamt    the Free Software Foundation; either version 3, or (at your option)
      8  1.1.1.1.4.2  yamt    any later version.
      9  1.1.1.1.4.2  yamt 
     10  1.1.1.1.4.2  yamt    GCC is distributed in the hope that it will be useful,
     11  1.1.1.1.4.2  yamt    but WITHOUT ANY WARRANTY; without even the implied warranty of
     12  1.1.1.1.4.2  yamt    MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
     13  1.1.1.1.4.2  yamt    GNU General Public License for more details.
     14  1.1.1.1.4.2  yamt 
     15  1.1.1.1.4.2  yamt    Under Section 7 of GPL version 3, you are granted additional
     16  1.1.1.1.4.2  yamt    permissions described in the GCC Runtime Library Exception, version
     17  1.1.1.1.4.2  yamt    3.1, as published by the Free Software Foundation.
     18  1.1.1.1.4.2  yamt 
     19  1.1.1.1.4.2  yamt    You should have received a copy of the GNU General Public License and
     20  1.1.1.1.4.2  yamt    a copy of the GCC Runtime Library Exception along with this program;
     21  1.1.1.1.4.2  yamt    see the files COPYING3 and COPYING.RUNTIME respectively.  If not, see
     22  1.1.1.1.4.2  yamt    <http://www.gnu.org/licenses/>.  */
     23  1.1.1.1.4.2  yamt 
     24  1.1.1.1.4.2  yamt #ifndef _X86INTRIN_H_INCLUDED
     25  1.1.1.1.4.2  yamt # error "Never use <fma4intrin.h> directly; include <x86intrin.h> instead."
     26  1.1.1.1.4.2  yamt #endif
     27  1.1.1.1.4.2  yamt 
     28  1.1.1.1.4.2  yamt #ifndef _FMA4INTRIN_H_INCLUDED
     29  1.1.1.1.4.2  yamt #define _FMA4INTRIN_H_INCLUDED
     30  1.1.1.1.4.2  yamt 
     31  1.1.1.1.4.2  yamt #ifndef __FMA4__
     32  1.1.1.1.4.2  yamt # error "FMA4 instruction set not enabled"
     33  1.1.1.1.4.2  yamt #else
     34  1.1.1.1.4.2  yamt 
     35  1.1.1.1.4.2  yamt /* We need definitions from the SSE4A, SSE3, SSE2 and SSE header files.  */
     36  1.1.1.1.4.2  yamt #include <ammintrin.h>
     37  1.1.1.1.4.2  yamt 
     38  1.1.1.1.4.2  yamt /* 128b Floating point multiply/add type instructions.  */
     39  1.1.1.1.4.2  yamt extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
     40  1.1.1.1.4.2  yamt _mm_macc_ps (__m128 __A, __m128 __B, __m128 __C)
     41  1.1.1.1.4.2  yamt {
     42  1.1.1.1.4.2  yamt   return (__m128) __builtin_ia32_vfmaddps ((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
     43  1.1.1.1.4.2  yamt }
     44  1.1.1.1.4.2  yamt 
     45  1.1.1.1.4.2  yamt extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
     46  1.1.1.1.4.2  yamt _mm_macc_pd (__m128d __A, __m128d __B, __m128d __C)
     47  1.1.1.1.4.2  yamt {
     48  1.1.1.1.4.2  yamt   return (__m128d) __builtin_ia32_vfmaddpd ((__v2df)__A, (__v2df)__B, (__v2df)__C);
     49  1.1.1.1.4.2  yamt }
     50  1.1.1.1.4.2  yamt 
     51  1.1.1.1.4.2  yamt extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
     52  1.1.1.1.4.2  yamt _mm_macc_ss (__m128 __A, __m128 __B, __m128 __C)
     53  1.1.1.1.4.2  yamt {
     54  1.1.1.1.4.2  yamt   return (__m128) __builtin_ia32_vfmaddss ((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
     55  1.1.1.1.4.2  yamt }
     56  1.1.1.1.4.2  yamt 
     57  1.1.1.1.4.2  yamt extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
     58  1.1.1.1.4.2  yamt _mm_macc_sd (__m128d __A, __m128d __B, __m128d __C)
     59  1.1.1.1.4.2  yamt {
     60  1.1.1.1.4.2  yamt   return (__m128d) __builtin_ia32_vfmaddsd ((__v2df)__A, (__v2df)__B, (__v2df)__C);
     61  1.1.1.1.4.2  yamt }
     62  1.1.1.1.4.2  yamt 
     63  1.1.1.1.4.2  yamt extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
     64  1.1.1.1.4.2  yamt _mm_msub_ps (__m128 __A, __m128 __B, __m128 __C)
     65  1.1.1.1.4.2  yamt 
     66  1.1.1.1.4.2  yamt {
     67  1.1.1.1.4.2  yamt   return (__m128) __builtin_ia32_vfmsubps ((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
     68  1.1.1.1.4.2  yamt }
     69  1.1.1.1.4.2  yamt 
     70  1.1.1.1.4.2  yamt extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
     71  1.1.1.1.4.2  yamt _mm_msub_pd (__m128d __A, __m128d __B, __m128d __C)
     72  1.1.1.1.4.2  yamt {
     73  1.1.1.1.4.2  yamt   return (__m128d) __builtin_ia32_vfmsubpd ((__v2df)__A, (__v2df)__B, (__v2df)__C);
     74  1.1.1.1.4.2  yamt }
     75  1.1.1.1.4.2  yamt 
     76  1.1.1.1.4.2  yamt extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
     77  1.1.1.1.4.2  yamt _mm_msub_ss (__m128 __A, __m128 __B, __m128 __C)
     78  1.1.1.1.4.2  yamt {
     79  1.1.1.1.4.2  yamt   return (__m128) __builtin_ia32_vfmsubss ((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
     80  1.1.1.1.4.2  yamt }
     81  1.1.1.1.4.2  yamt 
     82  1.1.1.1.4.2  yamt extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
     83  1.1.1.1.4.2  yamt _mm_msub_sd (__m128d __A, __m128d __B, __m128d __C)
     84  1.1.1.1.4.2  yamt {
     85  1.1.1.1.4.2  yamt   return (__m128d) __builtin_ia32_vfmsubsd ((__v2df)__A, (__v2df)__B, (__v2df)__C);
     86  1.1.1.1.4.2  yamt }
     87  1.1.1.1.4.2  yamt 
     88  1.1.1.1.4.2  yamt extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
     89  1.1.1.1.4.2  yamt _mm_nmacc_ps (__m128 __A, __m128 __B, __m128 __C)
     90  1.1.1.1.4.2  yamt {
     91  1.1.1.1.4.2  yamt   return (__m128) __builtin_ia32_vfnmaddps ((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
     92  1.1.1.1.4.2  yamt }
     93  1.1.1.1.4.2  yamt 
     94  1.1.1.1.4.2  yamt extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
     95  1.1.1.1.4.2  yamt _mm_nmacc_pd (__m128d __A, __m128d __B, __m128d __C)
     96  1.1.1.1.4.2  yamt {
     97  1.1.1.1.4.2  yamt   return (__m128d) __builtin_ia32_vfnmaddpd ((__v2df)__A, (__v2df)__B, (__v2df)__C);
     98  1.1.1.1.4.2  yamt }
     99  1.1.1.1.4.2  yamt 
    100  1.1.1.1.4.2  yamt extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    101  1.1.1.1.4.2  yamt _mm_nmacc_ss (__m128 __A, __m128 __B, __m128 __C)
    102  1.1.1.1.4.2  yamt {
    103  1.1.1.1.4.2  yamt   return (__m128) __builtin_ia32_vfnmaddss ((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
    104  1.1.1.1.4.2  yamt }
    105  1.1.1.1.4.2  yamt 
    106  1.1.1.1.4.2  yamt extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    107  1.1.1.1.4.2  yamt _mm_nmacc_sd (__m128d __A, __m128d __B, __m128d __C)
    108  1.1.1.1.4.2  yamt {
    109  1.1.1.1.4.2  yamt   return (__m128d) __builtin_ia32_vfnmaddsd ((__v2df)__A, (__v2df)__B, (__v2df)__C);
    110  1.1.1.1.4.2  yamt }
    111  1.1.1.1.4.2  yamt 
    112  1.1.1.1.4.2  yamt extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    113  1.1.1.1.4.2  yamt _mm_nmsub_ps (__m128 __A, __m128 __B, __m128 __C)
    114  1.1.1.1.4.2  yamt {
    115  1.1.1.1.4.2  yamt   return (__m128) __builtin_ia32_vfnmsubps ((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
    116  1.1.1.1.4.2  yamt }
    117  1.1.1.1.4.2  yamt 
    118  1.1.1.1.4.2  yamt extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    119  1.1.1.1.4.2  yamt _mm_nmsub_pd (__m128d __A, __m128d __B, __m128d __C)
    120  1.1.1.1.4.2  yamt {
    121  1.1.1.1.4.2  yamt   return (__m128d) __builtin_ia32_vfnmsubpd ((__v2df)__A, (__v2df)__B, (__v2df)__C);
    122  1.1.1.1.4.2  yamt }
    123  1.1.1.1.4.2  yamt 
    124  1.1.1.1.4.2  yamt extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    125  1.1.1.1.4.2  yamt _mm_nmsub_ss (__m128 __A, __m128 __B, __m128 __C)
    126  1.1.1.1.4.2  yamt {
    127  1.1.1.1.4.2  yamt   return (__m128) __builtin_ia32_vfnmsubss ((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
    128  1.1.1.1.4.2  yamt }
    129  1.1.1.1.4.2  yamt 
    130  1.1.1.1.4.2  yamt extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    131  1.1.1.1.4.2  yamt _mm_nmsub_sd (__m128d __A, __m128d __B, __m128d __C)
    132  1.1.1.1.4.2  yamt {
    133  1.1.1.1.4.2  yamt   return (__m128d) __builtin_ia32_vfnmsubsd ((__v2df)__A, (__v2df)__B, (__v2df)__C);
    134  1.1.1.1.4.2  yamt }
    135  1.1.1.1.4.2  yamt 
    136  1.1.1.1.4.2  yamt extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    137  1.1.1.1.4.2  yamt _mm_maddsub_ps (__m128 __A, __m128 __B, __m128 __C)
    138  1.1.1.1.4.2  yamt {
    139  1.1.1.1.4.2  yamt   return (__m128) __builtin_ia32_vfmaddsubps ((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
    140  1.1.1.1.4.2  yamt }
    141  1.1.1.1.4.2  yamt 
    142  1.1.1.1.4.2  yamt extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    143  1.1.1.1.4.2  yamt _mm_maddsub_pd (__m128d __A, __m128d __B, __m128d __C)
    144  1.1.1.1.4.2  yamt {
    145  1.1.1.1.4.2  yamt   return (__m128d) __builtin_ia32_vfmaddsubpd ((__v2df)__A, (__v2df)__B, (__v2df)__C);
    146  1.1.1.1.4.2  yamt }
    147  1.1.1.1.4.2  yamt 
    148  1.1.1.1.4.2  yamt extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    149  1.1.1.1.4.2  yamt _mm_msubadd_ps (__m128 __A, __m128 __B, __m128 __C)
    150  1.1.1.1.4.2  yamt {
    151  1.1.1.1.4.2  yamt   return (__m128) __builtin_ia32_vfmsubaddps ((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
    152  1.1.1.1.4.2  yamt }
    153  1.1.1.1.4.2  yamt 
    154  1.1.1.1.4.2  yamt extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    155  1.1.1.1.4.2  yamt _mm_msubadd_pd (__m128d __A, __m128d __B, __m128d __C)
    156  1.1.1.1.4.2  yamt {
    157  1.1.1.1.4.2  yamt   return (__m128d) __builtin_ia32_vfmsubaddpd ((__v2df)__A, (__v2df)__B, (__v2df)__C);
    158  1.1.1.1.4.2  yamt }
    159  1.1.1.1.4.2  yamt 
    160  1.1.1.1.4.2  yamt /* 256b Floating point multiply/add type instructions.  */
    161  1.1.1.1.4.2  yamt extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    162  1.1.1.1.4.2  yamt _mm256_macc_ps (__m256 __A, __m256 __B, __m256 __C)
    163  1.1.1.1.4.2  yamt {
    164  1.1.1.1.4.2  yamt   return (__m256) __builtin_ia32_vfmaddps256 ((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
    165  1.1.1.1.4.2  yamt }
    166  1.1.1.1.4.2  yamt 
    167  1.1.1.1.4.2  yamt extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    168  1.1.1.1.4.2  yamt _mm256_macc_pd (__m256d __A, __m256d __B, __m256d __C)
    169  1.1.1.1.4.2  yamt {
    170  1.1.1.1.4.2  yamt   return (__m256d) __builtin_ia32_vfmaddpd256 ((__v4df)__A, (__v4df)__B, (__v4df)__C);
    171  1.1.1.1.4.2  yamt }
    172  1.1.1.1.4.2  yamt 
    173  1.1.1.1.4.2  yamt extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    174  1.1.1.1.4.2  yamt _mm256_msub_ps (__m256 __A, __m256 __B, __m256 __C)
    175  1.1.1.1.4.2  yamt 
    176  1.1.1.1.4.2  yamt {
    177  1.1.1.1.4.2  yamt   return (__m256) __builtin_ia32_vfmsubps256 ((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
    178  1.1.1.1.4.2  yamt }
    179  1.1.1.1.4.2  yamt 
    180  1.1.1.1.4.2  yamt extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    181  1.1.1.1.4.2  yamt _mm256_msub_pd (__m256d __A, __m256d __B, __m256d __C)
    182  1.1.1.1.4.2  yamt {
    183  1.1.1.1.4.2  yamt   return (__m256d) __builtin_ia32_vfmsubpd256 ((__v4df)__A, (__v4df)__B, (__v4df)__C);
    184  1.1.1.1.4.2  yamt }
    185  1.1.1.1.4.2  yamt 
    186  1.1.1.1.4.2  yamt extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    187  1.1.1.1.4.2  yamt _mm256_nmacc_ps (__m256 __A, __m256 __B, __m256 __C)
    188  1.1.1.1.4.2  yamt {
    189  1.1.1.1.4.2  yamt   return (__m256) __builtin_ia32_vfnmaddps256 ((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
    190  1.1.1.1.4.2  yamt }
    191  1.1.1.1.4.2  yamt 
    192  1.1.1.1.4.2  yamt extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    193  1.1.1.1.4.2  yamt _mm256_nmacc_pd (__m256d __A, __m256d __B, __m256d __C)
    194  1.1.1.1.4.2  yamt {
    195  1.1.1.1.4.2  yamt   return (__m256d) __builtin_ia32_vfnmaddpd256 ((__v4df)__A, (__v4df)__B, (__v4df)__C);
    196  1.1.1.1.4.2  yamt }
    197  1.1.1.1.4.2  yamt 
    198  1.1.1.1.4.2  yamt extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    199  1.1.1.1.4.2  yamt _mm256_nmsub_ps (__m256 __A, __m256 __B, __m256 __C)
    200  1.1.1.1.4.2  yamt {
    201  1.1.1.1.4.2  yamt   return (__m256) __builtin_ia32_vfnmsubps256 ((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
    202  1.1.1.1.4.2  yamt }
    203  1.1.1.1.4.2  yamt 
    204  1.1.1.1.4.2  yamt extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    205  1.1.1.1.4.2  yamt _mm256_nmsub_pd (__m256d __A, __m256d __B, __m256d __C)
    206  1.1.1.1.4.2  yamt {
    207  1.1.1.1.4.2  yamt   return (__m256d) __builtin_ia32_vfnmsubpd256 ((__v4df)__A, (__v4df)__B, (__v4df)__C);
    208  1.1.1.1.4.2  yamt }
    209  1.1.1.1.4.2  yamt 
    210  1.1.1.1.4.2  yamt extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    211  1.1.1.1.4.2  yamt _mm256_maddsub_ps (__m256 __A, __m256 __B, __m256 __C)
    212  1.1.1.1.4.2  yamt {
    213  1.1.1.1.4.2  yamt   return (__m256) __builtin_ia32_vfmaddsubps256 ((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
    214  1.1.1.1.4.2  yamt }
    215  1.1.1.1.4.2  yamt 
    216  1.1.1.1.4.2  yamt extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    217  1.1.1.1.4.2  yamt _mm256_maddsub_pd (__m256d __A, __m256d __B, __m256d __C)
    218  1.1.1.1.4.2  yamt {
    219  1.1.1.1.4.2  yamt   return (__m256d) __builtin_ia32_vfmaddsubpd256 ((__v4df)__A, (__v4df)__B, (__v4df)__C);
    220  1.1.1.1.4.2  yamt }
    221  1.1.1.1.4.2  yamt 
    222  1.1.1.1.4.2  yamt extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    223  1.1.1.1.4.2  yamt _mm256_msubadd_ps (__m256 __A, __m256 __B, __m256 __C)
    224  1.1.1.1.4.2  yamt {
    225  1.1.1.1.4.2  yamt   return (__m256) __builtin_ia32_vfmsubaddps256 ((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
    226  1.1.1.1.4.2  yamt }
    227  1.1.1.1.4.2  yamt 
    228  1.1.1.1.4.2  yamt extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
    229  1.1.1.1.4.2  yamt _mm256_msubadd_pd (__m256d __A, __m256d __B, __m256d __C)
    230  1.1.1.1.4.2  yamt {
    231  1.1.1.1.4.2  yamt   return (__m256d) __builtin_ia32_vfmsubaddpd256 ((__v4df)__A, (__v4df)__B, (__v4df)__C);
    232  1.1.1.1.4.2  yamt }
    233  1.1.1.1.4.2  yamt 
    234  1.1.1.1.4.2  yamt #endif
    235  1.1.1.1.4.2  yamt 
    236  1.1.1.1.4.2  yamt #endif
    237