chris@160: /** chris@160: * Copyright (c) 2014, 2015, Enzien Audio Ltd. chris@160: * chris@160: * Permission to use, copy, modify, and/or distribute this software for any chris@160: * purpose with or without fee is hereby granted, provided that the above chris@160: * copyright notice and this permission notice appear in all copies. chris@160: * chris@160: * THE SOFTWARE IS PROVIDED "AS IS" AND THE AUTHOR DISCLAIMS ALL WARRANTIES WITH chris@160: * REGARD TO THIS SOFTWARE INCLUDING ALL IMPLIED WARRANTIES OF MERCHANTABILITY chris@160: * AND FITNESS. IN NO EVENT SHALL THE AUTHOR BE LIABLE FOR ANY SPECIAL, DIRECT, chris@160: * INDIRECT, OR CONSEQUENTIAL DAMAGES OR ANY DAMAGES WHATSOEVER RESULTING FROM chris@160: * LOSS OF USE, DATA OR PROFITS, WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE OR chris@160: * OTHER TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR chris@160: * PERFORMANCE OF THIS SOFTWARE. chris@160: */ chris@160: chris@160: #include "SignalVar.h" chris@160: chris@160: // __var~f chris@160: chris@160: static void sVarf_update(SignalVarf *o, float k, float step, bool reverse) { chris@160: #if HV_SIMD_AVX chris@160: if (reverse) o->v = _mm256_setr_ps(k+7.0f*step, k+6.0f*step, k+5.0f*step, k+4.0f*step, k+3.0f*step, k+2.0f*step, k+step, k); chris@160: else o->v = _mm256_set_ps(k+7.0f*step, k+6.0f*step, k+5.0f*step, k+4.0f*step, k+3.0f*step, k+2.0f*step, k+step, k); chris@160: #elif HV_SIMD_SSE chris@160: if (reverse) o->v = _mm_setr_ps(k+3.0f*step, k+2.0f*step, k+step, k); chris@160: else o->v = _mm_set_ps(k+3.0f*step, k+2.0f*step, k+step, k); chris@160: #elif HV_SIMD_NEON chris@160: if (reverse) o->v = (float32x4_t) {3.0f*step+k, 2.0f*step+k, step+k, k}; chris@160: else o->v = (float32x4_t) {k, step+k, 2.0f*step+k, 3.0f*step+k}; chris@160: #else // HV_SIMD_NONE chris@160: o->v = k; chris@160: #endif chris@160: } chris@160: chris@160: hv_size_t sVarf_init(SignalVarf *o, float k, float step, bool reverse) { chris@160: sVarf_update(o, k, step, reverse); chris@160: return 0; chris@160: } chris@160: chris@160: void sVarf_onMessage(HvBase *_c, SignalVarf *o, const HvMessage *m) { chris@160: if (msg_isFloat(m,0)) { chris@160: sVarf_update(o, msg_getFloat(m,0), msg_isFloat(m,1) ? msg_getFloat(m,1) : 0.0f, msg_getNumElements(m) == 3); chris@160: } chris@160: } chris@160: chris@160: chris@160: chris@160: // __var~i chris@160: chris@160: static void sVari_update(SignalVari *o, int k, int step, bool reverse) { chris@160: #if HV_SIMD_AVX chris@160: if (reverse) o->v = _mm256_setr_epi32(k+7*step, k+6*step, k+5*step, k+4*step, k+3*step, k+2*step, k+step, k); chris@160: else o->v = _mm256_set_epi32(k+7*step, k+6*step, k+5*step, k+4*step, k+3*step, k+2*step, k+step, k); chris@160: #elif HV_SIMD_SSE chris@160: if (reverse) o->v = _mm_setr_epi32(k+3*step, k+2*step, k+step, k); chris@160: else o->v = _mm_set_epi32(k+3*step, k+2*step, k+step, k); chris@160: #elif HV_SIMD_NEON chris@160: if (reverse) o->v = (int32x4_t) {3*step+k, 2*step+k, step+k, k}; chris@160: else o->v = (int32x4_t) {k, step+k, 2*step+k, 3*step+k}; chris@160: #else // HV_SIMD_NEON chris@160: o->v = k; chris@160: #endif chris@160: } chris@160: chris@160: hv_size_t sVari_init(SignalVari *o, int k, int step, bool reverse) { chris@160: sVari_update(o, k, step, reverse); chris@160: return 0; chris@160: } chris@160: chris@160: void sVari_onMessage(HvBase *_c, SignalVari *o, const HvMessage *m) { chris@160: if (msg_isFloat(m,0)) { chris@160: sVari_update(o, (int) msg_getFloat(m,0), msg_isFloat(m,1) ? (int) msg_getFloat(m,1) : 0, msg_getNumElements(m) == 3); chris@160: } chris@160: }