mirror of
https://github.com/mozilla/gecko-dev.git
synced 2024-11-07 04:05:49 +00:00
c689dbd103
This code is specific to Web Audio, and is not really part of the MediaStreamGraph code. I've always hated how these files being in two directories gets in the way while hacking on this code. --HG-- rename : content/media/AudioNodeEngine.cpp => content/media/webaudio/AudioNodeEngine.cpp rename : content/media/AudioNodeEngine.h => content/media/webaudio/AudioNodeEngine.h rename : content/media/AudioNodeEngineNEON.cpp => content/media/webaudio/AudioNodeEngineNEON.cpp rename : content/media/AudioNodeEngineNEON.h => content/media/webaudio/AudioNodeEngineNEON.h rename : content/media/AudioNodeExternalInputStream.cpp => content/media/webaudio/AudioNodeExternalInputStream.cpp rename : content/media/AudioNodeExternalInputStream.h => content/media/webaudio/AudioNodeExternalInputStream.h rename : content/media/AudioNodeStream.cpp => content/media/webaudio/AudioNodeStream.cpp rename : content/media/AudioNodeStream.h => content/media/webaudio/AudioNodeStream.h
226 lines
7.1 KiB
C++
226 lines
7.1 KiB
C++
/* -*- mode: c++; tab-width: 2; indent-tabs-mode: nil; c-basic-offset: 2 -*- */
|
|
/* this source code form is subject to the terms of the mozilla public
|
|
* license, v. 2.0. if a copy of the mpl was not distributed with this file,
|
|
* You can obtain one at http://mozilla.org/MPL/2.0/. */
|
|
|
|
#include "AudioNodeEngineNEON.h"
|
|
#include <arm_neon.h>
|
|
|
|
//#ifdef DEBUG
|
|
#if 0 // see bug 921099
|
|
#define ASSERT_ALIGNED(ptr) \
|
|
MOZ_ASSERT((((uintptr_t)ptr + 15) & ~0x0F) == (uintptr_t)ptr, \
|
|
#ptr " has to be aligned 16-bytes aligned.");
|
|
#else
|
|
#define ASSERT_ALIGNED(ptr)
|
|
#endif
|
|
|
|
#define ADDRESS_OF(array, index) ((float32_t*)&array[index])
|
|
|
|
namespace mozilla {
|
|
void AudioBufferAddWithScale_NEON(const float* aInput,
|
|
float aScale,
|
|
float* aOutput,
|
|
uint32_t aSize)
|
|
{
|
|
ASSERT_ALIGNED(aInput);
|
|
ASSERT_ALIGNED(aOutput);
|
|
|
|
float32x4_t vin0, vin1, vin2, vin3;
|
|
float32x4_t vout0, vout1, vout2, vout3;
|
|
float32x4_t vscale = vmovq_n_f32(aScale);
|
|
|
|
uint32_t dif = aSize % 16;
|
|
aSize -= dif;
|
|
unsigned i = 0;
|
|
for (; i < aSize; i+=16) {
|
|
vin0 = vld1q_f32(ADDRESS_OF(aInput, i));
|
|
vin1 = vld1q_f32(ADDRESS_OF(aInput, i+4));
|
|
vin2 = vld1q_f32(ADDRESS_OF(aInput, i+8));
|
|
vin3 = vld1q_f32(ADDRESS_OF(aInput, i+12));
|
|
|
|
vout0 = vld1q_f32(ADDRESS_OF(aOutput, i));
|
|
vout1 = vld1q_f32(ADDRESS_OF(aOutput, i+4));
|
|
vout2 = vld1q_f32(ADDRESS_OF(aOutput, i+8));
|
|
vout3 = vld1q_f32(ADDRESS_OF(aOutput, i+12));
|
|
|
|
vout0 = vmlaq_f32(vout0, vin0, vscale);
|
|
vout1 = vmlaq_f32(vout1, vin1, vscale);
|
|
vout2 = vmlaq_f32(vout2, vin2, vscale);
|
|
vout3 = vmlaq_f32(vout3, vin3, vscale);
|
|
|
|
vst1q_f32(ADDRESS_OF(aOutput, i), vout0);
|
|
vst1q_f32(ADDRESS_OF(aOutput, i+4), vout1);
|
|
vst1q_f32(ADDRESS_OF(aOutput, i+8), vout2);
|
|
vst1q_f32(ADDRESS_OF(aOutput, i+12), vout3);
|
|
}
|
|
|
|
for (unsigned j = 0; j < dif; ++i, ++j) {
|
|
aOutput[i] += aInput[i]*aScale;
|
|
}
|
|
}
|
|
void
|
|
AudioBlockCopyChannelWithScale_NEON(const float* aInput,
|
|
float aScale,
|
|
float* aOutput)
|
|
{
|
|
ASSERT_ALIGNED(aInput);
|
|
ASSERT_ALIGNED(aOutput);
|
|
|
|
float32x4_t vin0, vin1, vin2, vin3;
|
|
float32x4_t vout0, vout1, vout2, vout3;
|
|
float32x4_t vscale = vmovq_n_f32(aScale);
|
|
|
|
for (uint32_t i = 0; i < WEBAUDIO_BLOCK_SIZE; i+=16) {
|
|
vin0 = vld1q_f32(ADDRESS_OF(aInput, i));
|
|
vin1 = vld1q_f32(ADDRESS_OF(aInput, i+4));
|
|
vin2 = vld1q_f32(ADDRESS_OF(aInput, i+8));
|
|
vin3 = vld1q_f32(ADDRESS_OF(aInput, i+12));
|
|
|
|
vout0 = vmulq_f32(vin0, vscale);
|
|
vout1 = vmulq_f32(vin1, vscale);
|
|
vout2 = vmulq_f32(vin2, vscale);
|
|
vout3 = vmulq_f32(vin3, vscale);
|
|
|
|
vst1q_f32(ADDRESS_OF(aOutput, i), vout0);
|
|
vst1q_f32(ADDRESS_OF(aOutput, i+4), vout1);
|
|
vst1q_f32(ADDRESS_OF(aOutput, i+8), vout2);
|
|
vst1q_f32(ADDRESS_OF(aOutput, i+12), vout3);
|
|
}
|
|
}
|
|
|
|
void
|
|
AudioBlockCopyChannelWithScale_NEON(const float aInput[WEBAUDIO_BLOCK_SIZE],
|
|
const float aScale[WEBAUDIO_BLOCK_SIZE],
|
|
float aOutput[WEBAUDIO_BLOCK_SIZE])
|
|
{
|
|
ASSERT_ALIGNED(aInput);
|
|
ASSERT_ALIGNED(aScale);
|
|
ASSERT_ALIGNED(aOutput);
|
|
|
|
float32x4_t vin0, vin1, vin2, vin3;
|
|
float32x4_t vout0, vout1, vout2, vout3;
|
|
float32x4_t vscale0, vscale1, vscale2, vscale3;
|
|
|
|
for (uint32_t i = 0; i < WEBAUDIO_BLOCK_SIZE; i+=16) {
|
|
vin0 = vld1q_f32(ADDRESS_OF(aInput, i));
|
|
vin1 = vld1q_f32(ADDRESS_OF(aInput, i+4));
|
|
vin2 = vld1q_f32(ADDRESS_OF(aInput, i+8));
|
|
vin3 = vld1q_f32(ADDRESS_OF(aInput, i+12));
|
|
|
|
vscale0 = vld1q_f32(ADDRESS_OF(aScale, i));
|
|
vscale1 = vld1q_f32(ADDRESS_OF(aScale, i+4));
|
|
vscale2 = vld1q_f32(ADDRESS_OF(aScale, i+8));
|
|
vscale3 = vld1q_f32(ADDRESS_OF(aScale, i+12));
|
|
|
|
vout0 = vmulq_f32(vin0, vscale0);
|
|
vout1 = vmulq_f32(vin1, vscale1);
|
|
vout2 = vmulq_f32(vin2, vscale2);
|
|
vout3 = vmulq_f32(vin3, vscale3);
|
|
|
|
vst1q_f32(ADDRESS_OF(aOutput, i), vout0);
|
|
vst1q_f32(ADDRESS_OF(aOutput, i+4), vout1);
|
|
vst1q_f32(ADDRESS_OF(aOutput, i+8), vout2);
|
|
vst1q_f32(ADDRESS_OF(aOutput, i+12), vout3);
|
|
}
|
|
}
|
|
|
|
void
|
|
AudioBufferInPlaceScale_NEON(float* aBlock,
|
|
float aScale,
|
|
uint32_t aSize)
|
|
{
|
|
ASSERT_ALIGNED(aBlock);
|
|
|
|
float32x4_t vin0, vin1, vin2, vin3;
|
|
float32x4_t vout0, vout1, vout2, vout3;
|
|
float32x4_t vscale = vmovq_n_f32(aScale);
|
|
|
|
uint32_t dif = aSize % 16;
|
|
uint32_t vectorSize = aSize - dif;
|
|
uint32_t i = 0;
|
|
for (; i < vectorSize; i+=16) {
|
|
vin0 = vld1q_f32(ADDRESS_OF(aBlock, i));
|
|
vin1 = vld1q_f32(ADDRESS_OF(aBlock, i+4));
|
|
vin2 = vld1q_f32(ADDRESS_OF(aBlock, i+8));
|
|
vin3 = vld1q_f32(ADDRESS_OF(aBlock, i+12));
|
|
|
|
vout0 = vmulq_f32(vin0, vscale);
|
|
vout1 = vmulq_f32(vin1, vscale);
|
|
vout2 = vmulq_f32(vin2, vscale);
|
|
vout3 = vmulq_f32(vin3, vscale);
|
|
|
|
vst1q_f32(ADDRESS_OF(aBlock, i), vout0);
|
|
vst1q_f32(ADDRESS_OF(aBlock, i+4), vout1);
|
|
vst1q_f32(ADDRESS_OF(aBlock, i+8), vout2);
|
|
vst1q_f32(ADDRESS_OF(aBlock, i+12), vout3);
|
|
}
|
|
|
|
for (unsigned j = 0; j < dif; ++i, ++j) {
|
|
aBlock[i] *= aScale;
|
|
}
|
|
}
|
|
|
|
void
|
|
AudioBlockPanStereoToStereo_NEON(const float aInputL[WEBAUDIO_BLOCK_SIZE],
|
|
const float aInputR[WEBAUDIO_BLOCK_SIZE],
|
|
float aGainL, float aGainR, bool aIsOnTheLeft,
|
|
float aOutputL[WEBAUDIO_BLOCK_SIZE],
|
|
float aOutputR[WEBAUDIO_BLOCK_SIZE])
|
|
{
|
|
ASSERT_ALIGNED(aInputL);
|
|
ASSERT_ALIGNED(aInputR);
|
|
ASSERT_ALIGNED(aOutputL);
|
|
ASSERT_ALIGNED(aOutputR);
|
|
|
|
float32x4_t vinL0, vinL1;
|
|
float32x4_t vinR0, vinR1;
|
|
float32x4_t voutL0, voutL1;
|
|
float32x4_t voutR0, voutR1;
|
|
float32x4_t vscaleL = vmovq_n_f32(aGainL);
|
|
float32x4_t vscaleR = vmovq_n_f32(aGainR);
|
|
|
|
if (aIsOnTheLeft) {
|
|
for (uint32_t i = 0; i < WEBAUDIO_BLOCK_SIZE; i+=8) {
|
|
vinL0 = vld1q_f32(ADDRESS_OF(aInputL, i));
|
|
vinL1 = vld1q_f32(ADDRESS_OF(aInputL, i+4));
|
|
|
|
vinR0 = vld1q_f32(ADDRESS_OF(aInputR, i));
|
|
vinR1 = vld1q_f32(ADDRESS_OF(aInputR, i+4));
|
|
|
|
voutL0 = vmlaq_f32(vinL0, vinR0, vscaleL);
|
|
voutL1 = vmlaq_f32(vinL1, vinR1, vscaleL);
|
|
|
|
vst1q_f32(ADDRESS_OF(aOutputL, i), voutL0);
|
|
vst1q_f32(ADDRESS_OF(aOutputL, i+4), voutL1);
|
|
|
|
voutR0 = vmulq_f32(vinR0, vscaleR);
|
|
voutR1 = vmulq_f32(vinR1, vscaleR);
|
|
|
|
vst1q_f32(ADDRESS_OF(aOutputR, i), voutR0);
|
|
vst1q_f32(ADDRESS_OF(aOutputR, i+4), voutR1);
|
|
}
|
|
} else {
|
|
for (uint32_t i = 0; i < WEBAUDIO_BLOCK_SIZE; i+=8) {
|
|
vinL0 = vld1q_f32(ADDRESS_OF(aInputL, i));
|
|
vinL1 = vld1q_f32(ADDRESS_OF(aInputL, i+4));
|
|
|
|
vinR0 = vld1q_f32(ADDRESS_OF(aInputR, i));
|
|
vinR1 = vld1q_f32(ADDRESS_OF(aInputR, i+4));
|
|
|
|
voutL0 = vmulq_f32(vinL0, vscaleL);
|
|
voutL1 = vmulq_f32(vinL1, vscaleL);
|
|
|
|
vst1q_f32(ADDRESS_OF(aOutputL, i), voutL0);
|
|
vst1q_f32(ADDRESS_OF(aOutputL, i+4), voutL1);
|
|
|
|
voutR0 = vmlaq_f32(vinR0, vinL0, vscaleR);
|
|
voutR1 = vmlaq_f32(vinR1, vinL1, vscaleR);
|
|
|
|
vst1q_f32(ADDRESS_OF(aOutputR, i), voutR0);
|
|
vst1q_f32(ADDRESS_OF(aOutputR, i+4), voutR1);
|
|
}
|
|
}
|
|
}
|
|
}
|