Home
last modified time | relevance | path

Searched refs:temp (Results 1 – 25 of 78) sorted by relevance

1234

/dpdk/drivers/net/mlx5/windows/
H A Dmlx5_flow_os.c288 if (!temp) in mlx5_clear_thread_list()
295 while (temp) { in mlx5_clear_thread_list()
308 free(temp); in mlx5_clear_thread_list()
311 temp = next; in mlx5_clear_thread_list()
314 prev = temp; in mlx5_clear_thread_list()
315 temp = temp->next; in mlx5_clear_thread_list()
340 struct mlx5_workspace_thread *temp = calloc(1, sizeof(*temp)); in mlx5_add_workspace_to_list() local
342 if (!temp) { in mlx5_add_workspace_to_list()
350 free(temp); in mlx5_add_workspace_to_list()
358 first = temp; in mlx5_add_workspace_to_list()
[all …]
/dpdk/drivers/common/cnxk/
H A Droc_hash.c49 temp = (B ^ C ^ D) + _K[1]; in roc_hash_sha1_gen()
55 temp = lrot32(5, A) + temp + E + W[i]; in roc_hash_sha1_gen()
60 A = temp; in roc_hash_sha1_gen()
132 temp[1] = H + S1 + temp[0] + _K[i] + W[i]; in roc_hash_sha256_gen()
135 temp[3] = S0 + temp[2]; in roc_hash_sha256_gen()
140 E = D + temp[1]; in roc_hash_sha256_gen()
144 A = temp[1] + temp[3]; in roc_hash_sha256_gen()
244 temp[1] = H + S1 + temp[0] + _K[i] + W[i]; in roc_hash_sha512_gen()
247 temp[3] = S0 + temp[2]; in roc_hash_sha512_gen()
252 E = D + temp[1]; in roc_hash_sha512_gen()
[all …]
H A Droc_aes.c99 uint32_t temp; in aes_key_expand() local
105 temp = ks[i - 1]; in aes_key_expand()
107 temp = rot_word(temp); in aes_key_expand()
108 temp = sub_word(temp); in aes_key_expand()
109 temp ^= (uint32_t)GF8mul(1, 1 << ((i >> 2) - 1)); in aes_key_expand()
111 ks[i] = ks[i - 4] ^ temp; in aes_key_expand()
/dpdk/lib/net/
H A Dnet_crc_sse.c157 __m128i temp, fold, k; in crc32_eth_calc_pclmulqdq() local
172 fold = _mm_xor_si128(fold, temp); in crc32_eth_calc_pclmulqdq()
184 fold = _mm_xor_si128(fold, temp); in crc32_eth_calc_pclmulqdq()
194 fold = _mm_xor_si128(fold, temp); in crc32_eth_calc_pclmulqdq()
203 fold = _mm_xor_si128(fold, temp); in crc32_eth_calc_pclmulqdq()
230 temp = _mm_loadu_si128((const __m128i *) in crc32_eth_calc_pclmulqdq()
232 a = _mm_shuffle_epi8(fold, temp); in crc32_eth_calc_pclmulqdq()
234 temp = _mm_xor_si128(temp, in crc32_eth_calc_pclmulqdq()
236 b = _mm_shuffle_epi8(fold, temp); in crc32_eth_calc_pclmulqdq()
237 b = _mm_blendv_epi8(b, last16, temp); in crc32_eth_calc_pclmulqdq()
[all …]
H A Dnet_crc_neon.c131 uint64x2_t temp, fold, k; in crc32_eth_calc_pmull() local
135 temp = vreinterpretq_u64_u32(vsetq_lane_u32(crc, vmovq_n_u32(0), 0)); in crc32_eth_calc_pmull()
145 fold = veorq_u64(fold, temp); in crc32_eth_calc_pmull()
157 fold = veorq_u64(fold, temp); in crc32_eth_calc_pmull()
167 fold = veorq_u64(fold, temp); in crc32_eth_calc_pmull()
176 fold = veorq_u64(fold, temp); in crc32_eth_calc_pmull()
181 temp = vld1q_u64((const uint64_t *)&data[n]); in crc32_eth_calc_pmull()
182 fold = crcr32_folding_round(temp, k, fold); in crc32_eth_calc_pmull()
197 temp = vreinterpretq_u64_p128(vmull_p64( in crc32_eth_calc_pmull()
203 fold = veorq_u64(fold, temp); in crc32_eth_calc_pmull()
/dpdk/drivers/net/bnxt/hcapi/cfa/
H A Dhcapi_cfa_p58.c48 uint8_t temp[4]; in hcapi_cfa_crc32_hash() local
64 temp[3] = (uint8_t)(val1 >> 24); in hcapi_cfa_crc32_hash()
65 temp[2] = (uint8_t)(val1 >> 16); in hcapi_cfa_crc32_hash()
66 temp[1] = (uint8_t)(val1 >> 8); in hcapi_cfa_crc32_hash()
67 temp[0] = (uint8_t)(val1 & 0xff); in hcapi_cfa_crc32_hash()
72 val1 = hcapi_cfa_crc32i(~val1, temp, 4); in hcapi_cfa_crc32_hash()
80 val1 = hcapi_cfa_crc32i(~val1, temp, 4); in hcapi_cfa_crc32_hash()
H A Dhcapi_cfa_p4.c54 uint8_t temp[4]; in hcapi_cfa_crc32_hash() local
70 temp[3] = (uint8_t)(val1 >> 24); in hcapi_cfa_crc32_hash()
71 temp[2] = (uint8_t)(val1 >> 16); in hcapi_cfa_crc32_hash()
72 temp[1] = (uint8_t)(val1 >> 8); in hcapi_cfa_crc32_hash()
73 temp[0] = (uint8_t)(val1 & 0xff); in hcapi_cfa_crc32_hash()
78 val1 = hcapi_cfa_crc32i(~val1, temp, 4); in hcapi_cfa_crc32_hash()
85 val1 = hcapi_cfa_crc32i(~val1, temp, 4); in hcapi_cfa_crc32_hash()
/dpdk/drivers/net/mlx5/
H A Dmlx5_txq.c758 unsigned int temp; in txq_set_params() local
801 temp = RTE_ALIGN(temp, MLX5_WSEG_SIZE) + in txq_set_params()
803 temp = RTE_MIN(temp, MLX5_SEND_MAX_INLINE_LEN); in txq_set_params()
810 inlen_mode = temp; in txq_set_params()
836 temp = RTE_ALIGN(temp, MLX5_WQE_SIZE); in txq_set_params()
838 temp = RTE_MIN(temp, MLX5_WQE_SIZE_MAX + in txq_set_params()
843 temp = RTE_MIN(temp, MLX5_SEND_MAX_INLINE_LEN); in txq_set_params()
844 temp = RTE_MAX(temp, inlen_mode); in txq_set_params()
899 temp = RTE_ALIGN(temp, MLX5_WQE_SIZE); in txq_set_params()
901 temp = RTE_MIN(temp, MLX5_WQE_SIZE_MAX + in txq_set_params()
[all …]
/dpdk/examples/multi_process/client_server_mp/mp_server/
H A Dargs.c86 unsigned long temp; in parse_num_clients() local
91 temp = strtoul(clients, &end, 10); in parse_num_clients()
92 if (end == NULL || *end != '\0' || temp == 0) in parse_num_clients()
95 num_clients = (uint8_t)temp; in parse_num_clients()
/dpdk/examples/server_node_efd/server/
H A Dargs.c87 unsigned long temp; in parse_num_nodes() local
92 temp = strtoul(nodes, &end, 10); in parse_num_nodes()
93 if (end == NULL || *end != '\0' || temp == 0) in parse_num_nodes()
96 num_nodes = (uint8_t)temp; in parse_num_nodes()
/dpdk/lib/acl/
H A Dacl_run_sse.h128 xmm_t temp; in acl_match_check_x4() local
131 temp = (xmm_t)_mm_shuffle_ps((__m128)*indices1, (__m128)*indices2, in acl_match_check_x4()
134 temp = _mm_and_si128(match_mask, temp); in acl_match_check_x4()
136 while (!_mm_testz_si128(temp, temp)) { in acl_match_check_x4()
140 temp = (xmm_t)_mm_shuffle_ps((__m128)*indices1, in acl_match_check_x4()
143 temp = _mm_and_si128(match_mask, temp); in acl_match_check_x4()
H A Dacl_run_avx2.h139 ymm_t matches, temp; in acl_match_check_avx2x8() local
142 temp = _mm256_and_si256(match_mask, *tr_lo); in acl_match_check_avx2x8()
143 matches = _mm256_cmpeq_epi32(temp, match_mask); in acl_match_check_avx2x8()
150 temp = _mm256_and_si256(match_mask, *tr_lo); in acl_match_check_avx2x8()
151 matches = _mm256_cmpeq_epi32(temp, match_mask); in acl_match_check_avx2x8()
/dpdk/examples/flow_classify/
H A Dflow_classify.c411 uint32_t temp; in parse_ipv4_5tuple_rule() local
438 if (get_cb_field(&in[CB_FLD_SRC_PORT], &temp, 0, UINT16_MAX, 0)) in parse_ipv4_5tuple_rule()
440 ntuple_filter->src_port = (uint16_t)temp; in parse_ipv4_5tuple_rule()
448 ntuple_filter->src_port_mask = (uint16_t)temp; in parse_ipv4_5tuple_rule()
452 ntuple_filter->dst_port = (uint16_t)temp; in parse_ipv4_5tuple_rule()
460 ntuple_filter->dst_port_mask = (uint16_t)temp; in parse_ipv4_5tuple_rule()
462 if (get_cb_field(&in[CB_FLD_PROTO], &temp, 0, UINT8_MAX, '/')) in parse_ipv4_5tuple_rule()
464 ntuple_filter->proto = (uint8_t)temp; in parse_ipv4_5tuple_rule()
466 if (get_cb_field(&in[CB_FLD_PROTO], &temp, 0, UINT8_MAX, 0)) in parse_ipv4_5tuple_rule()
468 ntuple_filter->proto_mask = (uint8_t)temp; in parse_ipv4_5tuple_rule()
[all …]
/dpdk/buildtools/
H A Dgen-pmdinfo-cfile.py11 with tempfile.TemporaryDirectory(dir=tmp_root) as temp:
19 check=True, cwd=temp)
20 paths.append(os.path.join(temp, name))
/dpdk/drivers/mempool/dpaa2/
H A Ddpaa2_hw_mempool.c167 struct dpaa2_bp_list *prev = h_bp_list, *temp; in rte_hw_mbuf_free_pool() local
168 temp = h_bp_list->next; in rte_hw_mbuf_free_pool()
169 while (temp) { in rte_hw_mbuf_free_pool()
170 if (temp == bp) { in rte_hw_mbuf_free_pool()
171 prev->next = temp->next; in rte_hw_mbuf_free_pool()
175 prev = temp; in rte_hw_mbuf_free_pool()
176 temp = temp->next; in rte_hw_mbuf_free_pool()
/dpdk/lib/eal/common/
H A Deal_common_tailqs.c86 struct rte_tailq_elem *temp; in rte_eal_tailq_local_register() local
88 TAILQ_FOREACH(temp, &rte_tailq_elem_head, next) { in rte_eal_tailq_local_register()
89 if (!strncmp(t->name, temp->name, sizeof(temp->name))) in rte_eal_tailq_local_register()
/dpdk/drivers/net/dpaa/
H A Ddpaa_rxtx.c392 rte_pktmbuf_free_seg(temp); in dpaa_eth_sg_to_mbuf()
462 temp = (struct rte_mbuf *) in dpaa_free_mbuf()
487 rte_pktmbuf_free_seg(temp); in dpaa_free_mbuf()
800 struct rte_mbuf *temp, *mi; in dpaa_eth_mbuf_to_sg_fd() local
807 if (!temp) { in dpaa_eth_mbuf_to_sg_fd()
812 + temp->data_off)) { in dpaa_eth_mbuf_to_sg_fd()
832 temp->data_off = DEFAULT_TX_ICEOF in dpaa_eth_mbuf_to_sg_fd()
834 dcbz_64(temp->buf_addr); in dpaa_eth_mbuf_to_sg_fd()
838 sgt = temp->buf_addr + temp->data_off; in dpaa_eth_mbuf_to_sg_fd()
840 fd->addr = temp->buf_iova; in dpaa_eth_mbuf_to_sg_fd()
[all …]
/dpdk/app/test/
H A Dtest_rcu_qsbr.c307 struct rte_rcu_qsbr *temp; in test_rcu_qsbr_check_reader() local
311 temp = t[read_type]; in test_rcu_qsbr_check_reader()
318 rte_rcu_qsbr_thread_unregister(temp, in test_rcu_qsbr_check_reader()
965 struct rte_rcu_qsbr *temp; in test_rcu_qsbr_reader() local
973 temp = t[ti->ir]; in test_rcu_qsbr_reader()
980 rte_rcu_qsbr_lock(temp, lcore_id); in test_rcu_qsbr_reader()
987 rte_rcu_qsbr_unlock(temp, lcore_id); in test_rcu_qsbr_reader()
1004 struct rte_rcu_qsbr *temp; in test_rcu_qsbr_writer() local
1009 temp = t[ti->ir]; in test_rcu_qsbr_writer()
1020 token = rte_rcu_qsbr_start(temp); in test_rcu_qsbr_writer()
[all …]
H A Dtest_rcu_qsbr_perf.c285 struct rte_rcu_qsbr *temp; in test_rcu_qsbr_hash_reader() local
294 temp = t[read_type]; in test_rcu_qsbr_hash_reader()
297 rte_rcu_qsbr_thread_register(temp, thread_id); in test_rcu_qsbr_hash_reader()
302 rte_rcu_qsbr_thread_online(temp, thread_id); in test_rcu_qsbr_hash_reader()
304 rte_rcu_qsbr_lock(temp, thread_id); in test_rcu_qsbr_hash_reader()
311 rte_rcu_qsbr_unlock(temp, thread_id); in test_rcu_qsbr_hash_reader()
314 rte_rcu_qsbr_quiescent(temp, thread_id); in test_rcu_qsbr_hash_reader()
315 rte_rcu_qsbr_thread_offline(temp, thread_id); in test_rcu_qsbr_hash_reader()
323 rte_rcu_qsbr_thread_unregister(temp, thread_id); in test_rcu_qsbr_hash_reader()
/dpdk/drivers/common/sfc_efx/base/
H A Dsiena_nvram.c523 uint16_t temp[4]; variable
552 temp[0] = EFX_WORD_FIELD(verp->version_w, EFX_WORD_0);
553 temp[1] = EFX_WORD_FIELD(verp->version_x, EFX_WORD_0);
554 temp[2] = EFX_WORD_FIELD(verp->version_y, EFX_WORD_0);
555 temp[3] = EFX_WORD_FIELD(verp->version_z, EFX_WORD_0);
556 if (memcmp(version, temp, sizeof (temp)) < 0)
557 memcpy(version, temp, sizeof (temp));
/dpdk/lib/telemetry/
H A Dtelemetry.c199 char temp[buf_len]; in container_to_json() local
203 temp, buf_len) != 0) in container_to_json()
207 v->name, temp); in container_to_json()
266 char temp[buf_len]; in output_json() local
270 temp, buf_len) != 0) in output_json()
274 v->name, temp); in output_json()
308 char temp[buf_len]; in output_json() local
312 temp, buf_len) != 0) in output_json()
315 buf_len, used, temp); in output_json()
/dpdk/drivers/bus/fslmc/portal/
H A Ddpaa2_hw_dpio.c132 char *temp = NULL, *token = NULL; in dpaa2_affine_dpio_intr_to_respective_core() local
142 while (getline(&temp, &len, file) != -1) { in dpaa2_affine_dpio_intr_to_respective_core()
143 if ((strstr(temp, string)) != NULL) { in dpaa2_affine_dpio_intr_to_respective_core()
144 token = strtok(temp, ":"); in dpaa2_affine_dpio_intr_to_respective_core()
152 free(temp); in dpaa2_affine_dpio_intr_to_respective_core()
167 free(temp); in dpaa2_affine_dpio_intr_to_respective_core()
/dpdk/examples/multi_process/client_server_mp/mp_client/
H A Dclient.c71 unsigned long temp; in parse_client_num() local
76 temp = strtoul(client, &end, 10); in parse_client_num()
80 client_id = (uint8_t)temp; in parse_client_num()
/dpdk/drivers/net/dpaa2/
H A Ddpaa2_rxtx.c347 rte_mbuf_refcnt_set(temp, 1); in eth_sg_fd_to_mbuf()
350 (void **)&temp, 1, 1); in eth_sg_fd_to_mbuf()
352 rte_pktmbuf_free_seg(temp); in eth_sg_fd_to_mbuf()
419 temp = mbuf; in eth_mbuf_to_sg_fd()
420 if (rte_mbuf_refcnt_read(temp) > 1) { in eth_mbuf_to_sg_fd()
426 rte_mbuf_refcnt_update(temp, -1); in eth_mbuf_to_sg_fd()
431 (void **)&temp, 1, 0); in eth_mbuf_to_sg_fd()
436 temp = rte_pktmbuf_alloc(mp); in eth_mbuf_to_sg_fd()
437 if (temp == NULL) { in eth_mbuf_to_sg_fd()
445 (void **)&temp, 1, 0); in eth_mbuf_to_sg_fd()
[all …]
/dpdk/drivers/net/ice/
H A Dice_generic_flow.c1825 void *temp; in ice_flow_init() local
1861 void *temp; in ice_flow_uninit() local
1929 void *temp; in ice_register_parser() local
1947 node, temp) { in ice_register_parser()
1958 node, temp) { in ice_register_parser()
1985 void *temp; in ice_unregister_parser() local
1991 RTE_TAILQ_FOREACH_SAFE(p_parser, list, node, temp) { in ice_unregister_parser()
2321 void *temp; in ice_parse_engine_create() local
2354 void *temp; in ice_parse_engine_validate() local
2525 void *temp; in ice_flow_flush() local
[all …]

1234