173 lines
4.9 KiB
C
173 lines
4.9 KiB
C
/*
|
|
* This file is part of libsharp.
|
|
*
|
|
* libsharp 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.
|
|
*
|
|
* libsharp 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 libsharp; if not, write to the Free Software
|
|
* Foundation, Inc., 51 Franklin St, Fifth Floor, Boston, MA 02110-1301 USA
|
|
*/
|
|
|
|
/*
|
|
* libsharp is being developed at the Max-Planck-Institut fuer Astrophysik
|
|
* and financially supported by the Deutsches Zentrum fuer Luft- und Raumfahrt
|
|
* (DLR).
|
|
*/
|
|
|
|
/* \file sharp_complex_hacks.h
|
|
* support for converting vector types and complex numbers
|
|
*
|
|
* Copyright (C) 2012-2018 Max-Planck-Society
|
|
* Author: Martin Reinecke
|
|
*/
|
|
|
|
#ifndef SHARP_COMPLEX_HACKS_H
|
|
#define SHARP_COMPLEX_HACKS_H
|
|
|
|
#include <math.h>
|
|
#include "sharp_vecsupport.h"
|
|
|
|
#define UNSAFE_CODE
|
|
|
|
#if (VLEN==1)
|
|
|
|
static inline _Complex double vhsum_cmplx(Tv a, Tv b)
|
|
{ return a+_Complex_I*b; }
|
|
|
|
static inline void vhsum_cmplx2 (Tv a, Tv b, Tv c, Tv d,
|
|
_Complex double * restrict c1, _Complex double * restrict c2)
|
|
{ *c1 += a+_Complex_I*b; *c2 += c+_Complex_I*d; }
|
|
|
|
static inline void vhsum_cmplx_special (Tv a, Tv b, Tv c, Tv d,
|
|
_Complex double * restrict cc)
|
|
{ cc[0] += a+_Complex_I*b; cc[1] += c+_Complex_I*d; }
|
|
|
|
#endif
|
|
|
|
#if (VLEN==2)
|
|
|
|
static inline _Complex double vhsum_cmplx (Tv a, Tv b)
|
|
{
|
|
#if defined(__SSE3__)
|
|
Tv tmp = _mm_hadd_pd(a,b);
|
|
#else
|
|
Tv tmp = _mm_shuffle_pd(a,b,_MM_SHUFFLE2(0,1)) +
|
|
_mm_shuffle_pd(a,b,_MM_SHUFFLE2(1,0));
|
|
#endif
|
|
union {Tv v; _Complex double c; } u;
|
|
u.v=tmp; return u.c;
|
|
}
|
|
|
|
static inline void vhsum_cmplx2 (Tv a, Tv b, Tv c,
|
|
Tv d, _Complex double * restrict c1, _Complex double * restrict c2)
|
|
{
|
|
#ifdef UNSAFE_CODE
|
|
#if defined(__SSE3__)
|
|
*((__m128d *)c1) += _mm_hadd_pd(a,b);
|
|
*((__m128d *)c2) += _mm_hadd_pd(c,d);
|
|
#else
|
|
*((__m128d *)c1) += _mm_shuffle_pd(a,b,_MM_SHUFFLE2(0,1)) +
|
|
_mm_shuffle_pd(a,b,_MM_SHUFFLE2(1,0));
|
|
*((__m128d *)c2) += _mm_shuffle_pd(c,d,_MM_SHUFFLE2(0,1)) +
|
|
_mm_shuffle_pd(c,d,_MM_SHUFFLE2(1,0));
|
|
#endif
|
|
#else
|
|
union {Tv v; _Complex double c; } u1, u2;
|
|
#if defined(__SSE3__)
|
|
u1.v = _mm_hadd_pd(a,b); u2.v=_mm_hadd_pd(c,d);
|
|
#else
|
|
u1.v = _mm_shuffle_pd(a,b,_MM_SHUFFLE2(0,1)) +
|
|
_mm_shuffle_pd(a,b,_MM_SHUFFLE2(1,0));
|
|
u2.v = _mm_shuffle_pd(c,d,_MM_SHUFFLE2(0,1)) +
|
|
_mm_shuffle_pd(c,d,_MM_SHUFFLE2(1,0));
|
|
#endif
|
|
*c1+=u1.c; *c2+=u2.c;
|
|
#endif
|
|
}
|
|
|
|
static inline void vhsum_cmplx_special (Tv a, Tv b, Tv c, Tv d,
|
|
_Complex double * restrict cc)
|
|
{ vhsum_cmplx2(a,b,c,d,cc,cc+1); }
|
|
|
|
#endif
|
|
|
|
#if (VLEN==4)
|
|
|
|
static inline _Complex double vhsum_cmplx (Tv a, Tv b)
|
|
{
|
|
Tv tmp=_mm256_hadd_pd(a,b);
|
|
Tv tmp2=_mm256_permute2f128_pd(tmp,tmp,1);
|
|
tmp=_mm256_add_pd(tmp,tmp2);
|
|
#ifdef UNSAFE_CODE
|
|
_Complex double ret;
|
|
*((__m128d *)&ret)=_mm256_extractf128_pd(tmp, 0);
|
|
return ret;
|
|
#else
|
|
union {Tv v; _Complex double c[2]; } u;
|
|
u.v=tmp; return u.c[0];
|
|
#endif
|
|
}
|
|
|
|
static inline void vhsum_cmplx2 (Tv a, Tv b, Tv c, Tv d,
|
|
_Complex double * restrict c1, _Complex double * restrict c2)
|
|
{
|
|
Tv tmp1=_mm256_hadd_pd(a,b), tmp2=_mm256_hadd_pd(c,d);
|
|
Tv tmp3=_mm256_permute2f128_pd(tmp1,tmp2,49),
|
|
tmp4=_mm256_permute2f128_pd(tmp1,tmp2,32);
|
|
tmp1=tmp3+tmp4;
|
|
#ifdef UNSAFE_CODE
|
|
*((__m128d *)c1)=_mm_add_pd(*((__m128d *)c1),_mm256_extractf128_pd(tmp1, 0));
|
|
*((__m128d *)c2)=_mm_add_pd(*((__m128d *)c2),_mm256_extractf128_pd(tmp1, 1));
|
|
#else
|
|
union {Tv v; _Complex double c[2]; } u;
|
|
u.v=tmp1;
|
|
*c1+=u.c[0]; *c2+=u.c[1];
|
|
#endif
|
|
}
|
|
|
|
static inline void vhsum_cmplx_special (Tv a, Tv b, Tv c, Tv d,
|
|
_Complex double * restrict cc)
|
|
{
|
|
Tv tmp1=_mm256_hadd_pd(a,b), tmp2=_mm256_hadd_pd(c,d);
|
|
Tv tmp3=_mm256_permute2f128_pd(tmp1,tmp2,49),
|
|
tmp4=_mm256_permute2f128_pd(tmp1,tmp2,32);
|
|
tmp1=tmp3+tmp4;
|
|
#ifdef UNSAFE_CODE
|
|
_mm256_storeu_pd((double *)cc,
|
|
_mm256_add_pd(_mm256_loadu_pd((double *)cc),tmp1));
|
|
#else
|
|
union {Tv v; _Complex double c[2]; } u;
|
|
u.v=tmp1;
|
|
cc[0]+=u.c[0]; cc[1]+=u.c[1];
|
|
#endif
|
|
}
|
|
|
|
#endif
|
|
|
|
#if (VLEN==8)
|
|
|
|
static inline _Complex double vhsum_cmplx(Tv a, Tv b)
|
|
{ return _mm512_reduce_add_pd(a)+_Complex_I*_mm512_reduce_add_pd(b); }
|
|
|
|
static inline void vhsum_cmplx2 (Tv a, Tv b, Tv c, Tv d,
|
|
_Complex double * restrict c1, _Complex double * restrict c2)
|
|
{
|
|
*c1 += _mm512_reduce_add_pd(a)+_Complex_I*_mm512_reduce_add_pd(b);
|
|
*c2 += _mm512_reduce_add_pd(c)+_Complex_I*_mm512_reduce_add_pd(d);
|
|
}
|
|
|
|
static inline void vhsum_cmplx_special (Tv a, Tv b, Tv c, Tv d,
|
|
_Complex double * restrict cc)
|
|
{ vhsum_cmplx2(a,b,c,d,cc,cc+1); }
|
|
|
|
#endif
|
|
|
|
#endif
|