search for: __a

...h?rev=267690&r1=267689&r2=267690&view=diff ============================================================================== --- cfe/trunk/lib/Headers/avx512fintrin.h (original) +++ cfe/trunk/lib/Headers/avx512fintrin.h Wed Apr 27 05:44:15 2016 @@ -7324,6 +7324,30 @@ _mm512_kxor (__mmask16 __A, __mmask16 __ return (__mmask16) __builtin_ia32_kxorhi ((__mmask16) __A, (__mmask16) __B); } +static __inline__ void __DEFAULT_FN_ATTRS +_mm512_stream_si512 (__m512i * __P, __m512i __A) +{ + __builtin_ia32_movntdq512 ((__v8di *) __P, (__v8di) __A); +} + +static __inline__ __m512i __DEFAULT_FN...

...h?rev=267690&r1=267689&r2=267690&view=diff ============================================================================== --- cfe/trunk/lib/Headers/avx512fintrin.h (original) +++ cfe/trunk/lib/Headers/avx512fintrin.h Wed Apr 27 05:44:15 2016 @@ -7324,6 +7324,30 @@ _mm512_kxor (__mmask16 __A, __mmask16 __ return (__mmask16) __builtin_ia32_kxorhi ((__mmask16) __A, (__mmask16) __B); } +static __inline__ void __DEFAULT_FN_ATTRS +_mm512_stream_si512 (__m512i * __P, __m512i __A) +{ + __builtin_ia32_movntdq512 ((__v8di *) __P, (__v8di) __A); +} + +static __inline__ __m512i __DEFAULT_FN...

...ocator<llvm::MachineMove> > ' c:/Users/Greybird/Desktop/llvm/llvm-2.4/include/llvm/CodeGen/ MachineModuleInfo.h :1007: instantiated from here c:\mingw\bin\../lib/gcc/mingw32/4.3.0/include/c++/bits/ boost_concept_check.h:216 : error: '__gnu_cxx::_SGIAssignableConcept<_Tp>::__a' has incomplete type c:/Users/Greybird/Desktop/llvm/llvm-2.4/include/llvm/CodeGen/ MachineModuleInfo.h :53: error: forward declaration of 'struct llvm::MachineMove' c:\mingw\bin\../lib/gcc/mingw32/4.3.0/include/c++/bits/ boost_concept_check.h: In member function 'void __gnu_...

...ecific to some CPU targets? Let me take an example: /// Horizontally adds the adjacent pairs of values contained in two /// 128-bit vectors of [4 x float]. /// /// \headerfile <x86intrin.h> /// /// This intrinsic corresponds to the <c> VHADDPS </c> instruction. /// /// \param __a /// A 128-bit vector of [4 x float] containing one of the source operands. /// The horizontal sums of the values are stored in the lower bits of the /// destination. /// \param __b /// A 128-bit vector of [4 x float] containing one of the source operands. /// The horizontal sums of t...

...eck.h:296 >> : error: no match for 'operator==' in >> '((__gnu_cxx::_EqualOpConcept<llvm::BasicB >> lock, llvm::BasicBlock*>*)this)- >> >>> __gnu_cxx::_EqualOpConcept<llvm::BasicBlock, ll >>> >> vm::BasicBlock*>::__a == >> ((__gnu_cxx::_EqualOpConcept<llvm::BasicBlock, llvm::Ba >> sicBlock*>*)this)->__gnu_cxx::_EqualOpConcept<llvm::BasicBlock, >> llvm::BasicBlock >> *>::__b' >> c:/Users/Greybird/Desktop/llvm/llvm-2.4/include/llvm/ADT/APInt.h: >> B...

...: In file included from <some directory>/lib/clang/stable/include/immintrin.h:118: <some directory>/lib/clang/stable/include/avx512cdintrin.h:37:20: error: use of undeclared identifier '__builtin_ia32_vpconflictdi_512' return (__m512i) __builtin_ia32_vpconflictdi_512 ((__v8di) __A); ^ <some directory>/lib/clang/stable/include/avx512cdintrin.h:59:20: error: use of undeclared identifier '__builtin_ia32_vpconflictsi_512' return (__m512i) __builtin_ia32_vpconflictsi_512 ((__v16si) __A); ^ Any suggestions on what might be mess...

