Home
last modified time | relevance | path

Searched refs:addr (Results 1 – 25 of 442) sorted by relevance

12345678910>>...18

/net/core/
A Ddev_addr_lists_test.c71 memset(addr, 2, sizeof(addr)); in dev_addr_test_basic()
75 memset(addr, 3, sizeof(addr)); in dev_addr_test_basic()
90 memset(addr, 1, sizeof(addr)); in dev_addr_test_sync_one()
97 memset(addr, 2, sizeof(addr)); in dev_addr_test_sync_one()
121 memset(addr, i, sizeof(addr)); in dev_addr_test_add_del()
141 memset(addr, i, sizeof(addr)); in dev_addr_test_add_del()
158 memset(addr, 1, sizeof(addr)); in dev_addr_test_del_main()
186 memset(addr, i, sizeof(addr)); in dev_addr_test_add_set()
191 memset(addr, i, sizeof(addr)); in dev_addr_test_add_set()
195 memset(addr, 0, sizeof(addr)); in dev_addr_test_add_set()
[all …]
A Ddev_addr_lists.c31 diff = memcmp(new->addr, ha->addr, addr_len); in __hw_addr_insert()
63 memcpy(ha->addr, addr, addr_len); in __hw_addr_create()
88 diff = memcmp(addr, ha->addr, addr_len); in __hw_addr_add_ex()
176 int diff = memcmp(addr, ha->addr, addr_len); in __hw_addr_lookup()
342 err = sync(dev, ha->addr); in __hw_addr_sync_dev()
558 memset(addr, 0, sizeof(addr)); in dev_addr_init()
559 err = __hw_addr_add(&dev->dev_addrs, addr, sizeof(addr), in dev_addr_init()
568 dev->dev_addr = ha->addr; in dev_addr_init()
574 const void *addr, size_t len) in dev_addr_mod() argument
582 memcpy(&ha->addr[offset], addr, len); in dev_addr_mod()
[all …]
/net/sctp/
A Dbind_addr.c105 error = sctp_add_bind_addr(dest, &addr->a, sizeof(addr->a), in sctp_bind_addr_dup()
131 kfree_rcu(addr, rcu); in sctp_bind_addr_clean()
150 addr = kzalloc(sizeof(*addr), gfp); in sctp_add_bind_addr()
151 if (!addr) in sctp_add_bind_addr()
163 addr->valid = 1; in sctp_add_bind_addr()
191 addr->valid = 0; in sctp_del_bind_addr()
198 kfree_rcu(addr, rcu); in sctp_del_bind_addr()
268 union sctp_addr addr; in sctp_raw_to_bind_addrs() local
287 retval = sctp_add_bind_addr(bp, &addr, sizeof(addr), in sctp_raw_to_bind_addrs()
441 addr = addr_buf; in sctp_find_unmatch_addr()
[all …]
A Dipv6.c86 addr = kzalloc(sizeof(*addr), GFP_ATOMIC); in sctp_inet6addr_event()
87 if (addr) { in sctp_inet6addr_event()
89 addr->a.v6.sin6_addr = ifa->addr; in sctp_inet6addr_event()
91 addr->valid = 1; in sctp_inet6addr_event()
107 addr->valid = 0; in sctp_inet6addr_event()
474 addr = kzalloc(sizeof(*addr), GFP_ATOMIC); in sctp_v6_copy_addrlist()
475 if (addr) { in sctp_v6_copy_addrlist()
477 addr->a.v6.sin6_addr = ifp->addr; in sctp_v6_copy_addrlist()
591 addr->v6.sin6_addr = param->v6.addr; in sctp_v6_from_addr_param()
607 param->v6.addr = addr->v6.sin6_addr; in sctp_v6_to_addr_param()
[all …]
A Dprotocol.c88 addr = kzalloc(sizeof(*addr), GFP_ATOMIC); in sctp_v4_copy_addrlist()
89 if (addr) { in sctp_v4_copy_addrlist()
129 kfree(addr); in sctp_free_local_addr_list()
167 error = sctp_add_bind_addr(bp, &addr->a, sizeof(addr->a), in sctp_copy_local_addr_list()
239 memset(addr->v4.sin_zero, 0, sizeof(addr->v4.sin_zero)); in sctp_v4_from_sk()
264 addr->v4.sin_addr.s_addr = param->v4.addr.s_addr; in sctp_v4_from_addr_param()
265 memset(addr->v4.sin_zero, 0, sizeof(addr->v4.sin_zero)); in sctp_v4_from_addr_param()
280 param->v4.addr.s_addr = addr->v4.sin_addr.s_addr; in sctp_v4_to_addr_param()
315 memset(addr->v4.sin_zero, 0, sizeof(addr->v4.sin_zero)); in sctp_v4_inaddr_any()
617 memset(addr->v4.sin_zero, 0, sizeof(addr->v4.sin_zero)); in sctp_v4_addr_to_user()
[all …]
/net/can/j1939/
A Daddress-claim.c72 if (skcb->addr.dst_name || skcb->addr.da != J1939_NO_ADDR) { in j1939_ac_verify_outgoing()
83 u8 addr; in j1939_ac_fixup() local
97 if (ecu->addr != skcb->addr.sa) in j1939_ac_fixup()
103 addr = j1939_name_to_addr(priv, skcb->addr.src_name); in j1939_ac_fixup()
110 skcb->addr.sa = addr; in j1939_ac_fixup()
114 if (skcb->addr.dst_name) { in j1939_ac_fixup()
115 addr = j1939_name_to_addr(priv, skcb->addr.dst_name); in j1939_ac_fixup()
121 skcb->addr.da = addr; in j1939_ac_fixup()
169 if (ecu && ecu->addr == skcb->addr.sa) { in j1939_ac_process()
223 if (ecu->addr != skcb->addr.sa) in j1939_ac_process()
[all …]
A Dsocket.c229 if (jsk->addr.sa != skcb->addr.da) in j1939_sk_match_dst()
248 if (jsk->addr.da != skcb->addr.sa) in j1939_sk_match_dst()
518 jsk->addr.sa = addr->can_addr.j1939.addr; in j1939_sk_bind()
569 jsk->addr.da = addr->can_addr.j1939.addr; in j1939_sk_connect()
572 jsk->addr.pgn = addr->can_addr.j1939.pgn; in j1939_sk_connect()
592 addr->can_addr.j1939.pgn = jsk->addr.pgn; in j1939_sk_sock2sockaddr_can()
595 addr->can_addr.j1939.addr = jsk->addr.da; in j1939_sk_sock2sockaddr_can()
598 addr->can_addr.j1939.addr = jsk->addr.sa; in j1939_sk_sock2sockaddr_can()
842 sizeof(skcb->addr.da), &skcb->addr.da); in j1939_sk_recvmsg()
902 skcb->addr = jsk->addr; in j1939_sk_alloc_skb()
[all …]
/net/ceph/
A Ddecode.c11 struct ceph_entity_addr *addr) in ceph_decode_entity_addr_versioned() argument
26 ceph_decode_copy_safe(p, end, &addr->type, sizeof(addr->type), bad); in ceph_decode_entity_addr_versioned()
28 ceph_decode_copy_safe(p, end, &addr->nonce, sizeof(addr->nonce), bad); in ceph_decode_entity_addr_versioned()
34 memset(&addr->in_addr, 0, sizeof(addr->in_addr)); in ceph_decode_entity_addr_versioned()
38 addr->in_addr.ss_family = in ceph_decode_entity_addr_versioned()
63 ceph_decode_copy_safe(p, end, &addr->nonce, sizeof(addr->nonce), bad); in ceph_decode_entity_addr_legacy()
64 memset(&addr->in_addr, 0, sizeof(addr->in_addr)); in ceph_decode_entity_addr_legacy()
67 addr->in_addr.ss_family = in ceph_decode_entity_addr_legacy()
130 memcpy(addr, &tmp_addr, sizeof(*addr)); in ceph_decode_entity_addrvec()
187 ceph_encode_copy(p, &addr->type, sizeof(addr->type)); in ceph_encode_entity_addr()
[all …]
/net/dsa/
A Dtrace.h29 TP_ARGS(dp, addr, vid, db, err),
45 ether_addr_copy(__entry->addr, addr);
104 ether_addr_copy(__entry->addr, addr);
148 TP_ARGS(dp, addr, vid, db),
163 ether_addr_copy(__entry->addr, addr);
203 ether_addr_copy(__entry->addr, addr);
231 ether_addr_copy(__entry->addr, addr);
259 ether_addr_copy(__entry->addr, addr);
287 ether_addr_copy(__entry->addr, addr);
303 TP_ARGS(lag_dev, addr, vid, db),
[all …]
/net/mptcp/
A Dpm_kernel.c120 new_local->addr = entry->addr; in select_local_address()
151 new_local->addr = entry->addr; in select_signal_address()
408 locals[i].addr = entry->addr; in fill_local_addresses_vec()
550 if (mptcp_addresses_equal(&cur->addr, &entry->addr, in mptcp_pm_nl_append_new_local_addr()
551 cur->addr.port || entry->addr.port)) { in mptcp_pm_nl_append_new_local_addr()
575 entry->addr.id = cur->addr.id; in mptcp_pm_nl_append_new_local_addr()
667 mptcp_info2sockaddr(&entry->addr, &addr, entry->addr.family); in mptcp_pm_nl_create_listen_socket()
800 if (addr.addr.port && !address_use_port(&addr)) { in mptcp_pm_nl_add_addr_doit()
887 const struct mptcp_addr_info *addr = &entry->addr; in mptcp_nl_remove_subflow_and_signal_addr() local
989 if (addr.addr.id == 0) in mptcp_pm_nl_del_addr_doit()
[all …]
A Dpm_userspace.c37 if (mptcp_addresses_equal(&entry->addr, addr, false)) in mptcp_userspace_pm_lookup_addr()
58 addr_match = mptcp_addresses_equal(&e->addr, &entry->addr, true); in mptcp_userspace_pm_append_new_local_addr()
60 entry->addr.id = e->addr.id; in mptcp_userspace_pm_append_new_local_addr()
61 id_match = (e->addr.id == entry->addr.id); in mptcp_userspace_pm_append_new_local_addr()
83 ret = e->addr.id; in mptcp_userspace_pm_append_new_local_addr()
104 entry = mptcp_userspace_pm_lookup_addr(msk, &addr->addr); in mptcp_userspace_pm_delete_local_addr()
143 skc->addr.port = 0; in mptcp_userspace_pm_get_local_id()
191 struct nlattr *addr; in mptcp_pm_nl_announce_doit() local
407 local.addr = entry.addr; in mptcp_pm_nl_subflow_create_doit()
507 ipv6_addr_set_v4mapped(addr_l.addr.addr.s_addr, &addr_l.addr.addr6); in mptcp_pm_nl_subflow_destroy_doit()
[all …]
A Dpm.c17 struct mptcp_addr_info addr; member
60 addr_equals = a->addr.s_addr == b->addr.s_addr; in mptcp_addresses_equal()
87 addr->addr.s_addr = skc->skc_rcv_saddr; in mptcp_local_address()
100 addr->addr.s_addr = skc->skc_daddr; in mptcp_remote_address()
143 if (mptcp_addresses_equal(&entry->addr, addr, true)) in mptcp_lookup_anno_list_by_saddr()
255 if (!mptcp_addresses_equal(&local, addr, addr->port)) in mptcp_pm_mp_prio_send_ack()
286 if (!entry->addr.id) in mptcp_pm_add_timer()
326 if (entry && (!check_id || entry->addr.id == addr->id)) { in mptcp_pm_del_add_timer()
367 add_entry->addr = *addr; in mptcp_pm_alloc_anno_list()
615 } else if ((addr->id == 0 && !mptcp_pm_is_init_remote_addr(msk, addr)) || in mptcp_pm_add_addr_received()
[all …]
A Dpm_netlink.c63 if (addr->family != AF_INET in mptcp_pm_parse_pm_addr_attr()
65 && addr->family != AF_INET6 in mptcp_pm_parse_pm_addr_attr()
80 if (addr->family == AF_INET6) in mptcp_pm_parse_pm_addr_attr()
84 addr->addr.s_addr = nla_get_in_addr(tb[addr_addr]); in mptcp_pm_parse_pm_addr_attr()
93 struct mptcp_addr_info *addr) in mptcp_pm_parse_addr() argument
97 memset(addr, 0, sizeof(*addr)); in mptcp_pm_parse_addr()
133 struct mptcp_addr_info *addr = &entry->addr; in mptcp_nl_fill_addr() local
152 if (addr->family == AF_INET && in mptcp_nl_fill_addr()
154 addr->addr.s_addr)) in mptcp_nl_fill_addr()
179 struct mptcp_pm_addr_entry addr; in mptcp_pm_nl_get_addr_doit() local
[all …]
/net/vmw_vsock/
A Dvsock_addr.c16 memset(addr, 0, sizeof(*addr)); in vsock_addr_init()
17 addr->svm_family = AF_VSOCK; in vsock_addr_init()
18 addr->svm_cid = cid; in vsock_addr_init()
19 addr->svm_port = port; in vsock_addr_init()
27 if (!addr) in vsock_addr_validate()
30 if (addr->svm_family != AF_VSOCK) in vsock_addr_validate()
33 if (addr->svm_flags & ~svm_valid_flags) in vsock_addr_validate()
42 return addr->svm_port != VMADDR_PORT_ANY; in vsock_addr_bound()
55 return addr->svm_cid == other->svm_cid && in vsock_addr_equals_addr()
56 addr->svm_port == other->svm_port; in vsock_addr_equals_addr()
[all …]
/net/netlabel/
A Dnetlabel_addrlist.c46 struct netlbl_af4list *netlbl_af4list_search(__be32 addr, in netlbl_af4list_search() argument
52 if (iter->valid && (addr & iter->mask) == iter->addr) in netlbl_af4list_search()
77 if (iter->valid && iter->addr == addr && iter->mask == mask) in netlbl_af4list_search_exact()
103 ipv6_masked_addr_cmp(&iter->addr, &iter->mask, addr) == 0) in netlbl_af6list_search()
129 ipv6_addr_equal(&iter->addr, addr) && in netlbl_af6list_search_exact()
152 iter = netlbl_af4list_search(entry->addr, head); in netlbl_af4list_add()
154 iter->addr == entry->addr && iter->mask == entry->mask) in netlbl_af4list_add()
189 iter = netlbl_af6list_search(&entry->addr, head); in netlbl_af6list_add()
191 ipv6_addr_equal(&iter->addr, &entry->addr) && in netlbl_af6list_add()
312 __be32 addr, __be32 mask) in netlbl_af4list_audit_addr() argument
[all …]
/net/llc/
A Daf_llc.c85 return !memcmp(addr, &llc_ui_addrnull, sizeof(*addr)); in llc_ui_addr_null()
101 if (addr->sllc_test) in llc_ui_header_len()
103 else if (addr->sllc_xid) in llc_ui_header_len()
316 memcpy(&llc->addr, addr, sizeof(llc->addr)); in llc_ui_autobind()
382 if (!addr->sllc_sap) { in llc_ui_bind()
385 if (!addr->sllc_sap) in llc_ui_bind()
421 memcpy(&llc->addr, addr, sizeof(llc->addr)); in llc_ui_bind()
512 addr->sllc_mac, addr->sllc_sap); in llc_ui_connect()
734 memcpy(&newllc->addr, &llc->addr, sizeof(newllc->addr)); in llc_ui_accept()
945 if (addr) { in llc_ui_sendmsg()
[all …]
/net/bridge/
A Dbr_fdb.c214 memcpy(key.addr.addr, addr, sizeof(key.addr.addr)); in fdb_find_rcu()
290 dev_uc_del(p->dev, addr); in fdb_add_hw_addr()
307 dev_uc_del(p->dev, addr); in fdb_del_hw_addr()
317 fdb_del_hw_addr(br, f->key.addr.addr); in fdb_delete()
338 const unsigned char *addr = f->key.addr.addr; in fdb_delete_local() local
406 memcpy(fdb->key.addr.addr, addr, ETH_ALEN); in fdb_create()
451 fdb_add_hw_addr(br, addr); in fdb_add_local()
847 memcpy(fe->mac_addr, f->key.addr.addr, ETH_ALEN); in br_fdb_fillbuf()
1376 err = dev_uc_add(p->dev, f->key.addr.addr); in br_fdb_sync_static()
1392 dev_uc_del(p->dev, tmp->key.addr.addr); in br_fdb_sync_static()
[all …]
A Dbr_stp_bpdu.c94 buf[7] = bpdu->root.addr[0]; in br_send_config_bpdu()
95 buf[8] = bpdu->root.addr[1]; in br_send_config_bpdu()
96 buf[9] = bpdu->root.addr[2]; in br_send_config_bpdu()
97 buf[10] = bpdu->root.addr[3]; in br_send_config_bpdu()
98 buf[11] = bpdu->root.addr[4]; in br_send_config_bpdu()
99 buf[12] = bpdu->root.addr[5]; in br_send_config_bpdu()
202 bpdu.root.addr[0] = buf[4]; in br_stp_rcv()
203 bpdu.root.addr[1] = buf[5]; in br_stp_rcv()
204 bpdu.root.addr[2] = buf[6]; in br_stp_rcv()
205 bpdu.root.addr[3] = buf[7]; in br_stp_rcv()
[all …]
A Dbr_stp_if.c232 br_fdb_change_mac_address(br, addr); in br_stp_change_bridge_id()
235 memcpy(br->bridge_id.addr, addr, ETH_ALEN); in br_stp_change_bridge_id()
236 eth_hw_addr_set(br->dev, addr); in br_stp_change_bridge_id()
240 memcpy(p->designated_bridge.addr, addr, ETH_ALEN); in br_stp_change_bridge_id()
243 memcpy(p->designated_root.addr, addr, ETH_ALEN); in br_stp_change_bridge_id()
268 if (addr == br_mac_zero || in br_stp_recalculate_bridge_id()
270 addr = p->dev->dev_addr; in br_stp_recalculate_bridge_id()
274 if (ether_addr_equal(br->bridge_id.addr, addr)) in br_stp_recalculate_bridge_id()
277 br_stp_change_bridge_id(br, addr); in br_stp_recalculate_bridge_id()
349 id->addr[0], id->addr[1], id->addr[2], in br_show_bridge_id()
[all …]
/net/tipc/
A Deth_media.c41 static int tipc_eth_addr2str(struct tipc_media_addr *addr, in tipc_eth_addr2str() argument
47 sprintf(strbuf, "%pM", addr->value); in tipc_eth_addr2str()
52 static int tipc_eth_addr2msg(char *msg, struct tipc_media_addr *addr) in tipc_eth_addr2msg() argument
56 memcpy(msg + TIPC_MEDIA_ADDR_OFFSET, addr->value, ETH_ALEN); in tipc_eth_addr2msg()
62 struct tipc_media_addr *addr, in tipc_eth_raw2addr() argument
65 memset(addr, 0, sizeof(*addr)); in tipc_eth_raw2addr()
66 ether_addr_copy(addr->value, msg); in tipc_eth_raw2addr()
67 addr->media_id = TIPC_MEDIA_TYPE_ETH; in tipc_eth_raw2addr()
68 addr->broadcast = is_broadcast_ether_addr(addr->value); in tipc_eth_raw2addr()
74 struct tipc_media_addr *addr, in tipc_eth_msg2addr() argument
[all …]
A Dudp_media.c84 struct udp_media_addr addr; member
108 if (ntohs(addr->proto) == ETH_P_IP) in tipc_udp_is_mcast_addr()
283 struct udp_media_addr *addr) in tipc_udp_is_known_peer() argument
295 if (!memcmp(&rcast->addr, addr, sizeof(struct udp_media_addr))) in tipc_udp_is_known_peer()
321 memcpy(&rcast->addr, addr, sizeof(struct udp_media_addr)); in tipc_udp_rcast_add()
437 ip4.sin_port = addr->port; in __tipc_nl_add_udp_addr()
448 ip6.sin6_port = addr->port; in __tipc_nl_add_udp_addr()
594 addr->proto = htons(ETH_P_IP); in tipc_parse_udp_addr()
595 addr->port = ip4->sin_port; in tipc_parse_udp_addr()
603 addr->proto = htons(ETH_P_IPV6); in tipc_parse_udp_addr()
[all …]
/net/mac80211/
A Dfils_aead.c56 crypto_xor(d, addr[i], len[i]); in aes_s2v()
81 addr[num_elem] = plain; in aes_siv_encrypt()
160 addr[num_elem] = out; in aes_siv_decrypt()
222 const u8 *addr[5 + 1]; in fils_encrypt_assoc_req() local
245 addr[0] = mgmt->sa; in fils_encrypt_assoc_req()
248 addr[1] = mgmt->da; in fils_encrypt_assoc_req()
259 addr[4] = capab; in fils_encrypt_assoc_req()
274 const u8 *addr[5 + 1]; in fils_decrypt_assoc_resp() local
299 addr[0] = mgmt->sa; in fils_decrypt_assoc_resp()
302 addr[1] = mgmt->da; in fils_decrypt_assoc_resp()
[all …]
/net/atm/
A Dpvc.c31 struct sockaddr_atmpvc *addr; in pvc_bind() local
38 if (addr->sap_family != AF_ATMPVC) in pvc_bind()
48 addr->sap_addr.vpi = vcc->vpi; in pvc_bind()
50 addr->sap_addr.vci = vcc->vci; in pvc_bind()
52 error = vcc_connect(sock, addr->sap_addr.itf, addr->sap_addr.vpi, in pvc_bind()
53 addr->sap_addr.vci); in pvc_bind()
92 struct sockaddr_atmpvc *addr; in pvc_getname() local
98 memset(addr, 0, sizeof(*addr)); in pvc_getname()
99 addr->sap_family = AF_ATMPVC; in pvc_getname()
101 addr->sap_addr.vpi = vcc->vpi; in pvc_getname()
[all …]
/net/ethernet/
A Deth.c277 struct sockaddr *addr = p; in eth_prepare_mac_addr_change() local
294 struct sockaddr *addr = p; in eth_commit_mac_addr_change() local
296 eth_hw_addr_set(dev, addr->sa_data); in eth_commit_mac_addr_change()
489 unsigned char *addr; in eth_platform_get_mac_address() local
497 if (!addr) in eth_platform_get_mac_address()
500 ether_addr_copy(mac_addr, addr); in eth_platform_get_mac_address()
516 u8 addr[ETH_ALEN] __aligned(2); in platform_get_ethdev_address() local
521 eth_hw_addr_set(netdev, addr); in platform_get_ethdev_address()
571 if (!is_valid_ether_addr(addr)) in fwnode_get_mac_addr()
630 u8 addr[ETH_ALEN]; in device_get_ethdev_address() local
[all …]
/net/xdp/
A Dxsk_buff_pool.c492 u64 addr) in xp_addr_crosses_non_contig_pg() argument
499 *addr = xp_unaligned_extract_addr(*addr); in xp_check_unaligned()
500 if (*addr >= pool->addrs_cnt || in xp_check_unaligned()
509 *addr = xp_aligned_extract_addr(pool, *addr); in xp_check_aligned()
510 return *addr < pool->addrs_cnt; in xp_check_aligned()
532 u64 addr; in __xp_alloc() local
599 u64 addr; in xp_alloc_new_from_fq() local
712 return pool->unaligned ? xp_unaligned_add_offset_to_addr(addr) : addr; in __xp_raw_get_addr()
717 return pool->addrs + addr; in __xp_raw_get_data()
730 (addr & ~PAGE_MASK); in __xp_raw_get_dma()
[all …]

Completed in 49 milliseconds

12345678910>>...18