Home
last modified time | relevance | path

Searched refs:inet_sk (Results 26 – 50 of 101) sorted by relevance

12345

/openbmc/linux/net/ipv4/
H A Dinet_timewait_sock.c117 const struct inet_sock *inet = inet_sk(sk); in inet_twsk_hashdance()
188 const struct inet_sock *inet = inet_sk(sk); in inet_twsk_alloc()
H A Daf_inet.c135 struct inet_sock *inet = inet_sk(sk); in inet_sock_destruct()
178 inet = inet_sk(sk); in inet_autobind()
336 inet = inet_sk(sk); in inet_create()
476 struct inet_sock *inet = inet_sk(sk); in __inet_bind()
591 if (data_race(!inet_sk(sk)->inet_num) && inet_autobind(sk)) in inet_dgram_connect()
800 struct inet_sock *inet = inet_sk(sk); in inet_getname()
837 if (data_race(!inet_sk(sk)->inet_num) && !sk->sk_prot->no_autobind && in inet_send_prepare()
1255 struct inet_sock *inet = inet_sk(sk); in inet_sk_reselect_saddr()
1310 struct inet_sock *inet = inet_sk(sk); in inet_sk_rebuild_header()
H A Dip_output.c153 const struct inet_sock *inet = inet_sk(sk); in ip_build_and_send_pkt()
459 struct inet_sock *inet = inet_sk(sk); in __ip_queue_xmit()
549 return __ip_queue_xmit(sk, skb, fl, inet_sk(sk)->tos); in ip_queue_xmit()
961 struct inet_sock *inet = inet_sk(sk); in __ip_append_data()
1348 struct inet_sock *inet = inet_sk(sk); in ip_append_data()
1387 struct inet_sock *inet = inet_sk(sk); in __ip_make_skb()
1528 __ip_flush_pending_frames(sk, &sk->sk_write_queue, &inet_sk(sk)->cork.base); in ip_flush_pending_frames()
1628 inet_sk(sk)->tos = arg->tos & ~INET_ECN_MASK; in ip_send_unicast_reply()
H A Dtcp_ipv4.c211 struct inet_sock *inet = inet_sk(sk); in tcp_v4_connect()
357 struct inet_sock *inet = inet_sk(sk); in tcp_v4_mtu_reduced()
530 if (unlikely(iph->ttl < READ_ONCE(inet_sk(sk)->min_ttl))) { in tcp_v4_err()
659 const struct inet_sock *inet = inet_sk(sk); in tcp_v4_send_check()
1035 (inet_sk(sk)->tos & INET_ECN_MASK) : in tcp_v4_send_synack()
1036 inet_sk(sk)->tos; in tcp_v4_send_synack()
1591 newinet = inet_sk(newsk); in tcp_v4_syn_recv_sock()
2126 if (unlikely(iph->ttl < READ_ONCE(inet_sk(sk)->min_ttl))) { in tcp_v4_rcv()
2675 const struct inet_sock *inet = inet_sk(sk); in get_tcp4_sock()
3416 inet_sk(sk)->pmtudisc = IP_PMTUDISC_DO; in tcp_v4_init()
H A Draw_diag.c163 struct inet_sock *inet = inet_sk(sk); in raw_diag_dump()
H A Dinet_diag.c127 const struct inet_sock *inet = inet_sk(sk); in inet_diag_msg_attrs_fill()
789 struct inet_sock *inet = inet_sk(sk); in inet_diag_bc_sk()
1040 struct inet_sock *inet = inet_sk(sk); in inet_diag_dump_icsk()
1367 r->id.idiag_sport = inet_sk(sk)->inet_sport; in inet_diag_handler_get_info()
/openbmc/linux/net/mptcp/
H A Dsubflow.c121 return inet_sk(sk)->inet_sport != inet_sk((struct sock *)msk)->inet_sport; in subflow_use_different_sport()
219 ntohs(inet_sk(sk_listener)->inet_sport), in subflow_check_req()
220 ntohs(inet_sk((struct sock *)subflow_req->msk)->inet_sport)); in subflow_check_req()
419 return inet_sk(sk)->inet_dport != inet_sk((struct sock *)msk)->inet_dport; in subflow_use_different_dport()
563 ntohs(inet_sk(sk)->inet_dport), in subflow_finish_connect()
564 ntohs(inet_sk(parent)->inet_dport)); in subflow_finish_connect()
872 ntohs(inet_sk(sk)->inet_sport), in subflow_syn_recv_sock()
873 ntohs(inet_sk((struct sock *)owner)->inet_sport)); in subflow_syn_recv_sock()
H A Dprotocol.c3119 inet_sk(msk)->inet_num = inet_sk(ssk)->inet_num; in mptcp_copy_inaddrs()
3120 inet_sk(msk)->inet_dport = inet_sk(ssk)->inet_dport; in mptcp_copy_inaddrs()
3121 inet_sk(msk)->inet_sport = inet_sk(ssk)->inet_sport; in mptcp_copy_inaddrs()
3122 inet_sk(msk)->inet_daddr = inet_sk(ssk)->inet_daddr; in mptcp_copy_inaddrs()
3123 inet_sk(msk)->inet_saddr = inet_sk(ssk)->inet_saddr; in mptcp_copy_inaddrs()
3124 inet_sk(msk)->inet_rcv_saddr = inet_sk(ssk)->inet_rcv_saddr; in mptcp_copy_inaddrs()
3205 const struct inet_sock *inet = inet_sk(sk); in mptcp_copy_ip_options()
3208 newinet = inet_sk(newsk); in mptcp_copy_ip_options()
3240 inet_sk(nsk)->pinet6 = mptcp_inet6_sk(nsk); in mptcp_sk_clone_init()
H A Dpm_userspace.c136 inet_sk((struct sock *)msk))->inet_sport; in mptcp_userspace_pm_get_local_id()
418 issk = inet_sk(ssk); in mptcp_nl_find_ssk()
H A Dsockopt.c740 val = inet_sk(sk)->tos; in mptcp_setsockopt_v4_set_tos()
1106 const struct inet_sock *inet = inet_sk(sk); in mptcp_get_sub_addrs()
1390 return mptcp_put_int_option(msk, optval, optlen, inet_sk(sk)->tos); in mptcp_getsockopt_v4()
1458 __ip_sock_set_tos(ssk, inet_sk(sk)->tos); in sync_socket_options()
/openbmc/linux/net/ipv6/
H A Dping.c64 struct inet_sock *inet = inet_sk(sk); in ping_v6_sendmsg()
242 struct inet_sock *inet = inet_sk((struct sock *)v); in ping_v6_seq_show()
H A Dxfrm6_output.c37 fl6.fl6_dport = inet_sk(sk)->inet_dport; in xfrm6_local_error()
H A Ddatagram.c44 const struct inet_sock *inet = inet_sk(sk); in ip6_datagram_flow_key_init()
78 struct inet_sock *inet = inet_sk(sk); in ip6_datagram_dst_update()
144 struct inet_sock *inet = inet_sk(sk); in __ip6_datagram_connect()
527 if (inet_cmsg_flags(inet_sk(sk))) in ipv6_recv_error()
830 if (!ipv6_can_nonlocal_bind(net, inet_sk(sk)) && in ip6_datagram_send_ctl()
H A Dudp.c115 inet_sk(sk)->inet_num); in udp_v6_rehash()
138 inet = inet_sk(sk); in compute_score()
338 struct inet_sock *inet = inet_sk(sk); in udpv6_recvmsg()
812 const struct inet_sock *inet = inet_sk(sk); in __udp_v6_is_mcast_sock()
1325 err = udp_v6_send_skb(skb, &inet_sk(sk)->cork.fl.u.ip6, in udp_v6_push_pending_frames()
1326 &inet_sk(sk)->cork.base); in udp_v6_push_pending_frames()
1337 struct inet_sock *inet = inet_sk(sk); in udpv6_sendmsg()
1733 const struct inet_sock *inet = inet_sk((const struct sock *)v); in udp6_seq_show()
H A Daf_inet6.c205 inet = inet_sk(sk); in inet6_create()
220 inet_sk(sk)->pinet6 = np = inet6_sk_generic(sk); in inet6_create()
284 struct inet_sock *inet = inet_sk(sk); in __inet6_bind()
527 struct inet_sock *inet = inet_sk(sk); in inet6_getname()
830 struct inet_sock *inet = inet_sk(sk); in inet6_sk_rebuild_header()
/openbmc/linux/include/trace/events/
H A Dhandshake.h204 const struct inet_sock *inet = inet_sk(sk);
295 const struct inet_sock *inet = inet_sk(sk);
H A Dsock.h161 const struct inet_sock *inet = inet_sk(sk);
225 const struct inet_sock *inet = inet_sk(sk);
/openbmc/linux/net/ipv4/netfilter/
H A Dnf_tproxy_ipv4.c125 int wildcard = (inet_sk(sk)->inet_rcv_saddr == 0); in nf_tproxy_get_sock_v4()
/openbmc/linux/include/net/
H A Droute.h40 #define RT_CONN_FLAGS(sk) (RT_TOS(inet_sk(sk)->tos) | sock_flag(sk, SOCK_LOCALROUTE))
53 return RT_TOS(inet_sk(sk)->tos); in ip_sock_rt_tos()
/openbmc/linux/security/
H A Dlsm_audit.c320 const struct inet_sock *inet = inet_sk(sk); in dump_common_audit_data()
332 const struct inet_sock *inet = inet_sk(sk); in dump_common_audit_data()
/openbmc/linux/drivers/net/ethernet/chelsio/inline_crypto/chtls/
H A Dchtls_cm.c106 if (likely(!inet_sk(sk)->inet_rcv_saddr)) in chtls_find_netdev()
108 ndev = __ip_dev_find(&init_net, inet_sk(sk)->inet_rcv_saddr, false); in chtls_find_netdev()
689 inet_sk(sk)->inet_rcv_saddr, in chtls_listen_start()
690 inet_sk(sk)->inet_sport, 0, in chtls_listen_start()
706 inet_sk(sk)->inet_sport, in chtls_listen_start()
1187 newinet = inet_sk(newsk); in chtls_recv_sock()
1200 inet_sk(newsk)->pinet6 = &newtcp6sk->inet6; in chtls_recv_sock()
1469 atomic_set(&inet_sk(sk)->inet_id, get_random_u16()); in make_established()
/openbmc/linux/drivers/net/ethernet/netronome/nfp/crypto/
H A Dtls.c178 struct inet_sock *inet = inet_sk(sk); in nfp_net_tls_set_ipv4()
217 struct inet_sock *inet = inet_sk(sk); in nfp_net_tls_set_l4()
/openbmc/linux/net/netfilter/
H A Dnf_conntrack_proto.c270 const struct inet_sock *inet = inet_sk(sk); in getorigdst()
328 const struct inet_sock *inet = inet_sk(sk); in ipv6_getorigdst()
H A Dxt_socket.c70 inet_sk(sk)->inet_rcv_saddr == 0); in socket_match()
/openbmc/linux/net/rds/
H A Dtcp.c245 struct inet_sock *inet = inet_sk(tc->t_sock->sk); in rds_tcp_tc_info()
292 struct inet_sock *inet = inet_sk(sk); in rds6_tcp_tc_info()

12345