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

/linux-master/tools/testing/selftests/bpf/progs/
H A Dsock_destroy_prog_fail.c11 int bpf_sock_destroy(struct sock_common *sk) __ksym;
18 bpf_sock_destroy((struct sock_common *)sk);
H A Dsock_destroy_prog.c11 int bpf_sock_destroy(struct sock_common *sk) __ksym;
51 struct sock_common *sk_common = ctx->sk_common;
76 struct sock_common *sk_common = ctx->sk_common;
121 bpf_sock_destroy((struct sock_common *)sk);
140 bpf_sock_destroy((struct sock_common *)sk);
H A Dbpf_iter_bpf_sk_storage_helpers.c52 struct sock_common *sk_common = ctx->sk_common;
H A Dbpf_iter_setsockopt.c9 struct sock_common *_skc = skc; \
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.h93 struct sock_common *sk_common;
H A Dbpf_iter_tcp6.c214 struct sock_common *sk_common = ctx->sk_common;
H A Dbpf_iter_tcp4.c198 struct sock_common *sk_common = ctx->sk_common;
/linux-master/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;
/linux-master/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;
H A Dsock.h106 * struct sock_common - minimal network layer representation of sockets
150 struct sock_common { struct
343 * Now struct inet_timewait_sock also uses sock_common, so please just
346 struct sock_common __sk_common;
/linux-master/net/core/
H A Dfilter.c9694 BUILD_BUG_ON(sizeof_field(struct sock_common, skc_family) != 2);
9700 bpf_target_off(struct sock_common,
9705 BUILD_BUG_ON(sizeof_field(struct sock_common, skc_daddr) != 4);
9711 bpf_target_off(struct sock_common,
9716 BUILD_BUG_ON(sizeof_field(struct sock_common,
9723 bpf_target_off(struct sock_common,
9730 BUILD_BUG_ON(sizeof_field(struct sock_common,
9740 offsetof(struct sock_common,
9750 BUILD_BUG_ON(sizeof_field(struct sock_common,
9760 offsetof(struct sock_common,
[all...]
/linux-master/tools/include/linux/
H A Dbtf_ids.h175 * sock_common as the first argument in its memory layout.
184 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/linux-master/net/mptcp/
H A Dpm_netlink.c84 void mptcp_local_address(const struct sock_common *skc, struct mptcp_addr_info *addr)
96 static void remote_address(const struct sock_common *skc,
114 struct sock_common *skc;
117 skc = (struct sock_common *)mptcp_subflow_tcp_sock(subflow);
132 struct sock_common *skc;
135 skc = (struct sock_common *)mptcp_subflow_tcp_sock(subflow);
260 mptcp_local_address((struct sock_common *)sk, &saddr);
409 remote_address((struct sock_common *)sk, &remote);
436 remote_address((struct sock_common *)ssk, &addrs[i]);
535 mptcp_local_address((struct sock_common *)ms
[all...]
H A Dpm.c408 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc)
419 mptcp_local_address((struct sock_common *)msk, &msk_local);
420 mptcp_local_address((struct sock_common *)skc, &skc_local);
H A Dprotocol.h669 void mptcp_local_address(const struct sock_common *skc, struct mptcp_addr_info *addr);
1060 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
H A Dsubflow.c96 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req);
592 err = mptcp_pm_get_local_id(msk, (struct sock_common *)sk);
/linux-master/include/linux/
H A Dbtf_ids.h238 * sock_common as the first argument in its memory layout.
247 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/linux-master/net/ipv4/
H A Dtcp_ipv4.c2978 __bpf_md_ptr(struct sock_common *, sk_common);
2983 struct sock_common *sk_common, uid_t uid)
3521 struct sock_common *sk_common, uid_t uid)

Completed in 205 milliseconds