Gitiles
Code Review Sign In
gerrit-public.fairphone.software / toolchain / llvm-project / f0a1c65fb007d727ff93bd8ff9c438f689cde77d / . / clang / lib / Headers / fmaintrin.h
blob: 0e2ef0b1716bb59c80e289dd98f4bc89145e01dc [file] [log] [blame]
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]1/*===---- fma4intrin.h - FMA4 intrinsics -----------------------------------===
2 *
3 * Permission is hereby granted, free of charge, to any person obtaining a copy
4 * of this software and associated documentation files (the "Software"), to deal
5 * in the Software without restriction, including without limitation the rights
6 * to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
7 * copies of the Software, and to permit persons to whom the Software is
8 * furnished to do so, subject to the following conditions:
9 *
10 * The above copyright notice and this permission notice shall be included in
11 * all copies or substantial portions of the Software.
12 *
13 * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
14 * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
15 * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
16 * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
17 * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
18 * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
19 * THE SOFTWARE.
20 *
21 *===-----------------------------------------------------------------------===
22 */
23
24#ifndef __IMMINTRIN_H
25#error "Never use <fmaintrin.h> directly; include <immintrin.h> instead."
26#endif
27
28#ifndef __FMAINTRIN_H
29#define __FMAINTRIN_H
30
Eric Christopher4d1851682015-06-17 07:09:20 +0000[diff] [blame]31/* Define the default attributes for the functions in this file. */
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]32#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("fma")))
Eric Christopher4d1851682015-06-17 07:09:20 +0000[diff] [blame]33
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]34static __inline__ __m128 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]35_mm_fmadd_ps(__m128 __A, __m128 __B, __m128 __C)
36{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]37 return (__m128)__builtin_ia32_vfmaddps((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]38}
39
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]40static __inline__ __m128d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]41_mm_fmadd_pd(__m128d __A, __m128d __B, __m128d __C)
42{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]43 return (__m128d)__builtin_ia32_vfmaddpd((__v2df)__A, (__v2df)__B, (__v2df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]44}
45
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]46static __inline__ __m128 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]47_mm_fmadd_ss(__m128 __A, __m128 __B, __m128 __C)
48{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]49 return (__m128)__builtin_ia32_vfmaddss((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]50}
51
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]52static __inline__ __m128d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]53_mm_fmadd_sd(__m128d __A, __m128d __B, __m128d __C)
54{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]55 return (__m128d)__builtin_ia32_vfmaddsd((__v2df)__A, (__v2df)__B, (__v2df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]56}
57
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]58static __inline__ __m128 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]59_mm_fmsub_ps(__m128 __A, __m128 __B, __m128 __C)
60{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]61 return (__m128)__builtin_ia32_vfmsubps((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]62}
63
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]64static __inline__ __m128d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]65_mm_fmsub_pd(__m128d __A, __m128d __B, __m128d __C)
66{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]67 return (__m128d)__builtin_ia32_vfmsubpd((__v2df)__A, (__v2df)__B, (__v2df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]68}
69
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]70static __inline__ __m128 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]71_mm_fmsub_ss(__m128 __A, __m128 __B, __m128 __C)
72{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]73 return (__m128)__builtin_ia32_vfmsubss((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]74}
75
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]76static __inline__ __m128d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]77_mm_fmsub_sd(__m128d __A, __m128d __B, __m128d __C)
78{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]79 return (__m128d)__builtin_ia32_vfmsubsd((__v2df)__A, (__v2df)__B, (__v2df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]80}
81
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]82static __inline__ __m128 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]83_mm_fnmadd_ps(__m128 __A, __m128 __B, __m128 __C)
84{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]85 return (__m128)__builtin_ia32_vfnmaddps((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]86}
87
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]88static __inline__ __m128d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]89_mm_fnmadd_pd(__m128d __A, __m128d __B, __m128d __C)
90{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]91 return (__m128d)__builtin_ia32_vfnmaddpd((__v2df)__A, (__v2df)__B, (__v2df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]92}
93
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]94static __inline__ __m128 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]95_mm_fnmadd_ss(__m128 __A, __m128 __B, __m128 __C)
96{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]97 return (__m128)__builtin_ia32_vfnmaddss((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]98}
99
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]100static __inline__ __m128d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]101_mm_fnmadd_sd(__m128d __A, __m128d __B, __m128d __C)
102{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]103 return (__m128d)__builtin_ia32_vfnmaddsd((__v2df)__A, (__v2df)__B, (__v2df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]104}
105
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]106static __inline__ __m128 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]107_mm_fnmsub_ps(__m128 __A, __m128 __B, __m128 __C)
108{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]109 return (__m128)__builtin_ia32_vfnmsubps((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]110}
111
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]112static __inline__ __m128d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]113_mm_fnmsub_pd(__m128d __A, __m128d __B, __m128d __C)
114{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]115 return (__m128d)__builtin_ia32_vfnmsubpd((__v2df)__A, (__v2df)__B, (__v2df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]116}
117
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]118static __inline__ __m128 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]119_mm_fnmsub_ss(__m128 __A, __m128 __B, __m128 __C)
120{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]121 return (__m128)__builtin_ia32_vfnmsubss((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]122}
123
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]124static __inline__ __m128d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]125_mm_fnmsub_sd(__m128d __A, __m128d __B, __m128d __C)
126{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]127 return (__m128d)__builtin_ia32_vfnmsubsd((__v2df)__A, (__v2df)__B, (__v2df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]128}
129
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]130static __inline__ __m128 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]131_mm_fmaddsub_ps(__m128 __A, __m128 __B, __m128 __C)
132{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]133 return (__m128)__builtin_ia32_vfmaddsubps((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]134}
135
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]136static __inline__ __m128d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]137_mm_fmaddsub_pd(__m128d __A, __m128d __B, __m128d __C)
138{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]139 return (__m128d)__builtin_ia32_vfmaddsubpd((__v2df)__A, (__v2df)__B, (__v2df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]140}
141
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]142static __inline__ __m128 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]143_mm_fmsubadd_ps(__m128 __A, __m128 __B, __m128 __C)
144{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]145 return (__m128)__builtin_ia32_vfmsubaddps((__v4sf)__A, (__v4sf)__B, (__v4sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]146}
147
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]148static __inline__ __m128d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]149_mm_fmsubadd_pd(__m128d __A, __m128d __B, __m128d __C)
150{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]151 return (__m128d)__builtin_ia32_vfmsubaddpd((__v2df)__A, (__v2df)__B, (__v2df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]152}
153
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]154static __inline__ __m256 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]155_mm256_fmadd_ps(__m256 __A, __m256 __B, __m256 __C)
156{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]157 return (__m256)__builtin_ia32_vfmaddps256((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]158}
159
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]160static __inline__ __m256d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]161_mm256_fmadd_pd(__m256d __A, __m256d __B, __m256d __C)
162{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]163 return (__m256d)__builtin_ia32_vfmaddpd256((__v4df)__A, (__v4df)__B, (__v4df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]164}
165
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]166static __inline__ __m256 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]167_mm256_fmsub_ps(__m256 __A, __m256 __B, __m256 __C)
168{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]169 return (__m256)__builtin_ia32_vfmsubps256((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]170}
171
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]172static __inline__ __m256d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]173_mm256_fmsub_pd(__m256d __A, __m256d __B, __m256d __C)
174{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]175 return (__m256d)__builtin_ia32_vfmsubpd256((__v4df)__A, (__v4df)__B, (__v4df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]176}
177
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]178static __inline__ __m256 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]179_mm256_fnmadd_ps(__m256 __A, __m256 __B, __m256 __C)
180{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]181 return (__m256)__builtin_ia32_vfnmaddps256((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]182}
183
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]184static __inline__ __m256d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]185_mm256_fnmadd_pd(__m256d __A, __m256d __B, __m256d __C)
186{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]187 return (__m256d)__builtin_ia32_vfnmaddpd256((__v4df)__A, (__v4df)__B, (__v4df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]188}
189
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]190static __inline__ __m256 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]191_mm256_fnmsub_ps(__m256 __A, __m256 __B, __m256 __C)
192{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]193 return (__m256)__builtin_ia32_vfnmsubps256((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]194}
195
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]196static __inline__ __m256d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]197_mm256_fnmsub_pd(__m256d __A, __m256d __B, __m256d __C)
198{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]199 return (__m256d)__builtin_ia32_vfnmsubpd256((__v4df)__A, (__v4df)__B, (__v4df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]200}
201
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]202static __inline__ __m256 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]203_mm256_fmaddsub_ps(__m256 __A, __m256 __B, __m256 __C)
204{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]205 return (__m256)__builtin_ia32_vfmaddsubps256((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]206}
207
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]208static __inline__ __m256d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]209_mm256_fmaddsub_pd(__m256d __A, __m256d __B, __m256d __C)
210{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]211 return (__m256d)__builtin_ia32_vfmaddsubpd256((__v4df)__A, (__v4df)__B, (__v4df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]212}
213
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]214static __inline__ __m256 __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]215_mm256_fmsubadd_ps(__m256 __A, __m256 __B, __m256 __C)
216{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]217 return (__m256)__builtin_ia32_vfmsubaddps256((__v8sf)__A, (__v8sf)__B, (__v8sf)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]218}
219
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]220static __inline__ __m256d __DEFAULT_FN_ATTRS
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]221_mm256_fmsubadd_pd(__m256d __A, __m256d __B, __m256d __C)
222{
Craig Topper1aa231e2016-05-16 06:38:42 +0000[diff] [blame]223 return (__m256d)__builtin_ia32_vfmsubaddpd256((__v4df)__A, (__v4df)__B, (__v4df)__C);
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]224}
225
Michael Kupersteine45af542015-06-30 13:36:19 +0000[diff] [blame]226#undef __DEFAULT_FN_ATTRS
Eric Christopher4d1851682015-06-17 07:09:20 +0000[diff] [blame]227
Craig Topper2b1eda32012-06-04 03:42:47 +0000[diff] [blame]228#endif /* __FMAINTRIN_H */