Skip to content

O
OpenXG-RAN
Commit 12a0ca65 authored by Hongzhi Wang's avatar Hongzhi Wang
Browse files
Options

adding dpdk library and ldpc offload library

parent 530b74dd
Expand all Show whitespace changes
Inline Side-by-side
Showing with 20493 additions and 3 deletions
cmake_targets/CMakeLists.txt
View file @ 12a0ca65
......@@ -995,6 +995,27 @@ TARGET_LINK_LIBRARIES(benetel_5g pthread dl rt m numa)
##########################################################
# LDPC offload library
##########################################################
include_directories ("/usr/local/include")
set(HWLIB_LDPC_OFFLOAD_SOURCE
${OPENAIR1_DIR}/PHY/CODING/nrLDPC_decoder/nrLDPC_decoder_offload.c
# ${OPENAIR_TARGETS}/ARCH/test-bbdev/test_bbdev.c
${OPENAIR_TARGETS}/ARCH/test-bbdev/test_bbdev_perf.c
${OPENAIR_TARGETS}/ARCH/test-bbdev/test_bbdev_vector.c
)
add_library(ldpc_offload MODULE ${HWLIB_LDPC_OFFLOAD_SOURCE} )
set_target_properties(ldpc_offload PROPERTIES COMPILE_FLAGS "-include rte_config.h -march=native -I/usr/local/include")
SET(T1_DPDK_LIBS "-Wl,-rpath,/home/wang/dpdk-20.05/build/include -L/usr/local/lib64 -lrte_node -lrte_graph -lrte_bpf -lrte_flow_classify -lrte_pipeline -lrte_table -lrte_port -lrte_fib -lrte_ipsec -lrte_vhost -lrte_stack -lrte_security -lrte_sched -lrte_reorder -lrte_rib -lrte_rawdev -lrte_pdump -lrte_power -lrte_member -lrte_lpm -lrte_latencystats -lrte_kni -lrte_jobstats -lrte_ip_frag -lrte_gso -lrte_gro -lrte_eventdev -lrte_efd -lrte_distributor -lrte_cryptodev -lrte_compressdev -lrte_cfgfile -lrte_bitratestats -lrte_bbdev -lrte_acl -lrte_timer -lrte_hash -lrte_metrics -lrte_cmdline -lrte_pci -lrte_ethdev -lrte_meter -lrte_net -lrte_mbuf -lrte_mempool -lrte_rcu -lrte_ring -lrte_eal -lrte_telemetry -lrte_kvargs -Wl,--whole-archive -L/usr/local/lib64 -lrte_common_cpt -lrte_common_dpaax -lrte_common_iavf -lrte_common_octeontx -lrte_common_octeontx2 -lrte_bus_dpaa -lrte_bus_fslmc -lrte_bus_ifpga -lrte_bus_pci -lrte_bus_vdev -lrte_bus_vmbus -lrte_mempool_bucket -lrte_mempool_dpaa -lrte_mempool_dpaa2 -lrte_mempool_octeontx -lrte_mempool_octeontx2 -lrte_mempool_ring -lrte_mempool_stack -lrte_pmd_af_packet -lrte_pmd_ark -lrte_pmd_atlantic -lrte_pmd_avp -lrte_pmd_axgbe -lrte_pmd_bond -lrte_pmd_bnx2x -lrte_pmd_bnxt -lrte_pmd_cxgbe -lrte_pmd_dpaa -lrte_pmd_dpaa2 -lrte_pmd_e1000 -lrte_pmd_ena -lrte_pmd_enetc -lrte_pmd_enic -lrte_pmd_failsafe -lrte_pmd_fm10k -lrte_pmd_i40e -lrte_pmd_hinic -lrte_pmd_hns3 -lrte_pmd_iavf -lrte_pmd_ice -lrte_pmd_igc -lrte_pmd_ixgbe -lrte_pmd_kni -lrte_pmd_liquidio -lrte_pmd_memif -lrte_pmd_netvsc -lrte_pmd_nfp -lrte_pmd_null -lrte_pmd_octeontx -lrte_pmd_octeontx2 -lrte_pmd_pcap -lrte_pmd_pfe -lrte_pmd_qede -lrte_pmd_ring -lrte_pmd_sfc -lrte_pmd_softnic -lrte_pmd_tap -lrte_pmd_thunderx -lrte_pmd_vdev_netvsc -lrte_pmd_vhost -lrte_pmd_virtio -lrte_pmd_vmxnet3 -lrte_rawdev_dpaa2_cmdif -lrte_rawdev_dpaa2_qdma -lrte_rawdev_ioat -lrte_rawdev_ntb -lrte_rawdev_octeontx2_dma -lrte_rawdev_octeontx2_ep -lrte_rawdev_skeleton -lrte_pmd_caam_jr -lrte_pmd_ccp -lrte_pmd_dpaa_sec -lrte_pmd_dpaa2_sec -lrte_pmd_nitrox -lrte_pmd_null_crypto -lrte_pmd_octeontx_crypto -lrte_pmd_octeontx2_crypto -lrte_pmd_openssl -lrte_pmd_crypto_scheduler -lrte_pmd_virtio_crypto -lrte_pmd_octeontx_compress -lrte_pmd_qat -lrte_pmd_zlib -lrte_pmd_ifc -lrte_pmd_dpaa_event -lrte_pmd_dpaa2_event -lrte_pmd_octeontx2_event -lrte_pmd_opdl_event -lrte_pmd_skeleton_event -lrte_pmd_sw_event -lrte_pmd_dsw_event -lrte_pmd_octeontx_event -lrte_pmd_bbdev_null -lrte_pmd_bbdev_turbo_sw -lrte_pmd_bbdev_fpga_lte_fec -lrte_pmd_bbdev_fpga_5gnr_fec -Wl,--no-whole-archive -lrte_node -lrte_graph -lrte_bpf -lrte_flow_classify -lrte_pipeline -lrte_table -lrte_port -lrte_fib -lrte_ipsec -lrte_vhost -lrte_stack -lrte_security -lrte_sched -lrte_reorder -lrte_rib -lrte_rawdev -lrte_pdump -lrte_power -lrte_member -lrte_lpm -lrte_latencystats -lrte_kni -lrte_jobstats -lrte_ip_frag -lrte_gso -lrte_gro -lrte_eventdev -lrte_efd -lrte_distributor -lrte_cryptodev -lrte_compressdev -lrte_cfgfile -lrte_bitratestats -lrte_bbdev -lrte_acl -lrte_timer -lrte_hash -lrte_metrics -lrte_cmdline -lrte_pci -lrte_ethdev -lrte_meter -lrte_net -lrte_mbuf -lrte_mempool -lrte_rcu -lrte_ring -lrte_eal -lrte_telemetry -lrte_kvargs -Wl,-Bdynamic -pthread -lm -ldl -lnuma -lpcap")
TARGET_LINK_LIBRARIES(ldpc_offload ${T1_DPDK_LIBS})
TARGET_LINK_LIBRARIES(ldpc_offload pthread dl rt m numa)
##########################################################
include_directories ("${OPENAIR_TARGETS}/ARCH/COMMON")
Message("DEADLINE_SCHEDULER flag is ${DEADLINE_SCHEDULER}")
......
executables/nr-uesoftmodem.c
View file @ 12a0ca65
......@@ -434,6 +434,7 @@ int main( int argc, char **argv ) {
init_opt() ;
load_nrLDPClib();
load_nrLDPClib_offload();
if (ouput_vcd) {
vcd_signal_dumper_init("/tmp/openair_dump_nrUE.vcd");
......
openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_decoder_offload.c 0 → 100644
View file @ 12a0ca65
/*
* 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_offload.c
* \brief Defines the LDPC decoder
* \author openairinterface
* \date 12-06-2021
* \version 1.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"
#define NR_LDPC_ENABLE_PARITY_CHECK
//#define NR_LDPC_PROFILER_DETAIL
#ifdef NR_LDPC_DEBUG_MODE
#include "nrLDPC_tools/nrLDPC_debug.h"
#endif
#include <getopt.h>
#include <inttypes.h>
#include <stdio.h>
#include <string.h>
#include <stdbool.h>
#include <rte_eal.h>
#include <rte_common.h>
#include <rte_string_fns.h>
#include <rte_cycles.h>
#include <rte_lcore.h>
#include "nrLDPC_offload.h"
#include <math.h>
#include <rte_dev.h>
#include <rte_launch.h>
#include <rte_bbdev.h>
#include <rte_malloc.h>
#include <rte_random.h>
#include <rte_hexdump.h>
#include <rte_interrupts.h>
#define MAX_QUEUES RTE_MAX_LCORE
#define TEST_REPETITIONS 1000
/* Switch between PMD and Interrupt for throughput TC */
static bool intr_enabled;
/* LLR arithmetic representation for numerical conversion */
static int ldpc_llr_decimals;
static int ldpc_llr_size;
/* Keep track of the LDPC decoder device capability flag */
static uint32_t ldpc_cap_flags;
/* Represents tested active devices */
static struct active_device {
const char *driver_name;
uint8_t dev_id;
uint16_t supported_ops;
uint16_t queue_ids[MAX_QUEUES];
uint16_t nb_queues;
struct rte_mempool *ops_mempool;
struct rte_mempool *in_mbuf_pool;
struct rte_mempool *hard_out_mbuf_pool;
struct rte_mempool *soft_out_mbuf_pool;
struct rte_mempool *harq_in_mbuf_pool;
struct rte_mempool *harq_out_mbuf_pool;
} active_devs[RTE_BBDEV_MAX_DEVS];
static uint8_t nb_active_devs;
/* Data buffers used by BBDEV ops */
struct test_buffers {
struct rte_bbdev_op_data *inputs;
struct rte_bbdev_op_data *hard_outputs;
struct rte_bbdev_op_data *soft_outputs;
struct rte_bbdev_op_data *harq_inputs;
struct rte_bbdev_op_data *harq_outputs;
};
/* Operation parameters specific for given test case */
struct test_op_params {
struct rte_mempool *mp;
struct rte_bbdev_dec_op *ref_dec_op;
struct rte_bbdev_enc_op *ref_enc_op;
uint16_t burst_sz;
uint16_t num_to_process;
uint16_t num_lcores;
int vector_mask;
rte_atomic16_t sync;
struct test_buffers q_bufs[RTE_MAX_NUMA_NODES][MAX_QUEUES];
};
/* Contains per lcore params */
struct thread_params {
uint8_t dev_id;
uint16_t queue_id;
uint32_t lcore_id;
uint64_t start_time;
double ops_per_sec;
double mbps;
uint8_t iter_count;
double iter_average;
double bler;
rte_atomic16_t nb_dequeued;
rte_atomic16_t processing_status;
rte_atomic16_t burst_sz;
struct test_op_params *op_params;
struct rte_bbdev_dec_op *dec_ops[MAX_BURST];
struct rte_bbdev_enc_op *enc_ops[MAX_BURST];
};
/* Defines how many testcases can be specified as cmdline args */
#define MAX_CMDLINE_TESTCASES 8
static const char tc_sep = ',';
/* Declare structure for command line test parameters and options */
/*static struct test_params {
struct test_command *test_to_run[MAX_CMDLINE_TESTCASES];
unsigned int num_tests;
unsigned int num_ops;
unsigned int burst_sz;
unsigned int num_lcores;
double snr;
unsigned int iter_max;
char test_vector_filename[PATH_MAX];
bool init_device;
} test_params;
static struct test_commands_list commands_list =
TAILQ_HEAD_INITIALIZER(commands_list);
void
add_test_command(struct test_command *t)
{
TAILQ_INSERT_TAIL(&commands_list, t, next);
}
unsigned int
get_num_ops(void)
{
return test_params.num_ops;
}
unsigned int
get_burst_sz(void)
{
return test_params.burst_sz;
}
unsigned int
get_num_lcores(void)
{
return test_params.num_lcores;
}
double
get_snr(void)
{
return test_params.snr;
}
unsigned int
get_iter_max(void)
{
return test_params.iter_max;
}
bool
get_init_device(void)
{
return test_params.init_device;
}
static int
run_all_tests(void)
{
int ret = TEST_SUCCESS;
struct test_command *t;
TAILQ_FOREACH(t, &commands_list, next)
ret |= (int) t->callback();
return ret;
}
static int
run_parsed_tests(struct test_params *tp)
{
int ret = TEST_SUCCESS;
unsigned int i;
for (i = 0; i < tp->num_tests; ++i)
ret |= (int) tp->test_to_run[i]->callback();
return ret;
}
*/
int32_t nrLDPC_decod_offload(t_nrLDPC_dec_params* p_decParams, uint8_t C, uint8_t rv, uint32_t F, int8_t* w, int8_t* p_out)
{
uint32_t numIter = 0;
struct thread_params *t_params_tp;
uint16_t num_lcores=1;
/*uint16_t enq, deq;
const uint16_t queue_id = 1; //tp->queue_id;
const uint16_t burst_sz = 128; //tp->op_params->burst_sz;
const uint16_t num_ops = 128; //tp->op_params->num_to_process;
struct rte_bbdev_dec_op *ops_enq[num_ops];
struct rte_bbdev_dec_op *ops_deq[num_ops];
struct test_buffers *bufs = NULL;
int i, j, ret;
struct rte_bbdev_info info;
uint16_t num_to_enq;
*/
bool extDdr = check_bit(ldpc_cap_flags,
RTE_BBDEV_LDPC_INTERNAL_HARQ_MEMORY_OUT_ENABLE);
/* Allocate memory for thread parameters structure */
t_params_tp = rte_zmalloc(NULL, num_lcores * sizeof(struct thread_params),
RTE_CACHE_LINE_SIZE);
TEST_ASSERT_NOT_NULL(t_params_tp, "Failed to alloc %zuB for t_params",
RTE_ALIGN(sizeof(struct thread_params) * num_lcores,
RTE_CACHE_LINE_SIZE));
// throughput_pmd_lcore_ldpc_dec(&t_params_tp[0]);
return numIter;
}
openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_offload.h 0 → 100644
View file @ 12a0ca65
/* SPDX-License-Identifier: BSD-3-Clause
* Copyright(c) 2017 Intel Corporation
*/
#ifndef _MAIN_H_
#define _MAIN_H_
#include <stddef.h>
#include <sys/queue.h>
#include <rte_common.h>
#include <rte_hexdump.h>
#include <rte_log.h>
#define TEST_SUCCESS 0
#define TEST_FAILED -1
#define TEST_SKIPPED 1
#define MAX_BURST 512U
#define DEFAULT_BURST 32U
#define DEFAULT_OPS 64U
#define DEFAULT_ITER 6U
#define TEST_ASSERT(cond, msg, ...) do { \
if (!(cond)) { \
printf("TestCase %s() line %d failed: " \
msg "\n", __func__, __LINE__, ##__VA_ARGS__); \
return TEST_FAILED; \
} \
} while (0)
/* Compare two buffers (length in bytes) */
#define TEST_ASSERT_BUFFERS_ARE_EQUAL(a, b, len, msg, ...) do { \
if (memcmp((a), (b), len)) { \
printf("TestCase %s() line %d failed: " \
msg "\n", __func__, __LINE__, ##__VA_ARGS__); \
rte_memdump(stdout, "Buffer A", (a), len); \
rte_memdump(stdout, "Buffer B", (b), len); \
return TEST_FAILED; \
} \
} while (0)
#define TEST_ASSERT_SUCCESS(val, msg, ...) do { \
typeof(val) _val = (val); \
if (!(_val == 0)) { \
printf("TestCase %s() line %d failed (err %d): " \
msg "\n", __func__, __LINE__, _val, \
##__VA_ARGS__); \
return TEST_FAILED; \
} \
} while (0)
#define TEST_ASSERT_FAIL(val, msg, ...) \
TEST_ASSERT_SUCCESS(!(val), msg, ##__VA_ARGS__)
#define TEST_ASSERT_NOT_NULL(val, msg, ...) do { \
if ((val) == NULL) { \
printf("TestCase %s() line %d failed (null): " \
msg "\n", __func__, __LINE__, ##__VA_ARGS__); \
return TEST_FAILED; \
} \
} while (0)
struct unit_test_case {
int (*setup)(void);
void (*teardown)(void);
int (*testcase)(void);
const char *name;
};
#define TEST_CASE(testcase) {NULL, NULL, testcase, #testcase}
#define TEST_CASE_ST(setup, teardown, testcase) \
{setup, teardown, testcase, #testcase}
#define TEST_CASES_END() {NULL, NULL, NULL, NULL}
struct unit_test_suite {
const char *suite_name;
int (*setup)(void);
void (*teardown)(void);
struct unit_test_case unit_test_cases[];
};
int unit_test_suite_runner(struct unit_test_suite *suite);
typedef int (test_callback)(void);
TAILQ_HEAD(test_commands_list, test_command);
struct test_command {
TAILQ_ENTRY(test_command) next;
const char *command;
test_callback *callback;
};
void add_test_command(struct test_command *t);
/* Register a test function */
#define REGISTER_TEST_COMMAND(name, testsuite) \
static int test_func_##name(void) \
{ \
return unit_test_suite_runner(&testsuite); \
} \
static struct test_command test_struct_##name = { \
.command = RTE_STR(name), \
.callback = test_func_##name, \
}; \
RTE_INIT(test_register_##name) \
{ \
add_test_command(&test_struct_##name); \
}
const char *get_vector_filename(void);
unsigned int get_num_ops(void);
unsigned int get_burst_sz(void);
unsigned int get_num_lcores(void);
double get_snr(void);
unsigned int get_iter_max(void);
bool get_init_device(void);
#endif
openair1/PHY/CODING/nrLDPC_defs.h
View file @ 12a0ca65
......@@ -56,4 +56,5 @@ typedef int(*nrLDPC_encoderfunc_t)(unsigned char **,unsigned char **,int,int,sho
\param p_profiler LDPC profiler statistics
*/
typedef int32_t(*nrLDPC_decoderfunc_t)(t_nrLDPC_dec_params* , int8_t*, int8_t* , t_nrLDPC_procBuf* , t_nrLDPC_time_stats* );
typedef int32_t(*nrLDPC_decoffloadfunc_t)(t_nrLDPC_dec_params* , uint8_t , uint8_t, uint32_t , int8_t*, int8_t* );
#endif
openair1/PHY/CODING/nrLDPC_extern.h
View file @ 12a0ca65
......@@ -23,13 +23,17 @@
#ifdef LDPC_LOADER
nrLDPC_decoderfunc_t nrLDPC_decoder;
nrLDPC_encoderfunc_t nrLDPC_encoder;
nrLDPC_decoffloadfunc_t nrLDPC_decoder_offload;
#else
/* functions to load the LDPC shared lib, implemented in openair1/PHY/CODING/nrLDPC_load.c */
extern int load_nrLDPClib(void) ;
extern int load_nrLDPClib_offload(void) ;
extern int load_nrLDPClib_ref(char *libversion, nrLDPC_encoderfunc_t * nrLDPC_encoder_ptr); // for ldpctest
/* ldpc coder/decoder functions, as loaded by load_nrLDPClib(). */
extern nrLDPC_decoderfunc_t nrLDPC_decoder;
extern nrLDPC_encoderfunc_t nrLDPC_encoder;
extern nrLDPC_decoffloadfunc_t nrLDPC_decoder_offload;
// inline functions:
#include "openair1/PHY/CODING/nrLDPC_decoder/nrLDPC_init_mem.h"
#endif
openair1/PHY/CODING/nrLDPC_load.c
View file @ 12a0ca65
......@@ -61,6 +61,16 @@ int load_nrLDPClib(void) {
return 0;
}
int load_nrLDPClib_offload(void) {
loader_shlibfunc_t shlib_decoffload_fdesc;
shlib_decoffload_fdesc.fname = "nrLDPC_decod_offload";
int ret=load_module_shlib("ldpc_offload",&shlib_decoffload_fdesc,1,NULL);
AssertFatal( (ret >= 0),"Error loading ldpc decoder offload");
nrLDPC_decoder_offload = (nrLDPC_decoffloadfunc_t)shlib_decoffload_fdesc.fptr;
return 0;
}
int load_nrLDPClib_ref(char *libversion, nrLDPC_encoderfunc_t * nrLDPC_encoder_ptr) {
loader_shlibfunc_t shlib_encoder_fdesc;
......
targets/ARCH/test-bbdev/Makefile 0 → 100644
View file @ 12a0ca65
# SPDX-License-Identifier: BSD-3-Clause
# Copyright(c) 2017 Intel Corporation
include $(RTE_SDK)/mk/rte.vars.mk
#
# library name
#
APP = testbbdev
CFLAGS += -O3
CFLAGS += $(WERROR_FLAGS)
#
# all sources are stored in SRCS-y
#
SRCS-$(CONFIG_RTE_TEST_BBDEV) += main.c
SRCS-$(CONFIG_RTE_TEST_BBDEV) += test_bbdev.c
SRCS-$(CONFIG_RTE_TEST_BBDEV) += test_bbdev_perf.c
SRCS-$(CONFIG_RTE_TEST_BBDEV) += test_bbdev_vector.c
LDLIBS += -lm
ifeq ($(CONFIG_RTE_LIBRTE_PMD_BBDEV_FPGA_LTE_FEC),y)
LDLIBS += -lrte_pmd_bbdev_fpga_lte_fec
endif
ifeq ($(CONFIG_RTE_LIBRTE_PMD_BBDEV_FPGA_5GNR_FEC),y)
LDLIBS += -lrte_pmd_bbdev_fpga_5gnr_fec
endif
include $(RTE_SDK)/mk/rte.app.mk
targets/ARCH/test-bbdev/ldpc_dec_default.data 0 → 120000
View file @ 12a0ca65
test_vectors/ldpc_dec_v2342_drop.data
\ No newline at end of file
targets/ARCH/test-bbdev/ldpc_enc_default.data 0 → 120000
View file @ 12a0ca65
test_vectors/turbo_dec_c1_k6144_r0_e10376_crc24b_sbd_negllr_high_snr.data
\ No newline at end of file
targets/ARCH/test-bbdev/main.c 0 → 100644
View file @ 12a0ca65
/* SPDX-License-Identifier: BSD-3-Clause
* Copyright(c) 2017 Intel Corporation
*/
#include <getopt.h>
#include <inttypes.h>
#include <stdio.h>
#include <string.h>
#include <stdbool.h>
#include <rte_eal.h>
#include <rte_common.h>
#include <rte_string_fns.h>
#include <rte_cycles.h>
#include <rte_lcore.h>
#include "main.h"
/* Defines how many testcases can be specified as cmdline args */
#define MAX_CMDLINE_TESTCASES 8
static const char tc_sep = ',';
/* Declare structure for command line test parameters and options */
static struct test_params {
struct test_command *test_to_run[MAX_CMDLINE_TESTCASES];
unsigned int num_tests;
unsigned int num_ops;
unsigned int burst_sz;
unsigned int num_lcores;
double snr;
unsigned int iter_max;
char test_vector_filename[PATH_MAX];
bool init_device;
} test_params;
static struct test_commands_list commands_list =
TAILQ_HEAD_INITIALIZER(commands_list);
void
add_test_command(struct test_command *t)
{
TAILQ_INSERT_TAIL(&commands_list, t, next);
}
int
unit_test_suite_runner(struct unit_test_suite *suite)
{
int test_result = TEST_SUCCESS;
unsigned int total = 0, skipped = 0, succeeded = 0, failed = 0;
uint64_t start, end;
printf("\n===========================================================\n");
printf("Starting Test Suite : %s\n", suite->suite_name);
start = rte_rdtsc_precise();
if (suite->setup) {
test_result = suite->setup();
if (test_result == TEST_FAILED) {
printf(" + Test suite setup %s failed!\n",
suite->suite_name);
printf(" + ------------------------------------------------------- +\n");
return 1;
}
if (test_result == TEST_SKIPPED) {
printf(" + Test suite setup %s skipped!\n",
suite->suite_name);
printf(" + ------------------------------------------------------- +\n");
return 0;
}
}
while (suite->unit_test_cases[total].testcase) {
if (suite->unit_test_cases[total].setup)
test_result = suite->unit_test_cases[total].setup();
if (test_result == TEST_SUCCESS)
test_result = suite->unit_test_cases[total].testcase();
if (suite->unit_test_cases[total].teardown)
suite->unit_test_cases[total].teardown();
if (test_result == TEST_SUCCESS) {
succeeded++;
printf("TestCase [%2d] : %s passed\n", total,
suite->unit_test_cases[total].name);
} else if (test_result == TEST_SKIPPED) {
skipped++;
printf("TestCase [%2d] : %s skipped\n", total,
suite->unit_test_cases[total].name);
} else {
failed++;
printf("TestCase [%2d] : %s failed\n", total,
suite->unit_test_cases[total].name);
}
total++;
}
/* Run test suite teardown */
if (suite->teardown)
suite->teardown();
end = rte_rdtsc_precise();
printf(" + ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ +\n");
printf(" + Test Suite Summary : %s\n", suite->suite_name);
printf(" + Tests Total : %2d\n", total);
printf(" + Tests Skipped : %2d\n", skipped);
printf(" + Tests Passed : %2d\n", succeeded);
printf(" + Tests Failed : %2d\n", failed);
printf(" + Tests Lasted : %lg ms\n",
((end - start) * 1000) / (double)rte_get_tsc_hz());
printf(" + ~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~~ +\n");
return (failed > 0) ? 1 : 0;
}
const char *
get_vector_filename(void)
{
return test_params.test_vector_filename;
}
unsigned int
get_num_ops(void)
{
return test_params.num_ops;
}
unsigned int
get_burst_sz(void)
{
return test_params.burst_sz;
}
unsigned int
get_num_lcores(void)
{
return test_params.num_lcores;
}
double
get_snr(void)
{
return test_params.snr;
}
unsigned int
get_iter_max(void)
{
return test_params.iter_max;
}
bool
get_init_device(void)
{
return test_params.init_device;
}
static void
print_usage(const char *prog_name)
{
struct test_command *t;
printf("***Usage: %s [EAL params] [-- [-n/--num-ops NUM_OPS]\n"
"\t[-b/--burst-size BURST_SIZE]\n"
"\t[-v/--test-vector VECTOR_FILE]\n"
"\t[-c/--test-cases TEST_CASE[,TEST_CASE,...]]]\n",
prog_name);
printf("Available testcases: ");
TAILQ_FOREACH(t, &commands_list, next)
printf("%s ", t->command);
printf("\n");
}
static int
parse_args(int argc, char **argv, struct test_params *tp)
{
int opt, option_index;
unsigned int num_tests = 0;
bool test_cases_present = false;
bool test_vector_present = false;
struct test_command *t;
char *tokens[MAX_CMDLINE_TESTCASES];
int tc, ret;
static struct option lgopts[] = {
{ "num-ops", 1, 0, 'n' },
{ "burst-size", 1, 0, 'b' },
{ "test-cases", 1, 0, 'c' },
{ "test-vector", 1, 0, 'v' },
{ "lcores", 1, 0, 'l' },
{ "snr", 1, 0, 's' },
{ "iter_max", 6, 0, 't' },
{ "init-device", 0, 0, 'i'},
{ "help", 0, 0, 'h' },
{ NULL, 0, 0, 0 }
};
tp->iter_max = DEFAULT_ITER;
while ((opt = getopt_long(argc, argv, "hin:b:c:v:l:s:t:", lgopts,
&option_index)) != EOF)
switch (opt) {
case 'n':
TEST_ASSERT(strlen(optarg) > 0,
"Num of operations is not provided");
tp->num_ops = strtol(optarg, NULL, 10);
break;
case 'b':
TEST_ASSERT(strlen(optarg) > 0,
"Burst size is not provided");
tp->burst_sz = strtol(optarg, NULL, 10);
TEST_ASSERT(tp->burst_sz <= MAX_BURST,
"Burst size mustn't be greater than %u",
MAX_BURST);
break;
case 'c':
TEST_ASSERT(test_cases_present == false,
"Test cases provided more than once");
test_cases_present = true;
ret = rte_strsplit(optarg, strlen(optarg),
tokens, MAX_CMDLINE_TESTCASES, tc_sep);
TEST_ASSERT(ret <= MAX_CMDLINE_TESTCASES,
"Too many test cases (max=%d)",
MAX_CMDLINE_TESTCASES);
for (tc = 0; tc < ret; ++tc) {
/* Find matching test case */
TAILQ_FOREACH(t, &commands_list, next)
if (!strcmp(tokens[tc], t->command))
tp->test_to_run[num_tests] = t;
TEST_ASSERT(tp->test_to_run[num_tests] != NULL,
"Unknown test case: %s",
tokens[tc]);
++num_tests;
}
break;
case 'v':
TEST_ASSERT(test_vector_present == false,
"Test vector provided more than once");
test_vector_present = true;
TEST_ASSERT(strlen(optarg) > 0,
"Config file name is null");
snprintf(tp->test_vector_filename,
sizeof(tp->test_vector_filename),
"%s", optarg);
break;
case 's':
TEST_ASSERT(strlen(optarg) > 0,
"SNR is not provided");
tp->snr = strtod(optarg, NULL);
break;
case 't':
TEST_ASSERT(strlen(optarg) > 0,
"Iter_max is not provided");
tp->iter_max = strtol(optarg, NULL, 10);
break;
case 'l':
TEST_ASSERT(strlen(optarg) > 0,
"Num of lcores is not provided");
tp->num_lcores = strtol(optarg, NULL, 10);
TEST_ASSERT(tp->num_lcores <= RTE_MAX_LCORE,
"Num of lcores mustn't be greater than %u",
RTE_MAX_LCORE);
break;
case 'i':
/* indicate fpga fec config required */
tp->init_device = true;
break;
case 'h':
print_usage(argv[0]);
return 0;
default:
printf("ERROR: Unknown option: -%c\n", opt);
return -1;
}
if (tp->num_ops == 0) {
printf(
"WARNING: Num of operations was not provided or was set 0. Set to default (%u)\n",
DEFAULT_OPS);
tp->num_ops = DEFAULT_OPS;
}
if (tp->burst_sz == 0) {
printf(
"WARNING: Burst size was not provided or was set 0. Set to default (%u)\n",
DEFAULT_BURST);
tp->burst_sz = DEFAULT_BURST;
}
if (tp->num_lcores == 0) {
printf(
"WARNING: Num of lcores was not provided or was set 0. Set to value from RTE config (%u)\n",
rte_lcore_count());
tp->num_lcores = rte_lcore_count();
}
TEST_ASSERT(tp->burst_sz <= tp->num_ops,
"Burst size (%u) mustn't be greater than num ops (%u)",
tp->burst_sz, tp->num_ops);
tp->num_tests = num_tests;
return 0;
}
static int
run_all_tests(void)
{
int ret = TEST_SUCCESS;
struct test_command *t;
TAILQ_FOREACH(t, &commands_list, next)
ret |= (int) t->callback();
return ret;
}
static int
run_parsed_tests(struct test_params *tp)
{
int ret = TEST_SUCCESS;
unsigned int i;
for (i = 0; i < tp->num_tests; ++i)
ret |= (int) tp->test_to_run[i]->callback();
return ret;
}
int
main(int argc, char **argv)
{
int ret;
/* Init EAL */
ret = rte_eal_init(argc, argv);
if (ret < 0)
return 1;
argc -= ret;
argv += ret;
/* Parse application arguments (after the EAL ones) */
ret = parse_args(argc, argv, &test_params);
if (ret < 0) {
print_usage(argv[0]);
return 1;
}
/* If no argument provided - run all tests */
if (test_params.num_tests == 0)
return run_all_tests();
else
return run_parsed_tests(&test_params);
}
targets/ARCH/test-bbdev/main.h 0 → 100644
View file @ 12a0ca65
/* SPDX-License-Identifier: BSD-3-Clause
* Copyright(c) 2017 Intel Corporation
*/
#ifndef _MAIN_H_
#define _MAIN_H_
#include <stddef.h>
#include <sys/queue.h>
#include <rte_common.h>
#include <rte_hexdump.h>
#include <rte_log.h>
#define TEST_SUCCESS 0
#define TEST_FAILED -1
#define TEST_SKIPPED 1
#define MAX_BURST 512U
#define DEFAULT_BURST 32U
#define DEFAULT_OPS 64U
#define DEFAULT_ITER 6U
#define TEST_ASSERT(cond, msg, ...) do { \
if (!(cond)) { \
printf("TestCase %s() line %d failed: " \
msg "\n", __func__, __LINE__, ##__VA_ARGS__); \
return TEST_FAILED; \
} \
} while (0)
/* Compare two buffers (length in bytes) */
#define TEST_ASSERT_BUFFERS_ARE_EQUAL(a, b, len, msg, ...) do { \
if (memcmp((a), (b), len)) { \
printf("TestCase %s() line %d failed: " \
msg "\n", __func__, __LINE__, ##__VA_ARGS__); \
rte_memdump(stdout, "Buffer A", (a), len); \
rte_memdump(stdout, "Buffer B", (b), len); \
return TEST_FAILED; \
} \
} while (0)
#define TEST_ASSERT_SUCCESS(val, msg, ...) do { \
typeof(val) _val = (val); \
if (!(_val == 0)) { \
printf("TestCase %s() line %d failed (err %d): " \
msg "\n", __func__, __LINE__, _val, \
##__VA_ARGS__); \
return TEST_FAILED; \
} \
} while (0)
#define TEST_ASSERT_FAIL(val, msg, ...) \
TEST_ASSERT_SUCCESS(!(val), msg, ##__VA_ARGS__)
#define TEST_ASSERT_NOT_NULL(val, msg, ...) do { \
if ((val) == NULL) { \
printf("TestCase %s() line %d failed (null): " \
msg "\n", __func__, __LINE__, ##__VA_ARGS__); \
return TEST_FAILED; \
} \
} while (0)
struct unit_test_case {
int (*setup)(void);
void (*teardown)(void);
int (*testcase)(void);
const char *name;
};
#define TEST_CASE(testcase) {NULL, NULL, testcase, #testcase}
#define TEST_CASE_ST(setup, teardown, testcase) \
{setup, teardown, testcase, #testcase}
#define TEST_CASES_END() {NULL, NULL, NULL, NULL}
struct unit_test_suite {
const char *suite_name;
int (*setup)(void);
void (*teardown)(void);
struct unit_test_case unit_test_cases[];
};
int unit_test_suite_runner(struct unit_test_suite *suite);
typedef int (test_callback)(void);
TAILQ_HEAD(test_commands_list, test_command);
struct test_command {
TAILQ_ENTRY(test_command) next;
const char *command;
test_callback *callback;
};
void add_test_command(struct test_command *t);
/* Register a test function */
#define REGISTER_TEST_COMMAND(name, testsuite) \
static int test_func_##name(void) \
{ \
return unit_test_suite_runner(&testsuite); \
} \
static struct test_command test_struct_##name = { \
.command = RTE_STR(name), \
.callback = test_func_##name, \
}; \
RTE_INIT(test_register_##name) \
{ \
add_test_command(&test_struct_##name); \
}
const char *get_vector_filename(void);
unsigned int get_num_ops(void);
unsigned int get_burst_sz(void);
unsigned int get_num_lcores(void);
double get_snr(void);
unsigned int get_iter_max(void);
bool get_init_device(void);
#endif
targets/ARCH/test-bbdev/meson.build 0 → 100644
View file @ 12a0ca65
# SPDX-License-Identifier: BSD-3-Clause
# Copyright(c) 2018 Intel Corporation
sources = files('main.c',
'test_bbdev.c',
'test_bbdev_perf.c',
'test_bbdev_vector.c')
deps += ['bbdev', 'bus_vdev']
if dpdk_conf.has('RTE_LIBRTE_PMD_BBDEV_FPGA_LTE_FEC')
deps += ['pmd_bbdev_fpga_lte_fec']
endif
if dpdk_conf.has('RTE_LIBRTE_PMD_BBDEV_FPGA_5GNR_FEC')
deps += ['pmd_bbdev_fpga_5gnr_fec']
endif
targets/ARCH/test-bbdev/test-bbdev.py 0 → 100755
View file @ 12a0ca65
#!/usr/bin/env python
# SPDX-License-Identifier: BSD-3-Clause
# Copyright(c) 2017 Intel Corporation
import sys
import os
import argparse
import subprocess
import shlex
from threading import Timer
def kill(process):
print "ERROR: Test app timed out"
process.kill()
if "RTE_SDK" in os.environ:
dpdk_path = os.environ["RTE_SDK"]
else:
dpdk_path = "../.."
if "RTE_TARGET" in os.environ:
dpdk_target = os.environ["RTE_TARGET"]
else:
dpdk_target = "x86_64-native-linux-gcc"
parser = argparse.ArgumentParser(
description='BBdev Unit Test Application',
formatter_class=argparse.ArgumentDefaultsHelpFormatter)
parser.add_argument("-p", "--testapp-path",
help="specifies path to the bbdev test app",
default=dpdk_path + "/" + dpdk_target + "/app/testbbdev")
parser.add_argument("-e", "--eal-params",
help="EAL arguments which are passed to the test app",
default="--vdev=baseband_null0")
parser.add_argument("-t", "--timeout",
type=int,
help="Timeout in seconds",
default=300)
parser.add_argument("-c", "--test-cases",
nargs="+",
help="Defines test cases to run. Run all if not specified")
parser.add_argument("-v", "--test-vector",
nargs="+",
help="Specifies paths to the test vector files.",
default=[dpdk_path +
"/app/test-bbdev/test_vectors/bbdev_null.data"])
parser.add_argument("-n", "--num-ops",
type=int,
help="Number of operations to process on device.",
default=32)
parser.add_argument("-b", "--burst-size",
nargs="+",
type=int,
help="Operations enqueue/dequeue burst size.",
default=[32])
parser.add_argument("-l", "--num-lcores",
type=int,
help="Number of lcores to run.",
default=16)
parser.add_argument("-i", "--init-device",
action='store_true',
help="Initialise PF device with default values.")
args = parser.parse_args()
if not os.path.exists(args.testapp_path):
print "No such file: " + args.testapp_path
sys.exit(1)
params = [args.testapp_path]
if args.eal_params:
params.extend(shlex.split(args.eal_params))
params.extend(["--"])
if args.num_ops:
params.extend(["-n", str(args.num_ops)])
if args.num_lcores:
params.extend(["-l", str(args.num_lcores)])
if args.test_cases:
params.extend(["-c"])
params.extend([",".join(args.test_cases)])
if args.init_device:
params.extend(["-i"])
exit_status = 0
for vector in args.test_vector:
for burst_size in args.burst_size:
call_params = params[:]
call_params.extend(["-v", vector])
call_params.extend(["-b", str(burst_size)])
params_string = " ".join(call_params)
print("Executing: {}".format(params_string))
app_proc = subprocess.Popen(call_params)
if args.timeout > 0:
timer = Timer(args.timeout, kill, [app_proc])
timer.start()
try:
app_proc.communicate()
except:
print("Error: failed to execute: {}".format(params_string))
finally:
timer.cancel()
if app_proc.returncode != 0:
exit_status = 1
print("ERROR TestCase failed. Failed test for vector {}. Return code: {}".format(
vector, app_proc.returncode))
sys.exit(exit_status)
targets/ARCH/test-bbdev/test_bbdev.c 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/test_bbdev_perf.c 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/test_bbdev_vector.c 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/test_bbdev_vector.h 0 → 100644
View file @ 12a0ca65
/* SPDX-License-Identifier: BSD-3-Clause
* Copyright(c) 2017 Intel Corporation
*/
#ifndef TEST_BBDEV_VECTOR_H_
#define TEST_BBDEV_VECTOR_H_
#include <rte_bbdev_op.h>
/* Flags which are set when specific parameter is define in vector file */
enum {
TEST_BBDEV_VF_E = (1ULL << 0),
TEST_BBDEV_VF_EA = (1ULL << 1),
TEST_BBDEV_VF_EB = (1ULL << 2),
TEST_BBDEV_VF_K = (1ULL << 3),
TEST_BBDEV_VF_K_NEG = (1ULL << 4),
TEST_BBDEV_VF_K_POS = (1ULL << 5),
TEST_BBDEV_VF_C_NEG = (1ULL << 6),
TEST_BBDEV_VF_C = (1ULL << 7),
TEST_BBDEV_VF_CAB = (1ULL << 8),
TEST_BBDEV_VF_RV_INDEX = (1ULL << 9),
TEST_BBDEV_VF_ITER_MAX = (1ULL << 10),
TEST_BBDEV_VF_ITER_MIN = (1ULL << 11),
TEST_BBDEV_VF_EXPECTED_ITER_COUNT = (1ULL << 12),
TEST_BBDEV_VF_EXT_SCALE = (1ULL << 13),
TEST_BBDEV_VF_NUM_MAPS = (1ULL << 14),
TEST_BBDEV_VF_NCB = (1ULL << 15),
TEST_BBDEV_VF_NCB_NEG = (1ULL << 16),
TEST_BBDEV_VF_NCB_POS = (1ULL << 17),
TEST_BBDEV_VF_R = (1ULL << 18),
TEST_BBDEV_VF_BG = (1ULL << 19),
TEST_BBDEV_VF_ZC = (1ULL << 20),
TEST_BBDEV_VF_F = (1ULL << 21),
TEST_BBDEV_VF_QM = (1ULL << 22),
TEST_BBDEV_VF_CODE_BLOCK_MODE = (1ULL << 23),
TEST_BBDEV_VF_OP_FLAGS = (1ULL << 24),
TEST_BBDEV_VF_EXPECTED_STATUS = (1ULL << 25),
};
enum op_data_type {
DATA_INPUT = 0,
DATA_SOFT_OUTPUT,
DATA_HARD_OUTPUT,
DATA_HARQ_INPUT,
DATA_HARQ_OUTPUT,
DATA_NUM_TYPES,
};
struct op_data_buf {
uint32_t *addr;
uint32_t length;
};
struct op_data_entries {
struct op_data_buf segments[RTE_BBDEV_TURBO_MAX_CODE_BLOCKS];
unsigned int nb_segments;
};
struct test_bbdev_vector {
enum rte_bbdev_op_type op_type;
int expected_status;
int mask;
union {
struct rte_bbdev_op_turbo_dec turbo_dec;
struct rte_bbdev_op_turbo_enc turbo_enc;
struct rte_bbdev_op_ldpc_dec ldpc_dec;
struct rte_bbdev_op_ldpc_enc ldpc_enc;
};
/* Additional storage for op data entries */
struct op_data_entries entries[DATA_NUM_TYPES];
};
/* fills test vector parameters based on test file */
int
test_bbdev_vector_read(const char *filename,
struct test_bbdev_vector *vector);
#endif /* TEST_BBDEV_VECTOR_H_ */
targets/ARCH/test-bbdev/test_vectors/bbdev_null.data 0 → 100644
View file @ 12a0ca65
# SPDX-License-Identifier: BSD-3-Clause
# Copyright(c) 2017 Intel Corporation
op_type =
RTE_BBDEV_OP_NONE
\ No newline at end of file
targets/ARCH/test-bbdev/test_vectors/demo_dec_scn_5_rv0_drv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_DEC
input0 =
0x8181817f, 0x81817f7f, 0x817f817f, 0x7f7f817f, 0x81817f81, 0x817f7f81, 0x81818181, 0x7f817f7f, 0x7f7f7f7f, 0x817f817f, 0x7f7f817f, 0x817f7f7f, 0x81817f81, 0x7f7f817f, 0x8181817f, 0x817f817f, 0x817f8181, 0x817f817f, 0x7f7f7f7f, 0x81818181, 0x817f7f81, 0x817f817f, 0x817f7f81, 0x817f817f, 0x7f818181, 0x7f7f8181, 0x817f7f81, 0x817f8181, 0x817f7f81, 0x81817f7f, 0x817f8181, 0x7f817f81, 0x817f7f7f, 0x817f817f, 0x81818181, 0x81817f81, 0x7f7f7f81, 0x81818181, 0x7f81817f, 0x81818181, 0x7f817f81, 0x817f7f7f, 0x817f7f7f, 0x7f7f8181, 0x817f7f7f, 0x817f817f, 0x7f81817f, 0x817f7f7f, 0x81818181, 0x817f7f7f, 0x7f7f7f7f, 0x817f7f81, 0x7f817f81, 0x7f7f7f7f, 0x817f817f, 0x7f817f7f, 0x817f817f, 0x817f8181, 0x81817f81, 0x7f817f7f, 0x7f7f7f7f, 0x7f817f81, 0x817f7f81, 0x7f817f7f, 0x817f8181, 0x8181817f, 0x8181817f, 0x7f818181, 0x817f817f, 0x81817f7f, 0x8181817f, 0x7f81817f, 0x7f81817f, 0x81817f81, 0x817f7f81, 0x7f7f7f81, 0x8181817f, 0x7f7f8181, 0x81817f81, 0x7f818181, 0x7f817f81, 0x817f7f7f, 0x7f7f8181, 0x817f817f, 0x7f817f81, 0x817f8181, 0x7f817f7f, 0x7f7f7f7f, 0x7f7f7f81, 0x81817f81, 0x7f7f8181, 0x81817f81, 0x7f818181, 0x7f7f8181, 0x81817f7f, 0x7f7f7f7f, 0x817f817f, 0x81818181, 0x817f7f7f, 0x817f7f81, 0x81818181, 0x7f7f817f, 0x81817f7f, 0x7f7f817f, 0x7f7f817f, 0x7f7f817f, 0x81818181, 0x8181817f, 0x7f7f7f7f, 0x7f817f81, 0x8181817f, 0x7f81817f, 0x7f817f81, 0x7f818181, 0x817f7f7f, 0x7f7f8181, 0x8181817f, 0x7f817f81, 0x7f7f817f, 0x8181817f, 0x7f81817f, 0x7f7f8181, 0x7f7f7f7f, 0x817f7f7f, 0x7f7f7f81, 0x7f81817f, 0x7f7f817f, 0x7f7f7f81, 0x7f817f81, 0x7f7f8181, 0x7f7f7f81, 0x81818181, 0x817f7f81, 0x817f8181, 0x7f7f817f, 0x7f7f817f, 0x7f7f7f7f, 0x817f7f81, 0x7f817f81, 0x7f7f7f81, 0x817f817f, 0x81817f81, 0x7f817f7f, 0x7f817f81, 0x7f7f8181, 0x8181817f, 0x817f7f81, 0x7f7f817f, 0x7f7f817f, 0x7f817f7f, 0x81817f7f, 0x7f817f81, 0x81817f81, 0x7f81817f, 0x81817f7f, 0x817f8181, 0x7f7f7f7f, 0x7f818181, 0x7f81817f, 0x7f7f7f81, 0x7f7f8181, 0x817f8181, 0x817f817f, 0x8181817f, 0x7f81817f, 0x817f7f7f, 0x8181817f, 0x817f817f, 0x7f817f7f, 0x8181817f, 0x81817f7f, 0x81817f7f, 0x817f817f, 0x7f817f7f, 0x81817f81, 0x8181817f, 0x81818181, 0x7f817f81, 0x7f81817f, 0x7f7f817f, 0x817f7f81, 0x81817f7f, 0x817f8181, 0x7f7f7f81, 0x81817f81, 0x8181817f, 0x81818181, 0x7f7f8181, 0x7f7f817f, 0x81817f81, 0x8181817f, 0x7f817f81, 0x81817f81, 0x81818181, 0x7f7f7f7f, 0x817f7f7f, 0x817f7f7f, 0x81817f7f, 0x7f817f81, 0x7f818181, 0x817f817f, 0x817f7f81, 0x81817f81, 0x7f7f7f81, 0x7f817f7f, 0x81818181, 0x817f7f7f, 0x817f7f81, 0x7f817f7f, 0x817f7f7f, 0x817f7f81, 0x7f7f7f81, 0x81817f81, 0x817f7f7f, 0x7f7f7f7f, 0x817f7f7f, 0x7f7f7f81, 0x7f7f8181, 0x817f8181, 0x7f817f81, 0x7f7f7f7f, 0x7f818181, 0x8181817f, 0x81817f7f, 0x817f8181, 0x81817f81, 0x7f817f81, 0x817f8181, 0x7f7f817f, 0x7f818181, 0x817f7f81, 0x817f7f81, 0x7f7f817f, 0x817f7f81, 0x817f817f, 0x7f7f7f7f, 0x81818181, 0x81817f81, 0x81818181, 0x7f817f81, 0x7f81817f, 0x81818181, 0x7f7f7f81, 0x7f7f8181, 0x7f81817f, 0x7f817f81, 0x81817f81, 0x81817f7f, 0x7f817f7f, 0x7f817f81, 0x81818181, 0x7f817f81, 0x81817f81, 0x817f817f, 0x7f7f8181, 0x817f8181, 0x81818181, 0x7f81817f, 0x7f7f817f, 0x817f7f7f, 0x7f7f817f, 0x7f7f7f7f, 0x7f817f7f, 0x7f81817f, 0x817f7f81, 0x817f8181, 0x817f817f, 0x81817f81, 0x7f7f7f7f, 0x81817f81, 0x817f817f, 0x7f7f7f81, 0x7f7f7f7f, 0x7f817f7f, 0x817f7f81, 0x81817f81, 0x817f7f81, 0x81817f81, 0x81817f81, 0x81817f81, 0x817f7f7f, 0x817f817f, 0x817f7f81, 0x817f7f7f, 0x8181817f, 0x81817f7f, 0x81818181, 0x7f7f7f7f, 0x7f7f817f, 0x817f8181, 0x7f7f8181, 0x7f817f81, 0x7f817f81, 0x7f7f7f7f, 0x7f817f7f, 0x7f7f8181, 0x7f7f7f7f, 0x7f817f7f, 0x817f7f7f, 0x8181817f, 0x7f7f7f81, 0x817f7f81, 0x7f817f81, 0x7f7f8181, 0x7f7f8181, 0x7f7f7f7f, 0x817f7f81, 0x7f7f7f7f, 0x7f7f817f, 0x7f7f7f81, 0x817f7f7f, 0x817f7f7f, 0x7f7f8181, 0x817f7f7f, 0x817f7f7f, 0x81817f81, 0x7f7f7f81, 0x7f81817f, 0x7f818181, 0x81817f7f, 0x817f7f7f, 0x817f7f81, 0x7f81817f, 0x7f818181, 0x81818181, 0x817f8181, 0x81818181, 0x817f7f7f, 0x817f7f81, 0x7f818181, 0x7f7f7f7f, 0x7f7f8181, 0x81817f81, 0x817f8181, 0x817f7f7f, 0x7f817f81, 0x817f7f81, 0x7f7f8181, 0x8181817f, 0x7f817f7f, 0x7f817f81, 0x817f8181, 0x7f818181, 0x817f7f81, 0x7f7f817f, 0x81817f81, 0x7f7f8181, 0x817f7f7f, 0x817f8181, 0x7f817f7f, 0x7f81817f, 0x7f7f7f7f, 0x7f7f8181, 0x7f7f7f7f, 0x817f7f81, 0x7f7f7f7f, 0x81817f7f, 0x7f81817f, 0x7f7f8181, 0x81818181, 0x7f81817f, 0x7f81817f, 0x7f7f7f7f, 0x7f7f8181, 0x7f7f8181, 0x7f7f7f7f, 0x817f7f81, 0x7f81817f, 0x817f817f, 0x7f818181, 0x7f7f817f, 0x817f817f, 0x81817f7f, 0x7f817f81, 0x8181817f, 0x817f817f, 0x7f7f817f, 0x7f7f7f7f, 0x817f7f7f, 0x7f7f817f, 0x7f817f81, 0x7f7f8181, 0x7f7f817f, 0x81818181, 0x7f7f7f81, 0x81817f7f, 0x7f7f8181, 0x7f7f817f, 0x7f817f7f, 0x7f81817f, 0x8181817f, 0x817f7f7f, 0x81817f7f, 0x7f7f7f81, 0x817f8181, 0x81817f81, 0x7f7f8181, 0x817f817f, 0x817f7f7f, 0x81818181, 0x817f7f7f, 0x7f7f817f, 0x817f7f7f, 0x81818181, 0x7f7f7f81, 0x7f81817f, 0x81818181, 0x7f7f7f81, 0x7f7f8181, 0x817f7f7f, 0x817f8181, 0x81817f7f, 0x7f818181, 0x7f7f7f81, 0x7f817f81, 0x7f7f8181, 0x7f818181, 0x7f81817f, 0x7f817f7f, 0x7f7f817f, 0x817f817f, 0x8181817f, 0x7f817f81, 0x7f817f7f, 0x81817f81, 0x817f817f, 0x817f8181, 0x81817f7f, 0x81818181, 0x7f7f7f81, 0x81817f7f, 0x81817f7f, 0x7f817f81, 0x7f818181, 0x7f7f8181, 0x81817f7f, 0x817f8181, 0x7f7f8181, 0x7f818181, 0x7f7f7f7f, 0x7f7f817f, 0x7f817f7f, 0x7f81817f, 0x7f817f81, 0x7f81817f, 0x81817f7f, 0x7f7f817f, 0x7f817f7f, 0x7f7f7f7f, 0x817f8181, 0x817f8181, 0x817f8181, 0x81818181, 0x81817f81, 0x7f817f7f, 0x7f817f81, 0x7f7f817f, 0x7f7f817f, 0x81818181, 0x7f817f7f, 0x8181817f, 0x817f8181, 0x7f7f8181, 0x81818181, 0x7f818181, 0x7f817f81, 0x7f7f817f, 0x7f7f7f7f, 0x81817f7f, 0x7f7f8181, 0x8181817f, 0x81817f81, 0x7f817f81, 0x81817f7f, 0x7f7f817f, 0x7f817f81, 0x7f81817f, 0x81817f81, 0x81818181, 0x817f7f81, 0x7f818181, 0x8181817f, 0x81817f7f, 0x817f817f, 0x817f817f, 0x8181817f, 0x7f817f81, 0x8181817f, 0x81818181, 0x7f7f7f7f, 0x81818181, 0x817f817f, 0x7f7f7f81, 0x7f7f7f81, 0x7f81817f, 0x7f818181, 0x817f817f, 0x817f817f, 0x8181817f, 0x7f7f7f7f, 0x81818181, 0x817f817f, 0x817f7f7f, 0x7f818181, 0x817f7f81, 0x7f7f7f7f, 0x817f8181, 0x7f818181, 0x7f817f7f, 0x817f7f7f, 0x81818181, 0x81817f81, 0x81817f7f, 0x81817f7f, 0x7f818181, 0x7f817f7f, 0x817f8181, 0x7f818181, 0x7f7f7f81, 0x7f7f8181, 0x7f7f8181, 0x7f81817f, 0x817f7f81, 0x81817f81, 0x817f7f81, 0x8181817f, 0x817f817f, 0x7f817f81, 0x7f818181, 0x7f7f817f, 0x817f7f7f, 0x7f817f81, 0x7f81817f, 0x81817f7f, 0x8181817f, 0x7f81817f, 0x7f7f7f81, 0x817f7f81, 0x7f817f7f, 0x7f817f7f, 0x7f817f7f, 0x81817f81, 0x7f817f7f, 0x7f7f8181, 0x81817f7f, 0x817f7f81, 0x7f7f7f7f, 0x7f7f7f7f, 0x817f817f, 0x7f7f7f7f, 0x817f8181, 0x7f7f8181, 0x817f817f, 0x7f817f81, 0x7f818181, 0x817f7f81, 0x817f7f7f, 0x81817f7f, 0x7f817f81, 0x7f7f7f81
output0 =
0xea7bdad9, 0xabd8311a, 0x4e7ba2e2, 0x5c5c5c85, 0xc400ed50, 0x9bea8883, 0x04c2b70f, 0x392dc1c2, 0x6f7a1597, 0xe4bbe4c8, 0x350dc432, 0x926071f2, 0x372ea0eb, 0x36d61798, 0x1d5544a1, 0x37de9af4, 0x722e1ff0, 0x35abc04a, 0xff203abe, 0xca7f7d7a, 0x32a305d0, 0x5c08bf1b, 0xae11c62b, 0x9d832088, 0xe3b2ec27, 0x9438eea5, 0x89525b88, 0xe3007430, 0x836b5498, 0xee899e03, 0xe5c91dd4, 0x5117acf9, 0x6b0df72a, 0x7ed367f0, 0xa7cc1dd4, 0x4f8bc304, 0x939bba5d, 0x76a555c3, 0x1e3e0a60, 0x6f395cde, 0x5ca777f3, 0x79163b7d, 0x04f40cd1, 0xfe
basegraph=
1
z_c=
64
n_cb=
4224
q_m=
2
n_filler=
0
e=
2240
rv_index=
0
code_block_mode=
1
iter_max=
63
expected_iter_count=
4
op_flags=
RTE_BBDEV_LDPC_ITERATION_STOP_ENABLE, RTE_BBDEV_LDPC_CRC_TYPE_24B_DROP
expected_status=
OK
targets/ARCH/test-bbdev/test_vectors/demo_dec_scn_7_rv0_drv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_DEC
input0 =
0x7f7f7f81, 0x81817f7f, 0x7f817f7f, 0x7f817f81, 0x7f7f7f7f, 0x7f81817f, 0x7f817f7f, 0x81817f7f, 0x7f81817f, 0x81818181, 0x7f7f7f81, 0x817f7f81, 0x8181817f, 0x7f7f7f81, 0x81817f81, 0x7f818181, 0x81817f81, 0x817f7f7f, 0x7f7f7f81, 0x7f7f817f, 0x7f818181, 0x817f7f81, 0x81817f7f, 0x7f7f817f, 0x817f7f81, 0x7f817f81, 0x7f7f8181, 0x81818181, 0x7f817f81, 0x817f7f81, 0x8181817f, 0x7f7f7f7f, 0x817f817f, 0x81817f81, 0x7f7f7f7f, 0x817f7f81, 0x81818181, 0x817f817f, 0x7f81817f, 0x817f817f, 0x7f7f817f, 0x7f7f817f, 0x7f817f81, 0x8181817f, 0x817f7f7f, 0x7f818181, 0x8181817f, 0x8181817f, 0x81817f81, 0x7f817f81, 0x817f817f, 0x7f7f8181, 0x7f817f7f, 0x81817f81, 0x817f817f, 0x8181817f, 0x8181817f, 0x7f7f8181, 0x817f817f, 0x7f7f7f7f, 0x817f8181, 0x7f817f7f, 0x7f7f817f, 0x7f7f7f81, 0x7f817f81, 0x817f8181, 0x817f8181, 0x81817f81, 0x817f8181, 0x817f7f81, 0x817f7f7f, 0x817f7f7f, 0x817f817f, 0x7f7f8181, 0x81818181, 0x817f7f81, 0x817f7f7f, 0x81817f81, 0x8181817f, 0x81817f81, 0x817f7f81, 0x7f81817f, 0x7f7f7f81, 0x817f817f, 0x817f817f, 0x81817f7f, 0x7f817f7f, 0x81818181, 0x81817f81, 0x81817f7f, 0x7f81817f, 0x817f7f81, 0x7f7f817f, 0x81817f81, 0x81817f7f, 0x7f7f8181, 0x817f7f81, 0x817f8181, 0x817f817f, 0x7f81817f, 0x7f81817f, 0x817f7f7f, 0x7f81817f, 0x817f7f7f, 0x8181817f, 0x81817f7f, 0x7f81817f, 0x8181817f, 0x817f7f7f, 0x81817f7f, 0x81818181, 0x7f817f7f, 0x7f818181, 0x81817f81, 0x8181817f, 0x817f817f, 0x7f7f8181, 0x7f817f7f, 0x7f7f7f81, 0x7f7f8181, 0x81818181, 0x7f817f7f, 0x7f818181, 0x7f7f7f81, 0x7f7f7f7f, 0x7f818181, 0x81817f7f, 0x81818181, 0x81817f81, 0x7f818181, 0x7f7f817f, 0x817f817f, 0x817f817f, 0x7f817f7f, 0x81817f81, 0x81817f81, 0x7f7f7f7f, 0x7f7f7f81, 0x81817f81, 0x7f7f7f81, 0x7f817f7f, 0x7f817f81, 0x7f7f7f7f, 0x7f7f8181, 0x8181817f, 0x817f7f7f, 0x817f8181, 0x817f7f81, 0x7f817f81, 0x7f7f817f, 0x817f7f7f, 0x7f7f817f, 0x817f8181, 0x7f7f7f81, 0x817f8181, 0x81818181, 0x817f7f7f, 0x7f818181, 0x7f81817f, 0x7f81817f, 0x7f7f8181, 0x7f818181, 0x7f818181, 0x817f7f81, 0x817f817f, 0x81817f81, 0x7f7f8181, 0x817f8181, 0x817f817f, 0x7f7f8181, 0x817f817f, 0x817f817f, 0x7f817f81, 0x7f818181, 0x7f817f81, 0x7f818181, 0x81817f7f, 0x7f818181, 0x817f7f81, 0x817f8181, 0x8181817f, 0x7f817f81, 0x81818181, 0x7f81817f, 0x7f81817f, 0x81817f81, 0x7f818181, 0x7f817f81, 0x7f817f81, 0x817f7f7f, 0x7f7f8181, 0x817f7f81, 0x7f817f81, 0x7f81817f, 0x817f817f, 0x7f7f817f, 0x7f7f7f7f, 0x817f7f7f, 0x8181817f, 0x7f817f7f, 0x7f7f7f81, 0x7f7f8181, 0x7f7f817f, 0x81818181, 0x7f7f7f7f, 0x81818181, 0x817f7f7f, 0x817f7f81, 0x817f7f7f, 0x7f817f7f, 0x817f8181, 0x7f817f81, 0x817f7f81, 0x7f817f81, 0x81817f81, 0x81818181, 0x7f7f817f, 0x7f7f817f, 0x7f7f7f81, 0x817f7f7f, 0x7f817f7f, 0x8181817f, 0x7f817f81, 0x817f7f7f, 0x7f7f7f7f, 0x817f7f81, 0x7f7f8181, 0x7f818181, 0x7f817f81, 0x817f7f7f, 0x8181817f, 0x817f7f81, 0x817f7f7f, 0x7f81817f, 0x817f7f7f, 0x7f817f7f, 0x7f7f7f81, 0x7f7f8181, 0x81818181, 0x7f7f7f81, 0x817f8181, 0x817f7f7f, 0x7f7f8181, 0x7f7f7f7f, 0x7f7f817f, 0x7f7f8181, 0x7f7f817f, 0x7f7f817f, 0x7f7f8181, 0x817f817f, 0x817f817f, 0x81818181, 0x817f7f81, 0x7f817f7f, 0x7f818181, 0x7f817f7f, 0x817f817f, 0x817f8181, 0x8181817f, 0x81818181, 0x81817f81, 0x7f7f7f81, 0x81817f81, 0x7f7f7f7f, 0x7f7f7f81, 0x81818181, 0x817f817f, 0x7f7f7f81, 0x81817f81, 0x7f7f8181, 0x817f817f, 0x81818181, 0x817f7f81, 0x817f7f81, 0x81817f7f, 0x7f81817f, 0x7f818181, 0x817f7f81, 0x7f818181, 0x7f7f8181, 0x7f7f817f, 0x81817f81, 0x7f7f7f81, 0x7f7f7f7f, 0x7f7f8181, 0x7f817f7f, 0x7f817f7f, 0x817f7f7f, 0x817f7f81, 0x7f7f817f, 0x817f8181, 0x7f7f7f7f, 0x7f81817f, 0x7f817f7f, 0x817f8181, 0x81817f81, 0x81817f7f, 0x8181817f, 0x7f7f817f, 0x7f7f7f81, 0x7f7f7f81, 0x7f7f7f7f, 0x817f8181, 0x7f81817f, 0x817f7f7f, 0x81817f81, 0x817f7f7f, 0x817f7f7f, 0x7f81817f, 0x7f818181, 0x7f81817f, 0x7f7f7f7f, 0x7f7f7f7f, 0x7f7f7f7f, 0x7f7f817f, 0x817f817f, 0x7f817f81, 0x817f8181, 0x7f7f7f7f, 0x7f818181, 0x7f7f8181, 0x81817f7f, 0x7f7f7f81, 0x817f7f7f, 0x81817f7f, 0x7f817f7f, 0x7f81817f, 0x817f817f, 0x8181817f, 0x7f7f8181, 0x7f7f7f81, 0x81818181, 0x7f7f7f81, 0x7f7f7f7f, 0x7f7f7f7f, 0x81817f81, 0x817f817f, 0x817f7f7f, 0x817f817f, 0x81818181, 0x817f7f81, 0x7f817f7f, 0x81818181, 0x7f7f8181, 0x817f8181, 0x817f7f7f, 0x7f7f7f81, 0x8181817f, 0x81817f81, 0x7f7f8181, 0x81817f81, 0x7f7f8181, 0x7f818181, 0x8181817f, 0x81817f7f, 0x7f7f7f7f, 0x7f7f7f7f, 0x81817f7f, 0x7f818181, 0x81817f7f, 0x81817f81, 0x817f817f, 0x7f7f8181, 0x81817f7f, 0x7f818181, 0x817f7f81, 0x7f81817f, 0x7f81817f, 0x7f817f81, 0x81818181, 0x817f7f81, 0x7f817f7f, 0x7f7f7f81, 0x7f7f8181, 0x81817f81, 0x817f7f7f, 0x7f7f7f7f, 0x81817f7f, 0x7f817f7f, 0x81818181, 0x7f817f7f, 0x8181817f, 0x7f7f7f7f, 0x7f817f7f, 0x817f7f7f, 0x7f7f7f81, 0x817f8181, 0x7f7f7f81, 0x7f817f81, 0x81818181, 0x7f81817f, 0x7f817f81, 0x817f817f, 0x817f7f7f, 0x7f817f81, 0x81817f7f, 0x7f817f7f, 0x817f8181, 0x7f7f8181, 0x7f818181, 0x7f817f81, 0x81818181, 0x7f7f817f, 0x817f7f7f, 0x8181817f, 0x817f8181, 0x81817f7f, 0x81818181, 0x7f818181, 0x7f817f7f, 0x7f7f7f7f, 0x7f817f81, 0x81817f7f, 0x7f817f81, 0x7f817f81, 0x7f7f7f81, 0x81817f81, 0x81817f7f, 0x8181817f, 0x817f817f, 0x817f7f7f, 0x81817f7f, 0x81817f81, 0x7f817f7f, 0x7f817f81, 0x817f817f, 0x7f817f81, 0x7f7f7f7f, 0x817f8181, 0x817f8181, 0x81817f7f, 0x81818181, 0x817f7f7f, 0x7f7f817f, 0x7f81817f, 0x817f7f7f, 0x7f818181, 0x7f7f817f, 0x7f7f817f, 0x81817f81, 0x817f8181, 0x817f7f7f, 0x7f7f8181, 0x7f818181, 0x8181817f, 0x7f7f7f7f, 0x7f817f81, 0x81818181, 0x7f81817f, 0x7f817f7f, 0x81818181, 0x7f81817f, 0x7f7f8181, 0x7f817f81, 0x7f7f8181, 0x817f8181, 0x7f7f7f81, 0x8181817f, 0x817f7f81, 0x7f817f81, 0x817f7f81, 0x7f81817f, 0x817f817f, 0x7f817f81, 0x81818181, 0x817f817f, 0x7f7f817f, 0x7f818181, 0x8181817f, 0x7f817f7f, 0x7f81817f, 0x7f81817f, 0x817f8181, 0x817f7f81, 0x7f81817f, 0x7f81817f, 0x7f81817f, 0x81817f81, 0x7f81817f, 0x817f8181, 0x8181817f, 0x7f7f7f81, 0x817f817f, 0x817f817f, 0x7f7f7f7f, 0x7f7f7f7f, 0x817f8181, 0x817f7f81, 0x7f7f817f, 0x7f818181, 0x81817f81, 0x7f7f8181, 0x7f7f7f7f, 0x7f81817f, 0x7f818181, 0x7f7f7f81, 0x7f7f7f81, 0x817f7f81, 0x817f817f, 0x81818181, 0x7f818181, 0x7f817f81, 0x81817f7f, 0x817f8181, 0x7f7f7f81, 0x81818181, 0x7f81817f, 0x8181817f, 0x817f7f7f, 0x81817f7f, 0x7f817f7f, 0x7f7f8181, 0x817f817f, 0x7f7f7f7f, 0x8181817f, 0x7f7f817f, 0x7f81817f, 0x817f7f7f, 0x817f7f7f, 0x7f81817f, 0x7f817f81, 0x7f817f7f, 0x7f7f817f, 0x7f7f817f, 0x817f817f, 0x817f7f7f, 0x817f7f81, 0x7f817f81, 0x817f817f, 0x817f8181, 0x7f81817f, 0x7f81817f, 0x81817f81, 0x817f8181, 0x817f817f, 0x817f817f, 0x7f7f7f81, 0x81817f7f, 0x7f7f8181, 0x8181817f, 0x817f7f7f, 0x7f7f8181, 0x817f7f7f, 0x817f8181, 0x7f817f7f, 0x7f81817f, 0x81818181, 0x7f81817f, 0x81818181, 0x7f817f81, 0x7f7f7f7f, 0x7f7f8181, 0x81817f7f, 0x81818181, 0x7f818181, 0x7f81817f, 0x7f7f7f81, 0x7f7f7f7f, 0x81817f81, 0x8181817f, 0x7f81817f, 0x7f7f7f7f, 0x8181817f, 0x81817f7f, 0x7f7f8181, 0x7f818181, 0x81817f81, 0x817f7f81, 0x817f7f81, 0x81817f81, 0x817f8181, 0x817f7f7f, 0x81817f7f, 0x7f7f7f7f, 0x81817f81, 0x81817f7f, 0x817f8181, 0x7f7f8181, 0x7f7f817f, 0x7f7f8181, 0x817f7f7f, 0x7f818181, 0x81817f7f, 0x817f8181, 0x817f7f7f, 0x81817f7f, 0x8181817f, 0x817f817f, 0x81817f7f, 0x7f7f7f7f, 0x81818181, 0x7f7f817f, 0x817f7f7f, 0x7f7f8181, 0x81817f7f, 0x7f7f7f81, 0x8181817f, 0x81817f81, 0x7f81817f, 0x7f81817f, 0x7f817f81, 0x7f7f817f, 0x7f817f81, 0x7f818181, 0x817f7f7f, 0x7f7f7f81, 0x817f7f7f, 0x817f8181, 0x817f7f7f, 0x7f818181, 0x817f817f, 0x81817f7f, 0x7f817f81, 0x7f7f7f81, 0x817f7f7f, 0x7f7f7f7f, 0x7f81817f, 0x7f7f817f, 0x7f818181, 0x81817f81, 0x817f7f7f, 0x7f7f8181, 0x817f7f7f, 0x81817f7f, 0x81817f7f, 0x7f7f7f81, 0x81817f7f, 0x817f7f81, 0x7f7f7f81, 0x7f817f7f, 0x81817f7f, 0x81818181, 0x817f8181, 0x817f7f81, 0x7f7f8181, 0x8181817f, 0x8181817f, 0x7f7f817f, 0x7f81817f, 0x817f817f, 0x7f817f7f, 0x7f7f7f7f, 0x7f7f8181, 0x7f817f7f, 0x7f81817f, 0x81817f81, 0x7f817f7f, 0x7f7f8181, 0x7f7f7f7f, 0x817f7f7f, 0x7f7f817f, 0x8181817f, 0x7f7f7f7f, 0x817f8181, 0x7f7f817f, 0x817f8181
output0 =
0xea7bdad9, 0xabd8311a, 0x4e7ba2e2, 0x5c5c5c85, 0xc400ed50, 0x9bea8883, 0x04c2b70f, 0x392dc1c2, 0x6f7a1597, 0xe4bbe4c8, 0x350dc432, 0x926071f2, 0x372ea0eb, 0x36d61798, 0x1d5544a1, 0x37de9af4, 0x722e1ff0, 0x35abc04a, 0xff203abe, 0xca7f7d7a, 0x32a305d0, 0x5c08bf1b, 0xae11c62b, 0x9d832088, 0xe3b2ec27, 0x9438eea5, 0x89525b88, 0xe3007430, 0x836b5498, 0xee899e03, 0xe5c91dd4, 0x5117acf9, 0x6b0df72a, 0x7ed367f0, 0xa7cc1dd4, 0x4f8bc304, 0x939bba5d, 0x76a555c3, 0x1e3e0a60
basegraph=
2
z_c=
128
n_cb=
6400
q_m=
2
n_filler=
8
e =
2624
rv_index =
0
code_block_mode =
1
iter_max=
63
expected_iter_count=
4
op_flags =
RTE_BBDEV_LDPC_ITERATION_STOP_ENABLE, RTE_BBDEV_LDPC_CRC_TYPE_24B_DROP
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/demo_dec_scn_8_rv0_drv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_DEC
input0 =
0x7f817f81, 0x7f7f8181, 0x7f7f7f7f, 0x7f7f7f81, 0x7f7f8181, 0x817f8181, 0x7f7f7f7f, 0x817f8181, 0x8181817f, 0x81817f81, 0x817f7f81, 0x7f817f81, 0x81817f7f, 0x7f7f7f7f, 0x81818181, 0x817f7f81, 0x7f7f7f81, 0x7f7f817f, 0x81817f7f, 0x8181817f, 0x7f81817f, 0x7f81817f, 0x81817f81, 0x817f7f7f, 0x7f81817f, 0x7f81817f, 0x81817f81, 0x7f7f7f7f, 0x7f81817f, 0x7f81817f, 0x7f818181, 0x7f7f817f, 0x81817f7f, 0x81817f7f, 0x7f7f817f, 0x817f7f7f, 0x81818181, 0x7f7f7f81, 0x7f818181, 0x8181817f, 0x817f7f7f, 0x817f7f7f, 0x7f7f817f, 0x817f7f7f, 0x7f817f81, 0x817f817f, 0x81817f7f, 0x817f817f, 0x817f7f81, 0x7f7f7f7f, 0x7f7f7f7f, 0x81818181, 0x7f7f8181, 0x7f7f7f7f, 0x817f7f81, 0x7f7f7f7f, 0x81817f81, 0x7f7f8181, 0x817f7f81, 0x817f8181, 0x7f7f7f81, 0x7f817f7f, 0x7f7f7f81, 0x81817f81, 0x817f817f, 0x7f7f7f7f, 0x7f817f81, 0x7f817f81, 0x817f8181, 0x7f818181, 0x8181817f, 0x7f818181, 0x81818181, 0x7f7f7f7f, 0x7f7f817f, 0x7f7f7f81, 0x817f817f, 0x7f7f7f7f, 0x7f817f7f, 0x817f7f7f, 0x7f818181, 0x817f817f, 0x817f7f7f, 0x817f8181, 0x81818181, 0x817f7f7f, 0x817f817f, 0x81817f7f, 0x817f7f7f, 0x7f7f7f81, 0x7f818181, 0x8181817f, 0x7f7f817f, 0x7f817f81, 0x817f8181, 0x81817f7f, 0x7f7f7f81, 0x7f81817f, 0x8181817f, 0x81817f81, 0x7f7f7f7f, 0x7f81817f, 0x7f81817f, 0x7f817f7f, 0x8181817f, 0x7f818181, 0x7f7f8181, 0x817f7f81, 0x8181817f, 0x817f8181, 0x81817f81, 0x81817f81, 0x81818181, 0x7f7f817f, 0x7f7f8181, 0x817f817f, 0x817f7f81, 0x817f817f, 0x81818181, 0x817f7f81, 0x7f7f8181, 0x817f817f, 0x7f818181, 0x7f817f7f, 0x817f7f7f, 0x817f7f7f, 0x7f7f7f81, 0x81817f7f, 0x7f7f7f7f, 0x7f7f817f, 0x817f7f81, 0x81817f81, 0x7f7f817f, 0x817f7f7f, 0x817f8181, 0x81818181, 0x7f7f7f81, 0x817f817f, 0x7f7f7f81, 0x7f817f81, 0x7f7f7f81, 0x7f817f7f, 0x817f7f7f, 0x7f817f81, 0x7f7f8181, 0x817f8181, 0x81817f81, 0x81817f81, 0x81817f7f, 0x817f7f81, 0x7f7f7f81, 0x7f81817f, 0x7f817f7f, 0x817f817f, 0x8181817f, 0x817f8181, 0x817f7f7f, 0x81817f7f, 0x7f7f7f7f, 0x7f817f7f, 0x8181817f, 0x817f7f7f, 0x7f81817f, 0x7f7f7f81, 0x81817f7f, 0x817f817f, 0x817f817f, 0x7f817f7f, 0x7f7f7f81, 0x8181817f, 0x7f7f7f7f, 0x81817f7f, 0x7f817f7f, 0x817f8181, 0x7f7f8181, 0x7f817f81, 0x8181817f, 0x81818181, 0x7f81817f, 0x7f7f7f81, 0x81818181, 0x817f817f, 0x817f817f, 0x817f7f7f, 0x817f7f7f, 0x7f7f7f7f, 0x81817f81, 0x7f7f817f, 0x7f7f8181, 0x817f8181, 0x7f817f81, 0x817f7f81, 0x7f81817f, 0x7f7f817f, 0x7f7f817f, 0x7f81817f, 0x7f7f817f, 0x7f818181, 0x817f7f7f, 0x81817f81, 0x7f81817f, 0x817f817f, 0x817f7f81, 0x817f8181, 0x81817f7f, 0x7f818181, 0x817f7f7f, 0x817f7f81, 0x81818181, 0x7f81817f, 0x7f81817f, 0x81817f7f, 0x81817f7f, 0x7f7f8181, 0x7f817f81, 0x7f7f7f7f, 0x817f8181, 0x81817f7f, 0x8181817f, 0x81818181, 0x7f81817f, 0x81817f81, 0x81817f81, 0x7f817f7f, 0x7f7f7f81, 0x7f818181, 0x7f818181, 0x7f7f817f, 0x817f8181, 0x7f818181, 0x7f817f7f, 0x7f81817f, 0x7f818181, 0x81818181, 0x817f7f81, 0x81817f81, 0x7f817f7f, 0x817f8181, 0x817f7f81, 0x7f817f81, 0x81818181, 0x817f817f, 0x7f7f7f7f, 0x81817f81, 0x81817f81, 0x7f7f817f, 0x817f7f7f, 0x7f81817f, 0x7f81817f, 0x7f7f7f81, 0x81817f81, 0x81817f7f, 0x7f7f8181, 0x7f817f81, 0x7f7f7f7f, 0x7f7f7f7f, 0x81817f81, 0x817f7f7f, 0x7f7f8181, 0x7f7f817f, 0x817f7f7f, 0x7f81817f, 0x7f7f817f, 0x817f7f81, 0x817f8181, 0x8181817f, 0x817f8181, 0x817f8181, 0x7f7f7f81, 0x7f7f817f, 0x7f818181, 0x7f81817f, 0x7f81817f, 0x817f7f7f, 0x817f8181, 0x7f7f817f, 0x7f7f7f7f, 0x81818181, 0x81818181, 0x7f7f8181, 0x8181817f, 0x7f7f7f81, 0x81818181, 0x7f817f81, 0x7f817f81, 0x7f7f7f81, 0x817f7f7f, 0x7f7f8181, 0x7f7f7f7f, 0x7f7f7f81, 0x7f818181, 0x81817f7f, 0x81817f7f, 0x7f7f8181, 0x7f81817f, 0x7f7f817f, 0x817f7f81, 0x817f7f81, 0x7f818181, 0x81818181, 0x7f817f7f, 0x8181817f, 0x7f818181, 0x7f7f8181, 0x8181817f, 0x7f81817f, 0x7f7f8181, 0x7f817f81, 0x7f817f7f, 0x7f81817f, 0x7f818181, 0x8181817f, 0x817f7f7f, 0x817f8181, 0x7f7f8181, 0x7f7f817f, 0x7f818181, 0x81817f7f, 0x7f817f7f, 0x817f7f7f, 0x81818181, 0x7f817f81, 0x817f817f, 0x817f8181, 0x817f7f81, 0x7f818181, 0x7f7f7f7f, 0x817f8181, 0x7f817f81, 0x817f817f, 0x8181817f, 0x7f817f7f, 0x817f7f7f, 0x817f7f81, 0x7f7f817f, 0x7f81817f, 0x81817f81, 0x817f7f81, 0x7f818181, 0x81817f81, 0x81817f7f, 0x7f818181, 0x7f818181, 0x7f818181, 0x817f817f, 0x7f817f81, 0x7f817f7f, 0x7f7f817f, 0x817f7f81, 0x81817f81, 0x7f7f7f7f, 0x7f817f7f, 0x7f817f81, 0x81818181, 0x817f7f81, 0x7f7f8181, 0x7f7f7f7f, 0x7f81817f, 0x7f817f7f, 0x7f7f7f81, 0x7f81817f, 0x8181817f, 0x817f7f7f, 0x817f7f7f, 0x817f7f7f, 0x7f81817f, 0x817f8181, 0x7f7f7f81, 0x7f817f81, 0x81817f7f, 0x7f7f7f81, 0x7f7f7f7f, 0x7f7f8181, 0x7f7f7f81, 0x7f7f8181, 0x7f7f7f81, 0x7f7f7f81, 0x7f7f8181, 0x7f817f7f, 0x817f8181, 0x7f817f7f, 0x81817f81, 0x7f818181, 0x7f7f8181, 0x817f817f, 0x7f7f7f7f, 0x7f7f7f7f, 0x81817f7f, 0x7f817f7f, 0x817f7f81, 0x81817f81, 0x817f7f7f, 0x7f7f7f7f, 0x817f8181, 0x7f7f817f, 0x7f7f7f81, 0x81817f7f, 0x8181817f, 0x817f7f81, 0x81818181
output0 =
0xea7bdad9, 0xabd8311a, 0x4e7ba2e2, 0x5c5c5c85, 0xc400ed50, 0x9bea8883, 0x04c2b70f, 0x392dc1c2, 0x6f7a1597, 0xc8
basegraph=
2
z_c=
32
n_cb=
1600
q_m=
2
n_filler=
0
e=
1600
rv_index=
0
code_block_mode=
1
iter_max=
63
expected_iter_count=
4
op_flags=
RTE_BBDEV_LDPC_ITERATION_STOP_ENABLE, RTE_BBDEV_LDPC_CRC_TYPE_24B_DROP
expected_status=
OK
targets/ARCH/test-bbdev/test_vectors/demo_enc_scn_1_rv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0x9e8b30df, 0x3abedc68, 0xf6cfeee5, 0x787b3a9c, 0x6e06507c, 0xc9c3aaa5, 0xf2ba5dd9, 0xe520c3d1, 0x7e2bb833, 0xd60fe6cb, 0x8a54efb0, 0xa79f35e8, 0x772bb893, 0xc1c07991, 0xc7192ad6, 0x910c2e00, 0x2911da4a, 0xc7a5771c, 0xb9e4374d, 0x751104c1, 0x3ad46388, 0x4cd8fd10, 0x530ba0c5, 0xff5ebefe, 0xac7d5c04, 0x4e5203d5, 0xec0ff874, 0xb82f597b, 0x6c8522aa, 0xec19e86b, 0x49d70574, 0xac4f8e06, 0x274c23b0, 0xf61327dd, 0x9ce9a85e, 0x204383b4, 0xd9f0ed43, 0x23c11157, 0x3a0ab700, 0x72a13a3a, 0xd54745de, 0x57588c1b, 0x589b5bde, 0xdd8afc06, 0xcedcc8d4, 0x082a17c0, 0xff4586d7, 0x82925726, 0xfbc1a3cb, 0xc46faa49, 0xacefc0be, 0x746d62a3, 0xd724ae9d, 0x3766deb6, 0x2ab26543, 0x618b0fa5, 0x89837f30, 0x273a61cc, 0xe29f85ea, 0x589d28a3, 0x4ec6d6fc, 0xb29c1486, 0x79ad100c, 0xffd6d7d5, 0xd9804049, 0x37f910bf, 0x10bf8531, 0x69185f30, 0x4429674e, 0xc3f8526a, 0x39d8a153, 0xc3ae1663, 0xe9e28d1d, 0xcda89aa0, 0x8d2ce8db, 0xad933336, 0x5f8bcda1, 0x0daa3bb1, 0x8ec35f69, 0x13f52272, 0x05ffeb98, 0x0506f8ae, 0x6f4af993, 0x48a77fb4, 0xf01c92eb, 0x6cb26c8b, 0xfd504e3b, 0xb2
output0 =
0xd0cb4a0f, 0xad2b9e58, 0x7cbd8ee4, 0x69b3ea44, 0xeeac54df, 0xc9c02427, 0x774a91f9, 0x7a9cfbd2, 0xc0de1a96, 0x6b3a8b1c, 0x822e47d2, 0x46a001f0, 0xd9493df3, 0x7bb5d313, 0xb85d5514, 0x4282b041, 0xcde3d920, 0xd7080357, 0x2f3fa543, 0x6fb16289, 0x2f0aa375, 0x83df31a8, 0x304116e0, 0x263f1656, 0x1e3890c1, 0xdd0e31e6, 0xb3af5042, 0xf121c4a7, 0x14c927e0, 0x4e368b05, 0xa98ff8fe, 0xfefbe873, 0xe4637404, 0xe4cce32a, 0x5b5172e2, 0xac605c67, 0x85fb607a, 0xe1adaf14, 0xc673ce2f, 0xc0dbfa09, 0x4d5d99cd, 0xe46d2781, 0x94f98a6c, 0xf0fd9343, 0x3754602f, 0xd7242ea6, 0xe9852911, 0xf5cdfe60, 0x4e1900df, 0x2a48f574, 0x6b19a2b6, 0x38eb5f07, 0xc5ddbc66, 0xe4d797b8, 0x5ec0309f, 0x010c4b65, 0xe2a85f70, 0xc7f214ef, 0x07523e26, 0x1b5c12e5, 0x6fdb5500, 0xcd0a8d04, 0x991ecc5e, 0x1d7f56c8, 0x3760b9e2, 0x67e67b31, 0xb5c1de47, 0x7b27c063, 0x8e62edf3, 0x9062db82, 0xf0ba6801, 0xe2f689d4, 0x81f430f3, 0xbdb1e5b7, 0x2f1250b5, 0x9554c91d, 0x68857ff7, 0xefba6225, 0x7e723d48, 0x19854d96, 0x5f889ef4, 0x9abe12b5, 0x98dd9261, 0x24f1aa29, 0x55a0ed8b, 0xb0d8aba8, 0x0c284a99, 0x313eb738, 0xe988a692, 0x6ff36048, 0xfdf76d8b, 0x3f0e282d, 0x67285a34, 0x984d4dca, 0xef506288, 0x462ddbd1, 0xba6a415e, 0xc0
basegraph=
1
z_c=
128
n_cb=
3200
q_m=
2
n_filler=
0
e =
3112
rv_index =
0
code_block_mode =
1
op_flags =
RTE_BBDEV_LDPC_RATE_MATCH, RTE_BBDEV_LDPC_CRC_24B_ATTACH
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/demo_enc_scn_2_rv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0x9e8b30df, 0x3abedc68, 0xf6cfeee5, 0x787b3a9c, 0x6e06507c, 0xc9c3aaa5, 0xf2ba5dd9, 0xe520c3d1, 0x7e2bb833, 0xd60fe6cb, 0x8a54efb0, 0xa79f35e8, 0x772bb893, 0xc1c07991, 0xc7192ad6, 0x910c2e00, 0x2911da4a, 0xc7a5771c, 0xb9e4374d, 0x751104c1, 0x3ad46388, 0x4cd8fd10, 0x530ba0c5, 0xff5ebefe, 0xac7d5c04, 0x4e5203d5, 0xec0ff874, 0xb82f597b, 0x6c8522aa, 0xec19e86b, 0x49d70574, 0xac4f8e06, 0x274c23b0, 0xf61327dd, 0x9ce9a85e, 0x204383b4, 0xd9f0ed43, 0x23c11157, 0x3a0ab700, 0x72a13a3a, 0xd54745de, 0x57588c1b, 0x589b5bde, 0xdd8afc06, 0xcedcc8d4, 0x082a17c0, 0xff4586d7, 0x82925726, 0xfbc1a3cb, 0xc46faa49, 0xacefc0be, 0x746d62a3, 0xd724ae9d, 0x3766deb6, 0x2ab26543, 0x618b0fa5, 0x89837f30, 0x273a61cc, 0xe29f85ea, 0x589d28a3, 0x4ec6d6fc, 0xb29c1486, 0x79ad100c, 0xffd6d7d5, 0xd9804049, 0x37f910bf, 0x10bf8531, 0x69185f30, 0x4429674e, 0xc3f8526a, 0x39d8a153, 0xc3ae1663, 0xe9e28d1d, 0xcda89aa0, 0x8d2ce8db, 0xad933336, 0x5f8bcda1, 0x0daa3bb1, 0x8ec35f69, 0x13f52272, 0x05ffeb98, 0x0506f8ae, 0x6f4af993, 0x48a77fb4, 0xf01c92eb, 0x6cb26c8b, 0xfd504e3b, 0x9cae44b2, 0xb0bb6e72, 0xf10de0af, 0x512b983d, 0x319a51ec, 0xbf548277, 0x4e71789d, 0xc2645c23, 0x5fb92dfe, 0xd3f357f9, 0x661045e9, 0x75c0cbc6, 0x7a3f88f9, 0x338d9b23, 0x91cddcb1, 0x26653b44, 0x59456601, 0xc96175e8, 0x9eca4c28, 0xcf94eb4e, 0xf2de9546, 0x75a5437b, 0x6506329d, 0xdec978f8, 0x4fdc9af2, 0x0119faa3, 0x2547fa31, 0x1af33692, 0x1670fe27, 0x1640a17f, 0x4fa73a5b, 0x26e5696d, 0x0af49c1e, 0x0f986c62, 0x33edbcd7, 0x7d888c5a, 0x342f5ee7, 0x66cb8e8c, 0x07060a3a, 0x2188b6b9, 0xf3c51f6f, 0x6eb156a6, 0x73c51893, 0xded24f9c, 0x019af43a, 0xa5395f1a, 0xc283f30b, 0x7b995783, 0xa0001c41, 0x6d7b0601, 0x6bf0aacf, 0xb78d3d51, 0x7f48cf8f, 0x8b302f20, 0xbedc689e, 0xcfeee53a, 0x7b3a9cf6, 0x06507c78, 0xc3aaa56e, 0xba5dd9c9, 0x20c3d1f2, 0x2bb833e5, 0x0fe6cb7e, 0x54efb0d6, 0x9f35e88a, 0x2bb893a7, 0xc0799177, 0x192ad6c1, 0x0c2e00c7, 0x11da4a91, 0xa5771c29, 0xe4374dc7, 0x1104c1b9, 0xd4638875, 0xd8fd103a, 0x0ba0c54c, 0x5ebefe53, 0x7d5c04ff, 0x5203d5ac, 0x0ff8744e, 0x2f597bec, 0x8522aab8, 0x19e86b6c, 0xd70574ec, 0x4f8e0649, 0x4c23b0ac, 0x1327dd27, 0xe9a85ef6, 0x4383b49c, 0xf0ed4320, 0xc11157d9, 0x0ab70023, 0xa13a3a3a, 0x4745de72, 0x588c1bd5, 0x9b5bde57, 0x8afc0658, 0xdcc8d4dd, 0x2a17c0ce, 0x4586d708, 0x925726ff, 0xc1a3cb82, 0x6faa49fb, 0xefc0bec4, 0x6d62a3ac, 0x24ae9d74, 0x66deb6d7, 0xb2654337, 0x8b0fa52a, 0x837f3061, 0x3a61cc89, 0x9f85ea27, 0x9d28a3e2, 0xc6d6fc58, 0x9c14864e, 0xad100cb2, 0xd6d7d579, 0x804049ff, 0xf910bfd9, 0xbf853137, 0x185f3010, 0x29674e69, 0xf8526a44, 0xd8a153c3, 0xae166339, 0xe28d1dc3, 0xa89aa0e9, 0x2ce8dbcd, 0x9333368d, 0x8bcda1ad, 0xaa3bb15f, 0xc35f690d, 0xf522728e, 0xffeb9813, 0x06f8ae05, 0x4af99305, 0xa77fb46f, 0x1c92eb48, 0xb26c8bf0, 0x504e3b6c, 0xae44b2fd, 0xbb6e729c, 0x0de0afb0, 0x2b983df1, 0x9a51ec51, 0x54827731, 0x71789dbf, 0x645c234e, 0xb92dfec2, 0xf357f95f, 0x1045e9d3, 0xc0cbc666, 0x3f88f975, 0x8d9b237a, 0xcddcb133, 0x653b4491, 0x45660126, 0x6175e859, 0xca4c28c9, 0x94eb4e9e, 0xde9546cf, 0xa5437bf2, 0x06329d75, 0xc978f865, 0xdc9af2de, 0x19faa34f, 0x47fa3101, 0xf3369225, 0x70fe271a, 0x40a17f16, 0xa73a5b16, 0xe5696d4f, 0xf49c1e26, 0x986c620a, 0xedbcd70f, 0x888c5a33, 0x7d
output0 =
0xa1673514, 0xb589a27b, 0x1a0473b3, 0xe9254c23, 0x84ef742f, 0xf1e8aa50, 0xd7638a2f, 0xd0cbba1d, 0x4959dd98, 0xa56c6695, 0x84bd9e6c, 0xf1a88653, 0x2340702a, 0x97657fa2, 0xb9942d50, 0xb598fa31, 0x5a48108a, 0x7a59a420, 0x6a5ce2a6, 0x6cfe4a56, 0xc5d8b962, 0xb183c3bd, 0x1a91758b, 0x010d5e34, 0xf7b90b34, 0xd6b641bf, 0x02167b36, 0x0e5d47a1, 0x3f9f4504, 0x8d0e8d11, 0xcd0f8d1f, 0x583b0288, 0x2724e8e6, 0x63a37e31, 0xf0d59f03, 0x7e33c163, 0xcf22ecb2, 0xd562de86, 0xf1fe3d00, 0xe3e69c84, 0x84a175e7, 0xada0e5f7, 0x2e4754e5, 0xc140d948, 0x2cd13be7, 0xeaef3635, 0x7e332d49, 0x49954dd3, 0x5bd9cae1, 0x9eeb53a0, 0xccccc270, 0x74a5ba69, 0x10e0f98e, 0xf4ddabf8, 0x1d2c5e88, 0x306aa32d, 0xfdc9e2d6, 0x3ea3644c, 0xece27d9f, 0x2e4e7868, 0x273c1b35, 0xcd190ddf, 0xee056389, 0x0639ca81, 0xea7a041f, 0x86900a85, 0x177cb1e5, 0x7f199d1b, 0x73d5cdb9, 0x0ca8bb86, 0x941c0f88, 0x8532f2d7, 0x78f3b0fe, 0xbc213cf0, 0x201278d5, 0x589fa1d2, 0x1146a114, 0xd26be38d, 0x2ba333e6, 0xefba69e6, 0x51208774, 0x97e25490, 0x1156aa9e, 0x6e1bd2ea, 0x7280474f, 0x1507be9f, 0xbe66454a, 0xc63c8442, 0x3f2dad64, 0x2064d71c, 0x18278c6d, 0x5ef0c0fb, 0x16cd5e32, 0x960f95e2, 0x7c175b2c, 0x5ef4b8d8, 0xb385e246, 0xd7bd19ec, 0xc9875488, 0xe7e0c0d8, 0xd4b89af3, 0xf7c4a51c, 0x1e0b785f, 0xa2dc4fc7, 0xb6a14289, 0xbb76df90, 0xde4f438e, 0xf65589d9, 0xaf26d369, 0xe8905ee4, 0x0c580d3f, 0x0e4773ae, 0x8aedc1d2, 0x6305fbfe, 0x94ffad98, 0x26016950, 0x83bf4ec7, 0xee6dc970, 0xae7a74de, 0x80607fcd, 0x18d29fad, 0x00beb457, 0xb538dbc4, 0xb43809cf, 0xb970ca1e, 0xe3aa5473, 0x74750c9b, 0xa1d6b99d, 0xe82d197a, 0x019fdbca, 0x45a8afc9, 0x16efe255, 0xd597b35e, 0x57339b5c, 0x5732f5f8, 0x120b99c6, 0x4dc12b3a, 0xff8e6523, 0x957ba382, 0xa824167e, 0xe0765b5d, 0x5cb47468, 0xf658b8af, 0xaf3797da, 0x3b3296af, 0x5bf60aab, 0x626192e9, 0x69691102, 0x9fb439a1, 0x337b01e4, 0x908497ea, 0x8d2fab4e, 0xcb974e0c, 0x5e4ee785, 0xf1a7079b, 0x1793e6a1, 0xcb5a6535, 0x7c08737c, 0x3c791341, 0xc2723235, 0x376bc1a9, 0x87f4037c, 0xe535950c, 0xed96ccf0, 0xdeada935, 0xeaf475c2, 0x32823834, 0x49febdf2, 0x1e61da2b, 0x677b6298, 0x481ef2d2, 0x637d7d41, 0xc13b80fa, 0xb9e2d6f5, 0xc99308aa, 0xee74f0b6, 0xd9af5bc9, 0x17449347, 0xc8eb124b, 0x271d6e35, 0x690e08d3, 0x8c474bea, 0xfdaf2a1c, 0x2d57543b, 0x53d8ba6f, 0x2c074434, 0x9d5f8b26, 0xee317acc, 0xc679a779, 0x2d1972ad, 0xb5d7b943, 0x8c4164fa, 0xa078097c, 0xef158487, 0xe5de2bf3, 0x5b1ef3f8, 0xb1808963, 0xb67b9490, 0xed267ab9, 0x640aba19, 0xbd80e584, 0x2c6d8fe0, 0x9d14dc4a, 0x3e512944, 0x699a929a, 0x424cd494, 0xee13bb2c, 0x1eeb37a4, 0x68726dcd, 0xa97916cf, 0xc1571f97, 0x5a7a77a1, 0xea30e5d2, 0xe9b30ce3, 0x75ab881f, 0x47019996, 0xea23d812, 0x36dd921e, 0x4eef9f15, 0x5da10bd0, 0x3a234a95, 0xca3e93d2, 0xa1070324, 0x00894405, 0x39404211, 0xa36dde6e, 0x989cfff5, 0xde3800bf, 0xa34b4327, 0x6a8ea7d0, 0xaaf4fbc5, 0xbb6b9020, 0xee5d144d, 0xcb81055a, 0xd56dbc96, 0xeccee1f6, 0x72fc980a, 0xbba1b8bc, 0xa0972ceb, 0x9f6edc1f, 0xf12a816e, 0x2c040067, 0x27ccf828, 0x0af0cd8d, 0xc7b793a4, 0xddcff776, 0x07b359ef, 0x004d1be4, 0x0e1f37ec, 0x8f59c5cb, 0x9bf0f93e, 0xef517ded, 0x11da7da3, 0x6062efa8, 0x80f8c8d5, 0xea86625a, 0x0a876ac9, 0x9b5cc49a, 0x52d37f7e, 0x41b0d72a, 0x3df313a1, 0x9242d958, 0x15417eb0, 0xb005e90c, 0x8d604792, 0x5612ccb7, 0xe407875d, 0x72896e3a, 0xf3306fb4, 0x71fd3e1e, 0x12f0c6ce, 0x02477141, 0x8190676f, 0x70e70f79, 0x5542d84a, 0x80b2e3ee, 0x27b5f520, 0xca41149c, 0xacfb5e73, 0xec26f8de, 0x3114efbb, 0xf22af467, 0x32a3b48c, 0x48364a10, 0x342fa930, 0xab0490ea, 0xcf2ff5fd, 0xbb1dc322, 0xc8c990da, 0x67c40d0c, 0x8e2df179, 0x5094e8
basegraph=
1
z_c=
384
n_cb=
9600
q_m=
2
n_filler=
0
e =
9332
rv_index =
0
code_block_mode =
1
op_flags =
RTE_BBDEV_LDPC_RATE_MATCH, RTE_BBDEV_LDPC_CRC_24B_ATTACH
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/demo_enc_scn_3_rv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0x9e8b30df, 0x3abedc68, 0xf6cfeee5, 0x787b3a9c, 0x6e06507c, 0xc9c3aaa5, 0xf2ba5dd9, 0xe520c3d1, 0x7e2bb833, 0xd60fe6cb, 0x8a54efb0, 0xa79f35e8, 0x772bb893, 0xc1c07991, 0xc7192ad6, 0x910c2e00, 0x2911da4a, 0xc7a5771c, 0xb9e4374d, 0x751104c1, 0x3ad46388, 0x4cd8fd10, 0x530ba0c5, 0xff5ebefe, 0xac7d5c04, 0x4e5203d5, 0xec0ff874, 0xb82f597b, 0x6c8522aa, 0xec19e86b, 0x49d70574, 0xac4f8e06, 0x274c23b0, 0xf61327dd, 0x9ce9a85e, 0x204383b4, 0xd9f0ed43, 0x23c11157, 0x3a0ab700, 0x72a13a3a, 0xd54745de, 0x57588c1b, 0x589b5bde, 0xdd8afc06, 0xcedcc8d4, 0x082a17c0, 0xff4586d7, 0x82925726, 0xfbc1a3cb, 0xc46faa49, 0xacefc0be, 0x746d62a3, 0xd724ae9d, 0x3766deb6, 0x2ab26543, 0x618b0fa5, 0x89837f30, 0x273a61cc, 0xe29f85ea, 0x589d28a3, 0x4ec6d6fc, 0xb29c1486, 0x79ad100c, 0xffd6d7d5, 0xd9804049, 0x37f910bf, 0x10bf8531, 0x69185f30, 0x4429674e, 0xc3f8526a, 0x39d8a153, 0xc3ae1663, 0xe9e28d1d, 0xcda89aa0, 0x8d2ce8db, 0xad933336, 0x5f8bcda1, 0x0daa3bb1, 0x8ec35f69, 0x13f52272, 0x05ffeb98, 0x0506f8ae, 0x6f4af993, 0x48a77fb4, 0xf01c92eb, 0x6cb26c8b, 0xfd504e3b, 0x9cae44b2, 0xb0bb6e72, 0xf10de0af, 0x512b983d, 0x319a51ec, 0xbf548277, 0x4e71789d, 0xc2645c23, 0x5fb92dfe, 0xd3f357f9, 0x661045e9, 0x75c0cbc6, 0x7a3f88f9, 0x338d9b23, 0x91cddcb1, 0x26653b44, 0x59456601, 0xc96175e8, 0x9eca4c28, 0xcf94eb4e, 0xf2de9546, 0x75a5437b, 0x6506329d, 0xdec978f8, 0x4fdc9af2, 0x0119faa3, 0x2547fa31, 0x1af33692, 0x1670fe27, 0x1640a17f, 0x4fa73a5b, 0x26e5696d, 0x0af49c1e, 0x0f986c62, 0x33edbcd7, 0x7d888c5a, 0x342f5ee7, 0x66cb8e8c, 0x07060a3a, 0x2188b6b9, 0xf3c51f6f, 0x6eb156a6, 0x73c51893, 0xded24f9c, 0x019af43a, 0xa5395f1a, 0xc283f30b, 0x7b995783, 0xa0001c41, 0x6d7b0601, 0x6bf0aacf, 0xb78d3d51, 0x7f48cf8f, 0x8b302f20, 0xbedc689e, 0xcfeee53a, 0x7b3a9cf6, 0x06507c78, 0xc3aaa56e, 0xba5dd9c9, 0x20c3d1f2, 0x2bb833e5, 0x0fe6cb7e, 0x54efb0d6, 0x9f35e88a, 0x2bb893a7, 0xc0799177, 0x192ad6c1, 0x0c2e00c7, 0x11da4a91, 0xa5771c29, 0xe4374dc7, 0x1104c1b9, 0xd4638875, 0xd8fd103a, 0x0ba0c54c, 0x5ebefe53, 0x7d5c04ff, 0x5203d5ac, 0x0ff8744e, 0x2f597bec, 0x8522aab8, 0x19e86b6c, 0xd70574ec, 0x4f8e0649, 0x4c23b0ac, 0x1327dd27, 0xe9a85ef6, 0x35fb9a9c
output0 =
0x9db2cc75, 0x86491306, 0x2f7fb407, 0x3fa46689, 0x2a1ff675, 0xd79f34a9, 0x201003e4, 0x673b1603, 0x1f6cc485, 0xd91e75b2, 0xb3fe4116, 0xf42194a6, 0x10dd72e1, 0x0e36ce00, 0xe8cbf8be, 0xbffbfd22, 0xf1767045, 0xe499a72f, 0x4a4072e2, 0xbd745937, 0xd5ae743b, 0xf0e8ba05, 0xc772de6a, 0xc48fbe1c, 0x1c08cc88, 0xe16d3780, 0xc0e89e6d, 0xf5bc8306, 0x3350752b, 0x96642ff7, 0xa9c53c11, 0xa5c9fe34, 0x1b58408b, 0x7a49a535, 0x2e59f7b2, 0x6caf5e53, 0xc4c9b877, 0xe48383a8, 0x4b85759b, 0x45081b64, 0xa7e80f75, 0x87e204fa, 0x43433f33, 0x0b1847b5, 0x2a8a5001, 0x890a8844, 0xcd1f9c0a, 0x5d7a539c, 0x2275ece6, 0x23b36f34, 0xf1c0db07, 0x7f629567, 0xca32fdf2, 0x8026df97, 0xa0af7d04, 0xf6e3cdc0, 0xd0f160b6, 0xeca5f4e7, 0x7e5611f4, 0x9455dd58, 0x6c857ae3, 0xeabf6735, 0x2a33781d, 0x5c941c82, 0x4ecc9be4, 0xcbfa07f0, 0xd999c371, 0x24f5ee6d, 0x05f0a9db, 0xb1dcaaac, 0x486d0f8d, 0x743fe72c, 0xbcdce7d2, 0x3ef37508, 0xfdf628cf, 0x6e4a3839, 0x332d4a74, 0x9d4c5dcb, 0xea4527c9, 0x173dcf84, 0xeb3f014b, 0x83d00ad0, 0x462cb4f1, 0x3f58c90b, 0x768488a8, 0x09e9fa82, 0xc4594e98, 0xc126a383, 0x3db7f0ab, 0xbd7039e4, 0x35077990, 0x49cfb0d6, 0x1002a150, 0x933fa389, 0x2fb662e2, 0xeeaf38f3, 0x51758221, 0xd2b240d1, 0x0046bbda, 0x2f1bc7aa, 0x76c5565f, 0x5557fe9b, 0xfa33100a, 0xd26cd117, 0x2f28b971, 0x74308619, 0x4877983d, 0x5af4d5aa, 0x43994f37, 0xc24fd5a6, 0x2c064e6c, 0x5ab4b9c8, 0xe2d4e716, 0xd2fc49a9, 0x9982109d, 0xe3b095d9, 0xd4e89ea2, 0xf2c4f518, 0x0f0e284f, 0xb78c5a92, 0xb7a453d9, 0xbe778f81, 0xca4e569b, 0xf241c9dc, 0xef77c669, 0xec841ba5, 0x4c48092a, 0x4a4376bf, 0x9ae98593, 0x7640feaf, 0xc0eae9c9, 0x67503900, 0xc2bb0ed7, 0xbf3c9831, 0xfa2a749a, 0xc1747e88, 0x1dc2ceb8, 0x11aee152, 0xe1388ac5, 0xa42959ce, 0xa824ce4e, 0xa2fb0566, 0x61741d8f, 0xe1d6e8d9, 0xa8290d7a, 0x10cfdf8b, 0x45e9af8c, 0x47bab310, 0x9596e75a, 0x17729a18, 0x1662b4ac, 0x121bd883, 0x48843f3f, 0xfa8f7436, 0x902ae297, 0xec20067f, 0xb4361b5c, 0x18b5643d, 0xb25dbdfb, 0xae36838f, 0x6a7697fa, 0x1eb30feb, 0x326596e9, 0x396d4413, 0xdfb579e0, 0x622b04f4, 0xd5c1d3ee, 0x8c7ebe1a, 0xca824e1d, 0x1f0eb7c5, 0xa0f7578a, 0x5687b7f5, 0x8a5f7435, 0x69493629, 0x3d381245, 0xd6767264, 0x276f84f8, 0x96b1166d, 0xa471851c, 0xbdc698b0, 0xdeb9bd21, 0xfae52587, 0x76c27934, 0x4dbba8b2, 0x1e619b6b, 0x227b7698, 0x195ee786, 0x76396951, 0xc52b81be, 0xe9f393a4, 0x89c70cfb, 0xbb71f1e3, 0xccbe0b8c, 0x1200c647, 0x421a
basegraph=
1
z_c=
256
n_cb=
6400
q_m=
2
n_filler=
0
e =
6224
rv_index =
0
code_block_mode =
1
op_flags =
RTE_BBDEV_LDPC_RATE_MATCH, RTE_BBDEV_LDPC_CRC_24B_ATTACH
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/demo_enc_scn_4_rv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0xea7bdad9, 0xabd8311a, 0x4e7ba2e2, 0x5c5c5c85, 0xc400ed50, 0x9bea8883, 0x04c2b70f, 0x392dc1c2, 0x6f7a1597, 0xe4bbe4c8, 0x350dc432, 0x926071f2, 0x372ea0eb, 0x36d61798, 0x1d5544a1, 0x37de9af4, 0x722e1ff0, 0x35abc04a, 0xff203abe, 0xca7f7d7a, 0x32a305d0, 0x5c08bf1b, 0xae11c62b, 0x9d832088, 0xe3b2ec27, 0x9438eea5, 0x89525b88, 0xe3007430, 0x836b5498, 0xee899e03, 0xe5c91dd4, 0x5117acf9, 0x6b0df72a, 0x7ed367f0, 0xa7cc1dd4, 0x4f8bc304, 0x939bba5d, 0x76a555c3, 0x1e3e0a60, 0x6f395cde, 0x5ca777f3, 0x79163b7d, 0x04f40cd1, 0xf1f312fe, 0x8abcb1ed, 0xf3550fd6, 0x8060deb6, 0x82380005, 0xc1ea99de, 0xd0cfc143, 0x58fa9ca5, 0x5c2f5980, 0x39f24b7b, 0xc918a3ce, 0x656a8d76, 0xf6f8a3cf, 0x9d6d1184, 0x5c5060e0, 0x3171d366, 0xe77af42c, 0xf24290f4, 0x1df2f5e8, 0x56c1a6eb, 0x3be35b07, 0xdaee3c1b, 0x65dfcb90, 0x8ba0ede7, 0x311e72b1, 0x772ffa8a, 0xd863ce1d, 0x8974177a, 0x87d85875, 0x927596d1, 0x0481e7fa, 0x9768d335, 0x90a5f29b, 0x13e11b45, 0x73cbac15, 0x9301bfde, 0xf3026564, 0x794a8697, 0x552e6f6b, 0x2880a6cd, 0xe780e65f, 0xf68c45fe, 0x254e9ac4, 0x8509c8f8, 0xb5235ffc
output0 =
0x72176e87, 0xef78cd6b, 0x71b884e4, 0x64e89b8f, 0x35a0484a, 0x721ab211, 0x576e1cee, 0x09875528, 0x559cdeec, 0x6e4ee95d, 0x2b06d496, 0x2d5b79f7, 0x7474578d, 0xa7176633, 0x8d8661eb, 0x2f5bf8f2, 0xfb0205ff, 0x093ab91d, 0x10a19d30, 0x631ade9d, 0x894bac8f, 0xeaba510c, 0xe77a9c3f, 0xd9b0fe7a, 0x724110f2, 0x185f4e89, 0xfb9e9e02, 0xa4269001, 0x68e1db0d, 0xe9881752, 0x541dc095, 0xf3d65fc0, 0xe4ad7a49, 0x0be958cb, 0xb9bd36dc, 0x7096c51a, 0xce72c185, 0x87d41d23, 0x716a441e, 0x1ef80511, 0x20729182, 0x5bc5da2d, 0xb9864f01, 0xf9bd83d1, 0xf30225f7, 0x66ad97f0, 0xb0dd86bf, 0x02666b12, 0x3bbadc59, 0xde2ce355, 0x7e2941be, 0xe96f5ab6, 0xa74671b2, 0x7bddf4e4, 0x5ee57400, 0xaa31dad1, 0xdd9ff623, 0x0b938f82, 0x73675ab4, 0x2d7f22c8, 0x99410078, 0xb947ed1f, 0xf132f8a6, 0xab38961a, 0x2a3b0eff, 0xf0677e99, 0x8e5ae76e, 0x976e3907, 0xa00017f6, 0x210534aa, 0x4803bcfb, 0x12eb4bfb, 0x439be7e8, 0x98d1a09f, 0xba447cf6, 0x0bfe7263, 0xf9b738cb, 0x50c11478, 0x11017210, 0x18d0944b, 0x86d2a8b2, 0x12e19cb9, 0x16b04a21, 0x45b7fab0, 0xa0c6239c, 0x9073d9ae, 0xd3660485, 0xf072ba5c, 0x8f25cf3b, 0xc60f58ae, 0x4a9cbcb0, 0xd2a0c056, 0xa7c47c3f, 0x7629986d, 0x4ec9aaf4, 0x39bec0fb, 0x065674d4, 0xa296e279, 0x116900ac, 0xe0675076, 0x5fa3382d, 0x165e032b, 0x25afa51d, 0x6ffd9d7b, 0x45c375eb, 0x59ba4861, 0x26fbd5ec, 0xe7124cab, 0x7dcc8bf9, 0x7c3213f4, 0x8a676b05, 0xca0e4af9, 0xe05fdb56, 0x9da3ada9, 0xcee511d3, 0x777ceef7, 0xa6fc3ea8, 0xde8144cc, 0x0d2e46db, 0x165aa912, 0x99aad991, 0x6f6fbf08, 0xe9f4f313, 0xc4b64b7c, 0x6a02cd7e, 0xc280657f, 0xd476672e, 0x2f8094f6, 0x699213b2, 0x0d86733f, 0x3bfd99af, 0x34101685, 0x1ba2664f, 0x2fd29569, 0x49abdfc7, 0x148276d8, 0xde023764, 0x5a4256ed, 0xf0997352, 0x5f2bcae4, 0xaedab8b3, 0x0ac35311, 0x2669713d, 0x0efe1855, 0x69842e96, 0xc63fdc64, 0xee3cda68, 0x3323e84d, 0x799cb3b1, 0xd5580190, 0x2ca9ba22, 0x6fbd40d0, 0x3260b8be, 0x79aef4c0, 0xdcd365b4, 0x2249a834, 0x95b0d5ae, 0x66d48311, 0x3d73a5af, 0x47bc98aa, 0xcb8268f0, 0x767c3314, 0x35f998e7, 0xbee335e1, 0x5cce5171, 0x7efd26fb, 0x2c657d06, 0xdab1199b, 0x19dc335e, 0x43906378, 0x5d854831, 0x28e1cc04, 0x3f73e9f7, 0x0027b04d, 0x14f95dd1, 0xbe06dde2
basegraph=
1
z_c=
128
n_cb=
8448
q_m=
2
n_filler=
0
e =
5632
rv_index =
0
code_block_mode =
1
op_flags =
RTE_BBDEV_LDPC_RATE_MATCH, RTE_BBDEV_LDPC_CRC_24B_ATTACH
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/demo_enc_scn_5_rv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0xea7bdad9, 0xabd8311a, 0x4e7ba2e2, 0x5c5c5c85, 0xc400ed50, 0x9bea8883, 0x04c2b70f, 0x392dc1c2, 0x6f7a1597, 0xe4bbe4c8, 0x350dc432, 0x926071f2, 0x372ea0eb, 0x36d61798, 0x1d5544a1, 0x37de9af4, 0x722e1ff0, 0x35abc04a, 0xff203abe, 0xca7f7d7a, 0x32a305d0, 0x5c08bf1b, 0xae11c62b, 0x9d832088, 0xe3b2ec27, 0x9438eea5, 0x89525b88, 0xe3007430, 0x836b5498, 0xee899e03, 0xe5c91dd4, 0x5117acf9, 0x6b0df72a, 0x7ed367f0, 0xa7cc1dd4, 0x4f8bc304, 0x939bba5d, 0x76a555c3, 0x1e3e0a60, 0x6f395cde, 0x5ca777f3, 0x79163b7d, 0x04f40cd1, 0xfe
output0 =
0xf2b95473, 0x75b44105, 0x95950fd5, 0xda939dec, 0x6f8ffb15, 0x61151ca1, 0x52a009f1, 0x920ab25d, 0x76537ed7, 0xbe7c986b, 0x20adc5a1, 0x30eccb8b, 0x34f4195f, 0x760af744, 0x477a1cae, 0x4886016c, 0x449d8fac, 0x2a5ba809, 0x3a4294c7, 0x680e3db6, 0x756157cd, 0xb7523327, 0xd89364fa, 0x7a4bfcb7, 0xae1301bf, 0x192fb859, 0x01b19821, 0x730eda8c, 0x994eaddb, 0xfafb5049, 0xb36a8c6f, 0xcdb5fa2a, 0x264041f6, 0x580b5b9d, 0xbb9b9b02, 0xf0739115, 0x2ca0ca4d, 0xac891702, 0x114890c0, 0xe3861bc1, 0xf1fd6e19, 0x1abd0c9e, 0xe9ad729c, 0x60d2c14b, 0xcf3690c0, 0x96c00c66, 0x753a455e, 0x4fac1440, 0x7126c483, 0x1fc5db38, 0xf8861f14, 0xace8d3c1, 0xa25724e6, 0x33f8d3b5, 0xe0dcc3ae, 0x42636a42, 0x2afbdd0d, 0xcf7df244, 0x7b3c40ea, 0xf96b4aa3, 0xa75735e7, 0x6e88f5f0, 0x1ef57055, 0xfb21de90, 0x8cdee233, 0x5a979bc6, 0x76631ae4, 0x2c2b2289, 0xdc500039, 0xa813e95a
basegraph=
1
z_c=
64
n_cb=
4224
q_m=
2
n_filler=
0
e =
2240
rv_index =
0
code_block_mode =
1
op_flags =
RTE_BBDEV_LDPC_RATE_MATCH, RTE_BBDEV_LDPC_CRC_24B_ATTACH
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/demo_enc_scn_6_rv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0xea7bdad9, 0xabd8311a, 0x4e7ba2e2, 0x5c5c5c85, 0xc400ed50, 0x9bea8883, 0x04c2b70f, 0x392dc1c2, 0x6f7a1597, 0xe4bbe4c8, 0x350dc432, 0x926071f2, 0x372ea0eb, 0x36d61798, 0x1d5544a1, 0x37de9af4, 0x722e1ff0, 0x35abc04a, 0xff203abe, 0xca7f7d7a, 0x32a305d0, 0x5c08bf1b, 0xae11c62b, 0x9d832088, 0xe3b2ec27, 0x9438eea5, 0x89525b88, 0xe3007430, 0x836b5498, 0xee899e03, 0xe5c91dd4, 0x5117acf9, 0x6b0df72a, 0x7ed367f0, 0xa7cc1dd4, 0x4f8bc304, 0x939bba5d, 0x76a555c3, 0x1e3e0a60, 0x6f395cde, 0x5ca777f3, 0x79163b7d, 0x04f40cd1, 0xf1f312fe, 0x8abcb1ed, 0xf3550fd6, 0x8060deb6, 0x82380005, 0xc1ea99de, 0xd0cfc143, 0x58fa9ca5, 0x5c2f5980, 0x39f24b7b, 0xc918a3ce, 0x656a8d76, 0xf6f8a3cf, 0x9d6d1184, 0x5c5060e0, 0x3171d366, 0xe77af42c, 0xf24290f4, 0x1df2f5e8, 0x56c1a6eb, 0x3be35b07, 0xdaee3c1b, 0x65dfcb90, 0x8ba0ede7, 0x311e72b1, 0x772ffa8a, 0xd863ce1d, 0x8974177a, 0x87d85875, 0x927596d1, 0x0481e7fa, 0x9768d335, 0x90a5f29b, 0x13e11b45, 0x73cbac15, 0x9301bfde, 0x64
output0 =
0xfb5615fe, 0x4d6aa84c, 0x04b58965, 0x230fde89, 0xcc5fecca, 0xbfbf550c, 0xf67ad92b, 0xc8f1af3e, 0x370144b7, 0x494a1a9d, 0xea9b9b17, 0xb562c051, 0x3ce18b59, 0xacc91317, 0x155cc4d5, 0xb2820bc0, 0xa5f93b0d, 0x1fe9489e, 0xacfd67c9, 0x20c3914e, 0xcf239190, 0x87810976, 0x706e110b, 0x0fbd4550, 0x7567d4d3, 0x0fc18b28, 0xbdc21a14, 0xbced9791, 0xb21260a2, 0x27b9c3b5, 0xf49cc2bb, 0x12266f03, 0x2fff9d4c, 0x9e28b204, 0x2b6814ee, 0xf83a1fb2, 0xe75270a2, 0x6fd8b0a4, 0x5fb42455, 0xaa74cf95, 0xd88bb226, 0x5b828b86, 0x27624ee1, 0x382a36cc, 0x88405568, 0xfc53e81a, 0xb427b8f7, 0xfa3dc31b, 0x3e6b1efe, 0xf1263f88, 0xdb0aa37e, 0xc76f6953, 0xe04117f2, 0x345174ee, 0x1c13bcea, 0x17aa1eee, 0x02cae3a8, 0xd981f1df, 0xbf506ce6, 0x0eae2777, 0xfcf7789f, 0x10d5456c, 0x15047241, 0x4894851e, 0xc3c7f9f7, 0x03e18cb9, 0x12b01f64, 0x55b2bfe1, 0xa496679d, 0xc07289be, 0x826314c4, 0xf033eb1c, 0xca749a3a, 0xc65b19ea, 0x1f9db8b4, 0xc6e59002, 0xa790382b, 0x7728dd7c, 0x5f89fbe5, 0x28bbc5fb, 0x064320d0, 0xf393f369, 0x402810ad, 0xa4720036, 0x4ef67d2d, 0x024b166b, 0x34eaa55c, 0x7bacc96e, 0x45d220ae, 0x4dee5d75, 0x62fed1ed, 0xe21259aa, 0x3ccccab9, 0x697753f0, 0xdf266f01, 0x9a4f5ea8, 0xe51ede07, 0xdce7f8e9, 0xdfa05182, 0x6328afb6
basegraph=
2
z_c=
256
n_cb=
12800
q_m=
2
n_filler=
0
e =
3200
rv_index =
0
code_block_mode =
1
op_flags =
RTE_BBDEV_LDPC_RATE_MATCH, RTE_BBDEV_LDPC_CRC_24B_ATTACH
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/demo_enc_scn_7_rv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0xea7bdad9, 0xabd8311a, 0x4e7ba2e2, 0x5c5c5c85, 0xc400ed50, 0x9bea8883, 0x04c2b70f, 0x392dc1c2, 0x6f7a1597, 0xe4bbe4c8, 0x350dc432, 0x926071f2, 0x372ea0eb, 0x36d61798, 0x1d5544a1, 0x37de9af4, 0x722e1ff0, 0x35abc04a, 0xff203abe, 0xca7f7d7a, 0x32a305d0, 0x5c08bf1b, 0xae11c62b, 0x9d832088, 0xe3b2ec27, 0x9438eea5, 0x89525b88, 0xe3007430, 0x836b5498, 0xee899e03, 0xe5c91dd4, 0x5117acf9, 0x6b0df72a, 0x7ed367f0, 0xa7cc1dd4, 0x4f8bc304, 0x939bba5d, 0x76a555c3, 0x1e3e0a60
output0 =
0x23062a83, 0xbe78896f, 0x34e984b1, 0x70a9cf9a, 0x65f5095b, 0x771ea744, 0x572b5cba, 0x48d2507c, 0x11d9dbad, 0x7b1bf95c, 0x2f538596, 0x3c4b69b3, 0x6161569d, 0xf2136773, 0x8cc275eb, 0x3f0ee8f2, 0xbb5245be, 0x0c2ab808, 0x14a4d971, 0x661edfd8, 0xcd5be9ce, 0xaeae555c, 0xf67a9d3e, 0xc9a1ea6b, 0x720154a6, 0x190f4f8c, 0xbf9ada12, 0xa1278144, 0x79a1ce09, 0xf88c1216, 0x444cc0d1, 0xe2925fc5, 0xb0b87f5d, 0x5fbc588f, 0xece93699, 0x21c2804b, 0xdb62d094, 0xd6804837, 0x606e111b, 0x0ead4500, 0x653281c3, 0x0b808f7c, 0xfc925f51, 0xbcbc87d1, 0xe30330e7, 0x66e9c3b5, 0xb18c92af, 0x02272f03, 0x6aafd818, 0xce2da351, 0x3f7d41af, 0xa83a0ae2, 0xb21375b3, 0x3fdda0a5, 0x4be46114, 0xaf70ced1, 0xcdcaf662, 0x5a969a87, 0x66724ef5, 0x6d6b66d9, 0xd9005578, 0xe806bc4e, 0x3dea5f89, 0x2c13678f, 0x16617450, 0x9a5144a2, 0x55bd665d, 0x1d1cc783, 0x0cfaf626, 0xb780e63f, 0xb9ce7360, 0xb330d19b, 0x3d1e4cdc, 0xf4307513, 0x667b381c, 0x1d18aea4, 0x10a8531e, 0x131ceb64, 0x3f823938, 0x6574c7d9, 0x2c6bc220, 0x4d0d4701
basegraph=
2
z_c=
128
n_cb=
6400
q_m=
2
n_filler=
8
e =
2624
rv_index =
0
code_block_mode =
1
op_flags =
RTE_BBDEV_LDPC_RATE_MATCH, RTE_BBDEV_LDPC_CRC_24B_ATTACH
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/demo_enc_scn_8_rv0.data 0 → 100755
View file @ 12a0ca65
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0xea7bdad9, 0xabd8311a, 0x4e7ba2e2, 0x5c5c5c85, 0xc400ed50, 0x9bea8883, 0x04c2b70f, 0x392dc1c2, 0x6f7a1597, 0xc8
output0 =
0x0dcd08ac, 0xf9309a7b, 0xb1663784, 0xe466b066, 0xe7f84133, 0x35a54111, 0x90c00f90, 0x8b829dbc, 0x7edeaa50, 0x215048f0, 0x53f11de5, 0xd34ae718, 0x62067b86, 0xbb7dc97e, 0xf995c5f4, 0x8311e2c5, 0xdf419b04, 0x1a828a85, 0x8639bbcd, 0x02137d25, 0x52356871, 0xca2d0387, 0x51f5687f, 0xa9cdb410, 0x1b4e4664, 0x193e9d65, 0xa03c63f6, 0xb26b7fd3, 0x26dee48e, 0x9a2d9bef, 0x16b40bf5, 0x00cab368, 0x4916c4b1, 0xe684ddd7, 0xfc0fd461, 0x1ca8fa78, 0x643ce308, 0xec27ef99, 0xe726ca76, 0x21e3c41d, 0x0d9e5dfa, 0x461972a5, 0xee3eebb9, 0x029b245a, 0x28069caf, 0xd8161167, 0xc8c880a3, 0xec2b2d8c, 0xb1290350, 0x9f37480d
basegraph=
2
z_c=
32
n_cb=
1600
q_m=
2
n_filler=
0
e =
1600
rv_index =
0
code_block_mode =
1
op_flags =
RTE_BBDEV_LDPC_RATE_MATCH, RTE_BBDEV_LDPC_CRC_24B_ATTACH
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/ldpc_dec_HARQ_1_0.data 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/test_vectors/ldpc_dec_HARQ_1_1.data 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/test_vectors/ldpc_dec_HARQ_1_2.data 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/test_vectors/ldpc_dec_v11835.data 0 → 100644
View file @ 12a0ca65
# SPDX-License-Identifier: BSD-3-Clause
# Copyright(c) 2019 Intel Corporation
op_type =
RTE_BBDEV_OP_LDPC_DEC
input0 =
0x817F7F81, 0x817F817F, 0x7F818181, 0x7F818181, 0x7F817F81, 0x7F7F8181, 0x817F7F7F, 0x81817F81,
0x7F7F6B7F, 0x7F7F817F, 0x7F7F8181, 0x817F8181, 0x81817F7F, 0x7F818192, 0x7F81817F, 0x817F7F7F,
0x8181
output0 =
0x44FB08C0, 0x661CCC
basegraph=
2
z_c=
10
n_cb=
500
q_m=
6
n_filler=
44
e=
66
rv_index=
0
code_block_mode=
1
iter_max=
20
expected_iter_count=
4
op_flags=
RTE_BBDEV_LDPC_ITERATION_STOP_ENABLE
expected_status=
OK
targets/ARCH/test-bbdev/test_vectors/ldpc_dec_v2342_drop.data 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/test_vectors/ldpc_dec_v7813.data 0 → 100644
View file @ 12a0ca65
# SPDX-License-Identifier: BSD-3-Clause
# Copyright(c) 2019 Intel Corporation
op_type =
RTE_BBDEV_OP_LDPC_DEC
input0 =
0x7F817F81, 0x7F81817F, 0x7F7F7F7F, 0x81818181, 0x7F81817F, 0x817F8181, 0x817F7F7F, 0x7F817F81,
0x817F7F7F, 0x8181817F, 0x8181817F
output0 =
0x8C4DEB9F, 0x52
basegraph=
2
z_c=
7
n_cb=
350
q_m=
2
n_filler=
30
e =
44
rv_index =
0
code_block_mode =
1
iter_max =
8
expected_iter_count =
6
op_flags =
RTE_BBDEV_LDPC_ITERATION_STOP_ENABLE
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/ldpc_dec_v8480.data 0 → 100644
View file @ 12a0ca65
# SPDX-License-Identifier: BSD-3-Clause
# Copyright(c) 2019 Intel Corporation
op_type =
RTE_BBDEV_OP_LDPC_DEC
input0 =
0x81817F81, 0x817F7F7F, 0x7F817F7F, 0x7F817F7F, 0x8181817F, 0x817F817F, 0x817F817F, 0x7F818181,
0x7F817F7F, 0x81817F81, 0x81817F7F, 0x7F7F7F81, 0x7F817F81, 0x81817F7F, 0x8181817F, 0x81818181,
0x817F8181, 0x7F7F7F81, 0x7F818181, 0x817F7F7F, 0x7F7F7F7F, 0x7F7F7F81, 0x7F817F81, 0x817F7F81,
0x7F7F7F81, 0x817F8181, 0x7F818181, 0x817F817F, 0x7F7F817F, 0x7F817F7F, 0x7F817F7F, 0x7F81817F,
0x7F818181, 0x7F81817F, 0x81817F7F, 0x81817F7F, 0x7F81817F, 0x817F7F81, 0x81817F81, 0x817F817F,
0x7F7F8181, 0x817F7F81, 0x81818181, 0x7F7F7F7F, 0x7F7F7F7F, 0x817F817F, 0x7F81817F, 0x7F7F817F,
0x8181817F, 0x817F8181, 0x7F817F81, 0x817F8181, 0x8181817F, 0x817F8181, 0x7F817F81, 0x8181817F,
0x7F7F8181, 0x7F7F817F, 0x7F81817F, 0x81817F7F, 0x7F7F8181, 0x8181817F, 0x7F818181, 0x81817F81,
0x7F7F817F, 0x7F7F8181, 0x7F817F81, 0x7F81817F, 0x817F7F81, 0x81818181, 0x7F817F81, 0x7F7F7F7F,
0x7F817F7F, 0x81817F7F, 0x817F7F7F, 0x7F818181, 0x7F7F817F, 0x81817F81, 0x8181817F, 0x7F81817F,
0x8181817F, 0x817F8181, 0x7F817F7F, 0x817F817F, 0x81818181, 0x7F81817F, 0x817F817F, 0x81817F81,
0x7F7F8181, 0x817F7F7F, 0x7F818181, 0x7F7F8181, 0x81817F81, 0x7F81817F, 0x7F817F81, 0x81818181,
0x81817F81, 0x817F7F7F, 0x817F7F81, 0x7F7F817F, 0x7F818181, 0x7F817F7F, 0x817F817F, 0x7F7F817F,
0x81817F7F, 0x7F7F817F, 0x817F8181, 0x817F8181, 0x7F81817F, 0x817F817F, 0x817F7F7F, 0x81817F81,
0x81817F7F, 0x8181817F, 0x817F7F81, 0x81817F81, 0x7F7F817F, 0x7F7F8181, 0x7F7F817F, 0x81817F81,
0x81817F7F, 0x817F7F7F, 0x817F7F7F, 0x7F817F81, 0x8181817F, 0x81818181, 0x7F817F7F, 0x7F7F8181,
0x7F7F7F81, 0x7F7F7F81, 0x817F8181, 0x7F817F81, 0x81818181, 0x8181817F, 0x7F81817F, 0x7F818181,
0x7F7F817F, 0x7F7F7F81, 0x817F7F7F, 0x817F817F, 0x7F817F81, 0x817F7F7F, 0x7F81817F, 0x7F7F7F7F,
0x7F818181, 0x7F817F7F, 0x817F7F81, 0x7F81817F, 0x7F7F8181, 0x7F7F8181, 0x8181817F, 0x7F7F817F,
0x7F81817F, 0x7F81817F, 0x817F8181, 0x7F7F7F7F, 0x817F7F81, 0x7F7F8181, 0x817F8181, 0x817F7F7F,
0x7F7F817F, 0x817F8181, 0x81817F81, 0x81818181, 0x7F7F7F7F, 0x7F818181, 0x7F81817F, 0x81817F81,
0x7F7F817F, 0x8181817F, 0x817F817F, 0x7F7F7F7F, 0x7F818181, 0x7F7F817F, 0x7F818181, 0x817F7F81,
0x7F7F7F7F, 0x7F81817F, 0x817F7F7F, 0x81817F81, 0x7F817F81, 0x81818181, 0x7F7F8181, 0x817F817F,
0x7F817F81, 0x81817F81, 0x7F817F7F, 0x7F7F7F81, 0x7F7F7F7F, 0x81817F81, 0x817F7F81, 0x7F7F817F,
0x81818181, 0x7F7F7F7F, 0x817F817F, 0x817F7F81, 0x7F818181, 0x817F8181, 0x817F817F, 0x7F7F817F,
0x7F817F81
output0 =
0x76332859, 0x417B1254, 0xEC8A8CFE, 0xE7EFCD06, 0x43C5BDA2, 0x2EACD776, 0x6CD515AC, 0x6D6E04AC,
0xBC2D9F85, 0xD3643553, 0xD0C8DF8E, 0x235B434A, 0xD7AB7643, 0xA4D9C420, 0x372FA858, 0xF813CE10,
0xE0C238F6, 0x07853FD4, 0xE04E40F2, 0x0EE765A9, 0x6EEAFCBC, 0xA7059C68, 0xFBBC
basegraph=
2
z_c=
72
n_cb=
3600
q_m=
2
n_filler=
0
e =
804
rv_index =
0
code_block_mode =
1
iter_max =
8
expected_iter_count =
3
op_flags =
RTE_BBDEV_LDPC_ITERATION_STOP_ENABLE
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/ldpc_dec_v8568.data 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/test_vectors/ldpc_dec_v9503.data 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/test_vectors/ldpc_enc_v11835.data 0 → 100644
View file @ 12a0ca65
# SPDX-License-Identifier: BSD-3-Clause
# Copyright(c) 2019 Intel Corporation
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0x44FB08C0, 0x661CCC
output0 =
0x1BACEE95, 0x613ECD04, 0xC0
basegraph=
2
z_c=
10
n_cb=
500
q_m=
6
n_filler=
44
e=
66
rv_index=
0
code_block_mode=
1
op_flags=
RTE_BBDEV_LDPC_RATE_MATCH
expected_status=
OK
targets/ARCH/test-bbdev/test_vectors/ldpc_enc_v2342.data 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/test_vectors/ldpc_enc_v7813.data 0 → 100644
View file @ 12a0ca65
# SPDX-License-Identifier: BSD-3-Clause
# Copyright(c) 2017 Intel Corporation
# Origin : FEC5g_DL_1/7813
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0x8C4DEB9F, 0x52
output0 =
0x1A6D0FA6, 0x7017
basegraph=
2
z_c=
7
n_cb=
350
q_m=
2
n_filler=
30
e =
44
rv_index =
0
code_block_mode =
1
op_flags =
RTE_BBDEV_LDPC_RATE_MATCH
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/ldpc_enc_v8568.data 0 → 100644
View file @ 12a0ca65
# SPDX-License-Identifier: BSD-3-Clause
# Copyright(c) 2019 Intel Corporation
# Origin : FEC5g_DL_1/8568
op_type =
RTE_BBDEV_OP_LDPC_ENC
input0 =
0xB6D49CE2, 0x3E96B93F, 0xF02009F6, 0x2DF3D30D, 0x3B06C160, 0x646C69CC, 0x54439F0F, 0xCE0D12C3,
0x66E8BFD5, 0xA9D22B0C, 0xA9E7343B, 0x2B6EEF01, 0x6B6966C0, 0xB98FE144, 0xC3BF7BAD, 0x1B40DF1C,
0x973B12DC, 0x46E25E90, 0xB324ACCA, 0x5F0ED2B9, 0xBB4F
output0 =
0x8F1A7C00, 0x836CF0E5, 0x717CE52D, 0xEE86FB44, 0x21621E25, 0x58425AB5, 0xECA0F645, 0xAE9E63E6,
0x287D84BC, 0x9F19A401, 0xD68C4CA3, 0x354ACA5A, 0xD68D7FF8, 0xFAA84645, 0xCF0DBC28, 0x693C50F0,
0x9A3CD23C, 0x57E97520, 0x929BAF90, 0x8E2BA7D8, 0x5EF0FB8A, 0xFFE7B153, 0x9E164074, 0x4D06F0A2,
0x6BC68E5B, 0xB8274587, 0x69641DFC, 0xF5DC89A0, 0x4F8E741C, 0x1CB682DA, 0xEF36E914, 0x8BDEBA30,
0x4B6777E2, 0xEFBFD14C, 0x85F0DF67, 0x55DBD201, 0xCF29A01A, 0x862BD273, 0x1F43CFAF, 0x5CB128E9,
0x9C322654, 0xF8E4E47A, 0x0FCD1806, 0x0C7B6BC7, 0xF7B9748A, 0x6DE5D592, 0x0D119373, 0x5F7DC28C,
0x68F26F39, 0xAA47E18A, 0x479CDAAF, 0xE19DCBB3, 0xA72B475D, 0x2E781ED4, 0x4CBB910A, 0x5E5A5A1D,
0x2F668621, 0x86BD9FE1, 0xF1DC12E5, 0xB652E2C1, 0x2E0AC199, 0x059E43C4, 0x14F9B51E, 0x7DA378C5,
0x214E4D5F, 0x72ECE751, 0xF997A106, 0x3F362F62, 0x045DCA85, 0xAD27A58E, 0xB73B4390, 0xEB76C5D2,
0x58CE8B78, 0x73A1D1EA, 0x9705C8E4, 0x224703E8, 0xA0DE7885, 0x9CDBBEE0, 0xBAAFAE85, 0x1B5CFB8A,
0xF66B5209, 0x979335BB, 0x2AA6C7E2, 0x7E3958E7, 0xD39F8BC0, 0xD73BEA43, 0x24C74D3E, 0x9372C2D7,
0x49804670, 0xB3A983FC, 0xFA6DB662, 0x4E657550, 0xDDF757C2, 0xA7265DE7, 0x51BFA1A6, 0x63E1325D,
0x1FDBE953, 0x17348EDB, 0x6B6DC5C0, 0xE335772B, 0x32612617, 0xC13B63EB, 0x8C40891A, 0xF3566154,
0xF5345933, 0xAD9AB800, 0x4CF92B41, 0xF3B32673, 0x80577879, 0x19F8BB0E, 0xAD677483, 0x21B2EDC7,
0x3F96C8E2, 0x7B9211B7, 0x11909101, 0x6A9D9BF5, 0xC4A0E407, 0x5B013820, 0xD2102C31, 0xDC6F548A,
0xA4F6B72A, 0x79F19991, 0x6A21BE3C, 0x2E5CF7A5, 0xDCBB384B, 0xB05B5649, 0x1D61CCF1, 0x9DC122F3,
0x00CA6A82, 0xB7CECDF0, 0x605252A3, 0x0500B498, 0x61AA1618, 0x669788EF, 0xF0DB599F, 0x3ED04C4A,
0x17387F1E, 0xBDAC7B52, 0xEE7D1E0D, 0x58AF212C, 0x0CB064F8, 0x646239DB, 0x88CF9549, 0xD3C7C652,
0xB82109DB, 0x22225244, 0x305F8384, 0x9B4166D5, 0x704FA445, 0x956A0CA5, 0x89963D07, 0x5EF61FAB,
0xF71EAD06, 0xA47FB814, 0x86581A5C, 0xB81B9445, 0x4ECD608E, 0xE369E9A3, 0xFEB80EE5, 0x1399AB02,
0x30A74BEA, 0xCF08B948, 0xB0857028, 0xC81F8CD8, 0x64E13623, 0xAFF927F5, 0x592D7629, 0x7295DE02,
0xE98E2F04, 0x7407C828, 0x85EE9A47, 0xF9B6F671, 0x77F40DF0, 0x81CE7DA1, 0xB8732D5F, 0xC7AC742E,
0xF8623836, 0xE68F4E66, 0x18F29BB9, 0xF57E3350, 0x0E14399C, 0x114ACFA1, 0xFECFBDAA, 0xB0894694,
0xC8DF6D23, 0x7C71FB18, 0x91F00CF2, 0x6A45BC52, 0xFE99962D, 0x41FEBA3D, 0x5C1BB499, 0x51E50591,
0x04D9CDDE, 0x503FBB80, 0x2788B4EE, 0x82A545D8, 0x5F6DD45D, 0x7AE48BE2, 0x4C653419, 0x3C32D58C,
0x48788C71, 0x97A054A3, 0x7FC443B4, 0x805DFF9E, 0xA607D2C6, 0x02DA82C2, 0x884664C5
basegraph=
2
z_c=
72
n_cb=
3600
q_m=
2
n_filler=
64
e =
6624
rv_index =
0
code_block_mode =
1
op_flags =
RTE_BBDEV_LDPC_RATE_MATCH
expected_status =
OK
targets/ARCH/test-bbdev/test_vectors/ldpc_enc_v9503.data 0 → 100644
View file @ 12a0ca65
This diff is collapsed.
targets/ARCH/test-bbdev/turbo_dec_default.data 0 → 120000
View file @ 12a0ca65
test_vectors/turbo_dec_c1_k6144_r0_e10376_crc24b_sbd_negllr_high_snr.data
\ No newline at end of file
targets/ARCH/test-bbdev/turbo_enc_default.data 0 → 120000
View file @ 12a0ca65
This diff is collapsed.
Markdown is supported
0% or
You are about to add 0 people to the discussion. Proceed with caution.
Finish editing this message first!
Please register or to comment