Mercurial > hg > sv-dependency-builds
diff src/fftw-3.3.3/simd-support/amd64-cpuid.h @ 10:37bf6b4a2645
Add FFTW3
author | Chris Cannam |
---|---|
date | Wed, 20 Mar 2013 15:35:50 +0000 |
parents | |
children |
line wrap: on
line diff
--- /dev/null Thu Jan 01 00:00:00 1970 +0000 +++ b/src/fftw-3.3.3/simd-support/amd64-cpuid.h Wed Mar 20 15:35:50 2013 +0000 @@ -0,0 +1,89 @@ +/* + * Copyright (c) 2003, 2007-11 Matteo Frigo + * Copyright (c) 2003, 2007-11 Massachusetts Institute of Technology + * + * This program is free software; you can redistribute it and/or modify + * it under the terms of the GNU General Public License as published by + * the Free Software Foundation; either version 2 of the License, or + * (at your option) any later version. + * + * This program is distributed in the hope that it will be useful, + * but WITHOUT ANY WARRANTY; without even the implied warranty of + * MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the + * GNU General Public License for more details. + * + * You should have received a copy of the GNU General Public License + * along with this program; if not, write to the Free Software + * Foundation, Inc., 51 Franklin Street, Fifth Floor, Boston, MA 02110-1301 USA + * + */ + + +#ifdef _MSC_VER +#ifndef inline +#define inline __inline +#endif +#endif + +#ifdef _MSC_VER +#include <intrin.h> +#if (_MSC_VER >= 1600) && !defined(__INTEL_COMPILER) +#include <immintrin.h> +#endif +#endif + +static inline int cpuid_ecx(int op) +{ +# ifdef _MSC_VER +# ifdef __INTEL_COMPILER + int result; + _asm { + push rbx + mov eax,op + cpuid + mov result,ecx + pop rbx + } + return result; +# else + int cpu_info[4]; + __cpuid(cpu_info,op); + return cpu_info[2]; +# endif +# else + int eax, ecx, edx; + + __asm__("pushq %%rbx\n\tcpuid\n\tpopq %%rbx" + : "=a" (eax), "=c" (ecx), "=d" (edx) + : "a" (op)); + return ecx; +# endif +} + +static inline int xgetbv_eax(int op) +{ +# ifdef _MSC_VER +# ifdef __INTEL_COMPILER + int veax, vedx; + _asm { + mov ecx,op + xgetbv + mov veax,eax + mov vedx,edx + } + return veax; +# else +# if defined(_MSC_VER) && (_MSC_VER >= 1600) + unsigned __int64 result; + result = _xgetbv(op); + return (int)result; +# else +# error "Need at least Visual Studio 10 SP1 for AVX support" +# endif +# endif +# else + int eax, edx; + __asm__ (".byte 0x0f, 0x01, 0xd0" : "=a"(eax), "=d"(edx) : "c" (op)); + return eax; +#endif +}