- html - 出于某种原因,IE8 对我的 Sass 文件中继承的 html5 CSS 不友好?
- JMeter 在响应断言中使用 span 标签的问题
- html - 在 :hover and :active? 上具有不同效果的 CSS 动画
- html - 相对于居中的 html 内容固定的 CSS 重复背景?
当我查看 Atmel 软件框架中的一些驱动程序实现时,我遇到了几种使用内存屏障的情况。
障碍定义:
#define barrier() asm volatile("" ::: "memory")
示例 1(中断辅助函数):
static inline void cpu_irq_restore(irqflags_t flags)
{
barrier();
SREG = flags;
}
这个障碍对我来说很有意义。由于 cpu_irq_restore 是隐式内联的,因此它可以防止关键(从执行顺序角度来看)SREG 分配从实际函数调用位置重新排序。
作为旁注:SREG
被定义为特殊功能寄存器,定义为:
#define _SFR_MEM8(mem_addr) (*(volatile uint8_t *)(mem_addr))
示例 2(来自 AVR TWI 驱动程序):
static inline status_code_t twim_release(void)
{
/* First wait for the driver event handler to indicate something
* other than a transfer in-progress, then test the bus interface
* for an Idle bus state.
*/
while (OPERATION_IN_PROGRESS == transfer.status);
while (! twim_idle(transfer.bus)) { barrier(); }
status_code_t const status = transfer.status;
transfer.locked = false;
return status;
}
但是,我不清楚第二个用例。编译器可以通过什么方式优化该代码,使其在没有 barrier()
的情况下中断?
阅读 this article 后,我想我了解了软件内存障碍背后的基本推理。 .
在第二个示例中使用屏障的原因是什么?
最佳答案
twim_idle 函数可能会执行类似读取 TWI 相关特殊功能寄存器的值并检查其中某些位的操作。如果没有屏障,危险在于编译器可能会优化该寄存器的读取并将其移至第二个循环之前。那么第二个循环的行为将如下所示:
bool idle = twim_idle(transfer.bus);
while (!idle);
这是一种优化,可以使循环更快,并且对于读取普通变量是有效的,但在这种情况下显然会导致问题。在循环中放置障碍应该可以防止优化发生。
实际上,您不需要内存屏障,因为所有特殊功能寄存器都使用 volatile
关键字进行限定,因此编译器不会尝试缓存对它们的访问。
关于c - Atmel 驱动程序和 GCC 内存屏障用例,我们在Stack Overflow上找到一个类似的问题: https://stackoverflow.com/questions/37916566/
我有一个使用临界区的 Windows DLL(C 语言)。多次调用的特定例程需要在第一次调用时执行一些初始化代码,因此我使用了临界区。但是,由于它被调用了很多次,我试图避免每次调用时都进入该部分的开销
我想确保正确实现障碍。现在,每次调用 amStaticThreaded 时都会启动大量新线程。在我的主例程中,amStaticThreaded 之后的所有事情都只能由一个线程完成,但那部分速度非常快。
我想实现自定义 Java 屏障。我不想使用 CyclicBarrier class . 所以所有线程都在一个公共(public)点相遇。只有当所有线程都到达屏障时,线程才会继续。 我想使用 wait/
您好,很抱歉发布了一大堆代码,但我对 C 代码还很陌生,基本上我正在做一项大学作业,我必须实现一个“pthread_barrier”,现在我理解了屏障的概念(或者至少我认为我这样做)但我只是不确定我应
什么是boost:barrier,如何使用这种boost方法。你能不能给我一个清楚的例子,因为我找到了下面的例子: bool wait() { boost::mutex
我正在尝试在 cython 中使用 openmp。我需要在 cython 中做两件事: i) 在我的 cython 代码中使用 #pragma omp single{} 作用域。 ii) 使用#pra
所以这是代码: #pragma omp parallel private (myId) { set_affinity(); myId = omp_get_thread_num(); if
我正在尝试在 cython 中使用 openmp。我需要在 cython 中做两件事: i) 在我的 cython 代码中使用 #pragma omp single{} 作用域。 ii) 使用#pra
我正在尝试创建一个 C 代码来对具有多个线程的数组进行排序,因此我需要使用屏障来同步威胁 void sort(struct ThreadArguments* args){ struct
这些天我正在阅读有关内存栅栏和屏障的内容,作为同步多线程代码和避免代码重新排序的一种方法。 我通常在 Linux 操作系统下使用 C++ 进行开发,并且大量使用 boost 库,但我找不到任何与之相关
我正在编写一个 SMT 程序,并且正在尝试解决一个有趣的问题。 我需要所有函数一起退出,但是有些线程卡在障碍物上,即使我不希望它们这样做。 我的问题是:当我删除障碍时会发生什么?卡在屏障处的线程会释放
可能是我没有理解线程的屏障概念。但是我写了一段代码,我想了解它是否正确使用了 barrier。 代码如下: #!/usr/bin/env python3 # -*- coding: utf-8 -*-
我想编写可移植代码(Intel、ARM、PowerPC...)来解决一个经典问题的变体: Initially: X=Y=0 Thread A: X=1 if(!Y){ do something
我有一个 n 的二维网格x n元素。在一次迭代中,我通过平均相邻元素的值来计算一个元素的值。即: for(int i=0;i
我是 MPI 新手,在尝试使用障碍时遇到了 fatal error 。我有一个简单的 for 循环,它以循环方式将索引分配给每个进程,紧随其后的是 MPI 屏障: mpi.cc #include #
我正在使用 gdrive和 gshell为了与我的 Google 帐户交互并下载文件,请获取他们的信息。 当我运行时:gdrive about或 gdown about ,我收到以下消息 Initia
运行以下代码时,2个启动线程将被CyclicBarrier *对象锁定,并无限等待第三个线程解锁 import java.util.concurrent.BrokenBarrierException;
我是一名优秀的程序员,十分优秀!