From 63b28d3610152805cdabfadb77c722b80e2221eb Mon Sep 17 00:00:00 2001 From: Raymond Knopp Date: Tue, 3 May 2022 21:26:18 +0200 Subject: [PATCH] clean up (removal) of ldpc generated files on repository --- .../CODING/nrLDPC_decoder/nrLDPC_decoder.c | 14 +- .../generator_bnProc/bnProc_gen_BG2_avx2.c | 4 +- .../bnProcPc_gen_BG1_avx512.c | 4 +- .../bnProcPc_gen_BG2_avx512.c | 4 +- .../bnProc_gen_BG1_avx512.c | 2 +- .../bnProc_gen_BG2_avx512.c | 2 +- .../generator_cnProc/cnProc_gen_BG1_avx2.c | 2 +- .../cnProc_gen_BG2_avx512.c | 2 +- .../bnProc/nrLDPC_bnProc_BG1_R13_AVX2.h | 473 ---- .../bnProc/nrLDPC_bnProc_BG1_R23_AVX2.h | 168 -- .../bnProc/nrLDPC_bnProc_BG1_R89_AVX2.h | 78 - .../bnProc/nrLDPC_bnProc_BG2_R13_AVX2.c | 270 -- .../bnProc/nrLDPC_bnProc_BG2_R13_AVX2.h | 508 ---- .../bnProc/nrLDPC_bnProc_BG2_R15_AVX2.c | 483 ---- .../bnProc/nrLDPC_bnProc_BG2_R15_AVX2.h | 1005 ------- .../bnProc/nrLDPC_bnProc_BG2_R23_AVX2.c | 101 - .../bnProc/nrLDPC_bnProc_BG2_R23_AVX2.h | 198 -- .../bnProcPc/nrLDPC_bnProcPc_BG1_R13_AVX2.h | 729 ------ .../bnProcPc/nrLDPC_bnProcPc_BG1_R23_AVX2.h | 279 -- .../bnProcPc/nrLDPC_bnProcPc_BG1_R89_AVX2.h | 133 - .../bnProcPc/nrLDPC_bnProcPc_BG2_R13_AVX2.h | 427 --- .../bnProcPc/nrLDPC_bnProcPc_BG2_R15_AVX2.h | 737 ------ .../bnProcPc/nrLDPC_bnProcPc_BG2_R23_AVX2.h | 167 -- .../nrLDPC_bnProcPc_BG1_R13_AVX512.h | 0 .../nrLDPC_bnProcPc_BG1_R23_AVX512.h | 0 .../nrLDPC_bnProc_BG1_R13_AVX512.h | 473 ---- .../nrLDPC_bnProc_BG1_R23_AVX512.h | 168 -- .../nrLDPC_bnProc_BG1_R89_AVX512.h | 78 - .../nrLDPC_bnProc_BG2_R13_AVX512.h | 268 -- .../nrLDPC_bnProc_BG2_R15_AVX512.h | 481 ---- .../nrLDPC_bnProc_BG2_R23_AVX512.h | 99 - .../nrLDPC_bnProcPc_BG1_R13_AVX512.h | 743 ------ .../nrLDPC_bnProcPc_BG1_R23_AVX512.h | 293 --- .../nrLDPC_bnProcPc_BG1_R89_AVX512.h | 147 -- .../nrLDPC_bnProcPc_BG2_R13_AVX512.h | 441 ---- .../nrLDPC_bnProcPc_BG2_R15_AVX512.h | 751 ------ .../nrLDPC_bnProcPc_BG2_R23_AVX512.h | 181 -- .../cnProc/nrLDPC_cnProc_BG1_R13_AVX2.h | 2320 ----------------- .../cnProc/nrLDPC_cnProc_BG1_R23_AVX2.h | 2071 --------------- .../cnProc/nrLDPC_cnProc_BG1_R89_AVX2.h | 1151 -------- .../cnProc/nrLDPC_cnProc_BG2_R13_AVX2.h | 775 ------ .../cnProc/nrLDPC_cnProc_BG2_R15_AVX2.h | 815 ------ .../cnProc/nrLDPC_cnProc_BG2_R23_AVX2.h | 694 ----- .../nrLDPC_cnProc_BG1_R13_AVX512.h | 2320 ----------------- .../nrLDPC_cnProc_BG1_R23_AVX512.h | 2071 --------------- .../nrLDPC_cnProc_BG1_R89_AVX512.h | 1151 -------- .../nrLDPC_cnProc_BG2_R13_AVX512.h | 775 ------ .../nrLDPC_cnProc_BG2_R15_AVX512.h | 806 ------ .../nrLDPC_cnProc_BG2_R23_AVX512.h | 694 ----- 49 files changed, 17 insertions(+), 25539 deletions(-) delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG1_R13_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG1_R23_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG1_R89_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG2_R13_AVX2.c delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG2_R13_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG2_R15_AVX2.c delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG2_R15_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG2_R23_AVX2.c delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG2_R23_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProcPc/nrLDPC_bnProcPc_BG1_R13_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProcPc/nrLDPC_bnProcPc_BG1_R23_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProcPc/nrLDPC_bnProcPc_BG1_R89_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProcPc/nrLDPC_bnProcPc_BG2_R13_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProcPc/nrLDPC_bnProcPc_BG2_R15_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProcPc/nrLDPC_bnProcPc_BG2_R23_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProcPc_avx512/nrLDPC_bnProcPc_BG1_R13_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProcPc_avx512/nrLDPC_bnProcPc_BG1_R23_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc_avx512/nrLDPC_bnProc_BG1_R13_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc_avx512/nrLDPC_bnProc_BG1_R23_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc_avx512/nrLDPC_bnProc_BG1_R89_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc_avx512/nrLDPC_bnProc_BG2_R13_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc_avx512/nrLDPC_bnProc_BG2_R15_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc_avx512/nrLDPC_bnProc_BG2_R23_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bn_avx512/nrLDPC_bnProcPc_BG1_R13_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bn_avx512/nrLDPC_bnProcPc_BG1_R23_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bn_avx512/nrLDPC_bnProcPc_BG1_R89_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bn_avx512/nrLDPC_bnProcPc_BG2_R13_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bn_avx512/nrLDPC_bnProcPc_BG2_R15_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bn_avx512/nrLDPC_bnProcPc_BG2_R23_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc/nrLDPC_cnProc_BG1_R13_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc/nrLDPC_cnProc_BG1_R23_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc/nrLDPC_cnProc_BG1_R89_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc/nrLDPC_cnProc_BG2_R13_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc/nrLDPC_cnProc_BG2_R15_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc/nrLDPC_cnProc_BG2_R23_AVX2.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc_avx512/nrLDPC_cnProc_BG1_R13_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc_avx512/nrLDPC_cnProc_BG1_R23_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc_avx512/nrLDPC_cnProc_BG1_R89_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc_avx512/nrLDPC_cnProc_BG2_R13_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc_avx512/nrLDPC_cnProc_BG2_R15_AVX512.h delete mode 100644 openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/cnProc_avx512/nrLDPC_cnProc_BG2_R23_AVX512.h diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_decoder.c b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_decoder.c index 5a368228cf..3c95c9c69a 100644 --- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_decoder.c +++ b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_decoder.c @@ -155,13 +155,13 @@ static inline uint32_t nrLDPC_decoder_core(int8_t* p_llr, int8_t* p_out, uint32_ // int8_t* cnProcBuf= cnProcBuf; // int8_t* cnProcBufRes= cnProcBufRes; - int8_t cnProcBuf[NR_LDPC_SIZE_CN_PROC_BUF] __attribute__ ((aligned(32))) = {0}; - int8_t cnProcBufRes[NR_LDPC_SIZE_CN_PROC_BUF] __attribute__ ((aligned(32))) = {0}; - int8_t bnProcBuf[NR_LDPC_SIZE_BN_PROC_BUF] __attribute__ ((aligned(32))) = {0}; - int8_t bnProcBufRes[NR_LDPC_SIZE_BN_PROC_BUF] __attribute__ ((aligned(32))) = {0}; - int8_t llrRes[NR_LDPC_MAX_NUM_LLR] __attribute__ ((aligned(32))) = {0}; - int8_t llrProcBuf[NR_LDPC_MAX_NUM_LLR] __attribute__ ((aligned(32))) = {0}; - int8_t llrOut[NR_LDPC_MAX_NUM_LLR] __attribute__ ((aligned(32))) = {0}; + int8_t cnProcBuf[NR_LDPC_SIZE_CN_PROC_BUF] __attribute__ ((aligned(64))) = {0}; + int8_t cnProcBufRes[NR_LDPC_SIZE_CN_PROC_BUF] __attribute__ ((aligned(64))) = {0}; + int8_t bnProcBuf[NR_LDPC_SIZE_BN_PROC_BUF] __attribute__ ((aligned(64))) = {0}; + int8_t bnProcBufRes[NR_LDPC_SIZE_BN_PROC_BUF] __attribute__ ((aligned(64))) = {0}; + int8_t llrRes[NR_LDPC_MAX_NUM_LLR] __attribute__ ((aligned(64))) = {0}; + int8_t llrProcBuf[NR_LDPC_MAX_NUM_LLR] __attribute__ ((aligned(64))) = {0}; + int8_t llrOut[NR_LDPC_MAX_NUM_LLR] __attribute__ ((aligned(64))) = {0}; // Minimum number of iterations is 1 // 0 iterations means hard-decision on input LLRs uint32_t i = 1; diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc/bnProc_gen_BG2_avx2.c b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc/bnProc_gen_BG2_avx2.c index f07b631b1a..518fd8f3b5 100644 --- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc/bnProc_gen_BG2_avx2.c +++ b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc/bnProc_gen_BG2_avx2.c @@ -15,8 +15,8 @@ void nrLDPC_bnProc_BG2_generator_AVX2(int R) // system("mkdir -p ../ldpc_gen_files"); - char fname[50]; - sprintf(fname,"../ldpc_gen_files/bnProc/nrLDPC_bnProc_BG2_R%s_AVX2.c",ratestr[R]); + char fname[150]; + sprintf(fname,"../ldpc_gen_files/bnProc/nrLDPC_bnProc_BG2_R%s_AVX2.h",ratestr[R]); FILE *fd=fopen(fname,"w"); if (fd == NULL) {printf("Cannot create \n");abort();} diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProcPc_gen_BG1_avx512.c b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProcPc_gen_BG1_avx512.c index 24aa16349e..3be26012a5 100644 --- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProcPc_gen_BG1_avx512.c +++ b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProcPc_gen_BG1_avx512.c @@ -16,9 +16,9 @@ void nrLDPC_bnProcPc_BG1_generator_AVX512(int R) char fname[500]; - sprintf(fname,"../ldpc_gen_files/bn_avx512/nrLDPC_bnProcPc_BG1_R%s_AVX512.h",ratestr[R]); + sprintf(fname,"../ldpc_gen_files/bnProcPc_avx512/nrLDPC_bnProcPc_BG1_R%s_AVX512.h",ratestr[R]); FILE *fd=fopen(fname,"w"); - if (fd == NULL) {printf("Cannot create \n");abort();} + if (fd == NULL) {printf("Cannot create %s\n",fname);abort();} diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProcPc_gen_BG2_avx512.c b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProcPc_gen_BG2_avx512.c index caec9e7e8f..8b1a18ee25 100644 --- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProcPc_gen_BG2_avx512.c +++ b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProcPc_gen_BG2_avx512.c @@ -16,9 +16,9 @@ void nrLDPC_bnProcPc_BG2_generator_AVX512(int R) // system("mkdir -p ../ldpc_gen_files"); char fname[500]; - sprintf(fname,"../ldpc_gen_files/bn_avx512/nrLDPC_bnProcPc_BG2_R%s_AVX512.h",ratestr[R]); + sprintf(fname,"../ldpc_gen_files/bnProcPc_avx512/nrLDPC_bnProcPc_BG2_R%s_AVX512.h",ratestr[R]); FILE *fd=fopen(fname,"w"); - if (fd == NULL) {printf("Cannot create \n");abort();} + if (fd == NULL) {printf("Cannot create %s\n",fname);abort();} // fprintf(fd,"#include \n"); //fprintf(fd,"#include \n"); diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProc_gen_BG1_avx512.c b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProc_gen_BG1_avx512.c index 5985beda15..114f1b5422 100644 --- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProc_gen_BG1_avx512.c +++ b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProc_gen_BG1_avx512.c @@ -18,7 +18,7 @@ void nrLDPC_bnProc_BG1_generator_AVX512(int R) char fname[500]; sprintf(fname,"../ldpc_gen_files/bnProc_avx512/nrLDPC_bnProc_BG1_R%s_AVX512.h",ratestr[R]); FILE *fd=fopen(fname,"w"); - if (fd == NULL) {printf("Cannot create \n");abort();} + if (fd == NULL) {printf("Cannot create %s\n",fname);abort();} //fprintf(fd,"#include \n"); //fprintf(fd,"#include \n"); diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProc_gen_BG2_avx512.c b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProc_gen_BG2_avx512.c index 17a65b6501..780001bbe1 100644 --- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProc_gen_BG2_avx512.c +++ b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_bnProc_avx512/bnProc_gen_BG2_avx512.c @@ -18,7 +18,7 @@ void nrLDPC_bnProc_BG2_generator_AVX512(int R) char fname[500]; sprintf(fname,"../ldpc_gen_files/bnProc_avx512/nrLDPC_bnProc_BG2_R%s_AVX512.h",ratestr[R]); FILE *fd=fopen(fname,"w"); - if (fd == NULL) {printf("Cannot create \n");abort();} + if (fd == NULL) {printf("Cannot create %s\n",fname);abort();} fprintf(fd,"#include \n"); fprintf(fd,"#include \n"); diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_cnProc/cnProc_gen_BG1_avx2.c b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_cnProc/cnProc_gen_BG1_avx2.c index d860b3e633..8faec78584 100644 --- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_cnProc/cnProc_gen_BG1_avx2.c +++ b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_cnProc/cnProc_gen_BG1_avx2.c @@ -11,7 +11,7 @@ void nrLDPC_cnProc_BG1_generator_AVX2(int R) // system("mkdir -p ../ldpc_gen_files"); - char fname[50]; + char fname[150]; sprintf(fname,"../ldpc_gen_files/cnProc/nrLDPC_cnProc_BG1_R%s_AVX2.h",ratestr[R]); FILE *fd=fopen(fname,"w"); if (fd == NULL) {printf("Cannot create \n");abort();} diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_cnProc_avx512/cnProc_gen_BG2_avx512.c b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_cnProc_avx512/cnProc_gen_BG2_avx512.c index 846ad2659a..b046d8e2fa 100644 --- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_cnProc_avx512/cnProc_gen_BG2_avx512.c +++ b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/generator_cnProc_avx512/cnProc_gen_BG2_avx512.c @@ -13,7 +13,7 @@ void nrLDPC_cnProc_BG2_generator_AVX512(int R) // system("mkdir -p ../ldpc_gen_files"); - char fname[50]; + char fname[150]; sprintf(fname,"../ldpc_gen_files/cnProc_avx512/nrLDPC_cnProc_BG2_R%s_AVX512.h",ratestr[R]); FILE *fd=fopen(fname,"w"); if (fd == NULL) {printf("Cannot create \n");abort();} diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG1_R13_AVX2.h b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG1_R13_AVX2.h deleted file mode 100644 index bd46948100..0000000000 --- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/bnProc/nrLDPC_bnProc_BG1_R13_AVX2.h +++ /dev/null @@ -1,473 +0,0 @@ -static inline void nrLDPC_bnProc_BG1_R13_AVX2(int8_t* bnProcBuf,int8_t* bnProcBufRes, int8_t* llrRes, uint16_t Z ) { - uint32_t M, i; -// Process group with 2 CNs -// Process group with 3 CNs -// Process group with 4 CNs - M = (1*Z + 31)>>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i -#include -void nrLDPC_bnProc_BG2_R13_AVX2(int8_t* bnProcBuf,int8_t* bnProcBufRes, int8_t* llrRes, uint16_t Z ) { - __m256i* p_bnProcBuf; - __m256i* p_bnProcBufRes; - __m256i* p_llrRes; - __m256i* p_res; - uint32_t M, i; -// Process group with 2 CNs - M = (1*Z + 31)>>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [6912]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [6912]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [6912]; - for (i=0;i>5; - *p_res = _mm256_subs_epi8(*p_llrRes, p_bnProcBuf[0 + i]); - p_res++; - p_llrRes++; -} - p_res = &p_bnProcBufRes[12]; - p_llrRes = (__m256i*) &llrRes [6912]; - for (i=0;i>5; - *p_res = _mm256_subs_epi8(*p_llrRes, p_bnProcBuf[12 + i]); - p_res++; - p_llrRes++; -} -// Process group with 3 CNs -// Process group with 4 CNs - M = (2*Z + 31)>>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [7680]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [7680]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [7296]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [10752]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [10752]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [8064]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [12672]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [12672]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [8448]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [24192]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [24192]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [10368]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [26880]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [26880]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [10752]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [29952]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [29952]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [11136]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [34944]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [34944]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [11520]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [40320]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [40320]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [11904]; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i -#include -void nrLDPC_bnProc_BG2_R15_AVX2(int8_t* bnProcBuf,int8_t* bnProcBufRes, int8_t* llrRes, uint16_t Z ) { - __m256i* p_bnProcBuf; - __m256i* p_bnProcBufRes; - __m256i* p_llrRes; - __m256i* p_res; - uint32_t M, i; -// Process group with 2 CNs -// Process group with 3 CNs -// Process group with 4 CNs -// Process group with 5 CNs - M = (2*Z + 31)>>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [14592]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [14592]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [14592]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [18432]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [18432]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [15360]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [20736]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [20736]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [15744]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [23424]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [23424]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [16128]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [26496]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [26496]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [16512]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [33408]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [33408]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [17280]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [37248]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [37248]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [17664]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [41856]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [41856]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [18048]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [46848]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [46848]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [18432]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [52224]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [52224]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [18816]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [58368]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [58368]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [19200]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [66816]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [66816]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [19584]; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i>5; - for (i=0;i -#include -void nrLDPC_bnProc_BG2_R23_AVX2(int8_t* bnProcBuf,int8_t* bnProcBufRes, int8_t* llrRes, uint16_t Z ) { - __m256i* p_bnProcBuf; - __m256i* p_bnProcBufRes; - __m256i* p_llrRes; - __m256i* p_res; - uint32_t M, i; -// Process group with 2 CNs - M = (3*Z + 31)>>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [1152]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [1152]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [1152]; - for (i=0;i>5; - *p_res = _mm256_subs_epi8(*p_llrRes, p_bnProcBuf[0 + i]); - p_res++; - p_llrRes++; -} - p_res = &p_bnProcBufRes[36]; - p_llrRes = (__m256i*) &llrRes [1152]; - for (i=0;i>5; - *p_res = _mm256_subs_epi8(*p_llrRes, p_bnProcBuf[36 + i]); - p_res++; - p_llrRes++; -} -// Process group with 3 CNs - M = (5*Z + 31)>>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [3456]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [3456]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [2304]; - for (i=0;i>5; - *p_res = _mm256_subs_epi8(*p_llrRes, p_bnProcBuf[0 + i]); - p_res++; - p_llrRes++; -} - p_res = &p_bnProcBufRes[60]; - p_llrRes = (__m256i*) &llrRes [2304]; - for (i=0;i>5; - *p_res = _mm256_subs_epi8(*p_llrRes, p_bnProcBuf[60 + i]); - p_res++; - p_llrRes++; -} - p_res = &p_bnProcBufRes[120]; - p_llrRes = (__m256i*) &llrRes [2304]; - for (i=0;i>5; - *p_res = _mm256_subs_epi8(*p_llrRes, p_bnProcBuf[120 + i]); - p_res++; - p_llrRes++; -} -// Process group with 4 CNs - M = (3*Z + 31)>>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [9216]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [9216]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [4224]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [13824]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [13824]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [5376]; - for (i=0;i>5; - p_bnProcBuf = (__m256i*) &bnProcBuf [17664]; - p_bnProcBufRes = (__m256i*) &bnProcBufRes [17664]; - p_res = &p_bnProcBufRes[0]; - p_llrRes = (__m256i*) &llrRes [6144]; - for (i=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [16128]; - p_llrProcBuf = (__m128i*) &llrProcBuf [16128]; - p_llrRes = (__m256i*) &llrRes [16128]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [17664]; - p_llrProcBuf = (__m128i*) &llrProcBuf [16512]; - p_llrRes = (__m256i*) &llrRes [16512]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [19584]; - p_llrProcBuf = (__m128i*) &llrProcBuf [16896]; - p_llrRes = (__m256i*) &llrRes [16896]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [24192]; - p_llrProcBuf = (__m128i*) &llrProcBuf [17664]; - p_llrRes = (__m256i*) &llrRes [17664]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [34944]; - p_llrProcBuf = (__m128i*) &llrProcBuf [19200]; - p_llrRes = (__m256i*) &llrRes [19200]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [44160]; - p_llrProcBuf = (__m128i*) &llrProcBuf [20352]; - p_llrRes = (__m256i*) &llrRes [20352]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [47616]; - p_llrProcBuf = (__m128i*) &llrProcBuf [20736]; - p_llrRes = (__m256i*) &llrRes [20736]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [62976]; - p_llrProcBuf = (__m128i*) &llrProcBuf [22272]; - p_llrRes = (__m256i*) &llrRes [22272]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [75648]; - p_llrProcBuf = (__m128i*) &llrProcBuf [23424]; - p_llrRes = (__m256i*) &llrRes [23424]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [94080]; - p_llrProcBuf = (__m128i*) &llrProcBuf [24960]; - p_llrRes = (__m256i*) &llrRes [24960]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [99072]; - p_llrProcBuf = (__m128i*) &llrProcBuf [25344]; - p_llrRes = (__m256i*) &llrRes [25344]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [109824]; - p_llrProcBuf = (__m128i*) &llrProcBuf [25728]; - p_llrRes = (__m256i*) &llrRes [25728]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [3456]; - p_llrProcBuf = (__m128i*) &llrProcBuf [3456]; - p_llrRes = (__m256i*) &llrRes [3456]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [4224]; - p_llrProcBuf = (__m128i*) &llrProcBuf [3840]; - p_llrRes = (__m256i*) &llrRes [3840]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [9984]; - p_llrProcBuf = (__m128i*) &llrProcBuf [5760]; - p_llrRes = (__m256i*) &llrRes [5760]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [14592]; - p_llrProcBuf = (__m128i*) &llrProcBuf [6912]; - p_llrRes = (__m256i*) &llrRes [6912]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [28032]; - p_llrProcBuf = (__m128i*) &llrProcBuf [9600]; - p_llrRes = (__m256i*) &llrRes [9600]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [46464]; - p_llrProcBuf = (__m128i*) &llrProcBuf [12672]; - p_llrRes = (__m256i*) &llrRes [12672]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [50688]; - p_llrProcBuf = (__m128i*) &llrProcBuf [13056]; - p_llrRes = (__m256i*) &llrRes [13056]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [384]; - p_llrProcBuf = (__m128i*) &llrProcBuf [384]; - p_llrRes = (__m256i*) &llrRes [384]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [2688]; - p_llrProcBuf = (__m128i*) &llrProcBuf [1536]; - p_llrRes = (__m256i*) &llrRes [1536]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [26880]; - p_llrProcBuf = (__m128i*) &llrProcBuf [9600]; - p_llrRes = (__m256i*) &llrRes [9600]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [28416]; - p_llrProcBuf = (__m128i*) &llrProcBuf [9984]; - p_llrRes = (__m256i*) &llrRes [9984]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [6912]; - p_llrProcBuf = (__m128i*) &llrProcBuf [6912]; - p_llrRes = (__m256i*) &llrRes [6912]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [7680]; - p_llrProcBuf = (__m128i*) &llrProcBuf [7296]; - p_llrRes = (__m256i*) &llrRes [7296]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [10752]; - p_llrProcBuf = (__m128i*) &llrProcBuf [8064]; - p_llrRes = (__m256i*) &llrRes [8064]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [12672]; - p_llrProcBuf = (__m128i*) &llrProcBuf [8448]; - p_llrRes = (__m256i*) &llrRes [8448]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [24192]; - p_llrProcBuf = (__m128i*) &llrProcBuf [10368]; - p_llrRes = (__m256i*) &llrRes [10368]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [26880]; - p_llrProcBuf = (__m128i*) &llrProcBuf [10752]; - p_llrRes = (__m256i*) &llrRes [10752]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [29952]; - p_llrProcBuf = (__m128i*) &llrProcBuf [11136]; - p_llrRes = (__m256i*) &llrRes [11136]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [34944]; - p_llrProcBuf = (__m128i*) &llrProcBuf [11520]; - p_llrRes = (__m256i*) &llrRes [11520]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [40320]; - p_llrProcBuf = (__m128i*) &llrProcBuf [11904]; - p_llrRes = (__m256i*) &llrRes [11904]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [14592]; - p_llrProcBuf = (__m128i*) &llrProcBuf [14592]; - p_llrRes = (__m256i*) &llrRes [14592]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [18432]; - p_llrProcBuf = (__m128i*) &llrProcBuf [15360]; - p_llrRes = (__m256i*) &llrRes [15360]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [20736]; - p_llrProcBuf = (__m128i*) &llrProcBuf [15744]; - p_llrRes = (__m256i*) &llrRes [15744]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [23424]; - p_llrProcBuf = (__m128i*) &llrProcBuf [16128]; - p_llrRes = (__m256i*) &llrRes [16128]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [26496]; - p_llrProcBuf = (__m128i*) &llrProcBuf [16512]; - p_llrRes = (__m256i*) &llrRes [16512]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [33408]; - p_llrProcBuf = (__m128i*) &llrProcBuf [17280]; - p_llrRes = (__m256i*) &llrRes [17280]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [37248]; - p_llrProcBuf = (__m128i*) &llrProcBuf [17664]; - p_llrRes = (__m256i*) &llrRes [17664]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [41856]; - p_llrProcBuf = (__m128i*) &llrProcBuf [18048]; - p_llrRes = (__m256i*) &llrRes [18048]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [46848]; - p_llrProcBuf = (__m128i*) &llrProcBuf [18432]; - p_llrRes = (__m256i*) &llrRes [18432]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [52224]; - p_llrProcBuf = (__m128i*) &llrProcBuf [18816]; - p_llrRes = (__m256i*) &llrRes [18816]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [58368]; - p_llrProcBuf = (__m128i*) &llrProcBuf [19200]; - p_llrRes = (__m256i*) &llrRes [19200]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [66816]; - p_llrProcBuf = (__m128i*) &llrProcBuf [19584]; - p_llrRes = (__m256i*) &llrRes [19584]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [1152]; - p_llrProcBuf = (__m128i*) &llrProcBuf [1152]; - p_llrRes = (__m256i*) &llrRes [1152]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [3456]; - p_llrProcBuf = (__m128i*) &llrProcBuf [2304]; - p_llrRes = (__m256i*) &llrRes [2304]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [9216]; - p_llrProcBuf = (__m128i*) &llrProcBuf [4224]; - p_llrRes = (__m256i*) &llrRes [4224]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [13824]; - p_llrProcBuf = (__m128i*) &llrProcBuf [5376]; - p_llrRes = (__m256i*) &llrRes [5376]; - for (int i=0,j=0;i>5; - p_bnProcBuf = (__m128i*) &bnProcBuf [17664]; - p_llrProcBuf = (__m128i*) &llrProcBuf [6144]; - p_llrRes = (__m256i*) &llrRes [6144]; - for (int i=0,j=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i -#include -void nrLDPC_bnProc_BG2_R13_AVX512(int8_t* bnProcBuf,int8_t* bnProcBufRes, int8_t* llrRes, uint16_t Z ) { - uint32_t M, i; -// Process group with 2 CNs - M = (1*Z + 63)>>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i -#include -void nrLDPC_bnProc_BG2_R15_AVX512(int8_t* bnProcBuf,int8_t* bnProcBufRes, int8_t* llrRes, uint16_t Z ) { - uint32_t M, i; -// Process group with 2 CNs -// Process group with 3 CNs -// Process group with 4 CNs -// Process group with 5 CNs - M = (2*Z + 63)>>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i -#include -void nrLDPC_bnProc_BG2_R23_AVX512(int8_t* bnProcBuf,int8_t* bnProcBufRes, int8_t* llrRes, uint16_t Z ) { - uint32_t M, i; -// Process group with 2 CNs - M = (3*Z + 63)>>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [0]; - p_llrProcBuf = (__m256i*) &llrProcBuf [0]; - p_llrRes = (__m512i*) &llrRes [0]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [16128]; - p_llrProcBuf = (__m256i*) &llrProcBuf [16128]; - p_llrRes = (__m512i*) &llrRes [16128]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [17664]; - p_llrProcBuf = (__m256i*) &llrProcBuf [16512]; - p_llrRes = (__m512i*) &llrRes [16512]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [19584]; - p_llrProcBuf = (__m256i*) &llrProcBuf [16896]; - p_llrRes = (__m512i*) &llrRes [16896]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [24192]; - p_llrProcBuf = (__m256i*) &llrProcBuf [17664]; - p_llrRes = (__m512i*) &llrRes [17664]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [34944]; - p_llrProcBuf = (__m256i*) &llrProcBuf [19200]; - p_llrRes = (__m512i*) &llrRes [19200]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [44160]; - p_llrProcBuf = (__m256i*) &llrProcBuf [20352]; - p_llrRes = (__m512i*) &llrRes [20352]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [47616]; - p_llrProcBuf = (__m256i*) &llrProcBuf [20736]; - p_llrRes = (__m512i*) &llrRes [20736]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [62976]; - p_llrProcBuf = (__m256i*) &llrProcBuf [22272]; - p_llrRes = (__m512i*) &llrRes [22272]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [75648]; - p_llrProcBuf = (__m256i*) &llrProcBuf [23424]; - p_llrRes = (__m512i*) &llrRes [23424]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [94080]; - p_llrProcBuf = (__m256i*) &llrProcBuf [24960]; - p_llrRes = (__m512i*) &llrRes [24960]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [99072]; - p_llrProcBuf = (__m256i*) &llrProcBuf [25344]; - p_llrRes = (__m512i*) &llrRes [25344]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [109824]; - p_llrProcBuf = (__m256i*) &llrProcBuf [25728]; - p_llrRes = (__m512i*) &llrRes [25728]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [0]; - p_llrProcBuf = (__m256i*) &llrProcBuf [0]; - p_llrRes = (__m512i*) &llrRes [0]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [3456]; - p_llrProcBuf = (__m256i*) &llrProcBuf [3456]; - p_llrRes = (__m512i*) &llrRes [3456]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [4224]; - p_llrProcBuf = (__m256i*) &llrProcBuf [3840]; - p_llrRes = (__m512i*) &llrRes [3840]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [9984]; - p_llrProcBuf = (__m256i*) &llrProcBuf [5760]; - p_llrRes = (__m512i*) &llrRes [5760]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [14592]; - p_llrProcBuf = (__m256i*) &llrProcBuf [6912]; - p_llrRes = (__m512i*) &llrRes [6912]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [28032]; - p_llrProcBuf = (__m256i*) &llrProcBuf [9600]; - p_llrRes = (__m512i*) &llrRes [9600]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [46464]; - p_llrProcBuf = (__m256i*) &llrProcBuf [12672]; - p_llrRes = (__m512i*) &llrRes [12672]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [50688]; - p_llrProcBuf = (__m256i*) &llrProcBuf [13056]; - p_llrRes = (__m512i*) &llrRes [13056]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [0]; - p_llrProcBuf = (__m256i*) &llrProcBuf [0]; - p_llrRes = (__m512i*) &llrRes [0]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [384]; - p_llrProcBuf = (__m256i*) &llrProcBuf [384]; - p_llrRes = (__m512i*) &llrRes [384]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [2688]; - p_llrProcBuf = (__m256i*) &llrProcBuf [1536]; - p_llrRes = (__m512i*) &llrRes [1536]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [26880]; - p_llrProcBuf = (__m256i*) &llrProcBuf [9600]; - p_llrRes = (__m512i*) &llrRes [9600]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [28416]; - p_llrProcBuf = (__m256i*) &llrProcBuf [9984]; - p_llrRes = (__m512i*) &llrRes [9984]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [0]; - p_llrProcBuf = (__m256i*) &llrProcBuf [0]; - p_llrRes = (__m512i*) &llrRes [0]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [6912]; - p_llrProcBuf = (__m256i*) &llrProcBuf [6912]; - p_llrRes = (__m512i*) &llrRes [6912]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [7680]; - p_llrProcBuf = (__m256i*) &llrProcBuf [7296]; - p_llrRes = (__m512i*) &llrRes [7296]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [10752]; - p_llrProcBuf = (__m256i*) &llrProcBuf [8064]; - p_llrRes = (__m512i*) &llrRes [8064]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [12672]; - p_llrProcBuf = (__m256i*) &llrProcBuf [8448]; - p_llrRes = (__m512i*) &llrRes [8448]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [24192]; - p_llrProcBuf = (__m256i*) &llrProcBuf [10368]; - p_llrRes = (__m512i*) &llrRes [10368]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [26880]; - p_llrProcBuf = (__m256i*) &llrProcBuf [10752]; - p_llrRes = (__m512i*) &llrRes [10752]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [29952]; - p_llrProcBuf = (__m256i*) &llrProcBuf [11136]; - p_llrRes = (__m512i*) &llrRes [11136]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [34944]; - p_llrProcBuf = (__m256i*) &llrProcBuf [11520]; - p_llrRes = (__m512i*) &llrRes [11520]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [40320]; - p_llrProcBuf = (__m256i*) &llrProcBuf [11904]; - p_llrRes = (__m512i*) &llrRes [11904]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [0]; - p_llrProcBuf = (__m256i*) &llrProcBuf [0]; - p_llrRes = (__m512i*) &llrRes [0]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [14592]; - p_llrProcBuf = (__m256i*) &llrProcBuf [14592]; - p_llrRes = (__m512i*) &llrRes [14592]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [18432]; - p_llrProcBuf = (__m256i*) &llrProcBuf [15360]; - p_llrRes = (__m512i*) &llrRes [15360]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [20736]; - p_llrProcBuf = (__m256i*) &llrProcBuf [15744]; - p_llrRes = (__m512i*) &llrRes [15744]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [23424]; - p_llrProcBuf = (__m256i*) &llrProcBuf [16128]; - p_llrRes = (__m512i*) &llrRes [16128]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [26496]; - p_llrProcBuf = (__m256i*) &llrProcBuf [16512]; - p_llrRes = (__m512i*) &llrRes [16512]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [33408]; - p_llrProcBuf = (__m256i*) &llrProcBuf [17280]; - p_llrRes = (__m512i*) &llrRes [17280]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [37248]; - p_llrProcBuf = (__m256i*) &llrProcBuf [17664]; - p_llrRes = (__m512i*) &llrRes [17664]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [41856]; - p_llrProcBuf = (__m256i*) &llrProcBuf [18048]; - p_llrRes = (__m512i*) &llrRes [18048]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [46848]; - p_llrProcBuf = (__m256i*) &llrProcBuf [18432]; - p_llrRes = (__m512i*) &llrRes [18432]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [52224]; - p_llrProcBuf = (__m256i*) &llrProcBuf [18816]; - p_llrRes = (__m512i*) &llrRes [18816]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [58368]; - p_llrProcBuf = (__m256i*) &llrProcBuf [19200]; - p_llrRes = (__m512i*) &llrRes [19200]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [66816]; - p_llrProcBuf = (__m256i*) &llrProcBuf [19584]; - p_llrRes = (__m512i*) &llrRes [19584]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [0]; - p_llrProcBuf = (__m256i*) &llrProcBuf [0]; - p_llrRes = (__m512i*) &llrRes [0]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [1152]; - p_llrProcBuf = (__m256i*) &llrProcBuf [1152]; - p_llrRes = (__m512i*) &llrRes [1152]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [3456]; - p_llrProcBuf = (__m256i*) &llrProcBuf [2304]; - p_llrRes = (__m512i*) &llrRes [2304]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [9216]; - p_llrProcBuf = (__m256i*) &llrProcBuf [4224]; - p_llrRes = (__m512i*) &llrRes [4224]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [13824]; - p_llrProcBuf = (__m256i*) &llrProcBuf [5376]; - p_llrRes = (__m512i*) &llrRes [5376]; - for (int i=0,j=0;i>6; - p_bnProcBuf = (__m256i*) &bnProcBuf [17664]; - p_llrProcBuf = (__m256i*) &llrProcBuf [6144]; - p_llrRes = (__m512i*) &llrRes [6144]; - for (int i=0,j=0;i -#include -static inline void nrLDPC_cnProc_BG1_R13_AVX2(int8_t* cnProcBuf, int8_t* cnProcBufRes, uint16_t Z) { -//Process group with 3 BNs - __m256i ymm0, min, sgn,ones,maxLLR; - ones = _mm256_set1_epi8((char)1); - maxLLR = _mm256_set1_epi8((char)127); - uint32_t M; - M = (1*Z + 31)>>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i -#include -static inline void nrLDPC_cnProc_BG1_R23_AVX2(int8_t* cnProcBuf, int8_t* cnProcBufRes, uint16_t Z) { -//Process group with 3 BNs - __m256i ymm0, min, sgn,ones,maxLLR; - ones = _mm256_set1_epi8((char)1); - maxLLR = _mm256_set1_epi8((char)127); - uint32_t M; - M = (1*Z + 31)>>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i -#include -static inline void nrLDPC_cnProc_BG1_R89_AVX2(int8_t* cnProcBuf, int8_t* cnProcBufRes, uint16_t Z) { -//Process group with 3 BNs - __m256i ymm0, min, sgn,ones,maxLLR; - ones = _mm256_set1_epi8((char)1); - maxLLR = _mm256_set1_epi8((char)127); - uint32_t M; - M = (1*Z + 31)>>5; - for (int i=0;i>5; - for (int i=0;i -#include -static inline void nrLDPC_cnProc_BG2_R13_AVX2(int8_t* cnProcBuf, int8_t* cnProcBufRes, uint16_t Z) { -//Process group with 3 BNs - __m256i ymm0, min, sgn,ones,maxLLR; - ones = _mm256_set1_epi8((char)1); - maxLLR = _mm256_set1_epi8((char)127); - uint32_t M; -//Process group with 4 BNs - M = (8*Z + 31)>>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i -#include -static inline void nrLDPC_cnProc_BG2_R15_AVX2(int8_t* cnProcBuf, int8_t* cnProcBufRes, uint16_t Z) { -//Process group with 3 BNs - __m256i ymm0, min, sgn,ones,maxLLR; - ones = _mm256_set1_epi8((char)1); - maxLLR = _mm256_set1_epi8((char)127); - uint32_t M; - M = (6*Z + 31)>>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i -#include -static inline void nrLDPC_cnProc_BG2_R23_AVX2(int8_t* cnProcBuf, int8_t* cnProcBufRes, uint16_t Z) { -//Process group with 3 BNs - __m256i ymm0, min, sgn,ones,maxLLR; - ones = _mm256_set1_epi8((char)1); - maxLLR = _mm256_set1_epi8((char)127); - uint32_t M; -//Process group with 4 BNs - M = (1*Z + 31)>>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>5; - for (int i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i>6; - for (int i=0;i