- c - 在位数组中找到第一个零
- linux - Unix 显示有关匹配两种模式之一的文件的信息
- 正则表达式替换多个文件
- linux - 隐藏来自 xtrace 的命令
我最近买了一个 gy-521 board我正在尝试通过以下连接将它与 Raspberry Pi 3 一起使用
RPi3 | GY-521
---------------------
3.3V <-------> Vcc
GND <-------> GND
SCL <-------> SCL
SDA <-------> SDA
使用 i2cdetect -y 1
我得到以下内容
0 1 2 3 4 5 6 7 8 9 a b c d e f
00: -- -- -- -- -- -- -- -- -- -- -- -- --
10: -- -- -- -- -- -- -- -- -- -- -- -- -- -- -- --
20: -- -- -- -- -- -- -- -- -- -- -- -- -- -- -- --
30: -- -- -- -- -- -- -- -- -- -- -- -- -- -- -- --
40: -- -- -- -- -- -- -- -- -- -- -- -- -- -- -- --
50: -- -- -- -- -- -- -- -- -- -- -- -- -- -- -- --
60: -- -- -- -- -- -- -- -- 68 -- -- -- -- -- -- --
70: -- -- -- -- -- -- -- --
所以设备的地址是0x68。阅读datasheet我发现例如 X 轴上的加速度存储在寄存器 3B(高位)和 3C(低位)中。我的问题是如何访问这些寄存器?
我的想法是,如果我打开 /dev/i2c-1
作为文件描述符,我可以使用正常的 read
和 write
职能。然后,我可以在有新的可用数据的情况下使用 poll
,而不是一直获取数据。
我尝试按照 documentation 中的建议使用 read
函数但这不起作用(我只得到零)并且当我使用 poll
时,似乎另一侧没有人并且超时(100ms)到期。我想我应该对芯片说“给我 3B 寄存器的值”,但我不知道该怎么做。
代码
#include <stdio.h>
#include <stdlib.h>
#include <unistd.h>
#include <stdint.h>
#include <sys/types.h>
#include <sys/stat.h>
#include <fcntl.h>
#include <linux/i2c-dev.h>
#include <sys/ioctl.h>
#include <stdarg.h>
#include <poll.h>
#include <errno.h>
const char *filename = "/dev/i2c-1";
int DEBUG = 0;
int ADDRESS = 0x68;
struct pollfd pfd;
void debug(const char* format, ...)
{
if (DEBUG)
{
va_list argptr;
va_start(argptr, format);
fprintf(stdout, "### ");
vfprintf(stdout, format, argptr);
va_end(argptr);
}
}
void error_handler(const char *msg)
{
perror(msg);
exit(EXIT_FAILURE);
}
void set_debug(const char *deb_lev)
{
unsigned long num;
char *p;
errno = 0;
num = strtoul(deb_lev, &p, 10);
if (errno != 0 || *p != '\0')
error_handler("set_debug | strtoul");
DEBUG = (num > 0);
}
int open_file(const char *filename)
{
int fd;
if ((fd = open(filename, O_RDWR)) == -1)
error_handler("open_file | open");
debug("\"%s\" opened at %d\n", filename, fd);
return fd;
}
int8_t read_value(int fd)
{
debug("Reading from %d\n", fd);
int8_t num;
char *p = (char *)#
ssize_t size = sizeof(int8_t);
ssize_t r = 0;
while (size > 0)
{
if ((r = read(fd, p, size)) == -1)
error_handler("read_value | read");
size -= r;
p += r;
}
return num;
}
void command(uint16_t reg, int fd)
{
debug("Writing to %d\n", fd);
unsigned char reg_buf[2];
ssize_t w = 0;
ssize_t size = sizeof(unsigned char)*2;
reg_buf[0] = (reg >> 0) & 0xFF;
reg_buf[1] = (reg >> 8) & 0xFF;
if ((w = write(fd, reg_buf, size)) == -1)
error_handler("command | write");
}
void read_data_from_imu(struct pollfd *pfd)
{
int8_t val;
int p;
for (;;)
{
command(0x3b, pfd->fd);
switch (p = poll(pfd, 1, 100))
{
case -1:
error_handler("read_data_from_imu | poll");
case 0:
fprintf(stderr, "Timeout expired\n");
break;
default:
val = read_value(pfd->fd);
printf("Read: %u\n", val);
break;
}
}
}
int main(int argc, const char **argv)
{
if (argc < 2)
{
fprintf(stderr, "Usage: %s debug_flag\n", argv[0]);
return EXIT_FAILURE;
}
set_debug(argv[1]);
pfd.fd = open_file(filename);
debug("Setting slave address\n");
if (ioctl(pfd.fd, I2C_SLAVE, ADDRESS) == -1)
error_handler("main | ioctl");
read_data_from_imu(&pfd);
return EXIT_SUCCESS;
}
编辑
感谢Kennyhyun添加 write
解决了问题。
因此,如果您想读取x 轴上的加速度计测量值你必须做这样的事情
...
#define ACCEL_XOUT_H 0x3b
#define ACCEL_XOUT_L 0x3c
...
write_register(ACCEL_XOUT_H, pfd->fd);
x_data = read_value(pfd->fd);
write_register(ACCEL_XOUT_L, pfd->fd);
x_data = (x_data << 8) + read_value(pfd->fd);
...
编辑 2
此外,您还可以简化写入后直接读取2个字节的代码。你会得到这样的东西(省略错误处理)
int8_t buff[2];
write_register(ACCEL_XOUT_H, pfd->fd);
read(pfd->fd, buff, 2); //in this way you'll read both the ACCEL_XOUT_H register and the ACCEL_XOUT_L (the next one).
最佳答案
您可能需要了解 i2c 的基础知识。
http://www.ti.com/lit/an/slva704/slva704.pdf
3.2 从 I2C 总线上的从机读取
要读取I2C寄存器,需要写入slave addr、register addr和slave addr,然后从总线读取数据。但这是由司机完成的。从地址通过ioctl设置在fd中。但是你还需要写register addr。
从你的链接..
/* Using SMBus commands */
res = i2c_smbus_read_word_data(file, reg);
if (res < 0) {
/* ERROR HANDLING: i2c transaction failed */
} else {
/* res contains the read word */
}
i2c_smbus_read_word_data
有包含寄存器地址的 reg
。但 read() 不是。您需要 write(reg)
然后才能 read()
。
除非使用突发模式或其他方式,否则您只需读取 1 个字节。它读取 1 个字节,因为 size
是 1。但是在和 p++ 时没有意义。
在通过 command(0x3b, pfd->fd);
读取之前,您正在写入 3b。但它会像写作一样
68 > 3B , 68 > 00 , 68 <
并尝试阅读。 (其中 > 为读取位,0,< 为 1)也许您只需要 write(pfd->fd, 0x3b, 1)
而不是 command
。
关于c - 访问设备的寄存器 i2c,我们在Stack Overflow上找到一个类似的问题: https://stackoverflow.com/questions/39409124/
我无法理解如何使用一些旧的 VGA 代码在这个示例中设置序列 Controller 寄存器: mov dx,SC_INDEX mov ax,0604h out dx,ax
我希望对 zmm 0-31 寄存器集的四字元素执行整数算术运算并保留这些运算产生的进位位。看来这只有在通用寄存器集中处理数据时才有可能。 因此,我想将信息从 zmm 0-31 寄存器之一复制到通用寄存
ARM 64中包含多种寄存器,下面介绍一些常见的寄存器。 1 通用寄存器 ARM 64包含31个64bit寄存器,记为X0~X30。 每一个通用寄存器,它的低32bit都可以被访问,记为W0~W
1.寄存器 组合逻辑存在一个最大的缺点就是存在竞争与冒险,系统会产生不定态;使用时序逻辑电路就会极大的改善这种情况 寄存器具有存储功能,一般是由D触发器构成,由时钟脉冲控制,每个D触发器能够
使用 $gp 是否存在危险?注册以存储值?我想我的问题是 $gp 的真正功能是什么?它是否以某种方式在幕后调用,以便如果我使用它,事情可能会变得非常非常错误? 最佳答案 那么,$gp register
我遇到了这段代码的问题,我无法弄清楚问题出在哪里。所以当我运行这段代码时:if $row["count"] > 0 else块运行和 $_SESSION["error"]设置。 当$row["coun
所以我正在做二进制炸弹的变体。这就是阶段 0x0000000000401205 : sub $0x8,%rsp 0x0000000000401209 : cmp $0x3,
我在一个名为 (EmployeeDetailKey - varchar(10)) 的字段中获得了一个值,其中包含顺序值,例如 00001, 00002, 00003.... 它位于 Employeed
我有一个要求,应该为每个调用的线程分配一个计数器变量。但我没有得到预期的结果,实际上计数器在线程中重复。我创建了一个虚拟表和一个过程来将计数器值插入到表中。无论如何,是否可以更改代码以便线程获得递增的
预期输出:需要打印第4季度的wage_amt +--------------+--------------+--------------+--------------+ | wages_amt_q1
如何匹配模式 abc_[someArbitaryStringHere]_xyz? 为了澄清,我希望正则表达式能够匹配以下性质的字符串: abc_xyz、abc_asdfsdf_xyz、abc_32rw
从下拉列表(自定义)中选择一个值而不是常规下拉列表,它有很多下拉值 我可以用代码选择第一个值 find('.selected', :text=>arg1,exact: false).click 但无法
这个问题不太可能帮助任何 future 的访问者;它只与一个小的地理区域、一个特定的时间点或一个非常狭窄的情况有关,这些情况并不普遍适用于互联网的全局受众。为了帮助使这个问题更广泛地适用,visit
我有 .csv 文件中的数据,它包含 2 列 x 轴和 y 轴。从 .csv 文件读取轴,然后使用拉伸(stretch)指数函数拟合数据,但显示错误。 这里我给出示例数据以方便理解。 我的函数是f(x
我正在尝试使用以下汇编代码将磁盘扇区加载到内存中,但正如我在终端中使用一些 int 0x10 时发现的那样,它不起作用的原因是它陷入了无限循环。我以为循环会自动为我递减 cx 寄存器。下面是代码,其中
我正在尝试编写一个脚本,该脚本将在 vim 中打开一个文件并将其中的特定行复制到 vim 的寄存器之一中。当脚本再次运行时,它会决定再次打开文件,然后将 vim 寄存器中的值粘贴回。实际上,脚本应该在
我目前正在尝试弄清楚如何将指针寄存器 SI 指向的内存中的第一个字节添加到 AX 寄存器的当前内容中。 因此,如果 SI 包含某个地址,并且该地址在内存中的值是:00 和 01,我希望将 00 添加到
我试图将两个 16 位数字与以下 NASM 代码相乘: mov ax, [input1] mov bx, [input2] mul bx 前面代码的结果存储在 DX:AX 我试图使用来自单独库“pri
我正在尝试修改 rip 寄存器(只是为了好玩)。 buffer 应该是内存地址,所以不知道为什么会得到Error: operand type mismatch for 'movq' #include
我可以告诉gcc-style inline assembly把我的__m512i变量到特定 zmm注册,如 zmm31 ? 最佳答案 就像在根本没有特定寄存器约束的目标(如 ARM)上一样,使用 lo
我是一名优秀的程序员,十分优秀!