Gitiles
Code Review Sign In
gerrit-public.fairphone.software / toolchain / llvm-project / e45af54cdbdf6b61b6c0d11cbe6cdacda3075bff / . / clang / lib / Headers / fmaintrin.h
blob: 114a14380ea012e5e388ebd1731232ab1b689454 [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{
37 return (__m128)__builtin_ia32_vfmaddps(__A, __B, __C);
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{
43 return (__m128d)__builtin_ia32_vfmaddpd(__A, __B, __C);
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{
49 return (__m128)__builtin_ia32_vfmaddss(__A, __B, __C);
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{
55 return (__m128d)__builtin_ia32_vfmaddsd(__A, __B, __C);
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{
61 return (__m128)__builtin_ia32_vfmsubps(__A, __B, __C);
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{
67 return (__m128d)__builtin_ia32_vfmsubpd(__A, __B, __C);
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{
73 return (__m128)__builtin_ia32_vfmsubss(__A, __B, __C);
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{
79 return (__m128d)__builtin_ia32_vfmsubsd(__A, __B, __C);
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{
85 return (__m128)__builtin_ia32_vfnmaddps(__A, __B, __C);
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{
91 return (__m128d)__builtin_ia32_vfnmaddpd(__A, __B, __C);
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{
97 return (__m128)__builtin_ia32_vfnmaddss(__A, __B, __C);
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{
103 return (__m128d)__builtin_ia32_vfnmaddsd(__A, __B, __C);
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{
109 return (__m128)__builtin_ia32_vfnmsubps(__A, __B, __C);
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{
115 return (__m128d)__builtin_ia32_vfnmsubpd(__A, __B, __C);
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{
121 return (__m128)__builtin_ia32_vfnmsubss(__A, __B, __C);
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{
127 return (__m128d)__builtin_ia32_vfnmsubsd(__A, __B, __C);
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{
133 return (__m128)__builtin_ia32_vfmaddsubps(__A, __B, __C);
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{
139 return (__m128d)__builtin_ia32_vfmaddsubpd(__A, __B, __C);
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{
145 return (__m128)__builtin_ia32_vfmsubaddps(__A, __B, __C);
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{
151 return (__m128d)__builtin_ia32_vfmsubaddpd(__A, __B, __C);
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{
157 return (__m256)__builtin_ia32_vfmaddps256(__A, __B, __C);
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{
163 return (__m256d)__builtin_ia32_vfmaddpd256(__A, __B, __C);
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{
169 return (__m256)__builtin_ia32_vfmsubps256(__A, __B, __C);
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{
175 return (__m256d)__builtin_ia32_vfmsubpd256(__A, __B, __C);
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{
181 return (__m256)__builtin_ia32_vfnmaddps256(__A, __B, __C);
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{
187 return (__m256d)__builtin_ia32_vfnmaddpd256(__A, __B, __C);
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{
193 return (__m256)__builtin_ia32_vfnmsubps256(__A, __B, __C);
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{
199 return (__m256d)__builtin_ia32_vfnmsubpd256(__A, __B, __C);
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{
205 return (__m256)__builtin_ia32_vfmaddsubps256(__A, __B, __C);
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{
211 return (__m256d)__builtin_ia32_vfmaddsubpd256(__A, __B, __C);
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{
217 return (__m256)__builtin_ia32_vfmsubaddps256(__A, __B, __C);
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{
223 return (__m256d)__builtin_ia32_vfmsubaddpd256(__A, __B, __C);
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 */