/linux-6.6.21/tools/testing/selftests/bpf/progs/ |
D | sock_destroy_prog.c | 11 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()
|
D | sock_destroy_prog_fail.c | 11 int bpf_sock_destroy(struct sock_common *sk) __ksym; 18 bpf_sock_destroy((struct sock_common *)sk); in BPF_PROG()
|
D | test_tcp_estats.c | 54 struct sock_common { struct 75 struct sock_common __sk_common; argument
|
D | bpf_iter_bpf_sk_storage_helpers.c | 52 struct sock_common *sk_common = ctx->sk_common; in negate_socket_local_storage()
|
D | bpf_iter_setsockopt.c | 9 struct sock_common *_skc = skc; \
|
D | bpf_iter.h | 93 struct sock_common *sk_common;
|
D | bpf_iter_tcp4.c | 198 struct sock_common *sk_common = ctx->sk_common; in dump_tcp4()
|
D | bpf_iter_tcp6.c | 214 struct sock_common *sk_common = ctx->sk_common; in dump_tcp6()
|
/linux-6.6.21/tools/testing/selftests/bpf/ |
D | bpf_tcp_helpers.h | 25 struct sock_common { struct 37 struct sock_common __sk_common; argument 59 struct sock_common __req_common;
|
/linux-6.6.21/net/core/ |
D | filter.c | 9643 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 …]
|
/linux-6.6.21/net/mptcp/ |
D | pm_netlink.c | 90 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 *)msk->first, &mpc_addr); in mptcp_pm_create_subflow_or_signal_addr() [all …]
|
D | pm.c | 409 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()
|
D | protocol.h | 650 void mptcp_local_address(const struct sock_common *skc, struct mptcp_addr_info *addr); 1008 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
|
D | subflow.c | 97 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req); in subflow_token_join_request() 593 err = mptcp_pm_get_local_id(msk, (struct sock_common *)sk); in subflow_chk_local_id()
|
/linux-6.6.21/include/net/ |
D | inet_timewait_sock.h | 38 struct sock_common __tw_common;
|
D | request_sock.h | 54 struct sock_common __req_common;
|
D | sock.h | 163 struct sock_common { struct 362 struct sock_common __sk_common;
|
/linux-6.6.21/tools/include/linux/ |
D | btf_ids.h | 173 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
|
/linux-6.6.21/include/linux/ |
D | btf_ids.h | 234 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
|
/linux-6.6.21/net/ipv4/ |
D | tcp_ipv4.c | 2774 __bpf_md_ptr(struct sock_common *, sk_common); 2779 struct sock_common *sk_common, uid_t uid) in tcp_prog_seq_show() 3314 struct sock_common *sk_common, uid_t uid) in DEFINE_BPF_ITER_FUNC()
|