Skip to content
Projects
Groups
Snippets
Help
Loading...
Help
Support
Keyboard shortcuts
?
Submit feedback
Contribute to GitLab
Sign in / Register
Toggle navigation
O
OpenXG-RAN
Project overview
Project overview
Details
Activity
Releases
Repository
Repository
Files
Commits
Branches
Tags
Contributors
Graph
Compare
Issues
0
Issues
0
List
Boards
Labels
Milestones
Merge Requests
0
Merge Requests
0
CI / CD
CI / CD
Pipelines
Jobs
Schedules
Analytics
Analytics
CI / CD
Repository
Value Stream
Wiki
Wiki
Snippets
Snippets
Members
Members
Collapse sidebar
Close sidebar
Activity
Graph
Create a new issue
Jobs
Commits
Issue Boards
Open sidebar
canghaiwuhen
OpenXG-RAN
Commits
9c01cc66
Commit
9c01cc66
authored
Aug 14, 2020
by
Sakthivel Velumani
Browse files
Options
Browse Files
Download
Email Patches
Plain Diff
diabling avx2 for qpsk
parent
8aa88999
Changes
3
Hide whitespace changes
Inline
Side-by-side
Showing
3 changed files
with
6 additions
and
4 deletions
+6
-4
openair1/PHY/MODULATION/nr_modulation.c
openair1/PHY/MODULATION/nr_modulation.c
+4
-2
openair1/PHY/NR_REFSIG/nr_gen_mod_table.c
openair1/PHY/NR_REFSIG/nr_gen_mod_table.c
+1
-1
openair1/PHY/NR_REFSIG/nr_mod_table.h
openair1/PHY/NR_REFSIG/nr_mod_table.h
+1
-1
No files found.
openair1/PHY/MODULATION/nr_modulation.c
View file @
9c01cc66
...
@@ -38,7 +38,7 @@ void nr_modulation(uint32_t *in,
...
@@ -38,7 +38,7 @@ void nr_modulation(uint32_t *in,
uint32_t
bit_cnt
;
uint32_t
bit_cnt
;
uint64_t
x
,
x1
,
x2
;
uint64_t
x
,
x1
,
x2
;
#if defined(__AVX2__)
#if
0//
defined(__AVX2__)
uint16_t *in_2bytes = (uint16_t*) in;
uint16_t *in_2bytes = (uint16_t*) in;
__m256i *nr_mod_table256;
__m256i *nr_mod_table256;
__m256i *out256;
__m256i *out256;
...
@@ -113,7 +113,9 @@ void nr_modulation(uint32_t *in,
...
@@ -113,7 +113,9 @@ void nr_modulation(uint32_t *in,
out32
[
i
]
=
nr_mod_table32
[
in_bytes
[
i
]];
out32
[
i
]
=
nr_mod_table32
[
in_bytes
[
i
]];
return
;
return
;
#if defined(__AVX2__)
#if 0//defined(__AVX2__)
// disabling this as it is slower than SSE2
// (maybe because L1 cache could not hold the large table)
case 2:
case 2:
nr_mod_table256 = (__m256i*) nr_qpsk_2byte_mod_table;
nr_mod_table256 = (__m256i*) nr_qpsk_2byte_mod_table;
out256 = (__m256i*) out;
out256 = (__m256i*) out;
...
...
openair1/PHY/NR_REFSIG/nr_gen_mod_table.c
View file @
9c01cc66
...
@@ -34,7 +34,7 @@ void nr_generate_modulation_table() {
...
@@ -34,7 +34,7 @@ void nr_generate_modulation_table() {
short
nr_qpsk_mod_table
[
8
]
=
{
16384
,
16384
,
-
16384
,
16384
,
16384
,
-
16384
,
-
16384
,
-
16384
};
short
nr_qpsk_mod_table
[
8
]
=
{
16384
,
16384
,
-
16384
,
16384
,
16384
,
-
16384
,
-
16384
,
-
16384
};
#if defined(__AVX2__)
#if
0//
defined(__AVX2__)
//QPSK m256
//QPSK m256
table = (short*) nr_qpsk_2byte_mod_table;
table = (short*) nr_qpsk_2byte_mod_table;
for (i=0; i<65536; i++) {
for (i=0; i<65536; i++) {
...
...
openair1/PHY/NR_REFSIG/nr_mod_table.h
View file @
9c01cc66
...
@@ -31,7 +31,7 @@
...
@@ -31,7 +31,7 @@
short
nr_qpsk_mod_table
[
8
];
short
nr_qpsk_mod_table
[
8
];
#if defined(__AVX2__)
#if
0//
defined(__AVX2__)
__m256i nr_qpsk_2byte_mod_table[65536];
__m256i nr_qpsk_2byte_mod_table[65536];
#elif
defined
(
__SSE2__
)
#elif
defined
(
__SSE2__
)
__m128i
nr_qpsk_byte_mod_table
[
2048
];
__m128i
nr_qpsk_byte_mod_table
[
2048
];
...
...
Write
Preview
Markdown
is supported
0%
Try again
or
attach a new file
Attach a file
Cancel
You are about to add
0
people
to the discussion. Proceed with caution.
Finish editing this message first!
Cancel
Please
register
or
sign in
to comment