maki/openairinterface5g
1
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity

remove calls to clear SIMD registers, that was a historical issue

Browse Source
This commit is contained in:
Laurent THOMAS
2025-01-14 10:06:06 +01:00
parent f7d3b72851
commit a0d6057294
26 changed files with 3 additions and 348 deletions
Download Patch File Download Diff File Expand all files Collapse all files
openair1/PHY/CODING/3gpplte_sse.c
-2
View File
@@ -349,8 +349,6 @@ void threegpplte_turbo_encoder_sse(unsigned char *input,
#ifdef DEBUG_TURBO_ENCODER
printf("term: x0 %u, x1 %u, state1 %d\n",x[10],x[11],state1);
#endif // DEBUG_TURBO_ENCODER
simde_mm_empty();
simde_m_empty();
}
void init_encoder_sse (void) {
openair1/PHY/CODING/3gpplte_turbo_decoder_avx2_16bit.c
-2
View File
@@ -1258,8 +1258,6 @@ unsigned char phy_threegpplte_turbo_decoder16avx2(int16_t *y,
// fprintf(fdavx2,"crc %x, oldcrc %x\n",crc,oldcrc);
simde_mm_empty();
simde_m_empty();
#ifdef DEBUG_LOGMAP
fclose(fdavx2);
openair1/PHY/CODING/3gpplte_turbo_decoder_sse.c
-8
View File
@@ -364,8 +364,6 @@ void compute_gamma(llr_t *m11,llr_t *m10,llr_t *systematic,channel_t *y_parity,
simde_mm_extract_epi8(m11_128[k],15));
*/
#endif
simde_mm_empty();
simde_m_empty();
}
#define L 40
@@ -1183,8 +1181,6 @@ void compute_alpha(llr_t *alpha,llr_t *beta,llr_t *m_11,llr_t *m_10,unsigned sho
break;
}
simde_mm_empty();
simde_m_empty();
}
@@ -1747,8 +1743,6 @@ void compute_beta(llr_t *alpha,llr_t *beta,llr_t *m_11,llr_t *m_10,unsigned shor
break;
}
simde_mm_empty();
simde_m_empty();
}
void compute_ext(llr_t *alpha,llr_t *beta,llr_t *m_11,llr_t *m_10,llr_t *ext, llr_t *systematic,unsigned short frame_length) {
@@ -1910,8 +1904,6 @@ void compute_ext(llr_t *alpha,llr_t *beta,llr_t *m_11,llr_t *m_10,llr_t *ext, ll
}
#endif
simde_mm_empty();
simde_m_empty();
}
openair1/PHY/CODING/3gpplte_turbo_decoder_sse_16bit.c
-2
View File
@@ -1391,8 +1391,6 @@ uint8_t phy_threegpplte_turbo_decoder16(int16_t *y,
fclose(fdsse4);
#endif
#if defined(__x86_64__) || defined(__i386__)
simde_mm_empty();
simde_m_empty();
#endif
if (iteration_cnt > max_iterations)
set_abort(ab, true);
openair1/PHY/CODING/viterbi.c
-1
View File
@@ -314,7 +314,6 @@ void phy_viterbi_dot11_sse2(char *y,unsigned char *decoded_bytes,unsigned short
}
}
simde_mm_empty();
}
#ifdef TEST_DEBUG
openair1/PHY/CODING/viterbi_lte.c
-2
View File
@@ -279,8 +279,6 @@ void phy_viterbi_lte_sse2(int8_t *y,uint8_t *decoded_bytes,uint16_t n)
TB_ptr2-=64;
}
simde_mm_empty();
simde_m_empty();
}
#ifdef TEST_DEBUG
openair1/PHY/LTE_ESTIMATION/lte_ue_measurements.c
-14
View File
@@ -493,8 +493,6 @@ void conjch0_mult_ch1(int *ch0,
dl_ch1_128+=1;
ch0conj_ch1_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
void construct_HhH_elements(int *ch0conj_ch0, //00_00
@@ -567,8 +565,6 @@ void construct_HhH_elements(int *ch0conj_ch0, //00_00
after_mf_10_128+=1;
after_mf_11_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
@@ -595,8 +591,6 @@ void squared_matrix_element(int32_t *Hh_h_00,
Hh_h_00_sq_128+=1;
Hh_h_00_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
@@ -645,8 +639,6 @@ void det_HhH(int32_t *after_mf_00,
//after_mf_10_128+=1;
after_mf_11_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
void numer(int32_t *Hh_h_00_sq,
@@ -691,8 +683,6 @@ void numer(int32_t *Hh_h_00_sq,
h_h_10_sq_128+=1;
h_h_11_sq_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
void dlsch_channel_level_TM34_meas(int *ch00,
@@ -768,8 +758,6 @@ void dlsch_channel_level_TM34_meas(int *ch00,
avg_0[0] = min (avg_0[0], avg_1[0]);
avg_1[0] = avg_0[0];
simde_mm_empty();
simde_m_empty();
}
@@ -1339,8 +1327,6 @@ void lte_ue_measurements(PHY_VARS_UE *ue,
// printf("in lte_ue_measurements: selected rx_antenna[eNB_id==0]:%u\n", ue->measurements.selected_rx_antennas[eNB_id][i]);
} // eNB_id loop
simde_mm_empty();
simde_m_empty();
}
openair1/PHY/LTE_TRANSPORT/ulsch_demodulation.c
-12
View File
@@ -216,8 +216,6 @@ int32_t ulsch_qpsk_llr(LTE_DL_FRAME_PARMS *frame_parms,
(*llrp128)++;
}
simde_mm_empty();
simde_m_empty();
return(0);
}
@@ -245,8 +243,6 @@ void ulsch_16qam_llr(LTE_DL_FRAME_PARMS *frame_parms,
// print_bytes("rxF[i+1]",&rxF[i+1]);
}
simde_mm_empty();
simde_m_empty();
}
void ulsch_64qam_llr(LTE_DL_FRAME_PARMS *frame_parms,
@@ -289,8 +285,6 @@ void ulsch_64qam_llr(LTE_DL_FRAME_PARMS *frame_parms,
(*llrp32)+=12;
}
simde_mm_empty();
simde_m_empty();
}
void ulsch_detection_mrc(LTE_DL_FRAME_PARMS *frame_parms,
@@ -347,8 +341,6 @@ void ulsch_detection_mrc(LTE_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
void ulsch_extract_rbs_single(int32_t **rxdataF,
@@ -524,8 +516,6 @@ void ulsch_channel_compensation(int32_t **rxdataF_ext,
}
}
simde_mm_empty();
simde_m_empty();
}
void ulsch_channel_level(int32_t **drs_ch_estimates_ext,
@@ -556,8 +546,6 @@ void ulsch_channel_level(int32_t **drs_ch_estimates_ext,
((float *)&avg128U)[3])/(float)(nb_rb*12));
}
simde_mm_empty();
simde_m_empty();
}
static int ulsch_power_LUT[750];
openair1/PHY/LTE_UE_TRANSPORT/dci_ue.c
-8
View File
@@ -384,8 +384,6 @@ void pdcch_channel_level(int32_t **dl_ch_estimates_ext,
// printf("Channel level : %d\n",avg[(aatx<<1)+aarx]);
}
simde_mm_empty();
simde_m_empty();
}
@@ -433,8 +431,6 @@ void pdcch_detection_mrc_i(LTE_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -1078,8 +1074,6 @@ void pdcch_channel_compensation(int32_t **rxdataF_ext,
}
simde_mm_empty();
simde_m_empty();
}
void pdcch_detection_mrc(LTE_DL_FRAME_PARMS *frame_parms,
@@ -1103,8 +1097,6 @@ void pdcch_detection_mrc(LTE_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
openair1/PHY/LTE_UE_TRANSPORT/dlsch_demodulation.c
-36
View File
@@ -1481,8 +1481,6 @@ void dlsch_channel_compensation(int **rxdataF_ext,
}
}
simde_mm_empty();
simde_m_empty();
}
void dlsch_channel_compensation_core(int **rxdataF_ext,
@@ -1666,8 +1664,6 @@ void dlsch_channel_compensation_core(int **rxdataF_ext,
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -1706,8 +1702,6 @@ void prec2A_TM56_128(unsigned char pmi,simde__m128i *ch0,simde__m128i *ch1) {
ch0[0] = simde_mm_mulhi_epi16(ch0[0],amp);
ch0[0] = simde_mm_slli_epi16(ch0[0],1);
simde_mm_empty();
simde_m_empty();
}
// precoding is stream 0 .5(1,1) .5(1,-1) .5(1,1) .5(1,-1)
// stream 1 .5(1,-1) .5(1,1) .5(1,-1) .5(1,1)
@@ -1740,8 +1734,6 @@ void prec2A_TM3_128(simde__m128i *ch0,simde__m128i *ch1) {
//ch1[0] = simde_mm_srai_epi16(ch1[0],1);
// print_shorts("prec2A_TM3 ch0 (after):",ch0);
// print_shorts("prec2A_TM3 ch1 (after):",ch1);
simde_mm_empty();
simde_m_empty();
}
// pmi = 0 => stream 0 (1,1), stream 1 (1,-1)
@@ -1782,8 +1774,6 @@ void prec2A_TM4_128(int pmi,simde__m128i *ch0,simde__m128i *ch1) {
// ch1[0] = simde_mm_srai_epi16(ch1[0],1); //divide by 2
//print_shorts("prec2A_TM4 ch0 (end):",ch0);
//print_shorts("prec2A_TM4 ch1 (end):",ch1);
simde_mm_empty();
simde_m_empty();
// print_shorts("prec2A_TM4 ch0 (end):",ch0);
//print_shorts("prec2A_TM4 ch1 (end):",ch1);
}
@@ -2359,8 +2349,6 @@ void dlsch_channel_compensation_TM34(LTE_DL_FRAME_PARMS *frame_parms,
measurements->precoded_cqi_dB[eNB_id][1] = dB_fixed2(precoded_signal_strength1,measurements->n0_power_tot);
// printf("eNB_id %d, symbol %d: precoded CQI %d dB\n",eNB_id,symbol,
// measurements->precoded_cqi_dB[eNB_id][0]);
simde_mm_empty();
simde_m_empty();
}
@@ -2453,8 +2441,6 @@ void dlsch_dual_stream_correlation(LTE_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -2526,8 +2512,6 @@ void dlsch_detection_mrc(LTE_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
void dlsch_detection_mrc_TM34(LTE_DL_FRAME_PARMS *frame_parms,
@@ -2651,8 +2635,6 @@ void dlsch_detection_mrc_TM34(LTE_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
void dlsch_scale_channel(int **dl_ch_estimates_ext,
@@ -2765,8 +2747,6 @@ void dlsch_channel_level(int **dl_ch_estimates_ext,
((int32_t *)&avg128D)[3])/y;
}
simde_mm_empty();
simde_m_empty();
}
void dlsch_channel_level_core(int **dl_ch_estimates_ext,
@@ -2809,8 +2789,6 @@ void dlsch_channel_level_core(int **dl_ch_estimates_ext,
//printf("Channel level [%d]: %d\n",aatx*n_rx + aarx, avg[aatx*n_rx + aarx]);
}
simde_mm_empty();
simde_m_empty();
/* FIXME This part needs to be adapted like the one above */
}
@@ -2857,8 +2835,6 @@ void dlsch_channel_level_median(int **dl_ch_estimates_ext,
}
}
simde_mm_empty();
simde_m_empty();
}
void mmse_processing_oai(LTE_UE_PDSCH *pdsch_vars,
@@ -3189,8 +3165,6 @@ void dlsch_channel_aver_band(int **dl_ch_estimates_ext,
}
}
simde_mm_empty();
simde_m_empty();
}
void rxdataF_to_float(int32_t **rxdataF_ext,
@@ -3558,8 +3532,6 @@ void dlsch_channel_level_TM34(int **dl_ch_estimates_ext,
// printf("From Chan_level aver stream 1 final =%d\n", avg_1[0]);
avg_0[0] = min (avg_0[0], avg_1[0]);
avg_1[0] = avg_0[0];
simde_mm_empty();
simde_m_empty();
}
//compute average channel_level of effective (precoded) channel
@@ -3624,8 +3596,6 @@ void dlsch_channel_level_TM56(int **dl_ch_estimates_ext,
// choose maximum of the 2 effective channels
avg[0] = cmax(avg[0],avg[1]);
simde_mm_empty();
simde_m_empty();
}
//compute average channel_level for TM7
@@ -3684,8 +3654,6 @@ void dlsch_channel_level_TM7(int **dl_bf_ch_estimates_ext,
// printf("Channel level : %d\n",avg[(aatx<<1)+aarx]);
}
simde_mm_empty();
simde_m_empty();
}
//#define ONE_OVER_2_Q15 16384
void dlsch_alamouti(LTE_DL_FRAME_PARMS *frame_parms,
@@ -3753,8 +3721,6 @@ void dlsch_alamouti(LTE_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
//==============================================================================================
@@ -5587,8 +5553,6 @@ unsigned short dlsch_extract_rbs_TM7(int **rxdataF,
}
}
simde_mm_empty();
simde_m_empty();
return(nb_rb/frame_parms->nb_antennas_rx);
}
openair1/PHY/LTE_UE_TRANSPORT/dlsch_llr_computation_avx2.c
+1 -5
View File
@@ -1668,8 +1668,6 @@ void qam64_qam16_avx2(short *stream0_in,
}
simde_mm_empty();
simde_m_empty();
}
@@ -3499,8 +3497,6 @@ void qam64_qam64_avx2(int32_t *stream0_in,
}
simde_mm_empty();
simde_m_empty();
}
#endif
#endif
openair1/PHY/LTE_UE_TRANSPORT/pbch_ue.c
-6
View File
@@ -185,8 +185,6 @@ int pbch_channel_level(int **dl_ch_estimates_ext,
//msg("Channel level : %d, %d\n",avg1, avg2);
}
simde_mm_empty();
simde_m_empty();
return(avg2);
}
@@ -277,8 +275,6 @@ void pbch_channel_compensation(int **rxdataF_ext,
}
}
simde_mm_empty();
simde_m_empty();
}
void pbch_detection_mrc(LTE_DL_FRAME_PARMS *frame_parms,
@@ -302,8 +298,6 @@ void pbch_detection_mrc(LTE_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
void pbch_unscrambling(LTE_DL_FRAME_PARMS *frame_parms,
openair1/PHY/LTE_UE_TRANSPORT/pmch_ue.c
-24
View File
@@ -244,8 +244,6 @@ void mch_channel_level(int **dl_ch_estimates_ext,
// printf("Channel level : %d\n",avg[(aatx<<1)+aarx]);
}
simde_mm_empty();
simde_m_empty();
}
void mch_channel_level_khz_1dot25(int **dl_ch_estimates_ext,
@@ -285,8 +283,6 @@ void mch_channel_level_khz_1dot25(int **dl_ch_estimates_ext,
//printf("Channel level : %d\n",avg[(aatx<<1)+aarx]);
}
simde_mm_empty();
simde_m_empty();
}
@@ -393,8 +389,6 @@ void mch_channel_compensation(int **rxdataF_ext,
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -501,8 +495,6 @@ void mch_channel_compensation_khz_1dot25(int **rxdataF_ext,
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -533,8 +525,6 @@ void mch_detection_mrc(LTE_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -564,8 +554,6 @@ void mch_detection_mrc_khz_1dot25(LTE_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -603,8 +591,6 @@ int mch_qpsk_llr(LTE_DL_FRAME_PARMS *frame_parms,
}
*llr32p = (short *)llr32;
simde_mm_empty();
simde_m_empty();
return(0);
}
@@ -634,8 +620,6 @@ int mch_qpsk_llr_khz_1dot25(LTE_DL_FRAME_PARMS *frame_parms,
}
*llr32p = (short *)llr32;
simde_mm_empty();
simde_m_empty();
return(0);
}
@@ -700,8 +684,6 @@ void mch_16qam_llr(LTE_DL_FRAME_PARMS *frame_parms,
llr32 += 8;
}
simde_mm_empty();
simde_m_empty();
}
void mch_16qam_llr_khz_1dot25(LTE_DL_FRAME_PARMS *frame_parms,
@@ -750,8 +732,6 @@ void mch_16qam_llr_khz_1dot25(LTE_DL_FRAME_PARMS *frame_parms,
llr32 += 8;
}
simde_mm_empty();
simde_m_empty();
}
//----------------------------------------------------------------------------------------------
@@ -843,8 +823,6 @@ void mch_64qam_llr(LTE_DL_FRAME_PARMS *frame_parms,
}
*llr_save = llr;
simde_mm_empty();
simde_m_empty();
}
void mch_64qam_llr_khz_1dot25(LTE_DL_FRAME_PARMS *frame_parms,
@@ -924,8 +902,6 @@ void mch_64qam_llr_khz_1dot25(LTE_DL_FRAME_PARMS *frame_parms,
}
*llr_save = llr;
simde_mm_empty();
simde_m_empty();
}
int avg_pmch[4];
openair1/PHY/NR_TRANSPORT/nr_ulsch_demodulation.c
-14
View File
@@ -223,8 +223,6 @@ static void nr_ulsch_channel_level(int size_est,
}
}
simde_mm_empty();
simde_m_empty();
}
static void nr_ulsch_channel_compensation(c16_t *rxFext,
@@ -334,8 +332,6 @@ static void nr_ulsch_channel_compensation(c16_t *rxFext,
}
}
simde_mm_empty();
simde_m_empty();
}
// Zero Forcing Rx function: nr_det_HhH()
@@ -397,8 +393,6 @@ static void nr_ulsch_det_HhH (int32_t *after_mf_00,//a
after_mf_10_128+=1;
after_mf_11_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
/* Zero Forcing Rx function: nr_conjch0_mult_ch1()
@@ -444,8 +438,6 @@ static void nr_ulsch_conjch0_mult_ch1(int *ch0,
dl_ch1_128+=1;
ch0conj_ch1_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
static simde__m128i nr_ulsch_comp_muli_sum(simde__m128i input_x,
@@ -507,8 +499,6 @@ static simde__m128i nr_ulsch_comp_muli_sum(simde__m128i input_x,
//print_ints("unpack hi:",&tmp_z1[0]);
output = simde_mm_packs_epi32(tmp_z0,tmp_z1);
simde_mm_empty();
simde_m_empty();
return(output);
}
@@ -625,8 +615,6 @@ static void nr_ulsch_construct_HhH_elements(int *conjch00_ch00,
after_mf_10_128 += 1;
after_mf_11_128 += 1;
}
simde_mm_empty();
simde_m_empty();
}
// MMSE Rx function: nr_ulsch_mmse_2layers()
@@ -1017,8 +1005,6 @@ static uint8_t nr_ulsch_mmse_2layers(NR_DL_FRAME_PARMS *frame_parms,
after_mf_c_128 += 1;
after_mf_d_128 += 1;
}
simde_mm_empty();
simde_m_empty();
return(0);
}
openair1/PHY/NR_TRANSPORT/nr_ulsch_llr_computation.c
-3
View File
@@ -388,7 +388,6 @@ void nr_ulsch_qpsk_qpsk(c16_t *stream0_in, c16_t *stream1_in, c16_t *stream0_out
}
}
#endif
simde_mm_empty();
}
@@ -1056,7 +1055,6 @@ void nr_ulsch_qam16_qam16(c16_t *stream0_in,
stream0_128i_out[3] = simde_mm_unpackhi_epi32(xmm1_128, xmm3_128); // 8 LLRs, 2 REs
}
#endif
simde_mm_empty();
}
/*
@@ -1777,7 +1775,6 @@ void nr_ulsch_qam64_qam64(c16_t *stream0_in,
}
}
#endif
simde_mm_empty();
}
static void nr_ulsch_shift_llr(int16_t **llr_layers, uint32_t nb_re, uint32_t rxdataF_ext_offset, uint8_t mod_order, int shift)
openair1/PHY/NR_UE_TRANSPORT/csi_rx.c
-6
View File
@@ -86,8 +86,6 @@ void nr_det_A_MF_2x2(int32_t *a_mf_00,
a_mf_10_128+=1;
a_mf_11_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
void nr_squared_matrix_element(int32_t *a,
@@ -100,8 +98,6 @@ void nr_squared_matrix_element(int32_t *a,
a_sq_128+=1;
a_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
void nr_numer_2x2(int32_t *a_00_sq,
@@ -125,8 +121,6 @@ void nr_numer_2x2(int32_t *a_00_sq,
a_10_sq_128+=1;
a_11_sq_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
bool is_csi_rs_in_symbol(const fapi_nr_dl_config_csirs_pdu_rel15_t csirs_config_pdu, const int symbol) {
openair1/PHY/NR_UE_TRANSPORT/nr_dlsch_demodulation.c
-4
View File
@@ -1304,8 +1304,6 @@ static void nr_dlsch_detection_mrc(uint32_t rx_size_symbol,
rho128_0[i] = simde_mm_adds_epi16(simde_mm_srai_epi16(rho128_0[i],1),simde_mm_srai_epi16(rho128_1[i],1));
}*/
}
simde_mm_empty();
simde_m_empty();
}
}
@@ -1617,8 +1615,6 @@ void nr_conjch0_mult_ch1(int *ch0,
dl_ch1_128+=1;
ch0conj_ch1_128+=1;
}
simde_mm_empty();
simde_m_empty();
}
/*
openair1/PHY/NR_UE_TRANSPORT/nr_pbch.c
-2
View File
@@ -263,8 +263,6 @@ void nr_pbch_detection_mrc(NR_DL_FRAME_PARMS *frame_parms,
}
}
simde_mm_empty();
simde_m_empty();
}
void nr_pbch_unscrambling(int16_t *demod_pbch_e,
openair1/PHY/TOOLS/cadd_vv.c
-2
View File
@@ -47,8 +47,6 @@ int32_t sub_cpx_vector16(int16_t *x,
}
simde_mm_empty();
simde_m_empty();
return(0);
}
openair1/PHY/TOOLS/cmult_vv.c
-6
View File
@@ -87,8 +87,6 @@ int mult_cpx_conj_vector(int16_t *x1,
}
simde_mm_empty();
simde_m_empty();
return(0);
}
@@ -150,8 +148,6 @@ int mult_cpx_vector(int16_t *x1, //Q15
x2_128++;
y_128++;
}
simde_mm_empty();
simde_m_empty();
return(0);
}
@@ -207,7 +203,5 @@ int multadd_cpx_vector(int16_t *x1,
x2_128++;
y_128++;
}
simde_mm_empty();
simde_m_empty();
return(0);
}
openair1/PHY/TOOLS/oai_dfts.c
-180
View File
@@ -1661,8 +1661,6 @@ void dft64(int16_t *x,int16_t *y,unsigned char scale)
y256[7] = shiftright_int16_simd256(y256[7], 1);
}
simde_mm_empty();
simde_m_empty();
}
void idft64(int16_t *x,int16_t *y,unsigned char scale)
@@ -1760,8 +1758,6 @@ void idft64(int16_t *x,int16_t *y,unsigned char scale)
y256[7] = shiftright_int16_simd256(y256[7],3);
}
simde_mm_empty();
simde_m_empty();
}
static const int16_t tw128[128] __attribute__((aligned(32))) = { 32767,0,32727,-1608,32609,-3212,32412,-4808,32137,-6393,31785,-7962,31356,-9512,30851,-11039,30272,-12540,29621,-14010,28897,-15447,28105,-16846,27244,-18205,26318,-19520,25329,-20788,24278,-22005,23169,-23170,22004,-24279,20787,-25330,19519,-26319,18204,-27245,16845,-28106,15446,-28898,14009,-29622,12539,-30273,11038,-30852,9511,-31357,7961,-31786,6392,-32138,4807,-32413,3211,-32610,1607,-32728,0,-32767,-1608,-32728,-3212,-32610,-4808,-32413,-6393,-32138,-7962,-31786,-9512,-31357,-11039,-30852,-12540,-30273,-14010,-29622,-15447,-28898,-16846,-28106,-18205,-27245,-19520,-26319,-20788,-25330,-22005,-24279,-23170,-23170,-24279,-22005,-25330,-20788,-26319,-19520,-27245,-18205,-28106,-16846,-28898,-15447,-29622,-14010,-30273,-12540,-30852,-11039,-31357,-9512,-31786,-7962,-32138,-6393,-32413,-4808,-32610,-3212,-32728,-1608};
@@ -1998,8 +1994,6 @@ void dft256(int16_t *x,int16_t *y,unsigned char scale)
}
simde_mm_empty();
simde_m_empty();
}
void idft256(int16_t *x,int16_t *y,unsigned char scale)
@@ -2082,8 +2076,6 @@ void idft256(int16_t *x,int16_t *y,unsigned char scale)
}
simde_mm_empty();
simde_m_empty();
}
static const int16_t tw512[512] __attribute__((aligned(32))) = {
@@ -2307,8 +2299,6 @@ void dft1024(int16_t *x,int16_t *y,unsigned char scale)
}
simde_mm_empty();
simde_m_empty();
}
void idft1024(int16_t *x,int16_t *y,unsigned char scale)
@@ -2362,8 +2352,6 @@ void idft1024(int16_t *x,int16_t *y,unsigned char scale)
}
simde_mm_empty();
simde_m_empty();
}
int16_t tw2048[2048] __attribute__((aligned(32)));
@@ -2454,8 +2442,6 @@ void dft2048(int16_t *x,int16_t *y,unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
void idft2048(int16_t *x,int16_t *y,unsigned char scale)
@@ -2543,8 +2529,6 @@ void idft2048(int16_t *x,int16_t *y,unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
int16_t tw4096[3*2*1024];
@@ -2600,8 +2584,6 @@ void dft4096(int16_t *x,int16_t *y,unsigned char scale)
}
simde_mm_empty();
simde_m_empty();
}
void idft4096(int16_t *x,int16_t *y,unsigned char scale)
@@ -2655,8 +2637,6 @@ void idft4096(int16_t *x,int16_t *y,unsigned char scale)
}
simde_mm_empty();
simde_m_empty();
}
int16_t tw8192[2*4096] __attribute__((aligned(32)));
@@ -2747,8 +2727,6 @@ void dft8192(int16_t *x,int16_t *y,unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
void idft8192(int16_t *x,int16_t *y,unsigned char scale)
@@ -2836,8 +2814,6 @@ void idft8192(int16_t *x,int16_t *y,unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
int16_t tw16384[3*2*4096] __attribute__((aligned(32)));
@@ -2893,8 +2869,6 @@ void dft16384(int16_t *x,int16_t *y,unsigned char scale)
}
simde_mm_empty();
simde_m_empty();
}
void idft16384(int16_t *x,int16_t *y,unsigned char scale)
@@ -2948,8 +2922,6 @@ void idft16384(int16_t *x,int16_t *y,unsigned char scale)
}
simde_mm_empty();
simde_m_empty();
}
int16_t tw32768[2*16384] __attribute__((aligned(32)));
@@ -3040,8 +3012,6 @@ void dft32768(int16_t *x,int16_t *y,unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
void idft32768(int16_t *x,int16_t *y,unsigned char scale)
@@ -3129,8 +3099,6 @@ void idft32768(int16_t *x,int16_t *y,unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
int16_t twa768[512],twb768[512];
@@ -3183,8 +3151,6 @@ void idft768(int16_t *input, int16_t *output, unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
void dft768(int16_t *input, int16_t *output, unsigned char scale)
@@ -3246,8 +3212,6 @@ void dft768(int16_t *input, int16_t *output, unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
int16_t twa1536[1024],twb1536[1024];
@@ -3299,8 +3263,6 @@ void idft1536(int16_t *input, int16_t *output, unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
void dft1536(int16_t *input, int16_t *output, unsigned char scale)
@@ -3362,8 +3324,6 @@ void dft1536(int16_t *input, int16_t *output, unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
int16_t twa3072[2048] __attribute__((aligned(32)));
@@ -3415,8 +3375,6 @@ void dft3072(int16_t *input, int16_t *output,unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
void idft3072(int16_t *input, int16_t *output,unsigned char scale)
@@ -3465,8 +3423,6 @@ void idft3072(int16_t *input, int16_t *output,unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -3527,8 +3483,6 @@ void idft6144(int16_t *input, int16_t *output,unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -3590,8 +3544,6 @@ void dft6144(int16_t *input, int16_t *output,unsigned char scale)
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
}
int16_t twa12288[8192] __attribute__((aligned(32)));
@@ -3654,8 +3606,6 @@ void dft12288(int16_t *input, int16_t *output,unsigned char scale)
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
}
void idft12288(int16_t *input, int16_t *output,unsigned char scale)
@@ -3712,8 +3662,6 @@ void idft12288(int16_t *input, int16_t *output,unsigned char scale)
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
#ifndef MR_MAIN
if (LOG_DUMPFLAG(DEBUG_DFT)) {
LOG_M("idft12288out.m","out",output,6144,1,1);
@@ -3768,8 +3716,6 @@ void dft18432(int16_t *input, int16_t *output,unsigned char scale) {
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
}
void idft18432(int16_t *input, int16_t *output,unsigned char scale) {
@@ -3816,8 +3762,6 @@ void idft18432(int16_t *input, int16_t *output,unsigned char scale) {
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -3882,8 +3826,6 @@ void dft24576(int16_t *input, int16_t *output,unsigned char scale)
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
#ifndef MR_MAIN
if (LOG_DUMPFLAG(DEBUG_DFT)) {
LOG_M("out.m","out",output,24576,1,1);
@@ -3942,8 +3884,6 @@ void idft24576(int16_t *input, int16_t *output,unsigned char scale)
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
#ifndef MR_MAIN
if (LOG_DUMPFLAG(DEBUG_DFT)) {
LOG_M("idft24576out.m","out",output,24576,1,1);
@@ -4006,8 +3946,6 @@ void dft36864(int16_t *input, int16_t *output,uint8_t scale) {
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
#ifndef MR_MAIN
if (LOG_DUMPFLAG(DEBUG_DFT)) {
LOG_M("out.m","out",output,36864,1,1);
@@ -4059,8 +3997,6 @@ void idft36864(int16_t *input, int16_t *output,uint8_t scale) {
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
}
int16_t twa49152[32768] __attribute__((aligned(32)));
@@ -4111,8 +4047,6 @@ void dft49152(int16_t *input, int16_t *output,uint8_t scale) {
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
}
void idft49152(int16_t *input, int16_t *output,uint8_t scale) {
@@ -4159,8 +4093,6 @@ void idft49152(int16_t *input, int16_t *output,uint8_t scale) {
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
}
int16_t tw65536[3*2*16384] __attribute__((aligned(32)));
@@ -4216,8 +4148,6 @@ void idft65536(int16_t *x,int16_t *y,unsigned char scale)
}
simde_mm_empty();
simde_m_empty();
}
int16_t twa98304[65536] __attribute__((aligned(32)));
@@ -4267,8 +4197,6 @@ void dft98304(int16_t *input, int16_t *output,uint8_t scale) {
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
}
void idft98304(int16_t *input, int16_t *output,uint8_t scale) {
@@ -4315,8 +4243,6 @@ void idft98304(int16_t *input, int16_t *output,uint8_t scale) {
y128p+=16;
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -4470,8 +4396,6 @@ void dft12(int16_t *x,int16_t *y ,unsigned char scale_flag)
&y128[10],
&y128[11]);
simde_mm_empty();
simde_m_empty();
}
static const int16_t W1_12s_256[16] __attribute__((aligned(32))) =
@@ -4641,8 +4565,6 @@ void dft12_simd256(int16_t *x,int16_t *y)
&y256[10],
&y256[11]);
simde_mm_empty();
simde_m_empty();
}
static int16_t tw24[88]__attribute__((aligned(32)));
@@ -4735,8 +4657,6 @@ void dft24(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa36[88]__attribute__((aligned(32)));
@@ -4857,8 +4777,6 @@ void dft36(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa48[88]__attribute__((aligned(32)));
@@ -5017,8 +4935,6 @@ void dft48(int16_t *x, int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa60[88]__attribute__((aligned(32)));
@@ -5201,8 +5117,6 @@ void dft60(int16_t *x,int16_t *y,unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t tw72[280]__attribute__((aligned(32)));
@@ -5244,8 +5158,6 @@ void dft72(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t tw96[376]__attribute__((aligned(32)));
@@ -5289,8 +5201,6 @@ void dft96(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa108[280]__attribute__((aligned(32)));
@@ -5339,8 +5249,6 @@ void dft108(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t tw120[472]__attribute__((aligned(32)));
@@ -5380,8 +5288,6 @@ void dft120(int16_t *x,int16_t *y, unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa144[376]__attribute__((aligned(32)));
@@ -5430,8 +5336,6 @@ void dft144(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa180[472]__attribute__((aligned(32)));
@@ -5481,8 +5385,6 @@ void dft180(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa192[376]__attribute__((aligned(32)));
@@ -5539,8 +5441,6 @@ void dft192(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa216[568]__attribute__((aligned(32)));
@@ -5590,8 +5490,6 @@ void dft216(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa240[472]__attribute__((aligned(32)));
@@ -5648,8 +5546,6 @@ void dft240(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa288[760]__attribute__((aligned(32)));
@@ -5699,8 +5595,6 @@ void dft288(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa300[472]__attribute__((aligned(32)));
@@ -5764,8 +5658,6 @@ void dft300(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa324[107*2*4];
@@ -5814,8 +5706,6 @@ void dft324(int16_t *x,int16_t *y,unsigned char scale_flag) // 108 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa360[119*2*4];
@@ -5864,8 +5754,6 @@ void dft360(int16_t *x,int16_t *y,unsigned char scale_flag) // 120 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa384[95*2*4];
@@ -5921,8 +5809,6 @@ void dft384(int16_t *x,int16_t *y,unsigned char scale_flag) // 96 x 4
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa432[107*2*4];
@@ -5977,8 +5863,6 @@ void dft432(int16_t *x,int16_t *y,unsigned char scale_flag) // 108 x 4
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa480[119*2*4];
static int16_t twb480[119*2*4];
@@ -6033,8 +5917,6 @@ void dft480(int16_t *x,int16_t *y,unsigned char scale_flag) // 120 x 4
}
}
simde_mm_empty();
simde_m_empty();
};
@@ -6084,8 +5966,6 @@ void dft540(int16_t *x,int16_t *y,unsigned char scale_flag) // 180 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa576[191*2*4];
@@ -6135,8 +6015,6 @@ void dft576(int16_t *x,int16_t *y,unsigned char scale_flag) // 192 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
@@ -6179,8 +6057,6 @@ void dft600(int16_t *x,int16_t *y,unsigned char scale_flag) // 300 x 2
}
}
simde_mm_empty();
simde_m_empty();
};
@@ -6230,8 +6106,6 @@ void dft648(int16_t *x,int16_t *y,unsigned char scale_flag) // 216 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
@@ -6289,8 +6163,6 @@ void dft720(int16_t *x,int16_t *y,unsigned char scale_flag) // 180 x 4
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa768p[191*2*4];
@@ -6346,8 +6218,6 @@ void dft768p(int16_t *x,int16_t *y,unsigned char scale_flag) { // 192x 4;
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa384i[256];
@@ -6400,8 +6270,6 @@ void idft384(int16_t *input, int16_t *output, unsigned char scale)
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -6451,8 +6319,6 @@ void dft864(int16_t *x,int16_t *y,unsigned char scale_flag) // 288 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa900[299*2*4];
@@ -6501,8 +6367,6 @@ void dft900(int16_t *x,int16_t *y,unsigned char scale_flag) // 300 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
@@ -6560,8 +6424,6 @@ void dft960(int16_t *x,int16_t *y,unsigned char scale_flag) // 240 x 4
}
}
simde_mm_empty();
simde_m_empty();
};
@@ -6611,8 +6473,6 @@ void dft972(int16_t *x,int16_t *y,unsigned char scale_flag) // 324 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa1080[359*2*4];
@@ -6661,8 +6521,6 @@ void dft1080(int16_t *x,int16_t *y,unsigned char scale_flag) // 360 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa1152[287*2*4];
@@ -6719,8 +6577,6 @@ void dft1152(int16_t *x,int16_t *y,unsigned char scale_flag) // 288 x 4
}
}
simde_mm_empty();
simde_m_empty();
};
int16_t twa1200[4784];
@@ -6776,8 +6632,6 @@ void dft1200(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
@@ -6828,8 +6682,6 @@ void dft1296(int16_t *x,int16_t *y,unsigned char scale_flag) //432 * 3
}
}
simde_mm_empty();
simde_m_empty();
};
@@ -6879,8 +6731,6 @@ void dft1440(int16_t *x,int16_t *y,unsigned char scale_flag) // 480 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa1500[2392]__attribute__((aligned(32)));
@@ -6944,8 +6794,6 @@ void dft1500(int16_t *x,int16_t *y,unsigned char scale_flag)
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa1620[539*2*4];
@@ -6994,8 +6842,6 @@ void dft1620(int16_t *x,int16_t *y,unsigned char scale_flag) // 540 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa1728[575*2*4];
@@ -7044,8 +6890,6 @@ void dft1728(int16_t *x,int16_t *y,unsigned char scale_flag) // 576 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa1800[599*2*4];
@@ -7094,8 +6938,6 @@ void dft1800(int16_t *x,int16_t *y,unsigned char scale_flag) // 600 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa1920[479*2*4];
@@ -7150,8 +6992,6 @@ void dft1920(int16_t *x,int16_t *y,unsigned char scale_flag) // 480 x 4
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa1944[647*2*4];
@@ -7200,8 +7040,6 @@ void dft1944(int16_t *x,int16_t *y,unsigned char scale_flag) // 648 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa2160[719*2*4];
@@ -7250,8 +7088,6 @@ void dft2160(int16_t *x,int16_t *y,unsigned char scale_flag) // 720 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa2304[767*2*4];
@@ -7300,8 +7136,6 @@ void dft2304(int16_t *x,int16_t *y,unsigned char scale_flag) // 768 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa2400[599*2*4];
@@ -7357,8 +7191,6 @@ void dft2400(int16_t *x,int16_t *y,unsigned char scale_flag) // 600 x 4
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa2592[863*2*4];
@@ -7407,8 +7239,6 @@ void dft2592(int16_t *x,int16_t *y,unsigned char scale_flag) // 864 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa2700[899*2*4];
@@ -7457,8 +7287,6 @@ void dft2700(int16_t *x,int16_t *y,unsigned char scale_flag) // 900 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa2880[959*2*4];
@@ -7507,8 +7335,6 @@ void dft2880(int16_t *x,int16_t *y,unsigned char scale_flag) // 960 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa2916[971*2*4];
@@ -7557,8 +7383,6 @@ void dft2916(int16_t *x,int16_t *y,unsigned char scale_flag) // 972 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
static int16_t twa3000[599*8]__attribute__((aligned(32)));
@@ -7622,8 +7446,6 @@ void dft3000(int16_t *x,int16_t *y,unsigned char scale_flag) // 600 * 5
}
}
simde_mm_empty();
simde_m_empty();
}
static int16_t twa3240[1079*2*4];
@@ -7672,8 +7494,6 @@ void dft3240(int16_t *x,int16_t *y,unsigned char scale_flag) // 1080 x 3
}
}
simde_mm_empty();
simde_m_empty();
};
void init_rad4(int N,int16_t *tw) {
openair1/PHY/TOOLS/oai_dfts_neon.c
-2
View File
@@ -3633,8 +3633,6 @@ void idft65536(int16_t *x,int16_t *y,unsigned char scale)
}
simde_mm_empty();
simde_m_empty();
}
int16_t twa98304[65536] __attribute__((aligned(32)));
openair1/PHY/TOOLS/signal_energy.c
-2
View File
@@ -105,8 +105,6 @@ int32_t signal_energy_amp_shift(int32_t *input,uint32_t length)
temp -= temp2;
simde_mm_empty();
simde_m_empty();
return((temp>0)?temp:1);
}
openair1/PHY/TOOLS/simde_operations.c
+1 -1
View File
@@ -57,4 +57,4 @@ void simde_mm256_separate_real_imag_parts(simde__m256i *out_re, simde__m256i *ou
*out_re = simde_mm256_permute4x64_epi64(tmp0, 0xd8);
*out_im = simde_mm256_permute4x64_epi64(tmp1, 0xd8);
}
}
openair1/PHY/nr_phy_common/src/nr_phy_common.c
-3
View File
@@ -109,7 +109,6 @@ void nr_16qam_llr(int32_t *rxdataF_comp, int32_t *ch_mag_in, int16_t *llr, uint3
ch_mag_128++;
}
simde_mm_empty();
nb_re &= 0x3;
int16_t *rxDataF_i16 = (int16_t *)rxF_128;
@@ -238,7 +237,6 @@ void nr_64qam_llr(int32_t *rxdataF_comp, int32_t *ch_mag, int32_t *ch_mag2, int1
llr_i16[6 * i + 4] = saturating_sub(mag_realb, abs(llr_i16[6 * i + 2]));
llr_i16[6 * i + 5] = saturating_sub(mag_imagb, abs(llr_i16[6 * i + 3]));
}
simde_mm_empty();
}
void nr_256qam_llr(int32_t *rxdataF_comp, int32_t *ch_mag, int32_t *ch_mag2, int32_t *ch_mag3, int16_t *llr, uint32_t nb_re)
@@ -350,7 +348,6 @@ void nr_256qam_llr(int32_t *rxdataF_comp, int32_t *ch_mag, int32_t *ch_mag2, int
llr_i16[8 * i + 7] = saturating_sub(magc_imag, abs(llr_i16[8 * i + 5]));
}
}
simde_mm_empty();
}
void freq2time(uint16_t ofdm_symbol_size, int16_t *freq_signal, int16_t *time_signal)
openair1/SCHED_NR_UE/phy_frame_config_nr_ue.c
+1 -1
View File
@@ -139,4 +139,4 @@ int sl_nr_ue_slot_select(const sl_nr_phy_config_request_t *cfg, int slot, uint8_
}
return slot_type;
}
}