- r - 以节省内存的方式增长 data.frame
- ruby-on-rails - ruby/ruby on rails 内存泄漏检测
- android - 无法解析导入android.support.v7.app
- UNIX 域套接字与共享内存(映射文件)
我正在开发的Linux内核驱动程序之一是在内核中使用网络通信(sock_create()
、sock->ops->bind()
等)上)。
问题是会有多个套接字从中接收数据。所以我需要一些可以在内核空间中模拟 select()
或 poll()
的东西。由于这些函数使用文件描述符,我不能使用系统调用,除非我使用系统调用来创建套接字,但这似乎是不必要的,因为我在内核中工作。
所以我想在我自己的处理程序 (custom_sk_data_ready()
) 中包装默认的 sock->sk_data_ready
处理程序,这将解锁一个信号量。然后我可以编写自己的 kernel_select()
函数来尝试锁定信号量并进行阻塞等待直到它打开。这样内核函数就会进入休眠状态,直到信号量被 custom_sk_data_ready()
解锁。一旦 kernel_select()
获得锁,它就会解锁并调用 custom_sk_data_ready()
重新锁定它。因此,唯一的额外初始化是在绑定(bind)套接字之前运行 custom_sk_data_ready()
,这样第一次调用 custom_select()
就不会错误地触发。
我看到一个可能的问题。如果发生多次接收,则多次调用 custom_sk_data_ready()
将尝试解锁信号量。因此,为了不丢失多个调用并跟踪正在使用的 sock
,必须有一个表或列表指向正在使用的套接字。并且 custom_sk_data_ready()
必须在表/列表中标记它传递的是哪个套接字。
这个方法好吗?或者我应该在使用标准系统调用时解决用户/内核空间问题?
初步发现:
sock
结构中的所有回调函数都在中断上下文中调用。这意味着他们无法休眠。为了让主内核线程在准备就绪的套接字列表上休眠,使用了互斥锁,但是 custom_sk_data_ready()
必须像互斥锁上的自旋锁一样(调用 mutex_trylock()
重复)。这也意味着任何动态分配都必须使用 GFP_ATOMIC
标志。
其他可能性:
对于每个打开的套接字,将每个套接字的 sk_data_ready()
替换为自定义套接字 (custom_sk_data_ready()
) 并创建一个 worker (struct work_struct
) 和工作队列 (struct workqueue_struct
)。每个工作人员都将使用一个通用的 process_msg()
函数。创建一个内核模块级全局列表,其中每个列表元素都有一个指向套接字的指针并包含工作结构。当套接字上的数据就绪时,custom_sk_data_ready()
将执行并找到具有相同套接字的匹配列表元素,然后使用列表元素的工作队列调用 queue_work()
和 worker 。然后调用process_msg()
函数,可以通过struct work_struct *
参数(地址)的内容找到匹配的列表元素,也可以使用container_of()
宏来获取持有 worker 结构的列表结构的地址。
哪种技术最可靠?
最佳答案
你的第二个想法听起来更可行。
CEPH 代码看起来做了类似的事情,参见 net/ceph/messenger.c
。
关于linux - 模拟内核socket编程中select()和poll()的作用,我们在Stack Overflow上找到一个类似的问题: https://stackoverflow.com/questions/11336034/
我正在尝试打印 timeval 类型的值。实际上我可以打印它,但我收到以下警告: 该行有多个标记 格式“%ld”需要“long int”类型,但参数 2 的类型为“struct timeval” 程序
我正在编写自己的 unix 终端,但在执行命令时遇到问题: 首先,我获取用户输入并将其存储到缓冲区中,然后我将单词分开并将它们存储到我的 argv[] 数组中。IE命令是“firefox”以启动存储在
我是 CUDA 的新手。我有一个关于一个简单程序的问题,希望有人能注意到我的错误。 __global__ void ADD(float* A, float* B, float* C) { con
我有一个关于 C 语言 CGI 编程的一般性问题。 我使用嵌入式 Web 服务器来处理 Web 界面。为此,我在服务器中存储了一个 HTML 文件。在此 HTML 文件中包含 JavaScript 和
**摘要:**在代码的世界中,是存在很多艺术般的写法,这可能也是部分程序员追求编程这项事业的内在动力。 本文分享自华为云社区《【云驻共创】用4种代码中的艺术试图唤回你对编程的兴趣》,作者: break
我有一个函数,它的任务是在父对象中创建一个变量。我想要的是让函数在调用它的级别创建变量。 createVariable testFunc() [1] "test" > testFunc2() [1]
以下代码用于将多个连续的空格替换为1个空格。虽然我设法做到了,但我对花括号的使用感到困惑。 这个实际上运行良好: #include #include int main() { int ch, la
我正在尝试将文件写入磁盘,然后自动重新编译。不幸的是,某事似乎不起作用,我收到一条我还不明白的错误消息(我是 C 初学者 :-)。如果我手动编译生成的 hello.c,一切正常吗?! #include
如何将指针值传递给结构数组; 例如,在 txt 上我有这个: John Doe;xxxx@hotmail.com;214425532; 我的代码: typedef struct Person{
我尝试编写一些代码来检索 objectID,结果是 2B-06-01-04-01-82-31-01-03-01-01 . 这个值不正确吗? // Send a SysObjectId SNMP req
您好,提前感谢您的帮助, (请注意评论部分以获得更多见解:即,以下示例中的成本列已添加到此问题中;西蒙提供了一个很好的答案,但成本列本身并未出现在他的数据响应中,尽管他提供的功能与成本列一起使用) 我
我想知道是否有人能够提出一些解决非线性优化问题的软件包的方法,而非线性优化问题可以为优化解决方案提供整数变量?问题是使具有相等约束的函数最小化,该函数受某些上下边界约束的约束。 我已经在R中使用了'n
我是 R 编程的初学者,正在尝试向具有 50 列的矩阵添加一个额外的列。这个新列将是该行中前 10 个值的平均值。 randomMatrix <- generateMatrix(1,5000,100,
我在《K&R II C 编程 ANSI C》一书中读到,“>>”和“0; nwords--) sum += *buf++; sum = (sum >>
当下拉列表的选择发生变化时,我想: 1) 通过 div 在整个网站上显示一些 GUI 阻止覆盖 2)然后处理一些代码 3) 然后隐藏叠加层。 问题是,当我在事件监听器函数中编写此逻辑时,将执行 onC
我正在使用 Clojure 和 RESTEasy 设计 JAX-RS REST 服务器. 据我了解,用 Lisp 系列语言编写的应用程序比用“传统”命令式语言编写的应用程序更多地构建为“特定于领域的语
我目前正在研究一种替代出勤监控系统作为一项举措。目前,我设计的用户表单如下所示: Time Stamp Userform 它的工作原理如下: 员工将选择他/她将使用的时间戳类型:开始时间、超时、第一次
我是一名学生,试图自学编程,从在线资源和像您这样的人那里获得帮助。我在网上找到了一个练习来创建一个小程序来执行此操作: 编写一个程序,读取数字 a 和 b(长整型)并列出 a 和 b 之间有多少个数字
我正在尝试编写一个 shell 程序,给定一个参数,打印程序的名称和参数中的每个奇数词(即,不是偶数词)。但是,我没有得到预期的结果。在跟踪我的程序时,我注意到,尽管奇数词(例如,第 5 个词,5 %
只是想知道是否有任何 Java API 可以让您控制台式机/笔记本电脑外壳上的 LED? 或者,如果不可能,是否有可能? 最佳答案 如果你说的是前面的 LED 指示电源状态和 HDD 繁忙状态,恐怕没
我是一名优秀的程序员,十分优秀!