Home
last modified time | relevance | path

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

/openbmc/linux/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 Dtest_tcp_estats.c54 struct sock_common { struct
75 struct sock_common __sk_common; argument
H A Dbpf_iter_bpf_sk_storage_helpers.c52 struct sock_common *sk_common = ctx->sk_common; in negate_socket_local_storage()
H A Dbpf_iter_setsockopt.c9 struct sock_common *_skc = skc; \
H A Dbpf_iter.h93 struct sock_common *sk_common;
H A Dbpf_iter_tcp4.c198 struct sock_common *sk_common = ctx->sk_common; in dump_tcp4()
H A Dbpf_iter_tcp6.c214 struct sock_common *sk_common = ctx->sk_common; in dump_tcp6()
/openbmc/linux/tools/testing/selftests/bpf/
H A Dbpf_tcp_helpers.h25 struct sock_common { struct
37 struct sock_common __sk_common; argument
59 struct sock_common __req_common;
/openbmc/linux/net/mptcp/
H A Dpm.c401 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc) in mptcp_pm_get_local_id()
412 mptcp_local_address((struct sock_common *)msk, &msk_local); in mptcp_pm_get_local_id()
413 mptcp_local_address((struct sock_common *)skc, &skc_local); in mptcp_pm_get_local_id()
422 bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc) in mptcp_pm_is_backup()
426 mptcp_local_address((struct sock_common *)skc, &skc_local); in mptcp_pm_is_backup()
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()
146 remote_address((struct sock_common *)ssk, &cur); in lookup_subflow_by_daddr()
277 mptcp_local_address((struct sock_common *)sk, &saddr); in mptcp_pm_sport_in_anno_list()
432 remote_address((struct sock_common *)sk, &remote); in fill_remote_addresses_vec()
459 remote_address((struct sock_common *)ssk, &addrs[i]); in fill_remote_addresses_vec()
559 mptcp_local_address((struct sock_common *)msk->first, &mpc_addr); in mptcp_pm_create_subflow_or_signal_addr()
677 mptcp_local_address((struct sock_common *)msk, &mpc_addr); in fill_local_addresses_vec()
[all …]
H A Dprotocol.h657 void mptcp_local_address(const struct sock_common *skc, struct mptcp_addr_info *addr);
1033 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
1036 bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc);
H A Dsubflow.c97 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req); in subflow_token_join_request()
103 subflow_req->request_bkup = mptcp_pm_is_backup(msk, (struct sock_common *)req); in subflow_token_join_request()
611 err = mptcp_pm_get_local_id(msk, (struct sock_common *)sk); in subflow_chk_local_id()
616 subflow->request_bkup = mptcp_pm_is_backup(msk, (struct sock_common *)sk); in subflow_chk_local_id()
/openbmc/linux/net/core/
H A Dfilter.c9694 BUILD_BUG_ON(sizeof_field(struct sock_common, skc_family) != 2); in bpf_convert_ctx_access()
9700 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
9705 BUILD_BUG_ON(sizeof_field(struct sock_common, skc_daddr) != 4); in bpf_convert_ctx_access()
9711 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
9716 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
9723 bpf_target_off(struct sock_common, in bpf_convert_ctx_access()
9730 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
9740 offsetof(struct sock_common, in bpf_convert_ctx_access()
9750 BUILD_BUG_ON(sizeof_field(struct sock_common, in bpf_convert_ctx_access()
9760 offsetof(struct sock_common, in bpf_convert_ctx_access()
[all...]
/openbmc/linux/include/net/
H A Dinet_timewait_sock.h38 struct sock_common __tw_common;
H A Drequest_sock.h54 struct sock_common __req_common;
H A Dsock.h119 * struct sock_common - minimal network layer representation of sockets
163 struct sock_common { struct
359 * Now struct inet_timewait_sock also uses sock_common, so please just
362 struct sock_common __sk_common;
164 __anon3ba2e460020asock_common global() argument
171 __anon3ba2e460040asock_common global() argument
176 __anon3ba2e460050asock_common global() argument
184 skc_familysock_common global() argument
185 skc_statesock_common global() argument
186 skc_reusesock_common global() argument
187 skc_reuseportsock_common global() argument
188 skc_ipv6onlysock_common global() argument
189 skc_net_refcntsock_common global() argument
190 skc_bound_dev_ifsock_common global() argument
191 __anon3ba2e460070asock_common global() argument
195 skc_protsock_common global() argument
196 skc_netsock_common global() argument
199 skc_v6_daddrsock_common global() argument
200 skc_v6_rcv_saddrsock_common global() argument
203 skc_cookiesock_common global() argument
210 __anon3ba2e460080asock_common global() argument
220 skc_dontcopy_beginsock_common global() argument
222 __anon3ba2e460090asock_common global() argument
226 skc_tx_queue_mappingsock_common global() argument
228 skc_rx_queue_mappingsock_common global() argument
230 __anon3ba2e4600a0asock_common global() argument
236 skc_refcntsock_common global() argument
238 skc_dontcopy_endsock_common global() argument
239 __anon3ba2e4600b0asock_common global() argument
/openbmc/linux/tools/include/linux/
H A Dbtf_ids.h184 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/openbmc/linux/include/linux/
H A Dbtf_ids.h234 BTF_SOCK_TYPE(BTF_SOCK_TYPE_SOCK_COMMON, sock_common) \
/openbmc/linux/net/ipv4/
H A Dtcp_ipv4.c2789 __bpf_md_ptr(struct sock_common *, sk_common);
2794 struct sock_common *sk_common, uid_t uid) in tcp_prog_seq_show()
3341 struct sock_common *sk_common, uid_t uid) in DEFINE_BPF_ITER_FUNC()