- c - 在位数组中找到第一个零
- linux - Unix 显示有关匹配两种模式之一的文件的信息
- 正则表达式替换多个文件
- linux - 隐藏来自 xtrace 的命令
所以我尝试使用mutex_init()
、mutex_lock()
、mutex_unlock()
进行线程同步。
我目前正在尝试以循环方式安排线程(但一次可以运行超过 1 个线程)并且我将线程的当前状态设置为 TASK_INTERRUPTIBLE
,然后唤醒建立另一个线程,其 PID,我在列表中。
我需要根据我的逻辑迭代此列表。
据我了解,我需要在访问其元素时锁定此列表,否则另一个线程可能会在我对其进行更改时错过新条目。此外,由于一个互斥锁已锁定资源,因此在原始互斥锁释放资源之前,没有其他互斥锁可以解锁它。
但是,我仍然不确定我是否正确锁定了它。 (我在调用 schedule()
之前释放锁,然后重新锁定)
我在一个线程中本地声明一个互斥量并锁定列表。在我当前线程锁定之后
mutex_lock(&lock);
然后我遍历列表,直到找到一些东西(或者如果没有找到任何东西就结束),然后解锁。
mutex_unlock(&lock);
我假设在迭代时锁定是合法的。不过,我从未见过这样的例子。
此外,进程在持有互斥锁时处于 (TASK_UNINTERRUPTIBLE
) 状态是否正常?
编辑: 我正在根据以下答案添加更多信息。
我的程序有可能在单核虚拟机上运行。因此,我不想冒险使用 spin_lock()
进行无限轮询。
我正在尝试维护具有特定 ID 的线程之间的调度。例如,如果有 4 个线程。 “A”组中有 2 个,“B”组中有 2 个。我只允许在每组中运行 1 个线程。但是我在给定集合中的线程之间切换。但是,集合“A”中的线程不应切换到集合“B”中的任何线程
(我知道内核调度器不会是完美的,所以一个近似的切换就可以了)。
我对 TASK_STATE 的推理:
1) 创建的初始线程正在运行。
2) 如果同一组中的另一个线程正在运行(并且这个线程在给定时间内没有执行)。设置其他线程为TASK_INTERRUPTIPLE
,同时调用schedule()
; 注意:每个集合中可以有 2 个以上的线程,但为了简单起见,我们现在只考虑 2 个。
3) 如果已经执行了足够的时间,则将此任务设置为TASK_INTERRUPTIPLE
,将同一组中的其他任务设置为TASK_RUNNING
,同时调用schedule ()
;
当我访问某些被(现在)全局互斥锁锁定的数据结构时,所有这些逻辑都会发生。我在调用 schedule()
之前解锁互斥锁,然后立即重新锁定。在我的逻辑部分完成后,我完全解锁了互斥体。
这种方法有什么根本性的错误吗?
最佳答案
As I understand it, I need to lock this list as I access its elements
是的,确实如此。但是,如果您使用互斥锁,您会非常难过,因为对 lock
/unlock
的调用 是对调度程序的调用。因此,从调度程序内部调用它会导致死锁。您需要做什么取决于您的处理器是多核处理器还是(神秘的)单核处理器。 (这是一个虚拟系统吗?)在单核处理器上,您可以禁用中断。在多核处理器上,禁用中断是不够的(它只禁用了一个内核的中断,另一个内核可能仍然被中断)。在多核上最简单的事情就是使用自旋锁。与互斥锁不同,这两种锁定机制都可以从不同的线程解锁。
I set the current state of a thread to
TASK_INTERRUPTIBLE
线程是否正在脱离 CPU?如果是这样,它就没有运行,所以我怀疑 TASK_INTERRUPTIBLE
是错误的状态。如果您能为我列出可能的状态,或者您能描述该状态应该表示什么,那将会很有帮助。因为对我来说“TASK_INTERRUPTIBLE
”听起来像是一个正在运行的任务。
I declare a mutex locally within a thread and lock the list
本地互斥体是一个危险信号!您锁定的资源应该由具有相同范围的互斥体保护。如果列表是全局的,它应该有一个全局互斥锁来保护它。想要使用列表的线程必须首先获取它的互斥量。当然,正如我已经谈到的,您可能希望使用不同类型的锁定来保护准备运行进程的列表。
I assume locking while I iterate is legal
这是完全合法的(当然假设您的互斥方案没有错误)。事实上,这是必需的。例如,如果允许另一个线程在您读取列表时从列表中删除一个节点,您最终可能会取消引用已删除的节点。
Also, is it normal for the process to have a state of
TASK_UNINTERRUPTIBLE
while it holds a mutex lock?
不,如果进程当前正在 CPU 上运行,则不会在它持有锁时。用户代码可以使用互斥体。如果持有互斥锁使进程不可中断,则意味着进程可以通过简单地锁定互斥锁并且永远不会释放它来劫持系统。现在,您会发现lock
和unlock
功能需要在单核处理器上是不可中断的。然而,为进程设置状态是没有意义的,因为它实际上是调度程序不能被中断。
关于linux - 内核编程 - 互斥量,我们在Stack Overflow上找到一个类似的问题: https://stackoverflow.com/questions/52541014/
我正在尝试打印 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 繁忙状态,恐怕没
我是一名优秀的程序员,十分优秀!