From a7e6137408960c50fa7babdb5ee6a28060650455 Mon Sep 17 00:00:00 2001
From: Raymond Knopp <raymond.knopp@eurecom.fr>
Date: Sat, 9 May 2020 09:14:59 +0200
Subject: [PATCH] unrolled 2 BNs case in generator

---
 .../nrLDPC_decoder/nrLDPC_tools/cnProc_gen.c  |  39 +++++++++++++++---
 .../nrLDPC_decoder/nrLDPC_tools/cnProc_gen.o  | Bin 30856 -> 32264 bytes
 .../nrLDPC_decoder/nrLDPC_tools/gmon.out      | Bin 4138 -> 4354 bytes
 .../nrLDPC_cnProc_BG1_Z384_13.c               |  36 ++++++++++++++--
 4 files changed, 66 insertions(+), 9 deletions(-)

diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/cnProc_gen.c b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/cnProc_gen.c
index 1daff9c17a..eca8e886fc 100644
--- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/cnProc_gen.c
+++ b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/cnProc_gen.c
@@ -92,7 +92,7 @@ void nrLDPC_cnProc_BG1_generator(uint16_t Z,int R)
 	  //	  for (i=0; i<M; i++,iprime++)
 	  //            {
 	  
-	  fprintf(fd,"            for (int i=0;i<%d;i++) {\n",M);
+	  fprintf(fd,"            for (int i=0;i<%d;i+=2) {\n",M);
 	  // Abs and sign of 32 CNs (first BN)
 	  //                ymm0 = p_cnProcBuf[lut_idxCnProcG3[j][0] + i];
 	  fprintf(fd,"                ymm0 = ((__m256i*)cnProcBuf)[%d+i];\n",(lut_startAddrCnGroups[0]>>5)+lut_idxCnProcG3[j][0]);
@@ -117,6 +117,32 @@ void nrLDPC_cnProc_BG1_generator(uint16_t Z,int R)
 	  //                *p_cnProcBufResBit = _mm256_sign_epi8(min, sgn);
 	  //                p_cnProcBufResBit++;
 	  fprintf(fd,"                ((__m256i*)cnProcBufRes)[%d+i] = _mm256_sign_epi8(min, sgn);\n",(lut_startAddrCnGroups[0]>>5)+(j*bitOffsetInGroup));
+
+	  // Abs and sign of 32 CNs (first BN)
+	  //                ymm0 = p_cnProcBuf[lut_idxCnProcG3[j][0] + i];
+	  fprintf(fd,"                ymm0 = ((__m256i*)cnProcBuf)[%d+i];\n",(lut_startAddrCnGroups[0]>>5)+lut_idxCnProcG3[j][0]+1);
+	  //                sgn  = _mm256_sign_epi8(ones, ymm0);
+	  fprintf(fd,"                sgn  = _mm256_sign_epi8(ones, ymm0);\n");
+	  //                min  = _mm256_abs_epi8(ymm0);
+	  fprintf(fd,"                min  = _mm256_abs_epi8(ymm0);\n");
+	  
+	  // 32 CNs of second BN
+	  //                ymm0 = p_cnProcBuf[lut_idxCnProcG3[j][1] + i];
+	  fprintf(fd,"                ymm0 = ((__m256i*)cnProcBuf)[%d+i];\n",(lut_startAddrCnGroups[0]>>5)+lut_idxCnProcG3[j][1]+1);
+	  
+	  //                min  = _mm256_min_epu8(min, _mm256_abs_epi8(ymm0));
+	  fprintf(fd,"                min  = _mm256_min_epu8(min, _mm256_abs_epi8(ymm0));\n");
+	  
+	  //                sgn  = _mm256_sign_epi8(sgn, ymm0);
+	  fprintf(fd,"                sgn  = _mm256_sign_epi8(sgn, ymm0);\n");
+	  
+	  // Store result
+	  //                min = _mm256_min_epu8(min, maxLLR); // 128 in epi8 is -127
+	  fprintf(fd,"                min = _mm256_min_epu8(min, maxLLR);\n");
+	  //                *p_cnProcBufResBit = _mm256_sign_epi8(min, sgn);
+	  //                p_cnProcBufResBit++;
+	  fprintf(fd,"                ((__m256i*)cnProcBufRes)[%d+i] = _mm256_sign_epi8(min, sgn);\n",(lut_startAddrCnGroups[0]>>5)+(j*bitOffsetInGroup)+1);
+
 	  fprintf(fd,"            }\n");
         }
     }
