heavy-pico/hello-world/c/HvSignalPhasor.c

/**
 * Copyright (c) 2014-2018 Enzien Audio Ltd.
 *
 * Permission to use, copy, modify, and/or distribute this software for any
 * purpose with or without fee is hereby granted, provided that the above
 * copyright notice and this permission notice appear in all copies.
 *
 * THE SOFTWARE IS PROVIDED "AS IS" AND THE AUTHOR DISCLAIMS ALL WARRANTIES WITH
 * REGARD TO THIS SOFTWARE INCLUDING ALL IMPLIED WARRANTIES OF MERCHANTABILITY
 * AND FITNESS. IN NO EVENT SHALL THE AUTHOR BE LIABLE FOR ANY SPECIAL, DIRECT,
 * INDIRECT, OR CONSEQUENTIAL DAMAGES OR ANY DAMAGES WHATSOEVER RESULTING FROM
 * LOSS OF USE, DATA OR PROFITS, WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE OR
 * OTHER TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR
 * PERFORMANCE OF THIS SOFTWARE.
 */

#include "HvSignalPhasor.h"

#define HV_PHASOR_2_32 4294967296.0

#if HV_SIMD_AVX
static void sPhasor_updatePhase(SignalPhasor *o, float p) {
  o->phase = _mm256_set1_ps(p+1.0f); // o->phase is in range [1,2]
#elif HV_SIMD_SSE
  static void sPhasor_updatePhase(SignalPhasor *o, hv_uint32_t p) {
    o->phase = _mm_set1_epi32(p);
#elif HV_SIMD_NEON
  static void sPhasor_updatePhase(SignalPhasor *o, hv_uint32_t p) {
    o->phase =  vdupq_n_u32(p);
#else // HV_SIMD_NONE
  static void sPhasor_updatePhase(SignalPhasor *o, hv_uint32_t p) {
    o->phase = p;
#endif
}

// input phase is in the range of [0,1]. It is independent of o->phase.
#if HV_SIMD_AVX
static void sPhasor_k_updatePhase(SignalPhasor *o, float p) {
  o->phase = _mm256_set_ps(
      p+1.0f+7.0f*o->step.f2sc, p+1.0f+6.0f*o->step.f2sc,
      p+1.0f+5.0f*o->step.f2sc, p+1.0f+4.0f*o->step.f2sc,
      p+1.0f+3.0f*o->step.f2sc, p+1.0f+2.0f*o->step.f2sc,
      p+1.0f+o->step.f2sc,      p+1.0f);

  // ensure that o->phase is still in range [1,2]
  o->phase = _mm256_or_ps(_mm256_andnot_ps(
      _mm256_set1_ps(-INFINITY), o->phase), _mm256_set1_ps(1.0f));
#elif HV_SIMD_SSE
static void sPhasor_k_updatePhase(SignalPhasor *o, hv_uint32_t p) {
  o->phase = _mm_set_epi32(3*o->step.s+p, 2*o->step.s+p, o->step.s+p, p);
#elif HV_SIMD_NEON
static void sPhasor_k_updatePhase(SignalPhasor *o, hv_uint32_t p) {
  o->phase = (uint32x4_t) {p, o->step.s+p, 2*o->step.s+p, 3*o->step.s+p};
#else // HV_SIMD_NONE
static void sPhasor_k_updatePhase(SignalPhasor *o, hv_uint32_t p) {
  o->phase = p;
#endif
}

static void sPhasor_k_updateFrequency(SignalPhasor *o, float f, double r) {
#if HV_SIMD_AVX
  o->step.f2sc = (float) (f/r);
  o->inc = _mm256_set1_ps((float) (8.0f*f/r));
  sPhasor_k_updatePhase(o, o->phase[0]);
#elif HV_SIMD_SSE
  o->step.s = (hv_int32_t) (f*(HV_PHASOR_2_32/r));
  o->inc = _mm_set1_epi32(4*o->step.s);
  const hv_uint32_t *const p = (hv_uint32_t *) &o->phase;
  sPhasor_k_updatePhase(o, p[0]);
#elif HV_SIMD_NEON
  o->step.s = (hv_int32_t) (f*(HV_PHASOR_2_32/r));
  o->inc = vdupq_n_s32(4*o->step.s);
  sPhasor_k_updatePhase(o, vgetq_lane_u32(o->phase, 0));
#else // HV_SIMD_NONE
  o->step.s = (hv_int32_t) (f*(HV_PHASOR_2_32/r));
  o->inc = o->step.s;
  // no need to update phase
#endif
}

hv_size_t sPhasor_init(SignalPhasor *o, double samplerate) {
#if HV_SIMD_AVX
  o->phase = _mm256_set1_ps(1.0f);
  o->inc = _mm256_setzero_ps();
  o->step.f2sc = (float) (1.0/samplerate);
#elif HV_SIMD_SSE
  o->phase = _mm_setzero_si128();
  o->inc = _mm_setzero_si128();
  o->step.f2sc = (float) (HV_PHASOR_2_32/samplerate);
#elif HV_SIMD_NEON
  o->phase = vdupq_n_u32(0);
  o->inc = vdupq_n_s32(0);
  o->step.f2sc = (float) (HV_PHASOR_2_32/samplerate);
#else // HV_SIMD_NONE
  o->phase = 0;
  o->inc = 0;
  o->step.f2sc = (float) (HV_PHASOR_2_32/samplerate);
#endif
  return 0;
}

void sPhasor_onMessage(HeavyContextInterface *_c, SignalPhasor *o, int letIn, const HvMessage *m) {
  if (letIn == 1) {
    if (msg_isFloat(m,0)) {
      float p = msg_getFloat(m,0);
      while (p < 0.0f) p += 1.0f; // wrap phase to [0,1]
      while (p > 1.0f) p -= 1.0f;
#if HV_SIMD_AVX
      sPhasor_updatePhase(o, p);
#else // HV_SIMD_SSE || HV_SIMD_NEON || HV_SIMD_NONE
      sPhasor_updatePhase(o, (hv_uint32_t) (p * HV_PHASOR_2_32));
#endif
    }
  }
}

hv_size_t sPhasor_k_init(SignalPhasor *o, float frequency, double samplerate) {
  __hv_zero_i((hv_bOuti_t) &o->phase);
  sPhasor_k_updateFrequency(o, frequency, samplerate);
  return 0;
}

void sPhasor_k_onMessage(HeavyContextInterface *_c, SignalPhasor *o, int letIn, const HvMessage *m) {
  if (msg_isFloat(m,0)) {
    switch (letIn) {
      case 0: sPhasor_k_updateFrequency(o, msg_getFloat(m,0), hv_getSampleRate(_c)); break;
      case 1: {
        float p = msg_getFloat(m,0);
        while (p < 0.0f) p += 1.0f; // wrap phase to [0,1]
        while (p > 1.0f) p -= 1.0f;
#if HV_SIMD_AVX
        sPhasor_k_updatePhase(o, p);
#else // HV_SIMD_SSE || HV_SIMD_NEON || HV_SIMD_NONE
        sPhasor_k_updatePhase(o, (hv_uint32_t) (p * HV_PHASOR_2_32));
#endif
        break;
      }
      default: break;
    }
  }
}