Home
last modified time | relevance | path

Searched refs:sock_common (Results 1 - 25 of 36) sorted by relevance

12

/kernel/linux/linux-6.6/tools/testing/selftests/bpf/progs/
H A Dsock_destroy_prog.c11 int bpf_sock_destroy(struct sock_common *sk) __ksym;
51 struct sock_common *sk_common = ctx->sk_common; in iter_tcp6_client()
76 struct sock_common *sk_common = ctx->sk_common; in iter_tcp6_server()
121 bpf_sock_destroy((struct sock_common *)sk); in iter_udp6_client()
140 bpf_sock_destroy((struct sock_common *)sk); in iter_udp6_server()
H A Dsock_destroy_prog_fail.c11 int bpf_sock_destroy(struct sock_common *sk) __ksym;
18 bpf_sock_destroy((struct sock_common *)sk); in BPF_PROG()
H A Dbpf_iter_bpf_sk_storage_helpers.c52 struct sock_common *sk_common = ctx->sk_common; in negate_socket_local_storage()
H A Dtest_tcp_estats.c45 * Recursively, "sock" needs "sock_common" and "inet_sock".
54 struct sock_common { struct
75 struct sock_common __sk_common;
H A Dbpf_iter_setsockopt.c9 struct sock_common *_skc = skc; \
H A Dbpf_iter.h93 struct sock_common *sk_common;
/kernel/linux/linux-5.10/tools/testing/selftests/bpf/
H A Dbpf_tcp_helpers.h17 struct sock_common { struct
29 struct sock_common __sk_common;
50 struct sock_common __req_common;
/kernel/linux/linux-6.6/tools/testing/selftests/bpf/
H A Dbpf_tcp_helpers.h25 struct sock_common { struct
37 struct sock_common __sk_common;
59 struct sock_common __req_common;
/kernel/linux/linux-6.6/net/core/
H A Dfilter.c9643 BUILD_BUG_ON(sizeof_field(struct sock_common, skc_family) != 2); in bpf_convert_ctx_access()
9649 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
9654 BUILD_BUG_ON(sizeof_field(struct sock_common, skc_daddr) != 4); in bpf_convert_ctx_access()
9660 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
9665 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
9672 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
9679 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
9689 offsetof(struct sock_common, in bpf_convert_ctx_access()
9699 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
9709 offsetof(struct sock_common, in bpf_convert_ctx_access()
[all...]
/kernel/linux/linux-5.10/net/core/
H A Dfilter.c8628 BUILD_BUG_ON(sizeof_field(struct sock_common, skc_family) != 2); in bpf_convert_ctx_access()
8634 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
8639 BUILD_BUG_ON(sizeof_field(struct sock_common, skc_daddr) != 4); in bpf_convert_ctx_access()
8645 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
8650 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
8657 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
8664 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
8674 offsetof(struct sock_common, in bpf_convert_ctx_access()
8684 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
8694 offsetof(struct sock_common, in bpf_convert_ctx_access()
[all...]
/kernel/linux/linux-5.10/tools/testing/selftests/bpf/progs/
H A Dtest_tcp_estats.c45 * Recursively, "sock" needs "sock_common" and "inet_sock".
54 struct sock_common { struct
75 struct sock_common __sk_common;
H A Dbpf_iter.h77 struct sock_common *sk_common;
H A Dbpf_iter_tcp4.c199 struct sock_common *sk_common = ctx->sk_common; in dump_tcp4()
/kernel/linux/linux-5.10/net/mptcp/
H A Dpm_netlink.c87 static void local_address(const struct sock_common *skc, in local_address()
100 static void remote_address(const struct sock_common *skc, in remote_address()
118 struct sock_common *skc; in lookup_subflow_by_saddr()
121 skc = (struct sock_common *)mptcp_subflow_tcp_sock(subflow); in lookup_subflow_by_saddr()
340 remote_address((struct sock_common *)sk, &remote); in mptcp_pm_create_subflow_or_signal_addr()
518 int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk, struct sock_common *skc) in mptcp_pm_nl_get_local_id()
532 local_address((struct sock_common *)msk, &msk_local); in mptcp_pm_nl_get_local_id()
533 local_address((struct sock_common *)skc, &skc_local); in mptcp_pm_nl_get_local_id()
H A Dprotocol.h481 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
490 int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
H A Dpm.c223 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc) in mptcp_pm_get_local_id()
/kernel/linux/linux-6.6/net/mptcp/
H A Dpm.c409 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc) in mptcp_pm_get_local_id()
420 mptcp_local_address((struct sock_common *)msk, &msk_local); in mptcp_pm_get_local_id()
421 mptcp_local_address((struct sock_common *)skc, &skc_local); in mptcp_pm_get_local_id()
H A Dpm_netlink.c90 void mptcp_local_address(const struct sock_common *skc, struct mptcp_addr_info *addr) in mptcp_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()
266 mptcp_local_address((struct sock_common *)sk, &saddr); in mptcp_pm_sport_in_anno_list()
415 remote_address((struct sock_common *)sk, &remote); in fill_remote_addresses_vec()
442 remote_address((struct sock_common *)ssk, &addrs[i]); in fill_remote_addresses_vec()
544 mptcp_local_address((struct sock_common *)ms in mptcp_pm_create_subflow_or_signal_addr()
[all...]
/kernel/linux/linux-5.10/include/net/
H A Dinet_timewait_sock.h35 * Now struct sock also uses sock_common, so please just
38 struct sock_common __tw_common;
H A Drequest_sock.h54 struct sock_common __req_common;
/kernel/linux/linux-5.10/tools/include/linux/
H A Dbtf_ids.h160 * sock_common as the first argument in its memory layout.
169 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/kernel/linux/linux-5.10/include/linux/
H A Dbtf_ids.h160 * sock_common as the first argument in its memory layout.
169 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/kernel/linux/linux-6.6/include/net/
H A Dinet_timewait_sock.h35 * Now struct sock also uses sock_common, so please just
38 struct sock_common __tw_common;
/kernel/linux/linux-6.6/tools/include/linux/
H A Dbtf_ids.h173 * sock_common as the first argument in its memory layout.
182 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/kernel/linux/linux-6.6/include/linux/
H A Dbtf_ids.h225 * sock_common as the first argument in its memory layout.
234 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \

Completed in 39 milliseconds

12