@@ -250,7 +276,7 @@ void nrLDPC_cnProc_BG1_generator(uint16_t Z,int R)
 
   // =====================================================================
   // Process group with 6 BNs
-
+  fprintf(fd,"//Process group with 6 BNs\n");
   // Offset is 8*384/32 = 96
   const uint16_t lut_idxCnProcG6[6][5] = {{96,192,288,384,480}, {0,192,288,384,480},
 					  {0,96,288,384,480}, {0,96,192,384,480},
@@ -316,7 +342,7 @@ void nrLDPC_cnProc_BG1_generator(uint16_t Z,int R)
 
   // =====================================================================
   // Process group with 7 BNs
-
+  fprintf(fd,"//Process group with 7 BNs\n");
   // Offset is 5*384/32 = 60
   const uint16_t lut_idxCnProcG7[7][6] = {{60,120,180,240,300,360}, {0,120,180,240,300,360},
 					  {0,60,180,240,300,360},   {0,60,120,240,300,360},
@@ -384,7 +410,7 @@ void nrLDPC_cnProc_BG1_generator(uint16_t Z,int R)
 
   // =====================================================================
   // Process group with 8 BNs
-
+  fprintf(fd,"//Process group with 8 BNs\n");
   // Offset is 2*384/32 = 24
   const uint8_t lut_idxCnProcG8[8][7] = {{24,48,72,96,120,144,168}, {0,48,72,96,120,144,168},
 					 {0,24,72,96,120,144,168}, {0,24,48,96,120,144,168},
@@ -452,7 +478,7 @@ void nrLDPC_cnProc_BG1_generator(uint16_t Z,int R)
 
   // =====================================================================
   // Process group with 9 BNs
-
+  fprintf(fd,"//Process group with 9 BNs\n");
   // Offset is 2*384/32 = 24
   const uint8_t lut_idxCnProcG9[9][8] = {{24,48,72,96,120,144,168,192}, {0,48,72,96,120,144,168,192},
 					 {0,24,72,96,120,144,168,192}, {0,24,48,96,120,144,168,192},
@@ -522,7 +548,7 @@ void nrLDPC_cnProc_BG1_generator(uint16_t Z,int R)
 
   // =====================================================================
   // Process group with 10 BNs
-
+  fprintf(fd,"//Process group with 10 BNs\n");
   // Offset is 1*384/32 = 12
   const uint8_t lut_idxCnProcG10[10][9] = {{12,24,36,48,60,72,84,96,108}, {0,24,36,48,60,72,84,96,108},
 					   {0,12,36,48,60,72,84,96,108}, {0,12,24,48,60,72,84,96,108},
@@ -593,6 +619,7 @@ void nrLDPC_cnProc_BG1_generator(uint16_t Z,int R)
 
   // =====================================================================
   // Process group with 19 BNs
+  fprintf(fd,"//Process group with 19 BNs\n");
   // Offset is 4*384/32 = 12
   const uint16_t lut_idxCnProcG19[19][18] = {{48,96,144,192,240,288,336,384,432,480,528,576,624,672,720,768,816,864}, {0,96,144,192,240,288,336,384,432,480,528,576,624,672,720,768,816,864},
 					     {0,48,144,192,240,288,336,384,432,480,528,576,624,672,720,768,816,864}, {0,48,96,192,240,288,336,384,432,480,528,576,624,672,720,768,816,864},
diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/cnProc_gen.o b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/cnProc_gen.o
index 5d68165250ea59f7e9f3a2e3acea1c505d165252..b4dce96552df1786339bd3159aca5df15b3ef6ae 100644
GIT binary patch
delta 8840
zcmZ{pe^gaf7RT?s@9};h2&nOR{@{m^0~RQ1_$(zM@mGzB+RCOfOrtDo07WUYr~SYz
zbHLNEjHv{h)XW*N*UyR7Xk(d9e~?X<PMKP($;M?cwOqBdn0?OOn|JP}d)9*Y&i;J&
zIs2Tw@41)DW8LOs7tF>y>;3vYBd@cpH!QKrD!1;iL`wfGamdpzcE<9X;)E6Qc0M`V
z6kUN#aUrcxyyr<tdF_$%(w?54l-Kr}y==AT=D4siWpIL(((s3$#aiF6*f{TbuXxy(
z85<Myd(@YSNp<qekl3D-N9`}g13&i!r$15t&GhyA{x(#cGzY~l3e|c8y_QmIU~Jux
zTddfrVO2igq%rx~s}f_gaz8Q?4B5np+&qypVx&kIaZy5XcG;|D;?|2p3FGNoFe1Mt
z8rj+6+$FgQ6Ugo>8ckmZ7Ab3@u{u!=sfKOM%Z@!bVxwjLRV3$UTQ_FKM&<v<>UU$7
zEis>I5IL9SW;Q?+o~AX?RB1K`HLLF42h*w+8)o`8vFNg!qVFhM`-8Tm<#W|-#qQA`
zRkv&P05w3^9O#n+wqyS$vrzRrAF%lrbB5|SV*g8XvFh(#W%GP1s`@AHxBJyrOIR7&
z>jv6^8^#-!{q1IPeZj@^)_4uWj_jqWV7Hnk8@<XyrmcLTS93;cJWU<Zxac&B{s|&`
z(gN{8!H^red;2w}?e&W0^(}gZVEMM!Yp811REJSDsaJJDloSr>x2U&YCKeawM4zzi
z8U7qKjHIt1M45-=19Ck^QWJb^qkfU$3w#HLq<Qd5X2w>j-=^W;1r~*5mXy(h!}t$K
zR0Uo#W6J2Y1%^L*ikQrvvL@IH!~ZiOnMh^y*#g6#0Twlx%&9W^ZGqt*OGu_y83VS!
z@XsP7Gp&rlsI4&kOC+m;7+Z)9P$<ptKO#{*pxuN5cHaGW?FUQH14uRh7E&H1WdbUf
zo^>h@N+oP$)bRKzOq5n<fJGbhdyuL!^Vg1XBg?OKBP*)<618)yz@B^nvTlTN`1=~2
z(z~H+PrPcU8(F=-FHyrE1-sfn+JUuaoyvpIO@;LvhX3I}z_DT*N%H7$H?nSGU!o?i
z0K1wv8H0bk%Bd`cuDz@cYXUI8w$*X8v8At*8h$qoKMV(XYQIytrFZz|<8Ea0k3{79
zVV!ZOX9olwA;rm-%iKuY)V@R&>`h=-dqKf&t9B}{i9%mVA0??D*R`X?DXk;rZc=(t
zxpTi$xkW0gU|B~=Nz?!3tW$X~2<ul;58OXgq%{5R46taa`JM(XASF$|r_8Aw23@tJ
z8%UXsfxf!bshpMw^{1q3Ng71y>&;GS4Rr0Id9&R~)Rin(`!0<^({&tkDqn@JTI_eE
z3>x;`&;Pc!pJTOOkTeW-$7Qs)(5VbUH>m)oznYX;80bIdJC$RhYcJv5+Fp_ko^WRN
zq5~UxkxgPxkE=A{9xmFl(#_ei0mY5x)O5r0TGqHh@*~iyes8r+7pYEL+!RpXtpcU>
zObI*($n?$hdEPO^E8|<dBcBVjirJBwn<5F~*~kp}aXK=?HjkTdZKC9!MC+W_6lWq+
zH$}X$&I#)RVt!ffK=nLP+CR0yx;okCnU|I14?vLN*p9MKy+L}|7%SSQg<`GKsuRtR
zL{3F0dIC>tc_*I;KNsMkOty1qhmAMjzGLiwQ&+b0n*K`YlRgdZ(Xx^L1nSe#F2~pP
zlWe=#J|`_YQ`6`%RI)Ks;fR#&c1^F3xr*uMqh3Ck$i`!6w(Zg0pyh!t+n-z<-eMEH
zkNWpDy}p3sOrH+NoNQle`YYv`PrK-sTMdnN@e*`MLOWl<A*P>>`cE{y9#Ar7g~qRz
zeR<{%M!?HpG;^RbxLnigDY%B|sSIYj=r@C1o%xQ4AfOjC2Ym%^u?eUq_G)@Ppd(CA
zHSzDbKI$mU9_Bzb;l*6@6kLLKS^(9Ad^VAd@91=<PnY*x*?y}z=qspU4)<b?SGee(
zLQVluO|+q%2Xs)BULT4caiM3}XjA~*nqH6A5BDY6Xm%=qB((GGn{M0V*Ptp%7~p!%
zK`(&2*#uMo@=h)rpP+&1sQ{jE=(TI`CFVc{(C%=EU$Y-FJr%%lO|LKD2c~~q?xd`N
zpEL)3OXUq*Hrmq7xb?%)&R5(5w=7*x1+X3MyZ}yuUF6;{D0<dK;7xK4NHq{dI}ad>
z>8S>CUGz(Ad*2#Zp*iSVxPeVTHPEE#^&Q;K^i%`89D1z=I++92z{d`UcnzFmda40W
zvb}SB%fo1=l&Twptbt6;L0>@`b9e=7V492m(iCUPs0Jcv=K<A%UC!TIWONxuT^#<%
zCZL*V(e(NP+L@ke;?=m`c@AG-4ir#OJ+t*aSF_MgTS_&NtLgQCu3-B4ezktXxXQ(0
z5p$rLxYI?yp6RJ3nl-&%)Vu6w-*^h>X<?7%ps(O#HbE!W#4#8B2kPxee0-{jqiB!v
zqDaNpH?*acf?;Uq`msz;H4)MD`T}M-^-+V0Vy=tBGfoGC0(w!?>s$JFrl*?Nuj%6f
zMSFUVF$X#*zW7y#o*vI2=VeAU5kR}#q4)$nJ^4&eHBl_>vi|s%UdtTlc3j~yK^@co
zj5Tq;i~h6p_yVHxp^=K>Gy)z_S}5)y^^}54v~&G9rl*>ipy_dkVE>_A#~i38=Jj<@
z`lpzl0&3IrdQH5}^i&faA-w*1&JHsNs)<ju3G^JFXL_m$Bg5V~K7J0`6XpDJOQ|Rd
zH3xkKQ^*1JbWY6B^m;(|Fnt)GGisSWhyDtgGsKRRu6wG9TSfP+p>Q*!wBgT78hw*d
z%J<u7=d1r0(^I;Sy6A@wb;d@skFxFJH<fAOa;Bja&lDAvp>QRml+W80UC$_GZ=<5S
z8KqQph#VOCFr$>1Pn7R@MvE~GhA3SaDoPsWTvsL1W@e{cJTGb%hQh}grQP_iq){`|
zIVR=8hjyNep-fM?$Z^pxVS1W<g>8@aIn6dO2TDwn%LLn*o>H~TMc?Vr!}Ubj``E?d
zoWmi0>3Op3os&B>5q{{(2&0{@49ak(roWQ(m&5r~#vJBiTBrS*1L)^w#lBs5))zjl
zy?z-51J+~zC((UpC>+$@D@eK-X;|be35D|+{SN>2F+o%;2}NfyI#jL^+AV08Vrg25
zuMlco^lO=3zAKguU#h4FNf{fBzs=T14VqvY{<WdMRM8ziU=w`WUyW~^bP4ExOn)Cf
z*68n4M#-BjMU;Unq=44rEw2FWGRb;CB~0Hl*bZo}i+(ZFUo9_Ic?i_GIJ67%?ohY`
zUqHyPP^jiPCW?T5&FE;w48toH0;LOze5WJL6iq-!;u`~^6-XmuAJ8d`{toFJ(G7F~
zql=I}Aaa(5!jCapjkH-*0Nu)HBhq%U7H9{f?MRP_JwU%^^bpb?#7UqA79Fjq6KQ{u
zc26ign9(Ch^F%4oag2V3bdIP2x`5GBNSBH>p!JM)A#D&J0^P*uFGwN3_riJ^O_jkz
zJ0yyL9$|De(yzoqpk0j4M*53r0-A`23++ZV(hRW=XfC6TNXLk7pe2m9BfVMV{5}-E
zlhG4M8$<=rO^jCJkplSz+QH}=q>x{rUo+Z@)GJN`O_kRmG&!BT7ET~76lv9=@D+@9
zA)PNufi7m$z(evOQ3G@%qm@XX5p6(sFxrUpJ@FyX!;J1l+9k}IQ1}9)T}TIuBA_Gi
z)T0%7@zk0k76P5kXg1OXq6z3-j7~;cFZKa_gi(5XzDaZgeHN(<P9ADcVg_G~<<zcI
z|IpaEtT?g#IzZ4mL*m<I#n#j6-y9;cJdeKCFV9PC#d}v$lGwStIJoOl+vjC*dii*3
z%^hNRU5T||ytoZM9*T&q@bSh<ajLE)_;SQn&J+17##`U46t}G?v3!%nR`>{%i&OAX
uTrU5yA|fmEtVp@IZDomN)Qhd~Q4JhECSN0l*Ow$_)Y~Jq8)E0O%>M%iF2;cX

delta 8043
zcmZ{p3s98T7018*7Iy(bSya|lF`%`gND*Vj2%(}S!;qwkqczoNc&JG<4?v9~;s=x9
zqj^EEI#MkORuiN3!E92En)qtsBT1`flEG=xsENkZQ6ZVBX=_8zz27--zeBz|BfIzf
zf9KwF&$;)0yX)FJp0(|s`V=#Nam&alrn$u<s?0pk{le2HNz9Gt6~1Lgc*NAW9%4%D
zfC#hq>RrDJB!#E-_;*BjL3Fe?{Cw<kZ+LK^&KrKW@8{m|pZhO~2<IivF~i&Ln&<PS
zj!3GCHp0Dr`mslRn$k}UP3hMs$<eB#jp}GIF*PYXc*IMlXSdj$nq+QH4F4_lYqRI(
zL_;;tmO63lXFnNS*TXQp4K-Grw0in(P~D@e0t@CDo`mhfn?Bn*rfmCG*+|W2s{1N-
zkK9(>wrX4Li1*3y_EpEL@p3(Bs(*H+-LLcHtA0K9PkTyL|7ex1_cm9l{>2q`e}>uU
z>#qh}+DC;Af3|q+ceBO6(uYpBA`HWxy5T;sn++3<PVx+r+d7%^lJPbiwz{Bi5IO^p
zJ!v2D<miDJZJqs@9^30p&Fi1&l>n=^y|#$AM-S|o-Pyk^zJPv7XFo;s$Vj%zOna<t
zmSMzv1;NOK$DWjt8!-*=vYq-FhA;9K7-FWwA6WvMQhz;$e-~JkB+H?UUL3~%zLXY#
zmn@AkM%aMiw=R(;>!hqbY{Ky0AxV}@8GSZj_=8|klga8Squ&M${}_^FA(b)G1`Pj$
zB*~g8W0YkRhW|0CEr1vsNsCuf!0<mSrR5;)At}<Xuz%qRuta%5QqA8)WGj(9kbL5X
zlRPC!NTg+$ehL%OvLINrLB9o5Z76?5hMThFemCWr`P~(jxfNiKJqcAeLO6Wo%T9D5
zbnS_&-f&Z@Pjpw*@U38138W0v-f)tqpc@D4Hz2|ONXLq8Nh)>8Zpxah?uwdtD%jP;
zu^9Ys=R3)X(6yKKf)xq#YpL#%UTW;_q=w%^!zbb(>rXhzrq1Cve(t7hx=o5)KdiIM
z=?{S@M@U`DE2(Zub6$5vZP;00SGk~IUwhg~7Ff_%=yQbnaa}tao#+xG_YfI@<jxaL
zvPqH)U|Fq1()7D;ILT8{uzrP_(HJRBzc&aLtu)`#preSS>05H0<RIv(CH<Pn1Pt`8
zMNaa*XxM)WtsyiD(fu2oXc=_vP4o6%r=m`>T<u?I44Urn1t<9?bk$;S5*cOKk2(Ll
z-ky%t{)5o|V0Rp&qiIeu61p*IF#RMV@4`S&%yg1tpldJTz4A^a2|VG>?37ME-znKj
zctU282Oid<I61)+7Y>iF_r&)x%m~vvH?j#{J-z~;H$|+Q@OyJqlNg>=;7e;V|6_(k
zYSuupJ}cEsYZ5223Zxjwen7qytCw&~_L@kMnK!JD`T&sID{i$pIo9Xhm>A=agvmnT
zwRx=(QS|BHZc$qh4A&HtMO(-5zJ(MS@PsfD;4H~@6743u&w_t<I_!3x@xzdBbK&>E
zb5=GQUp``FJ7nAA;lXGa+3=4hXcx6Jg4Pe{#?`(uMrbtL4je9ob{=jz<1ZpV)`eeb
z+pW$C%Ftn*=AeiB3Y#DfE@IiXX}q4lgN%O&`6CV<4l?EAOXg6I4%ZwGU3?S<Oc|2b
zzibI;=NTQvc(noKMVg^G=qs4P9CC37%yQwEV*nHo?SMM8^MH1PU0vklKqWZn;&7Ht
zKzrg7jn@}&o$<6M+Pe5&jy*q01b!2=?!k5Pc&DJ9!lfNBUE}rX7c!o9z|$`L%eK91
zOVSQl@8a+ln}Bw}agEova4X~IU|&9PWwXzewk1pDQlZg`siN{)myKs=C*!H0`(5~t
z7_SQY01SLybI?<IjX6+7Z@BPdMDpyQ^$WP1W#i$_K)ZC7hl~n3OXKy~%NS1uUFyO&
z+V<`RZE|rq!X}`CeyH(!K`%3&?)0xUK1-f4x??WH$~<&0=vB1y3?=n)@>I|?v~zwk
z<5fZB8PC@o^pwtJ4ph)m7k($>DWLrtuV?5ZusiM;s_}WvK@aE}n}BM3!-Ws@c4mmq
zYy#RLLzd%?$z%>x<6m|;I3AO;7*92RMC0`ZJQ8pQl<!mPH;gAx;5GXrbD)&&bK&1-
zJl(<{XuKZKC5t&wjjy^mq^mFDU7M5w%0@e1z%<5FiD#nSk`8)APcjFpafLR4&TnKq
z)p)ZDf7r=e2G#hq=AiG=FPsj>BD|2l(s(_f>HT<(?S3)Zof)z^I@U1<O6kTQb?E5$
z6XU7IEgG)}bdvE@;t!==?mu3Fm;~nvD4-D9oh#_*NM}6Nc&x_j0TpPxCGU2s@e~(_
z#hQcUsm9A)_(sN4iC@!rEHUIC+F|BE=lGcBps!$W$eE#h{M2<A?L0%@F`hDN48Zfx
z9TEmOC!iV+L_0582IHy5<6L-)csajJDMj>x=AfT~t>l0_)%bOd*E94E<Eg~Q8E?_k
z?<#Yk8eeA)#K#PDW{7GWLOaiBI^(g#CB|6IAq&Q&34X;KYVh2*GCS4&iZ+g(xg^nE
z8nn^|+2QiACZnA`=1`&YHC~TuF5{`tr7rv~+b(XG20{lkCR<zSUq$k~VCZ8_)o1)h
z6wV74-*i#q@uzNzpUM_QJKw0|8Bb-)6Xo-RC9|1I=dj3SwC5PV5^J>1h2M}EUij!u
zU+9|l{W%>nu^ju~i}I&}p-Ao9vQ#&r+Fvw-n!?mu_$&2zaqg+0^&nFR$pk=q80`|4
zrrFppcj0RoKMcPXZE)eY+jh&K3F7cm_dyqj57-2&@l)nS7rveGG57(&CvOjEa=LW+
zIH45>QJ{c4_!t`HaOmRiW&Fc<XHIkBOBr7$&!60-OI#fGirTVZ=n!7jGAsn)onc%M
zEudau>S(3Ge`knGp!UWhkZ(S!i6T%Q42@uFA*z`o7u3m2orP+lC<k>8Q%g~;63w8l
zVQLww8^k$Ko0(dV>R#cgfb}wUAF3Bb2B=q<dIr_+L@}rxOg)QgtY`o=goll?@hPgq
z#W7ItX6k3C7K(OI>Dw*&UPg71NM0NaEn~iIsMd)>P#c)~1FBG8P!BORPEG;sv}ghK
z6Q+(v^-FOH)LTrQit7JFU`a3(1wYryMlqM68Wg#p4rOXRsu`jj)O(q_57pVC8PrFa
zdJ)w+aSqf5rWWCq0`*-A>t$*Us!(50uQ2shRK21Y)ZTbU$m!%+xQJ?+XaMydrnaFv
zQyc@8etsZd124&1(GKd1%(n>D%_8}kVCZ$G)}#8KC<OH!Q;(v0OVon;U#8Meo*~f!
z>M;CrO;JVQtu<L(0(A;glTe)_0?UG-$C)}2)ny_V)MuGmgldB*2XzaoGC29jco8eO
zBiy`fjry&5WaYT%v-0N?Xrudyg_YyXzpG!M#evEcdi#B4O7um1c8%&OMy?na6*I#2
zX%UaF$TW=-v2{g``Oa8z8D1{^TnwqoF~?VklB%4jz&M-iE8eKeG#{%Fmq8mgK@3@$
zV-BArO5kP2B>9`SIIuFsd}xxm43?S-F{C=jtOp%lit@$Q>YV6J74}H`3^B5D@c#if
C{7KmW

diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/gmon.out b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/gmon.out
index 7baa8bca3099ba92e71ae1fcce590668d150fd4a..a89f942e8ff56a7d12117b412b9d9be3676ad794 100644
GIT binary patch
delta 46
pcmZ3b(4;g$mMcTUfdK>}I5w)k<DVFCLzHoYIz-5q141(br2ztN2&Vu5

delta 43
mcmZotTBR^SmTQNa0|N-WVc)3!j$f4VgDQmY%K@PofpP%pY6uMg

diff --git a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/nrLDPC_cnProc_BG1_Z384_13.c b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/nrLDPC_cnProc_BG1_Z384_13.c
index 52a5155524..dc0c67e5df 100644
--- a/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/nrLDPC_cnProc_BG1_Z384_13.c
+++ b/openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_tools/ldpc_gen_files/nrLDPC_cnProc_BG1_Z384_13.c
@@ -5,7 +5,7 @@ void nrLDPC_cnProc_BG1_Z384_13(int8_t* cnProcBuf,int8_t* cnProcBufRes) {
                 __m256i ymm0, min, sgn,ones,maxLLR;
                 ones   = _mm256_set1_epi8((char)1);
                 maxLLR = _mm256_set1_epi8((char)127);
-            for (int i=0;i<12;i++) {
+            for (int i=0;i<12;i+=2) {
                 ymm0 = ((__m256i*)cnProcBuf)[12+i];
                 sgn  = _mm256_sign_epi8(ones, ymm0);
                 min  = _mm256_abs_epi8(ymm0);
@@ -14,8 +14,16 @@ void nrLDPC_cnProc_BG1_Z384_13(int8_t* cnProcBuf,int8_t* cnProcBufRes) {
                 sgn  = _mm256_sign_epi8(sgn, ymm0);
                 min = _mm256_min_epu8(min, maxLLR);
                 ((__m256i*)cnProcBufRes)[0+i] = _mm256_sign_epi8(min, sgn);
+                ymm0 = ((__m256i*)cnProcBuf)[13+i];
+                sgn  = _mm256_sign_epi8(ones, ymm0);
+                min  = _mm256_abs_epi8(ymm0);
+                ymm0 = ((__m256i*)cnProcBuf)[25+i];
+                min  = _mm256_min_epu8(min, _mm256_abs_epi8(ymm0));
+                sgn  = _mm256_sign_epi8(sgn, ymm0);
+                min = _mm256_min_epu8(min, maxLLR);
+                ((__m256i*)cnProcBufRes)[1+i] = _mm256_sign_epi8(min, sgn);
             }
-            for (int i=0;i<12;i++) {
+            for (int i=0;i<12;i+=2) {
                 ymm0 = ((__m256i*)cnProcBuf)[0+i];
                 sgn  = _mm256_sign_epi8(ones, ymm0);
                 min  = _mm256_abs_epi8(ymm0);
@@ -24,8 +32,16 @@ void nrLDPC_cnProc_BG1_Z384_13(int8_t* cnProcBuf,int8_t* cnProcBufRes) {
                 sgn  = _mm256_sign_epi8(sgn, ymm0);
                 min = _mm256_min_epu8(min, maxLLR);
                 ((__m256i*)cnProcBufRes)[12+i] = _mm256_sign_epi8(min, sgn);
+                ymm0 = ((__m256i*)cnProcBuf)[1+i];
+                sgn  = _mm256_sign_epi8(ones, ymm0);
+                min  = _mm256_abs_epi8(ymm0);
+                ymm0 = ((__m256i*)cnProcBuf)[25+i];
+                min  = _mm256_min_epu8(min, _mm256_abs_epi8(ymm0));
+                sgn  = _mm256_sign_epi8(sgn, ymm0);
+                min = _mm256_min_epu8(min, maxLLR);
+                ((__m256i*)cnProcBufRes)[13+i] = _mm256_sign_epi8(min, sgn);
             }
-            for (int i=0;i<12;i++) {
+            for (int i=0;i<12;i+=2) {
                 ymm0 = ((__m256i*)cnProcBuf)[0+i];
                 sgn  = _mm256_sign_epi8(ones, ymm0);
                 min  = _mm256_abs_epi8(ymm0);
@@ -34,6 +50,14 @@ void nrLDPC_cnProc_BG1_Z384_13(int8_t* cnProcBuf,int8_t* cnProcBufRes) {
                 sgn  = _mm256_sign_epi8(sgn, ymm0);
                 min = _mm256_min_epu8(min, maxLLR);
                 ((__m256i*)cnProcBufRes)[24+i] = _mm256_sign_epi8(min, sgn);
+                ymm0 = ((__m256i*)cnProcBuf)[1+i];
+                sgn  = _mm256_sign_epi8(ones, ymm0);
+                min  = _mm256_abs_epi8(ymm0);
+                ymm0 = ((__m256i*)cnProcBuf)[13+i];
+                min  = _mm256_min_epu8(min, _mm256_abs_epi8(ymm0));
+                sgn  = _mm256_sign_epi8(sgn, ymm0);
+                min = _mm256_min_epu8(min, maxLLR);
+                ((__m256i*)cnProcBufRes)[25+i] = _mm256_sign_epi8(min, sgn);
             }
 //Process group with 4 BNs
             for (int i=0;i<60;i++) {
@@ -169,6 +193,7 @@ void nrLDPC_cnProc_BG1_Z384_13(int8_t* cnProcBuf,int8_t* cnProcBufRes) {
                 min = _mm256_min_epu8(min, maxLLR);
                 ((__m256i*)cnProcBufRes)[1140+i] = _mm256_sign_epi8(min, sgn);
            }
+//Process group with 6 BNs
             for (int i=0;i<96;i++) {
                 ymm0 = ((__m256i*)cnProcBuf)[1452+i];
                 sgn  = _mm256_sign_epi8(ones, ymm0);
@@ -283,6 +308,7 @@ void nrLDPC_cnProc_BG1_Z384_13(int8_t* cnProcBuf,int8_t* cnProcBufRes) {
                 min = _mm256_min_epu8(min, maxLLR);
                 ((__m256i*)cnProcBufRes)[1836+i] = _mm256_sign_epi8(min, sgn);
             }
+//Process group with 7 BNs
             for (int i=0;i<60;i++) {
                 ymm0 = ((__m256i*)cnProcBuf)[1992+i];
                 sgn  = _mm256_sign_epi8(ones, ymm0);
@@ -437,6 +463,7 @@ void nrLDPC_cnProc_BG1_Z384_13(int8_t* cnProcBuf,int8_t* cnProcBufRes) {
                 min = _mm256_min_epu8(min, maxLLR);
                 ((__m256i*)cnProcBufRes)[2292+i] = _mm256_sign_epi8(min, sgn);
             }
+//Process group with 8 BNs
             for (int i=0;i<24;i++) {
                 ymm0 = ((__m256i*)cnProcBuf)[2376+i];
                 sgn  = _mm256_sign_epi8(ones, ymm0);
@@ -637,6 +664,7 @@ void nrLDPC_cnProc_BG1_Z384_13(int8_t* cnProcBuf,int8_t* cnProcBufRes) {
                 min = _mm256_min_epu8(min, maxLLR);
                 ((__m256i*)cnProcBufRes)[2520+i] = _mm256_sign_epi8(min, sgn);
               }
+//Process group with 9 BNs
             for (int i=0;i<24;i++) {
                 ymm0 = ((__m256i*)cnProcBuf)[2568+i];
                 sgn  = _mm256_sign_epi8(ones, ymm0);
@@ -889,6 +917,7 @@ void nrLDPC_cnProc_BG1_Z384_13(int8_t* cnProcBuf,int8_t* cnProcBufRes) {
                 min = _mm256_min_epu8(min, maxLLR);
                 ((__m256i*)cnProcBufRes)[2736+i] = _mm256_sign_epi8(min, sgn);
             }
+//Process group with 10 BNs
             for (int i=0;i<12;i++) {
                 ymm0 = ((__m256i*)cnProcBuf)[2772+i];
                 sgn  = _mm256_sign_epi8(ones, ymm0);
@@ -1199,6 +1228,7 @@ void nrLDPC_cnProc_BG1_Z384_13(int8_t* cnProcBuf,int8_t* cnProcBufRes) {
                 min = _mm256_min_epu8(min, maxLLR);
                 ((__m256i*)cnProcBufRes)[2868+i] = _mm256_sign_epi8(min, sgn);
             }
+//Process group with 19 BNs
             for (int i=0;i<48;i++) {
                 ymm0 = ((__m256i*)cnProcBuf)[2928+i];
                 sgn  = _mm256_sign_epi8(ones, ymm0);