1644 lines
57 KiB
C
1644 lines
57 KiB
C
/*
|
|
* Licensed to the OpenAirInterface (OAI) Software Alliance under one or more
|
|
* contributor license agreements. See the NOTICE file distributed with
|
|
* this work for additional information regarding copyright ownership.
|
|
* The OpenAirInterface Software Alliance licenses this file to You under
|
|
* the OAI Public License, Version 1.1 (the "License"); you may not use this file
|
|
* except in compliance with the License.
|
|
* You may obtain a copy of the License at
|
|
*
|
|
* http://www.openairinterface.org/?page_id=698
|
|
*
|
|
* Unless required by applicable law or agreed to in writing, software
|
|
* distributed under the License is distributed on an "AS IS" BASIS,
|
|
* WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
|
|
* See the License for the specific language governing permissions and
|
|
* limitations under the License.
|
|
*-------------------------------------------------------------------------------
|
|
* For more information about the OpenAirInterface (OAI) Software Alliance:
|
|
* contact@openairinterface.org
|
|
*/
|
|
|
|
/*!\file nrLDPC_decoder.c
|
|
* \brief Defines the LDPC decoder
|
|
* \author Sebastian Wagner (TCL Communications) Email: <mailto:sebastian.wagner@tcl.com>
|
|
* \date 30-09-2019
|
|
* \version 2.0
|
|
* \note
|
|
* \warning
|
|
*/
|
|
|
|
#include <stdint.h>
|
|
#include <immintrin.h>
|
|
#include "nrLDPCdecoder_defs.h"
|
|
#include "nrLDPC_types.h"
|
|
#include "nrLDPC_init.h"
|
|
#include "nrLDPC_mPass.h"
|
|
#include "nrLDPC_cnProc.h"
|
|
#include "nrLDPC_bnProc.h"
|
|
//include files-> AVX2
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z384_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z352_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z320_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z288_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z256_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z240_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z224_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z208_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z192_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z176_13_AVX2.c"
|
|
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z160_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z144_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z128_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z120_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z112_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z104_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z96_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z88_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z80_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z72_13_AVX2.c"
|
|
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z64_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z60_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z56_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z52_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z48_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z44_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z40_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z36_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z32_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z30_13_AVX2.c"
|
|
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z28_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z26_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z24_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z22_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z20_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z18_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z16_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z15_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z14_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z13_13_AVX2.c"
|
|
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z12_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z11_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z10_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z9_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z8_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z7_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z6_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z5_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z4_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z3_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z2_13_AVX2.c"
|
|
|
|
|
|
//include files for -->AVX512
|
|
|
|
//#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z384_13_AVX2.c"
|
|
/*#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z352_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z320_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z288_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z256_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z240_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z224_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z208_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z192_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z176_13_AVX2.c"
|
|
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z160_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z144_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z128_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z120_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z112_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z104_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z96_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z88_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z80_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z72_13_AVX2.c"
|
|
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z64_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z60_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z56_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z52_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z48_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z44_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z40_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z36_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z32_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z30_13_AVX2.c"
|
|
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z28_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z26_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z24_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z22_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z20_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z18_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z16_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z15_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z14_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z13_13_AVX2.c"
|
|
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z12_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z11_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z10_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z9_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z8_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z7_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z6_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z5_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z4_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z3_13_AVX2.c"
|
|
#include "nrLDPC_tools/ldpc_gen_files/avx2/nrLDPC_cnProc_BG1_Z2_13_AVX2.c"
|
|
*/
|
|
#define NR_LDPC_ENABLE_PARITY_CHECK
|
|
#define NR_LDPC_PROFILER_DETAIL
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
#include "nrLDPC_tools/nrLDPC_debug.h"
|
|
#endif
|
|
|
|
static inline uint32_t nrLDPC_decoder_core(int8_t* p_llr, int8_t* p_out, t_nrLDPC_procBuf* p_procBuf, uint32_t numLLR, t_nrLDPC_lut* p_lut, t_nrLDPC_dec_params* p_decParams, t_nrLDPC_time_stats* p_profiler);
|
|
|
|
int32_t nrLDPC_decod(t_nrLDPC_dec_params* p_decParams, int8_t* p_llr, int8_t* p_out, t_nrLDPC_procBuf* p_procBuf, t_nrLDPC_time_stats* p_profiler)
|
|
{
|
|
uint32_t numLLR;
|
|
uint32_t numIter = 0;
|
|
t_nrLDPC_lut lut;
|
|
t_nrLDPC_lut* p_lut = &lut;
|
|
|
|
//printf("p_procBuf->cnProcBuf = %p\n", p_procBuf->cnProcBuf);
|
|
|
|
// Initialize decoder core(s) with correct LUTs
|
|
numLLR = nrLDPC_init(p_decParams, p_lut);
|
|
|
|
// Launch LDPC decoder core for one segment
|
|
numIter = nrLDPC_decoder_core(p_llr, p_out, p_procBuf, numLLR, p_lut, p_decParams, p_profiler);
|
|
|
|
return numIter;
|
|
}
|
|
|
|
/**
|
|
\brief Performs LDPC decoding of one code block
|
|
\param p_llr Input LLRs
|
|
\param p_out Output vector
|
|
\param numLLR Number of LLRs
|
|
\param p_lut Pointer to decoder LUTs
|
|
\param p_decParams LDPC decoder parameters
|
|
\param p_profiler LDPC profiler statistics
|
|
*/
|
|
static inline uint32_t nrLDPC_decoder_core(int8_t* p_llr, int8_t* p_out, t_nrLDPC_procBuf* p_procBuf, uint32_t numLLR, t_nrLDPC_lut* p_lut, t_nrLDPC_dec_params* p_decParams, t_nrLDPC_time_stats* p_profiler)
|
|
{
|
|
uint16_t Z = p_decParams->Z;
|
|
uint8_t BG = p_decParams->BG;
|
|
uint8_t numMaxIter = p_decParams->numMaxIter;
|
|
e_nrLDPC_outMode outMode = p_decParams->outMode;
|
|
int8_t* cnProcBuf= p_procBuf->cnProcBuf;
|
|
int8_t* cnProcBufRes=p_procBuf->cnProcBufRes;
|
|
|
|
// Minimum number of iterations is 1
|
|
// 0 iterations means hard-decision on input LLRs
|
|
uint32_t i = 1;
|
|
// Initialize with parity check fail != 0
|
|
int32_t pcRes = 1;
|
|
int8_t* p_llrOut;
|
|
|
|
if (outMode == nrLDPC_outMode_LLRINT8)
|
|
{
|
|
p_llrOut = p_out;
|
|
}
|
|
else
|
|
{
|
|
// Use LLR processing buffer as temporary output buffer
|
|
p_llrOut = p_procBuf->llrProcBuf;
|
|
// Clear llrProcBuf
|
|
memset(p_llrOut,0, NR_LDPC_MAX_NUM_LLR*sizeof(int8_t));
|
|
}
|
|
|
|
|
|
// Initialization
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->llr2llrProcBuf);
|
|
#endif
|
|
nrLDPC_llr2llrProcBuf(p_lut, p_llr, p_procBuf, Z, BG);
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->llr2llrProcBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_initBuffer2File(nrLDPC_buffers_LLR_PROC);
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_LLR_PROC, p_procBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->llr2CnProcBuf);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
nrLDPC_llr2CnProcBuf_BG1(p_lut, p_llr, p_procBuf, Z);
|
|
}
|
|
else
|
|
{
|
|
nrLDPC_llr2CnProcBuf_BG2(p_lut, p_llr, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->llr2CnProcBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_initBuffer2File(nrLDPC_buffers_CN_PROC);
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_CN_PROC, p_procBuf);
|
|
#endif
|
|
|
|
// First iteration
|
|
|
|
// CN processing
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->cnProc);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
// depend on Z
|
|
switch (Z)
|
|
{
|
|
case 384:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z384_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z384_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 352:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z352_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z352_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 320:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z320_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
//nrLDPC_cnProc_BG1_Z320_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 288:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z288_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z288_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 256:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z256_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
//LDPC_cnProc_BG1_Z256_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 240:
|
|
{
|
|
|
|
nrLDPC_cnProc_BG1_Z240_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z240_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 224:
|
|
{
|
|
|
|
nrLDPC_cnProc_BG1_Z224_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
//nrLDPC_cnProc_BG1_Z224_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 208:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z208_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z208_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 192:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z192_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z192_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 176:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z176_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z176_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 160:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z176_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z176_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 144:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z144_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z144_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 128:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z128_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z128_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 120:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z120_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z120_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 112:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z112_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z112_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
|
|
case 104:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z104_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z104_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 96:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z96_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z96_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 88:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z88_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z88_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 80:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z80_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z80_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 72:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z72_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z72_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 64:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z64_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z64_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 60:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z60_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z60_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 56:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z56_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z56_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 52:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z52_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z52_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 48:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z48_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z48_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 44:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z44_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z44_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 40:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z40_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z40_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 36:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z36_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z36_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 32:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z32_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z32_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 30:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z30_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z30_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 28:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z28_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z28_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 26:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z26_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z26_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 24:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z24_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z24_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 22:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z22_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z22_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 20:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z20_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z20_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 18:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z18_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z18_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 16:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z16_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z16_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 15:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z15_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z15_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 14:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z14_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z14_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 13:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z13_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z13_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 12:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z12_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z12_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 11:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z11_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z11_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 10:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z10_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z10_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 9:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z9_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z9_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 8:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z8_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z8_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 7:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z7_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z7_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 6:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z6_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z6_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 5:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z5_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z5_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 4:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z4_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z4_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 3:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z3_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z3_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 2:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z2_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z2_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
}//end switch(Z)
|
|
}
|
|
else
|
|
{
|
|
nrLDPC_cnProc_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->cnProc);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_initBuffer2File(nrLDPC_buffers_CN_PROC_RES);
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_CN_PROC_RES, p_procBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->cn2bnProcBuf);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
nrLDPC_cn2bnProcBuf_BG1(p_lut, p_procBuf, Z);
|
|
}
|
|
else
|
|
{
|
|
nrLDPC_cn2bnProcBuf_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->cn2bnProcBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_initBuffer2File(nrLDPC_buffers_BN_PROC);
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_BN_PROC, p_procBuf);
|
|
#endif
|
|
|
|
// BN processing
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->bnProcPc);
|
|
#endif
|
|
nrLDPC_bnProcPc(p_lut, p_procBuf, Z);
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->bnProcPc);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_initBuffer2File(nrLDPC_buffers_LLR_RES);
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_LLR_RES, p_procBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->bnProc);
|
|
#endif
|
|
nrLDPC_bnProc(p_lut, p_procBuf, Z);
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->bnProc);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_initBuffer2File(nrLDPC_buffers_BN_PROC_RES);
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_BN_PROC_RES, p_procBuf);
|
|
#endif
|
|
|
|
// BN results to CN processing buffer
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->bn2cnProcBuf);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
nrLDPC_bn2cnProcBuf_BG1(p_lut, p_procBuf, Z);
|
|
}
|
|
else
|
|
{
|
|
nrLDPC_bn2cnProcBuf_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->bn2cnProcBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_CN_PROC, p_procBuf);
|
|
#endif
|
|
|
|
// Parity Check not necessary here since it will fail
|
|
// because first 2 cols/BNs in BG are punctured and cannot be
|
|
// estimated after only one iteration
|
|
|
|
// First iteration finished
|
|
|
|
while ( (i < (numMaxIter-1)) && (pcRes != 0) )
|
|
{
|
|
// Increase iteration counter
|
|
i++;
|
|
|
|
// CN processing
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->cnProc);
|
|
#endif
|
|
if (BG == 1){
|
|
// depend on Z
|
|
switch (Z)
|
|
{
|
|
case 384:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z384_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z384_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 352:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z352_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z352_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 320:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z320_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
//nrLDPC_cnProc_BG1_Z320_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 288:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z288_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z288_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 256:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z256_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
//LDPC_cnProc_BG1_Z256_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 240:
|
|
{
|
|
|
|
nrLDPC_cnProc_BG1_Z240_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z240_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 224:
|
|
{
|
|
|
|
nrLDPC_cnProc_BG1_Z224_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
//nrLDPC_cnProc_BG1_Z224_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 208:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z208_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z208_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 192:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z192_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
//nrLDPC_cnProc_BG1_Z192_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 176:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z176_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z176_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 160:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z176_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z176_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 144:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z144_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z144_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 128:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z128_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z128_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 120:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z120_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z120_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 112:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z112_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z112_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 104:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z104_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z104_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 96:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z96_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z96_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 88:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z88_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z88_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 80:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z80_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z80_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 72:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z72_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z72_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 64:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z64_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z64_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 60:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z60_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z60_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 56:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z56_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z56_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 52:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z52_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z52_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 48:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z48_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z48_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 44:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z44_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z44_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 40:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z40_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z40_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 36:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z36_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z36_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 32:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z32_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z32_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 30:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z30_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z30_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 28:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z28_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z28_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 26:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z26_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z26_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 24:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z24_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z24_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 22:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z22_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z22_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 20:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z20_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z20_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 18:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z18_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z18_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 16:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z16_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z16_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 15:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z15_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z15_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 14:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z14_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z14_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 13:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z13_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z13_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 12:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z12_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z12_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 11:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z11_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z11_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 10:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z10_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z10_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 9:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z9_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z9_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 8:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z8_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z8_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 7:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z7_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z7_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 6:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z6_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z6_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 5:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z5_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z5_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 4:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z4_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z4_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 3:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z3_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z3_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 2:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z2_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z2_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
}//end switch(Z)
|
|
|
|
|
|
|
|
}
|
|
else
|
|
{
|
|
nrLDPC_cnProc_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->cnProc);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_CN_PROC_RES, p_procBuf);
|
|
#endif
|
|
|
|
// Send CN results back to BNs
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->cn2bnProcBuf);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
nrLDPC_cn2bnProcBuf_BG1(p_lut, p_procBuf, Z);
|
|
}
|
|
else
|
|
{
|
|
nrLDPC_cn2bnProcBuf_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->cn2bnProcBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_BN_PROC, p_procBuf);
|
|
#endif
|
|
|
|
// BN Processing
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->bnProcPc);
|
|
#endif
|
|
nrLDPC_bnProcPc(p_lut, p_procBuf, Z);
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->bnProcPc);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_LLR_RES, p_procBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->bnProc);
|
|
#endif
|
|
nrLDPC_bnProc(p_lut, p_procBuf, Z);
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->bnProc);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_BN_PROC_RES, p_procBuf);
|
|
#endif
|
|
|
|
// BN results to CN processing buffer
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->bn2cnProcBuf);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
nrLDPC_bn2cnProcBuf_BG1(p_lut, p_procBuf, Z);
|
|
}
|
|
else
|
|
{
|
|
nrLDPC_bn2cnProcBuf_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->bn2cnProcBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_CN_PROC, p_procBuf);
|
|
#endif
|
|
|
|
// Parity Check
|
|
#ifdef NR_LDPC_ENABLE_PARITY_CHECK
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->cnProcPc);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
pcRes = nrLDPC_cnProcPc_BG1(p_lut, p_procBuf, Z);
|
|
}
|
|
else
|
|
{
|
|
pcRes = nrLDPC_cnProcPc_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->cnProcPc);
|
|
#endif
|
|
#endif
|
|
}
|
|
|
|
// Last iteration
|
|
if ( (i < numMaxIter) && (pcRes != 0) )
|
|
{
|
|
// Increase iteration counter
|
|
i++;
|
|
|
|
// CN processing
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->cnProc);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
// depend on Z
|
|
switch (Z)
|
|
{
|
|
case 384:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z384_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z384_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 352:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z352_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z352_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 320:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z320_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
//nrLDPC_cnProc_BG1_Z320_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 288:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z288_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z288_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 256:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z256_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
//LDPC_cnProc_BG1_Z256_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 240:
|
|
{
|
|
|
|
nrLDPC_cnProc_BG1_Z240_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z240_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 224:
|
|
{
|
|
|
|
nrLDPC_cnProc_BG1_Z224_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
//nrLDPC_cnProc_BG1_Z224_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 208:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z208_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z208_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 192:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z192_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z192_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 176:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z176_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z176_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 160:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z176_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z176_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 144:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z144_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z144_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 128:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z128_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z128_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 120:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z120_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z120_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 112:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z112_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z112_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
|
|
case 104:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z104_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z104_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 96:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z96_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z96_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 88:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z88_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z88_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 80:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z80_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z80_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 72:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z72_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z72_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 64:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z64_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z64_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 60:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z60_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z60_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 56:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z56_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z56_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 52:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z52_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z52_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 48:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z48_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z48_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 44:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z44_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z44_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 40:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z40_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z40_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 36:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z36_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z36_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 32:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z32_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z32_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 30:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z30_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z30_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 28:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z28_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z28_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 26:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z26_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z26_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 24:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z24_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z24_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 22:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z22_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z22_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 20:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z20_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z20_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 18:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z18_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z18_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 16:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z16_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z16_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 15:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z15_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z15_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 14:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z14_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z14_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 13:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z13_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z13_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 12:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z12_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z12_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 11:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z11_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z11_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 10:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z10_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z10_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 9:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z9_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z9_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 8:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z8_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z8_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 7:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z7_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z7_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 6:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z6_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z6_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 5:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z5_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z5_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 4:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z4_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z4_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
|
|
case 3:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z3_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z3_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
case 2:
|
|
{
|
|
nrLDPC_cnProc_BG1_Z2_13_AVX2(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
// nrLDPC_cnProc_BG1_Z2_13_AVX512(p_procBuf->cnProcBuf,p_procBuf->cnProcBufRes);
|
|
break;
|
|
}
|
|
}//end switch(Z)
|
|
|
|
}
|
|
else
|
|
{
|
|
nrLDPC_cnProc_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->cnProc);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_CN_PROC_RES, p_procBuf);
|
|
#endif
|
|
|
|
// Send CN results back to BNs
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->cn2bnProcBuf);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
nrLDPC_cn2bnProcBuf_BG1(p_lut, p_procBuf, Z);
|
|
}
|
|
else
|
|
{
|
|
nrLDPC_cn2bnProcBuf_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->cn2bnProcBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_BN_PROC, p_procBuf);
|
|
#endif
|
|
|
|
// BN Processing
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->bnProcPc);
|
|
#endif
|
|
nrLDPC_bnProcPc(p_lut, p_procBuf, Z);
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->bnProcPc);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_LLR_RES, p_procBuf);
|
|
#endif
|
|
|
|
// If parity check not enabled, no need to send the BN proc results
|
|
// back to CNs
|
|
#ifdef NR_LDPC_ENABLE_PARITY_CHECK
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->bnProc);
|
|
#endif
|
|
nrLDPC_bnProc(p_lut, p_procBuf, Z);
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->bnProc);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_BN_PROC_RES, p_procBuf);
|
|
#endif
|
|
|
|
// BN results to CN processing buffer
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->bn2cnProcBuf);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
nrLDPC_bn2cnProcBuf_BG1(p_lut, p_procBuf, Z);
|
|
}
|
|
else
|
|
{
|
|
nrLDPC_bn2cnProcBuf_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->bn2cnProcBuf);
|
|
#endif
|
|
|
|
#ifdef NR_LDPC_DEBUG_MODE
|
|
nrLDPC_debug_writeBuffer2File(nrLDPC_buffers_CN_PROC, p_procBuf);
|
|
#endif
|
|
|
|
// Parity Check
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->cnProcPc);
|
|
#endif
|
|
if (BG == 1)
|
|
{
|
|
pcRes = nrLDPC_cnProcPc_BG1(p_lut, p_procBuf, Z);
|
|
}
|
|
else
|
|
{
|
|
pcRes = nrLDPC_cnProcPc_BG2(p_lut, p_procBuf, Z);
|
|
}
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->cnProcPc);
|
|
#endif
|
|
#endif
|
|
}
|
|
|
|
// If maximum number of iterations reached an PC still fails increase number of iterations
|
|
// Thus, i > numMaxIter indicates that PC has failed
|
|
|
|
#ifdef NR_LDPC_ENABLE_PARITY_CHECK
|
|
if (pcRes != 0)
|
|
{
|
|
i++;
|
|
}
|
|
#endif
|
|
|
|
// Assign results from processing buffer to output
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->llrRes2llrOut);
|
|
#endif
|
|
nrLDPC_llrRes2llrOut(p_lut, p_llrOut, p_procBuf, Z, BG);
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->llrRes2llrOut);
|
|
#endif
|
|
|
|
// Hard-decision
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
start_meas(&p_profiler->llr2bit);
|
|
#endif
|
|
if (outMode == nrLDPC_outMode_BIT)
|
|
{
|
|
nrLDPC_llr2bitPacked(p_out, p_llrOut, numLLR);
|
|
}
|
|
else if (outMode == nrLDPC_outMode_BITINT8)
|
|
{
|
|
nrLDPC_llr2bit(p_out, p_llrOut, numLLR);
|
|
}
|
|
|
|
#ifdef NR_LDPC_PROFILER_DETAIL
|
|
stop_meas(&p_profiler->llr2bit);
|
|
#endif
|
|
|
|
return i;
|
|
}
|