Home
last modified time | relevance | path

Searched refs:lsk (Results 1 - 25 of 27) sorted by relevance

12

/kernel/linux/linux-6.6/tools/testing/selftests/net/
H A Dsctp_hello.c77 int lsk, csk, ret, len; in main() local
94 lsk = socket(ss.ss_family, SOCK_STREAM, IPPROTO_SCTP); in main()
95 if (lsk < 0) { in main()
96 printf("failed to create lsk\n"); in main()
101 ret = setsockopt(lsk, SOL_SOCKET, SO_BINDTODEVICE, in main()
110 ret = bind(lsk, (struct sockaddr *)&ss, len); in main()
116 ret = listen(lsk, 5); in main()
122 csk = accept(lsk, (struct sockaddr *)NULL, (socklen_t *)NULL); in main()
134 close(lsk); in main()
/kernel/linux/linux-5.10/drivers/net/ethernet/chelsio/inline_crypto/chtls/
H A Dchtls_cm.c623 struct sock *listen_sk = listen_ctx->lsk; in chtls_reset_synq()
674 ctx->lsk = sk; in chtls_listen_start()
779 cxgb4_free_stid(cdev->tids, stid, listen_ctx->lsk->sk_family); in chtls_pass_open_rpl()
780 sock_put(listen_ctx->lsk); in chtls_pass_open_rpl()
802 cxgb4_free_stid(cdev->tids, stid, listen_ctx->lsk->sk_family); in chtls_close_listsrv_rpl()
803 sock_put(listen_ctx->lsk); in chtls_close_listsrv_rpl()
891 static void bl_pass_open_abort(struct sock *lsk, struct sk_buff *skb) in bl_pass_open_abort() argument
893 pass_open_abort(skb->sk, lsk, skb); in bl_pass_open_abort()
920 parent = ((struct listen_ctx *)data)->lsk; in chtls_pass_open_arp_failure()
1073 struct sock *lsk, struc in inet_inherit_port()
1072 inet_inherit_port(struct inet_hashinfo *hash_info, struct sock *lsk, struct sock *newsk) inet_inherit_port() argument
1109 chtls_recv_sock(struct sock *lsk, struct request_sock *oreq, void *network_hdr, const struct cpl_pass_accept_req *req, struct chtls_dev *cdev) chtls_recv_sock() argument
1432 struct sock *lsk; chtls_pass_accept_req() local
1536 add_pass_open_to_parent(struct sock *child, struct sock *lsk, struct chtls_dev *cdev) add_pass_open_to_parent() argument
1562 bl_add_pass_open_to_parent(struct sock *lsk, struct sk_buff *skb) bl_add_pass_open_to_parent() argument
1575 struct sock *lsk, *sk; chtls_pass_establish() local
2053 bl_abort_syn_rcv(struct sock *lsk, struct sk_buff *skb) bl_abort_syn_rcv() argument
[all...]
H A Dchtls.h190 struct sock *lsk; member
/kernel/linux/linux-6.6/drivers/net/ethernet/chelsio/inline_crypto/chtls/
H A Dchtls_cm.c623 struct sock *listen_sk = listen_ctx->lsk; in chtls_reset_synq()
674 ctx->lsk = sk; in chtls_listen_start()
779 cxgb4_free_stid(cdev->tids, stid, listen_ctx->lsk->sk_family); in chtls_pass_open_rpl()
780 sock_put(listen_ctx->lsk); in chtls_pass_open_rpl()
802 cxgb4_free_stid(cdev->tids, stid, listen_ctx->lsk->sk_family); in chtls_close_listsrv_rpl()
803 sock_put(listen_ctx->lsk); in chtls_close_listsrv_rpl()
891 static void bl_pass_open_abort(struct sock *lsk, struct sk_buff *skb) in bl_pass_open_abort() argument
893 pass_open_abort(skb->sk, lsk, skb); in bl_pass_open_abort()
920 parent = ((struct listen_ctx *)data)->lsk; in chtls_pass_open_arp_failure()
1072 static void inet_inherit_port(struct sock *lsk, struc argument
1108 chtls_recv_sock(struct sock *lsk, struct request_sock *oreq, void *network_hdr, const struct cpl_pass_accept_req *req, struct chtls_dev *cdev) chtls_recv_sock() argument
1432 struct sock *lsk; chtls_pass_accept_req() local
1536 add_pass_open_to_parent(struct sock *child, struct sock *lsk, struct chtls_dev *cdev) add_pass_open_to_parent() argument
1562 bl_add_pass_open_to_parent(struct sock *lsk, struct sk_buff *skb) bl_add_pass_open_to_parent() argument
1575 struct sock *lsk, *sk; chtls_pass_establish() local
2053 bl_abort_syn_rcv(struct sock *lsk, struct sk_buff *skb) bl_abort_syn_rcv() argument
[all...]
H A Dchtls.h192 struct sock *lsk; member
/kernel/linux/linux-5.10/net/core/
H A Drequest_sock.c91 struct sock *lsk = req->rsk_listener; in reqsk_fastopen_remove() local
94 fastopenq = &inet_csk(lsk)->icsk_accept_queue.fastopenq; in reqsk_fastopen_remove()
103 if (!reset || lsk->sk_state != TCP_LISTEN) { in reqsk_fastopen_remove()
/kernel/linux/linux-6.6/net/core/
H A Drequest_sock.c91 struct sock *lsk = req->rsk_listener; in reqsk_fastopen_remove() local
94 fastopenq = &inet_csk(lsk)->icsk_accept_queue.fastopenq; in reqsk_fastopen_remove()
103 if (!reset || lsk->sk_state != TCP_LISTEN) { in reqsk_fastopen_remove()
/kernel/linux/linux-6.6/net/mptcp/
H A Dmptcp_diag.c210 struct sock *lsk = READ_ONCE(msk->first); in mptcp_diag_get_info() local
212 if (lsk) { in mptcp_diag_get_info()
216 r->idiag_rqueue = READ_ONCE(lsk->sk_ack_backlog); in mptcp_diag_get_info()
217 r->idiag_wqueue = READ_ONCE(lsk->sk_max_ack_backlog); in mptcp_diag_get_info()
H A Dpm_netlink.c901 if (entry->lsk) in __mptcp_pm_release_addr_entry()
902 sock_release(entry->lsk); in __mptcp_pm_release_addr_entry()
1015 SOCK_STREAM, IPPROTO_MPTCP, &entry->lsk); in mptcp_pm_nl_create_listen_socket()
1019 newsk = entry->lsk->sk; in mptcp_pm_nl_create_listen_socket()
1098 entry->lsk = NULL; in mptcp_pm_nl_get_local_id()
H A Dprotocol.h244 struct socket *lsk; member
/kernel/linux/linux-5.10/net/nfc/
H A Dllcp_sock.c406 struct nfc_llcp_sock *lsk, *n, *llcp_parent; in nfc_llcp_accept_dequeue() local
411 list_for_each_entry_safe(lsk, n, &llcp_parent->accept_queue, in nfc_llcp_accept_dequeue()
413 sk = &lsk->sk; in nfc_llcp_accept_dequeue()
423 list_del_init(&lsk->accept_queue); in nfc_llcp_accept_dequeue()
614 struct nfc_llcp_sock *lsk, *n; in llcp_sock_release() local
617 list_for_each_entry_safe(lsk, n, &llcp_sock->accept_queue, in llcp_sock_release()
619 accept_sk = &lsk->sk; in llcp_sock_release()
622 nfc_llcp_send_disconnect(lsk); in llcp_sock_release()
H A Dllcp_core.c90 struct nfc_llcp_sock *lsk, *n; in nfc_llcp_socket_release() local
93 list_for_each_entry_safe(lsk, n, in nfc_llcp_socket_release()
96 accept_sk = &lsk->sk; in nfc_llcp_socket_release()
/kernel/linux/linux-6.6/net/nfc/
H A Dllcp_sock.c411 struct nfc_llcp_sock *lsk, *n, *llcp_parent; in nfc_llcp_accept_dequeue() local
416 list_for_each_entry_safe(lsk, n, &llcp_parent->accept_queue, in nfc_llcp_accept_dequeue()
418 sk = &lsk->sk; in nfc_llcp_accept_dequeue()
428 list_del_init(&lsk->accept_queue); in nfc_llcp_accept_dequeue()
619 struct nfc_llcp_sock *lsk, *n; in llcp_sock_release() local
622 list_for_each_entry_safe(lsk, n, &llcp_sock->accept_queue, in llcp_sock_release()
624 accept_sk = &lsk->sk; in llcp_sock_release()
627 nfc_llcp_send_disconnect(lsk); in llcp_sock_release()
H A Dllcp_core.c88 struct nfc_llcp_sock *lsk, *n; in nfc_llcp_socket_release() local
91 list_for_each_entry_safe(lsk, n, in nfc_llcp_socket_release()
94 accept_sk = &lsk->sk; in nfc_llcp_socket_release()
/kernel/linux/linux-5.10/net/l2tp/
H A Dl2tp_ip6.c424 struct l2tp_ip6_sock *lsk = l2tp_ip6_sk(sk); in l2tp_ip6_getname() local
431 if (!lsk->peer_conn_id) in l2tp_ip6_getname()
433 lsa->l2tp_conn_id = lsk->peer_conn_id; in l2tp_ip6_getname()
443 lsa->l2tp_conn_id = lsk->conn_id; in l2tp_ip6_getname()
H A Dl2tp_ip.c354 struct l2tp_ip_sock *lsk = l2tp_ip_sk(sk); in l2tp_ip_getname() local
362 lsa->l2tp_conn_id = lsk->peer_conn_id; in l2tp_ip_getname()
369 lsa->l2tp_conn_id = lsk->conn_id; in l2tp_ip_getname()
/kernel/linux/linux-6.6/net/l2tp/
H A Dl2tp_ip6.c423 struct l2tp_ip6_sock *lsk = l2tp_ip6_sk(sk); in l2tp_ip6_getname() local
430 if (!lsk->peer_conn_id) in l2tp_ip6_getname()
432 lsa->l2tp_conn_id = lsk->peer_conn_id; in l2tp_ip6_getname()
442 lsa->l2tp_conn_id = lsk->conn_id; in l2tp_ip6_getname()
H A Dl2tp_ip.c356 struct l2tp_ip_sock *lsk = l2tp_ip_sk(sk); in l2tp_ip_getname() local
364 lsa->l2tp_conn_id = lsk->peer_conn_id; in l2tp_ip_getname()
371 lsa->l2tp_conn_id = lsk->conn_id; in l2tp_ip_getname()
/kernel/linux/linux-5.10/net/smc/
H A Daf_smc.c1149 struct sock *lsk = &lsmc->sk; in smc_clcsock_accept() local
1153 release_sock(lsk); in smc_clcsock_accept()
1154 new_sk = smc_sock_alloc(sock_net(lsk), NULL, lsk->sk_protocol); in smc_clcsock_accept()
1157 lsk->sk_err = ENOMEM; in smc_clcsock_accept()
1159 lock_sock(lsk); in smc_clcsock_accept()
1168 lock_sock(lsk); in smc_clcsock_accept()
1170 lsk->sk_err = -rc; in smc_clcsock_accept()
1171 if (rc < 0 || lsk->sk_state == SMC_CLOSED) { in smc_clcsock_accept()
1814 struct sock *lsk in smc_tcp_listen_work() local
[all...]
/kernel/linux/linux-6.6/net/smc/
H A Daf_smc.c1723 struct sock *lsk = &lsmc->sk; in smc_clcsock_accept() local
1727 release_sock(lsk); in smc_clcsock_accept()
1728 new_sk = smc_sock_alloc(sock_net(lsk), NULL, lsk->sk_protocol); in smc_clcsock_accept()
1731 lsk->sk_err = ENOMEM; in smc_clcsock_accept()
1733 lock_sock(lsk); in smc_clcsock_accept()
1742 lock_sock(lsk); in smc_clcsock_accept()
1744 lsk->sk_err = -rc; in smc_clcsock_accept()
1745 if (rc < 0 || lsk->sk_state == SMC_CLOSED) { in smc_clcsock_accept()
2539 struct sock *lsk in smc_tcp_listen_work() local
[all...]
/kernel/linux/linux-5.10/include/uapi/linux/
H A Dcdrom.h692 struct dvd_send_key lsk; member
/kernel/linux/linux-6.6/include/uapi/linux/
H A Dcdrom.h711 struct dvd_send_key lsk; member
/kernel/linux/patches/linux-5.10/prebuilts/usr/include/linux/
H A Dcdrom.h427 struct dvd_send_key lsk; member
/kernel/linux/patches/linux-6.6/prebuilts/usr/include/linux/
H A Dcdrom.h427 struct dvd_send_key lsk; member
/kernel/linux/patches/linux-4.19/prebuilts/usr/include/linux/
H A Dcdrom.h432 struct dvd_send_key lsk; member

Completed in 39 milliseconds

12