-
Notifications
You must be signed in to change notification settings - Fork 1
/
Copy pathStageProcNeonV4.hpp
115 lines (65 loc) · 2.79 KB
/
StageProcNeonV4.hpp
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
108
109
110
111
112
113
114
115
/*****************************************************************************
StageProcNeonV4.hpp
Author: Laurent de Soras, 2016
--- Legal stuff ---
This program is free software. It comes without any warranty, to
the extent permitted by applicable law. You can redistribute it
and/or modify it under the terms of the Do What The Fuck You Want
To Public License, Version 2, as published by Sam Hocevar. See
http://sam.zoy.org/wtfpl/COPYING for more details.
*Tab=3***********************************************************************/
#if ! defined (hiir_StageProcNeonV4_CODEHEADER_INCLUDED)
#define hiir_StageProcNeonV4_CODEHEADER_INCLUDED
/*\\\ INCLUDE FILES \\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\*/
#include "hiir/fnc_neon.h"
#include "hiir/StageDataNeonV4.h"
namespace hiir
{
/*\\\ PUBLIC \\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\*/
template <int CUR>
void StageProcNeonV4 <CUR>::process_sample_pos (StageDataNeonV4 *stage_ptr, float32x4_t &y, float32x4_t &mem)
{
StageProcNeonV4 <CUR>::process_sample_pos_rec (stage_ptr, y, mem);
storea (stage_ptr [CUR]._mem, y);
}
template <int CUR>
void StageProcNeonV4 <CUR>::process_sample_neg (StageDataNeonV4 *stage_ptr, float32x4_t &y, float32x4_t &mem)
{
StageProcNeonV4 <CUR>::process_sample_neg_rec (stage_ptr, y, mem);
storea (stage_ptr [CUR]._mem, y);
}
template <int CUR>
void StageProcNeonV4 <CUR>::process_sample_pos_rec (StageDataNeonV4 *stage_ptr, float32x4_t &y, float32x4_t &mem)
{
StageProcNeonV4 <CUR - 1>::process_sample_pos_rec (stage_ptr, y, mem);
const float32x4_t x = mem;
storea (stage_ptr [CUR - 1]._mem, y);
mem = load4a (stage_ptr [CUR]._mem);
y = vmlaq_f32 (x, y - mem, load4a (stage_ptr [CUR]._coef));
}
template <>
inline void StageProcNeonV4 <0>::process_sample_pos_rec (StageDataNeonV4 * /* stage_ptr */, float32x4_t & /* y */, float32x4_t & /* mem */)
{
// Nothing, stops the recursion
}
template <int CUR>
void StageProcNeonV4 <CUR>::process_sample_neg_rec (StageDataNeonV4 *stage_ptr, float32x4_t &y, float32x4_t &mem)
{
StageProcNeonV4 <CUR - 1>::process_sample_neg_rec (stage_ptr, y, mem);
const float32x4_t x = mem;
storea (stage_ptr [CUR - 1]._mem, y);
mem = load4a (stage_ptr [CUR]._mem);
y += mem;
y *= load4a (stage_ptr [CUR]._coef);
y -= x;
}
template <>
inline void StageProcNeonV4 <0>::process_sample_neg_rec (StageDataNeonV4 * /* stage_ptr */, float32x4_t & /* y */, float32x4_t & /* mem */)
{
// Nothing, stops the recursion
}
/*\\\ PROTECTED \\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\*/
/*\\\ PRIVATE \\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\*/
} // namespace hiir
#endif // hiir_StageProcNeonV4_CODEHEADER_INCLUDED
/*\\\ EOF \\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\\*/