Home
last modified time | relevance | path

Searched refs:sock_common (Results 1 – 18 of 18) sorted by relevance

/linux-6.1.9/tools/testing/selftests/bpf/
Dbpf_tcp_helpers.h25 struct sock_common { struct
37 struct sock_common __sk_common; argument
59 struct sock_common __req_common;
/linux-6.1.9/net/mptcp/
Dpm_netlink.c89 static void local_address(const struct sock_common *skc, in local_address()
102 static void remote_address(const struct sock_common *skc, in remote_address()
120 struct sock_common *skc; in lookup_subflow_by_saddr()
123 skc = (struct sock_common *)mptcp_subflow_tcp_sock(subflow); in lookup_subflow_by_saddr()
138 struct sock_common *skc; in lookup_subflow_by_daddr()
141 skc = (struct sock_common *)mptcp_subflow_tcp_sock(subflow); in lookup_subflow_by_daddr()
277 local_address((struct sock_common *)sk, &saddr); in mptcp_pm_sport_in_anno_list()
437 remote_address((struct sock_common *)sk, &remote); in fill_remote_addresses_vec()
451 remote_address((struct sock_common *)ssk, &addrs[i]); in fill_remote_addresses_vec()
547 local_address((struct sock_common *)msk->first, &mpc_addr); in mptcp_pm_create_subflow_or_signal_addr()
[all …]
Dprotocol.h893 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
900 int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
Dpm.c399 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc) in mptcp_pm_get_local_id()
Dsubflow.c96 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req); in subflow_token_join_request()
501 err = mptcp_pm_get_local_id(msk, (struct sock_common *)sk); in subflow_chk_local_id()
/linux-6.1.9/tools/testing/selftests/bpf/progs/
Dtest_tcp_estats.c54 struct sock_common { struct
75 struct sock_common __sk_common; argument
Dbpf_iter_bpf_sk_storage_helpers.c52 struct sock_common *sk_common = ctx->sk_common; in negate_socket_local_storage()
Dbpf_iter_setsockopt.c9 struct sock_common *_skc = skc; \
Dbpf_iter.h93 struct sock_common *sk_common;
Dbpf_iter_tcp4.c198 struct sock_common *sk_common = ctx->sk_common; in dump_tcp4()
Dbpf_iter_tcp6.c214 struct sock_common *sk_common = ctx->sk_common; in dump_tcp6()
/linux-6.1.9/net/core/
Dfilter.c9426 BUILD_BUG_ON(sizeof_field(struct sock_common, skc_family) != 2); in bpf_convert_ctx_access()
9432 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
9437 BUILD_BUG_ON(sizeof_field(struct sock_common, skc_daddr) != 4); in bpf_convert_ctx_access()
9443 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
9448 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
9455 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
9462 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
9472 offsetof(struct sock_common, in bpf_convert_ctx_access()
9482 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
9492 offsetof(struct sock_common, in bpf_convert_ctx_access()
[all …]
/linux-6.1.9/include/net/
Dinet_timewait_sock.h38 struct sock_common __tw_common;
Drequest_sock.h54 struct sock_common __req_common;
Dsock.h163 struct sock_common { struct
358 struct sock_common __sk_common;
/linux-6.1.9/tools/include/linux/
Dbtf_ids.h173 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/linux-6.1.9/include/linux/
Dbtf_ids.h234 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/linux-6.1.9/net/ipv4/
Dtcp_ipv4.c2712 __bpf_md_ptr(struct sock_common *, sk_common);
2717 struct sock_common *sk_common, uid_t uid) in tcp_prog_seq_show()
3242 struct sock_common *sk_common, uid_t uid) in DEFINE_BPF_ITER_FUNC()