Jean-Marc Valin wrote: >> I recently found a .. weird bug on Win32 SSE with GCC 4.2.1. >> >> In libspeex/cb_search_sse.h, the following union is used: >> >> union { >> float __a[4]; >> __m128 __v; >> } __u; >> >> For some odd reason, this particular version of GCC will not 16-byte >> align the union. IE; the alignment requirement of __v isn't propagated. >> Changing it into this: >> >> union { >> float __a[4...

...can view it (if it isn't spam) or label similar future email. If you have any questions, see the administrator of that system for details. Content preview: I recently found a .. weird bug on Win32 SSE with GCC 4.2.1. In libspeex/cb_search_sse.h, the following union is used: union { float __a[4]; __m128 __v; } __u; [...] Content analysis details: (4.0 points, 3.0 required) pts rule name description ---- ---------------------- -------------------------------------------------- 0.0 BAYES_50 BODY: Bayesian spam probability is 40 to 60%...

...ectory>/lib/clang/stable/include/immintrin.h:118: > > <some directory>/lib/clang/stable/include/avx512cdintrin.h:37:20: error: use of undeclared identifier '__builtin_ia32_vpconflictdi_512' > > return (__m512i) __builtin_ia32_vpconflictdi_512 ((__v8di) __A); > > ^ > > <some directory>/lib/clang/stable/include/avx512cdintrin.h:59:20: error: use of undeclared identifier '__builtin_ia32_vpconflictsi_512' > > return (__m512i) __builtin_ia32_vpconflictsi_512 ((__v16si) __A);...

Hi there, I've recently encountered a piece of code that uses some SSE2 intrinsics and builds with gcc46, but not clang: clang can't find _mm_movpi64_epi64(), while gcc46 defines it in its lib/gcc46/gcc/.../4.6.3/include/emmintrin.h: extern __inline __m128i __attribute__((__gnu_inline__, __always_inline__, __artificial__)) _mm_movpi64_epi64 (__m64 __A) { return _mm_set_epi64 ((__m64)0LL, __A); } extern __inline __m128i __attribute__((__gnu_inline__, __always_inline__, __artificial__)) _mm_set_epi64x (long long __q1, long long __q0) {...

Thanks Serge! This means for every new intrinsic set, a systematic change should be made to LLVM to support the new intrinsic set, right? The change should include frontend change, IR instruction set change, as well as low level code generation changes? On Tue, Jan 9, 2018 at 12:39 AM, serge guelton via llvm-dev < llvm-dev at lists.llvm.org> wrote: > > The vast majority of the

...r de Oliveira Costa <gcosta@redhat.com> Index: clean-start/include/asm-x86_64/msr.h =================================================================== --- clean-start.orig/include/asm-x86_64/msr.h +++ clean-start/include/asm-x86_64/msr.h @@ -2,6 +2,62 @@ #define X86_64_MSR_H 1 #ifndef __ASSEMBLY__ +#include <asm/errno.h> + +static inline void native_cpuid(unsigned int *eax, unsigned int *ebx, + unsigned int *ecx, unsigned int *edx) +{ + __asm__("cpuid" + : "=a" (*eax), + "=b" (*ebx), + "=c" (*ecx), + "=d" (*edx) +...

...r de Oliveira Costa <gcosta@redhat.com> Index: clean-start/include/asm-x86_64/msr.h =================================================================== --- clean-start.orig/include/asm-x86_64/msr.h +++ clean-start/include/asm-x86_64/msr.h @@ -2,6 +2,62 @@ #define X86_64_MSR_H 1 #ifndef __ASSEMBLY__ +#include <asm/errno.h> + +static inline void native_cpuid(unsigned int *eax, unsigned int *ebx, + unsigned int *ecx, unsigned int *edx) +{ + __asm__("cpuid" + : "=a" (*eax), + "=b" (*ebx), + "=c" (*ecx), + "=d" (*edx) +...

...ontally adds the adjacent pairs of values contained in two >> /// 128-bit vectors of [4 x float]. >> /// >> /// \headerfile <x86intrin.h> >> /// >> /// This intrinsic corresponds to the <c> VHADDPS </c> instruction. >> /// >> /// \param __a >> /// A 128-bit vector of [4 x float] containing one of the source >> operands. >> /// The horizontal sums of the values are stored in the lower bits of >> the >> /// destination. >> /// \param __b >> /// A 128-bit vector of [4 x float] contain...

...ux-gnu/4.8/../../../../include/c++/4.8/utility:70: In file included from /usr/lib/gcc/x86_64-linux-gnu/4.8/../../../../include/c++/4.8/bits/stl_pair.h:59: /usr/lib/gcc/x86_64-linux-gnu/4.8/../../../../include/c++/4.8/bits/move.h:185:5: error: conflicting types for 'swap' swap(_Tp (&__a)[_Nm], _Tp (&__b)[_Nm]) ^ /usr/lib/gcc/x86_64-linux-gnu/4.8/../../../../include/c++/4.8/bits/move.h:166:5: note: previous definition is here swap(_Tp& __a, _Tp& __b) -------------------------------------------------------------------------------- In file included from LLVMDIB...

...nclude" -ferror-limit=1000 and the followings are error codes. Thanks and regards, Seung-yeon. In file included from helloneon.c:4: d:/llvm_projects/llvm-3.0rc4/bin/../lib/clang/3.0/include\arm_neon.h:41:24: error: invalid vector element type 'int32_t' (aka 'long') typedef __attribute__((neon_vector_type(2))) int32_t int32x2_t; ^ d:/llvm_projects/llvm-3.0rc4/bin/../lib/clang/3.0/include\arm_neon.h:42:24: error: invalid vector element type 'int32_t' (aka 'long') typedef __attribute__((neon_vector_type(4))) int32_t int32x4_t;...

...ot/indexer-worker'. Program terminated with signal 11, Segmentation fault. #0 0x00007f30f7ad056d in __exchange_and_add (__val=-1, __mem=0xfffffffffffffff8) at /usr/src/debug/gcc-4.8.5-20150702/obj-x86_64-redhat-linux/x86_64-redhat-linux/libstdc++-v3/include/ext/atomicity.h:49 49 { return __atomic_fetch_add(__mem, __val, __ATOMIC_ACQ_REL); } (gdb) bt full #0 0x00007f30f7ad056d in __exchange_and_add (__val=-1, __mem=0xfffffffffffffff8) at /usr/src/debug/gcc-4.8.5-20150702/obj-x86_64-redhat-linux/x86_64-redhat-linux/libstdc++-v3/include/ext/atomicity.h:49 No locals. #1 __exchange_a...

...!tbaa !1 store i32 %1, i32* %max_value.sroa.0 for.body: %max_value.sroa.0.0.max_value.sroa.0.0.6 = load i32, i32* %max_value.sroa.0 %3 = bitcast i32 %max_value.sroa.0.0.max_value.sroa.0.0.6 to float %max_value.sroa.0.0.max_value.sroa_cast8 = bitcast i32* %max_value.sroa.0 to float* %__b.__a.i = select i1 %cmp.i, float* %arrayidx1, float* %max_value.sroa.0.0.max_value.sroa_cast8 %5 = bitcast float* %__b.__a.i to i32* %6 = load i32, i32* %5, align 4, !tbaa !1 store i32 %6, i32* %max_value.sroa.0 -------------------- After SROA when Canonicalization is turned off------------------...

...libc.so.6 #1 0xb76d2942 in std::string::_S_copy_chars () from /usr/lib/gcc/i686-pc-linux-gnu/4.1.2/libstdc++.so.6 #2 0xb7302315 in std::string::_S_construct<char const*> (__beg=0x9fe020c "!I4\thC6\tH#6\nçÃ6\npÆF·+", __end=0x13344334 <Address 0x13344334 out of bounds>, __a=@0xbf856e3f) at /usr/lib/gcc/i686-pc-linux-gnu/4.1.2/include/g++-v4/bits/basic_string.tcc:152 #3 0xb7302361 in std::string::_S_construct_aux<char const*> (__beg=0x9fe020c "!I4\thC6\tH#6\nçÃ6\npÆF·+", __end=0x13344334 <Address 0x13344334 out of bounds>, __a=@0xbf856e3f)...

...GLOBAL__sub_I_chacha_avx.cpp at string:1322, queue = 'com.apple.main-thread', stop reason = EXC_BAD_INSTRUCTION (code=EXC_I386_INVOP, subcode=0x0) frame #0: 0x000000010016ec49 cryptest.exe`_GLOBAL__sub_I_chacha_avx.cpp at string:1322 1319 { 1320 size_type (&__a)[__n_words] = __r_.first().__r.__words; 1321 for (unsigned __i = 0; __i < __n_words; ++__i) -> 1322 __a[__i] = 0; 1323 } 1324 1325 template <size_type __a> static And: (lldb) disass cryptest.exe`_GLOBAL__sub_I_chacha_avx.cpp at chach...