Home
last modified time | relevance | path

Searched refs:buffer (Results 1 – 25 of 173) sorted by relevance

1234567

/dpdk/lib/eal/common/
H A Deal_filesystem.h39 static char buffer[PATH_MAX]; /* static so auto-zeroed */ in eal_runtime_config_path() local
41 snprintf(buffer, sizeof(buffer), "%s/%s", rte_eal_get_runtime_dir(), in eal_runtime_config_path()
43 return buffer; in eal_runtime_config_path()
51 static char buffer[PATH_MAX]; /* static so auto-zeroed */ in eal_mp_socket_path() local
53 snprintf(buffer, sizeof(buffer), "%s/%s", rte_eal_get_runtime_dir(), in eal_mp_socket_path()
55 return buffer; in eal_mp_socket_path()
60 eal_get_fbarray_path(char *buffer, size_t buflen, const char *name) { in eal_get_fbarray_path() argument
61 snprintf(buffer, buflen, FBARRAY_NAME_FMT, rte_eal_get_runtime_dir(), in eal_get_fbarray_path()
63 return buffer; in eal_get_fbarray_path()
71 static char buffer[PATH_MAX]; /* static so auto-zeroed */ in eal_hugepage_info_path() local
[all …]
H A Deal_private.h730 int eal_asprintf(char **buffer, const char *format, ...);
732 #define asprintf(buffer, format, ...) \ argument
733 eal_asprintf(buffer, format, ##__VA_ARGS__)
/dpdk/drivers/net/cnxk/
H A Dcnxk_rep_flow.c51 populate_attr_data(void *buffer, uint32_t *length, const struct rte_flow_attr *attr) in populate_attr_data() argument
56 cnxk_rep_msg_populate_type(buffer, length, CNXK_TYPE_ATTR, sz); in populate_attr_data()
60 rte_memcpy(RTE_PTR_ADD(buffer, len), attr, sz); in populate_attr_data()
114 populate_pattern_data(void *buffer, uint32_t *length, const struct rte_flow_item *pattern, in populate_pattern_data() argument
125 cnxk_rep_msg_populate_type(buffer, length, CNXK_TYPE_PATTERN, sz); in populate_pattern_data()
129 rte_memcpy(RTE_PTR_ADD(buffer, len), pattern_data, sz); in populate_pattern_data()
252 populate_action_data(void *buffer, uint32_t *length, const struct rte_flow_action *action, in populate_action_data() argument
263 cnxk_rep_msg_populate_type(buffer, length, CNXK_TYPE_ACTION, sz); in populate_action_data()
267 rte_memcpy(RTE_PTR_ADD(buffer, len), action_data, sz); in populate_action_data()
278 void *buffer; in process_flow_destroy() local
[all …]
H A Dcnxk_rep_msg.c160 send_control_message(struct cnxk_eswitch_dev *eswitch_dev, void *buffer, uint32_t len) in send_control_message() argument
165 sz = send_message_on_socket(eswitch_dev->sock_fd, buffer, len, 0); in send_control_message()
184 cnxk_rep_msg_populate_msg_end(void *buffer, uint32_t *length) in cnxk_rep_msg_populate_msg_end() argument
186 cnxk_rep_msg_populate_command(buffer, length, CNXK_REP_MSG_END, 0); in cnxk_rep_msg_populate_msg_end()
190 cnxk_rep_msg_populate_type(void *buffer, uint32_t *length, cnxk_type_t type, uint32_t sz) in cnxk_rep_msg_populate_type() argument
201 rte_memcpy(RTE_PTR_ADD(buffer, len), &data, sizeof(cnxk_type_data_t)); in cnxk_rep_msg_populate_type()
208 cnxk_rep_msg_populate_header(void *buffer, uint32_t *length) in cnxk_rep_msg_populate_header() argument
213 cnxk_rep_msg_populate_type(buffer, length, CNXK_TYPE_HEADER, sizeof(cnxk_header_t)); in cnxk_rep_msg_populate_header()
221 rte_memcpy(RTE_PTR_ADD(buffer, len), &hdr, sizeof(cnxk_header_t)); in cnxk_rep_msg_populate_header()
228 cnxk_rep_msg_populate_command(void *buffer, uint32_t *length, cnxk_rep_msg_t type, uint32_t size) in cnxk_rep_msg_populate_command() argument
[all …]
H A Dcnxk_rep_ops.c501 void *buffer; in process_eth_stats() local
505 buffer = plt_zmalloc(size, 0); in process_eth_stats()
506 if (!buffer) { in process_eth_stats()
512 cnxk_rep_msg_populate_header(buffer, &len); in process_eth_stats()
515 cnxk_rep_msg_populate_command_meta(buffer, &len, &msg_st_meta, in process_eth_stats()
517 cnxk_rep_msg_populate_msg_end(buffer, &len); in process_eth_stats()
519 rc = cnxk_rep_msg_send_process(rep_dev, buffer, len, adata); in process_eth_stats()
525 rte_free(buffer); in process_eth_stats()
529 rte_free(buffer); in process_eth_stats()
662 void *buffer; in cnxk_rep_mac_addr_set() local
[all …]
/dpdk/drivers/crypto/qat/
H A Dqat_ec.h14 } buffer; typedef
25 buffer x;
26 buffer y;
27 buffer n;
28 buffer p;
29 buffer a;
30 buffer b;
31 buffer h;
/dpdk/lib/telemetry/
H A Dtelemetry_legacy.c34 char *buffer, int buf_len);
81 char *buffer __rte_unused, int buf_len __rte_unused) in register_client()
181 parse_client_request(char *buffer, int buf_len, int s) in parse_client_request() argument
184 char *data = buffer + buf_len; in parse_client_request()
187 if (buffer[0] != '{' || buffer[buf_len - 1] != '}') in parse_client_request()
190 if (strstr(buffer, CLIENTS_UNREG_ACTION) && strstr(buffer, CLIENTS_CMD) in parse_client_request()
191 && strstr(buffer, CLIENTS_DATA)) in parse_client_request()
195 char *action_ptr = strstr(buffer, callbacks[i].action); in parse_client_request()
196 char *cmd_ptr = strstr(buffer, callbacks[i].cmd); in parse_client_request()
197 char *data_ptr = strstr(buffer, callbacks[i].data); in parse_client_request()
[all …]
/dpdk/drivers/common/dpaax/caamflib/rta/
H A Dsec_run_time_asm.h389 uint32_t *buffer; member
398 uint32_t *buffer, unsigned int offset) in rta_program_cntxt_init() argument
404 program->buffer = buffer; in rta_program_cntxt_init()
454 program->buffer[program->current_pc] = program->bswap ? in __rta_out32()
462 program->buffer[program->current_pc] = cpu_to_be32(val); in __rta_out_be32()
469 program->buffer[program->current_pc] = cpu_to_le32(val); in __rta_out_le32()
565 uint8_t *tmp = (uint8_t *)&program->buffer[program->current_pc]; in rta_copy_data()
593 uint8_t *tmp = (uint8_t *)&program->buffer[program->current_pc]; in __rta_inline_data()
600 __rta_dma_data(&program->buffer[program->current_pc], data, in __rta_inline_data()
607 rta_desc_len(uint32_t *buffer) in rta_desc_len() argument
[all …]
/dpdk/drivers/net/qede/
H A Dqede_regs.c80 uint32_t *buffer = regs->data; in qede_get_regs() local
91 if (buffer == NULL) { in qede_get_regs()
98 memset(buffer, 0, regs->length); in qede_get_regs()
112 qdev->ops->common->dbg_idle_chk(edev, (uint8_t *)buffer + in qede_get_regs()
114 *(uint32_t *)((uint8_t *)buffer + offset) = in qede_get_regs()
122 qdev->ops->common->dbg_idle_chk(edev, (uint8_t *)buffer + in qede_get_regs()
124 *(uint32_t *)((uint8_t *)buffer + offset) = in qede_get_regs()
132 qdev->ops->common->dbg_reg_fifo(edev, (uint8_t *)buffer + in qede_get_regs()
134 *(uint32_t *)((uint8_t *)buffer + offset) = in qede_get_regs()
142 qdev->ops->common->dbg_igu_fifo(edev, (uint8_t *)buffer + in qede_get_regs()
[all …]
H A Dqede_if.h197 void *buffer,
202 void *buffer,
207 void *buffer,
212 void *buffer,
216 int (*dbg_protection_override)(struct ecore_dev *edev, void *buffer,
221 int (*dbg_igu_fifo)(struct ecore_dev *edev, void *buffer,
224 int (*dbg_fw_asserts)(struct ecore_dev *edev, void *buffer,
229 int (*dbg_ilt)(struct ecore_dev *edev, void *buffer,
H A Dqede_debug.h14 int qed_dbg_grc(struct ecore_dev *edev, void *buffer, u32 *num_dumped_bytes);
16 int qed_dbg_idle_chk(struct ecore_dev *edev, void *buffer,
19 int qed_dbg_reg_fifo(struct ecore_dev *edev, void *buffer,
22 int qed_dbg_igu_fifo(struct ecore_dev *edev, void *buffer,
25 int qed_dbg_protection_override(struct ecore_dev *edev, void *buffer,
28 int qed_dbg_fw_asserts(struct ecore_dev *edev, void *buffer,
31 int qed_dbg_ilt(struct ecore_dev *edev, void *buffer, u32 *num_dumped_bytes);
33 int qed_dbg_mcp_trace(struct ecore_dev *edev, void *buffer,
36 int qed_dbg_all_data(struct ecore_dev *edev, void *buffer);
40 int qed_dbg_feature(struct ecore_dev *edev, void *buffer,
/dpdk/lib/cfgfile/
H A Drte_cfgfile.c172 char buffer[CFG_NAME_LEN + CFG_VALUE_LEN + 4]; in rte_cfgfile_load_with_params() local
185 while (fgets(buffer, sizeof(buffer), f) != NULL) { in rte_cfgfile_load_with_params()
187 size_t len = strnlen(buffer, sizeof(buffer)); in rte_cfgfile_load_with_params()
189 if ((len >= sizeof(buffer) - 1) && (buffer[len-1] != '\n')) { in rte_cfgfile_load_with_params()
195 pos = memchr(buffer, params->comment_character, len); in rte_cfgfile_load_with_params()
197 (pos == buffer || *(pos-1) != '\\')) { in rte_cfgfile_load_with_params()
199 len = pos - buffer; in rte_cfgfile_load_with_params()
202 len = _strip(buffer, len); in rte_cfgfile_load_with_params()
204 if (buffer[0] != '[' && memchr(buffer, '=', len) == NULL) in rte_cfgfile_load_with_params()
207 if (buffer[0] == '[') { in rte_cfgfile_load_with_params()
[all …]
/dpdk/examples/multi_process/client_server_mp/shared/
H A Dcommon.h50 static char buffer[sizeof(MP_CLIENT_RXQ_NAME) + 2]; in get_rx_queue_name() local
52 snprintf(buffer, sizeof(buffer), MP_CLIENT_RXQ_NAME, id); in get_rx_queue_name()
53 return buffer; in get_rx_queue_name()
/dpdk/examples/server_node_efd/shared/
H A Dcommon.h62 static char buffer[sizeof(MP_NODE_RXQ_NAME) + 2]; in get_rx_queue_name() local
64 snprintf(buffer, sizeof(buffer), MP_NODE_RXQ_NAME, id); in get_rx_queue_name()
65 return buffer; in get_rx_queue_name()
/dpdk/drivers/common/sfc_efx/
H A Dsfc_efx_mcdi.c195 char *buffer, void *data, size_t data_size, in sfc_efx_mcdi_do_log() argument
209 buffer[position] = '\0'; in sfc_efx_mcdi_do_log()
210 sfc_efx_log_mcdi(mcdi, "%s \\", buffer); in sfc_efx_mcdi_do_log()
214 position += snprintf(buffer + position, in sfc_efx_mcdi_do_log()
228 char buffer[SFC_MCDI_LOG_BUF_SIZE]; in sfc_efx_mcdi_logger() local
245 pfxsize = snprintf(buffer, sizeof(buffer), "MCDI RPC %s:", in sfc_efx_mcdi_logger()
248 start = sfc_efx_mcdi_do_log(mcdi, buffer, header, header_size, in sfc_efx_mcdi_logger()
250 start = sfc_efx_mcdi_do_log(mcdi, buffer, data, data_size, in sfc_efx_mcdi_logger()
253 buffer[start] = '\0'; in sfc_efx_mcdi_logger()
254 sfc_efx_log_mcdi(mcdi, "%s", buffer); in sfc_efx_mcdi_logger()
/dpdk/lib/cmdline/
H A Dcmdline.c137 const char *history, *buffer; in cmdline_in() local
149 buffer = rdline_get_buffer(&cl->rdl); in cmdline_in()
153 same = !memcmp(buffer, history, histlen) && in cmdline_in()
154 buffer[histlen] == '\n'; in cmdline_in()
158 buflen = strnlen(buffer, RDLINE_BUF_SIZE); in cmdline_in()
160 rdline_add_history(&cl->rdl, buffer); in cmdline_in()
/dpdk/drivers/net/atlantic/hw_atl/
H A Dhw_atl_llh_internal.h547 #define HW_ATL_RPB_RXBHI_THRESH_ADR(buffer) (0x00005714 + (buffer) * 0x10) argument
566 #define HW_ATL_RPB_RXBLO_THRESH_ADR(buffer) (0x00005714 + (buffer) * 0x10) argument
603 #define HW_ATL_RPB_RXBBUF_SIZE_ADR(buffer) (0x00005710 + (buffer) * 0x10) argument
622 #define HW_ATL_RPB_RXBXOFF_EN_ADR(buffer) (0x00005714 + (buffer) * 0x10) argument
1887 #define HW_ATL_TPB_TXBHI_THRESH_ADR(buffer) (0x00007914 + (buffer) * 0x10) argument
1906 #define HW_ATL_TPB_TXBLO_THRESH_ADR(buffer) (0x00007914 + (buffer) * 0x10) argument
1943 #define HW_ATL_TPB_TXBBUF_SIZE_ADR(buffer) (0x00007910 + (buffer) * 0x10) argument
/dpdk/drivers/raw/ifpga/base/
H A Difpga_fme_pr.c226 static int fme_pr(struct ifpga_hw *hw, u32 port_id, const char *buffer, in fme_pr() argument
236 if (!buffer || size == 0) in fme_pr()
272 ret = fpga_pr_buf_load(fme, &info, buffer, size); in fme_pr()
283 int do_pr(struct ifpga_hw *hw, u32 port_id, const char *buffer, in do_pr() argument
292 if (!buffer || size == 0) { in do_pr()
297 bts_hdr = (const struct bts_header *)buffer; in do_pr()
306 buf = buffer + header_size; in do_pr()
/dpdk/drivers/net/mana/
H A Dgdma.c24 return ((uint8_t *)queue->buffer) + offset_in_bytes; in gdma_get_wqe_pointer()
157 if (wq_buffer_pointer >= ((uint8_t *)queue->buffer) + queue->size) in gdma_post_work_request()
160 write_scatter_gather_list((uint8_t *)queue->buffer, in gdma_post_work_request()
161 (uint8_t *)queue->buffer + queue->size, in gdma_post_work_request()
355 struct gdma_hardware_completion_entry *buffer = cq->buffer; in gdma_poll_completion_queue() local
358 cqe = &buffer[cq->head % cq->count]; in gdma_poll_completion_queue()
/dpdk/lib/power/
H A Dguest_channel.c
/dpdk/drivers/common/sfc_efx/base/
H A Def10_image.c35 uint8_t *buffer; member
52 if (cursor == NULL || cursor->buffer == NULL || cursor->length < 2) { in efx_asn1_parse_header_match_tag()
57 cursor->tag = cursor->buffer[0]; in efx_asn1_parse_header_match_tag()
70 if ((cursor->buffer[1] & 0x80) == 0) { in efx_asn1_parse_header_match_tag()
73 cursor->val_size = cursor->buffer[1]; in efx_asn1_parse_header_match_tag()
76 uint32_t nbytes = cursor->buffer[1] & 0x7F; in efx_asn1_parse_header_match_tag()
98 (cursor->val_size << 8) | cursor->buffer[offset]; in efx_asn1_parse_header_match_tag()
153 cursor->buffer += cursor->hdr_size; in efx_asn1_enter_tag()
195 if (memcmp(cursor->buffer + cursor->hdr_size, valp, val_size) != 0) { in efx_asn1_match_tag_value()
200 cursor->buffer += cursor->hdr_size + cursor->val_size; in efx_asn1_match_tag_value()
[all …]
/dpdk/lib/net/
H A Dnet_crc_sse.c178 alignas(16) uint8_t buffer[16]; in crc32_eth_calc_pclmulqdq() local
180 memset(buffer, 0, sizeof(buffer)); in crc32_eth_calc_pclmulqdq()
181 memcpy(buffer, data, data_len); in crc32_eth_calc_pclmulqdq()
183 fold = _mm_load_si128((const __m128i *)buffer); in crc32_eth_calc_pclmulqdq()
H A Dnet_crc_neon.c152 alignas(16) uint8_t buffer[16]; in crc32_eth_calc_pmull() local
154 memset(buffer, 0, sizeof(buffer)); in crc32_eth_calc_pmull()
155 memcpy(buffer, data, data_len); in crc32_eth_calc_pmull()
157 fold = vld1q_u64((uint64_t *)buffer); in crc32_eth_calc_pmull()
/dpdk/app/test-crypto-perf/
H A Ddpdk-graph-crypto-perf.py49 def boxplot_graph(self, x_axis_label, burst, buffer): argument
55 ", Buffer Size: " + buffer,
75 def histogram_graph(self, x_axis_label, burst, buffer): argument
89 buffer, height=1400, width=2400)
137 for (burst, buffer), group in clean_data.groupby(['Burst Size',
140 grapher.histogram_graph("time (us)", burst, buffer)
141 grapher.boxplot_graph("time (us)", burst, buffer)
/dpdk/drivers/common/dpaax/caamflib/
H A Drta.h67 #define PROGRAM_CNTXT_INIT(program, buffer, offset) \ argument
68 rta_program_cntxt_init(program, buffer, offset)
135 #define DESC_LEN(buffer) rta_desc_len(buffer) argument
143 #define DESC_BYTES(buffer) rta_desc_bytes(buffer) argument

1234567