Home
last modified time | relevance | path

Searched refs:skc (Results 1 – 5 of 5) sorted by relevance

/linux/net/mptcp/
H A Dpm.c83 void mptcp_local_address(const struct sock_common *skc, in mptcp_local_address() argument
86 addr->family = skc->skc_family; in mptcp_local_address()
87 addr->port = htons(skc->skc_num); in mptcp_local_address()
89 addr->addr.s_addr = skc->skc_rcv_saddr; in mptcp_local_address()
92 addr->addr6 = skc->skc_v6_rcv_saddr; in mptcp_local_address()
96 void mptcp_remote_address(const struct sock_common *skc, in mptcp_remote_address() argument
99 addr->family = skc->skc_family; in mptcp_remote_address()
100 addr->port = skc->skc_dport; in mptcp_remote_address()
102 addr->addr.s_addr = skc->skc_daddr; in mptcp_remote_address()
105 addr->addr6 = skc->skc_v6_daddr; in mptcp_remote_address()
[all …]
H A Dpm_userspace.c144 struct mptcp_pm_addr_entry *skc) in mptcp_userspace_pm_get_local_id() argument
152 entry = mptcp_userspace_pm_lookup_addr(msk, &skc->addr); in mptcp_userspace_pm_get_local_id()
159 if (skc->addr.port == msk_sport) in mptcp_userspace_pm_get_local_id()
160 skc->addr.port = 0; in mptcp_userspace_pm_get_local_id()
162 return mptcp_userspace_pm_append_new_local_addr(msk, skc, true); in mptcp_userspace_pm_get_local_id()
166 struct mptcp_addr_info *skc) in mptcp_userspace_pm_is_backup() argument
172 entry = mptcp_userspace_pm_lookup_addr(msk, skc); in mptcp_userspace_pm_is_backup()
H A Dprotocol.h838 void mptcp_local_address(const struct sock_common *skc,
840 void mptcp_remote_address(const struct sock_common *skc,
1216 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
1218 struct mptcp_pm_addr_entry *skc);
1220 struct mptcp_pm_addr_entry *skc);
1221 bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc);
1222 bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
1223 bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
H A Dpm_kernel.c919 struct mptcp_pm_addr_entry *skc) in mptcp_pm_nl_get_local_id() argument
928 entry = __lookup_addr(pernet, &skc->addr); in mptcp_pm_nl_get_local_id()
935 entry = kmemdup(skc, sizeof(*skc), GFP_ATOMIC); in mptcp_pm_nl_get_local_id()
947 bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc) in mptcp_pm_nl_is_backup() argument
954 entry = __lookup_addr(pernet, skc); in mptcp_pm_nl_is_backup()
/linux/tools/testing/selftests/bpf/progs/
H A Dtest_tcp_custom_syncookie.c510 struct bpf_sock *skc; in tcp_handle_ack()
531 skc = bpf_skc_lookup_tcp(ctx->skb, &tuple, tuple_size, -1, 0); in tcp_handle_ack()
532 if (!skc) in tcp_handle_ack()
535 if (skc->state != TCP_LISTEN) in tcp_handle_ack()
538 sk = (struct sock *)bpf_skc_to_tcp_sock(skc); in tcp_handle_ack()
555 bpf_sk_release(skc); in tcp_handle_ack()
508 struct bpf_sock *skc; tcp_handle_ack() local