- html - 出于某种原因,IE8 对我的 Sass 文件中继承的 html5 CSS 不友好?
- JMeter 在响应断言中使用 span 标签的问题
- html - 在 :hover and :active? 上具有不同效果的 CSS 动画
- html - 相对于居中的 html 内容固定的 CSS 重复背景?
我已经编写了一个内核模块。该模块是关于智能手机安全主题的论文的一部分。模块读取文件并通过 UDP 套接字发送其内容。
该模块在 Ubuntu 上正常工作。我已经为正确的 android 内核(2.6.29)编译了它。在 Android 下: Insmod 工作正常。
收到 UDP 数据包时出现一些错误。
我怀疑它与文件读取有关。
首先是错误信息:
hiJack: Starting LKM!
hiJack: Sending answer!
hiJack: Reading queue!
hiJack: Opening File!
Unable to handle kernel NULL pointer dereference at virtual address 0000001e
pgd = c0004000
[0000001e] *pgd=00000000
Internal error: Oops: 817 [#1]
Modules linked in: hiJack
CPU: 0 Not tainted (2.6.29 #3)
PC is at readFile+0x84/0xec [hiJack]
LR is at call_rcu+0x28/0x48
pc : [<bf0000ac>] lr : [<c0069f14>] psr: a0000013
sp : c2a27ef0 ip : 000007ff fp : c2a27f0c
r10: c2a27f38 r9 : c2a27f1c r8 : 00000000
r7 : 00000000 r6 : 00000000 r5 : 00000000 r4 : fffffffe
r3 : 00000000 r2 : 00000000 r1 : bf000b38 r0 : fffffffe
Flags: NzCv IRQs on FIQs on Mode SVC_32 ISA ARM Segment kernel
Control: 00093177 Table: 02bfc000 DAC: 00000017
LR: 0xc0069e94:
9e94 e5831000 e121f002 e89da810 c02fd2d8 e1a0c00d e92dd830 e24cb004 e5801004
9eb4 e10f4000 e3843080 e121f003 e59f101c e59f201c ebffffc7 e3140080 0a000001
9ed4 e121f004 e89da830 e121f004 e89da830 c02fd2ec c03280ec e1a0c00d e92dd830
9ef4 e24cb004 e5801004 e10f4000 e3843080 e121f003 e59f101c e59f201c ebffffb5
9f14 e3140080 0a000001 e121f004 e89da830 e121f004 e89da830 c02fd2d8 c03280b0
9f34 e1a0c00d e92dd8f0 e24cb004 e5913010 e1a04001 e3530000 e1a05000 0a00004c
9f54 e10f2000 e3823080 e121f003 e5903004 e591100c e0610003 e3500000 a594301c
9f74 a5843014 a5843018 aa000003 e2611001 e1710003 55943018 55843014 e5941014
SP: 0xc2a27e70:
7e70 c2a27e94 c2a27e80 60000013 00000004 c6043430 c0312fb8 ffffffff c2a27edc
7e90 00000000 00000000 c2a27f0c c2a27ea8 c024580c c00221d4 fffffffe bf000b38
7eb0 00000000 00000000 fffffffe 00000000 00000000 00000000 00000000 c2a27f1c
7ed0 c2a27f38 c2a27f0c 000007ff c2a27ef0 c0069f14 bf0000ac a0000013 ffffffff
7ef0 c2a26000 00000000 00000000 c783a2c0 c2a27f7c c2a27f10 bf000170 bf000034
7f10 c024778c bf000b24 c02f201c c6043400 00000017 c02f4e10 c6043400 c02f4f80
7f30 c2a27f54 c2a27f40 c0247814 c0247764 c0312f80 c2a26000 c2a27f9c c2a27f58
7f50 c0243e4c c2988240 c2a26000 bf000114 00000000 00000000 00000000 00000000
FP: 0xc2a27e8c:
7e8c c2a27edc 00000000 00000000 c2a27f0c c2a27ea8 c024580c c00221d4 fffffffe
7eac bf000b38 00000000 00000000 fffffffe 00000000 00000000 00000000 00000000
7ecc c2a27f1c c2a27f38 c2a27f0c 000007ff c2a27ef0 c0069f14 bf0000ac a0000013
7eec ffffffff c2a26000 00000000 00000000 c783a2c0 c2a27f7c c2a27f10 bf000170
7f0c bf000034 c024778c bf000b24 c02f201c c6043400 00000017 c02f4e10 c6043400
7f2c c02f4f80 c2a27f54 c2a27f40 c0247814 c0247764 c0312f80 c2a26000 c2a27f9c
7f4c c2a27f58 c0243e4c c2988240 c2a26000 bf000114 00000000 00000000 00000000
7f6c 00000000 c2a27f9c c2a27f80 c004aaec bf000120 c2988240 c2a26000 c2a27fa4
R9: 0xc2a27e9c:
7e9c c2a27ea8 c024580c c00221d4 fffffffe bf000b38 00000000 00000000 fffffffe
7ebc 00000000 00000000 00000000 00000000 c2a27f1c c2a27f38 c2a27f0c 000007ff
7edc c2a27ef0 c0069f14 bf0000ac a0000013 ffffffff c2a26000 00000000 00000000
7efc c783a2c0 c2a27f7c c2a27f10 bf000170 bf000034 c024778c bf000b24 c02f201c
7f1c c6043400 00000017 c02f4e10 c6043400 c02f4f80 c2a27f54 c2a27f40 c0247814
7f3c c0247764 c0312f80 c2a26000 c2a27f9c c2a27f58 c0243e4c c2988240 c2a26000
7f5c bf000114 00000000 00000000 00000000 00000000 c2a27f9c c2a27f80 c004aaec
7f7c bf000120 c2988240 c2a26000 c2a27fa4 c2988248 c2a27fd4 c2a27fa0 c004b1f0
R10: 0xc2a27eb8:
7eb8 fffffffe 00000000 00000000 00000000 00000000 c2a27f1c c2a27f38 c2a27f0c
7ed8 000007ff c2a27ef0 c0069f14 bf0000ac a0000013 ffffffff c2a26000 00000000
7ef8 00000000 c783a2c0 c2a27f7c c2a27f10 bf000170 bf000034 c024778c bf000b24
7f18 c02f201c c6043400 00000017 c02f4e10 c6043400 c02f4f80 c2a27f54 c2a27f40
7f38 c0247814 c0247764 c0312f80 c2a26000 c2a27f9c c2a27f58 c0243e4c c2988240
7f58 c2a26000 bf000114 00000000 00000000 00000000 00000000 c2a27f9c c2a27f80
7f78 c004aaec bf000120 c2988240 c2a26000 c2a27fa4 c2988248 c2a27fd4 c2a27fa0
7f98 c004b1f0 c004aa38 d0fe328e 00000000 c6043400 c004eecc c2a27fb0 c2a27fb0
Process hiJack-workqueu (pid: 305, stack limit = 0xc2a26268)
Stack: (0xc2a27ef0 to 0xc2a28000)
7ee0: c2a26000 00000000 00000000 c783a2c0
7f00: c2a27f7c c2a27f10 bf000170 bf000034 c024778c bf000b24 c02f201c c6043400
7f20: 00000017 c02f4e10 c6043400 c02f4f80 c2a27f54 c2a27f40 c0247814 c0247764
7f40: c0312f80 c2a26000 c2a27f9c c2a27f58 c0243e4c c2988240 c2a26000 bf000114
7f60: 00000000 00000000 00000000 00000000 c2a27f9c c2a27f80 c004aaec bf000120
7f80: c2988240 c2a26000 c2a27fa4 c2988248 c2a27fd4 c2a27fa0 c004b1f0 c004aa38
7fa0: d0fe328e 00000000 c6043400 c004eecc c2a27fb0 c2a27fb0 c2a26000 c004b0ec
7fc0: c2988240 00000000 c2a27ff4 c2a27fd8 c004e9b0 c004b0f8 00000000 00000000
7fe0: 00000000 00000000 00000000 c2a27ff8 c003da58 c004e964 00000000 0000001b
Backtrace:
[<bf000028>] (readFile+0x0/0xec [hiJack]) from [<bf000170>] (send_answer+0x5c/0x174 [hiJack])
r7:c783a2c0 r6:00000000 r5:00000000 r4:c2a26000
[<bf000114>] (send_answer+0x0/0x174 [hiJack]) from [<c004aaec>] (run_workqueue+0xc0/0x148)
[<c004aa2c>] (run_workqueue+0x0/0x148) from [<c004b1f0>] (worker_thread+0x104/0x118)
r7:c2988248 r6:c2a27fa4 r5:c2a26000 r4:c2988240
[<c004b0ec>] (worker_thread+0x0/0x118) from [<c004e9b0>] (kthread+0x58/0x94)
r7:00000000 r6:c2988240 r5:c004b0ec r4:c2a26000
[<c004e958>] (kthread+0x0/0x94) from [<c003da58>] (do_exit+0x0/0x6e0)
r7:00000000 r6:00000000 r5:00000000 r4:00000000
Code: ee032f10 e1a02007 e1a03fc2 e59f105c (e1c022f0)
Kernel panic - not syncing: Fatal exception
hiJack: Starting LKM!
hiJack: IN Port: 44552
hiJack: Sending answer!
hiJack: Reading queue!
hiJack: Opening File!
Unable to handle kernel paging request at virtual address fffffffe
pgd = c0004000
[fffffffe] *pgd=004a0031, *pte=00000000, *ppte=00000000
Internal error: Oops: 17 [#1]
Modules linked in: hiJack
CPU: 0 Not tainted (2.6.29 #3)
PC is at send_answer+0x5c/0x198 [hiJack]
LR is at call_rcu+0x28/0x48
pc : [<bf00017c>] lr : [<c0069f14>] psr: 20000013
sp : c4ef5f10 ip : 00000000 fp : c4ef5f7c
r10: c4ef5f38 r9 : c4ef5f1c r8 : 00000000
r7 : 00000000 r6 : c28a36a0 r5 : 00000000 r4 : c4ef4000
r3 : 0000000a r2 : c03280b0 r1 : 00002710 r0 : fffffffe
Flags: nzCv IRQs on FIQs on Mode SVC_32 ISA ARM Segment kernel
Control: 00093177 Table: 00d58000 DAC: 00000017
LR: 0xc0069e94:
9e94 e5831000 e121f002 e89da810 c02fd2d8 e1a0c00d e92dd830 e24cb004 e5801004
9eb4 e10f4000 e3843080 e121f003 e59f101c e59f201c ebffffc7 e3140080 0a000001
9ed4 e121f004 e89da830 e121f004 e89da830 c02fd2ec c03280ec e1a0c00d e92dd830
9ef4 e24cb004 e5801004 e10f4000 e3843080 e121f003 e59f101c e59f201c ebffffb5
9f14 e3140080 0a000001 e121f004 e89da830 e121f004 e89da830 c02fd2d8 c03280b0
9f34 e1a0c00d e92dd8f0 e24cb004 e5913010 e1a04001 e3530000 e1a05000 0a00004c
9f54 e10f2000 e3823080 e121f003 e5903004 e591100c e0610003 e3500000 a594301c
9f74 a5843014 a5843018 aa000003 e2611001 e1710003 55943018 55843014 e5941014
SP: 0xc4ef5e90:
5e90 c4ef5ee4 00000001 00000000 c2832ee0 00000000 c28a36a0 ffffffff c4ef5efc
5eb0 c28a36a0 00000000 c4ef5f7c c4ef5ec8 c024580c c00221d4 fffffffe 00002710
5ed0 c03280b0 0000000a c4ef4000 00000000 c28a36a0 00000000 00000000 c4ef5f1c
5ef0 c4ef5f38 c4ef5f7c 00000000 c4ef5f10 c0069f14 bf00017c 20000013 ffffffff
5f10 c024778c bf000b94 c4eb801c c59fa400 00000015 c02f4e10 c59fa400 c5dc8000
5f30 c4ef5f54 c4ef5f40 c0247814 c0247764 c0312f80 c4ef4000 c4ef5f9c c4ef5f58
5f50 c0243e4c c2816d60 c4ef4000 bf000120 00000000 00000000 00000000 00000000
5f70 c4ef5f9c c4ef5f80 c004aaec bf00012c c2816d60 c4ef4000 c4ef5fa4 c2816d68
FP: 0xc4ef5efc:
5efc c4ef5f10 c0069f14 bf00017c 20000013 ffffffff c024778c bf000b94 c4eb801c
5f1c c59fa400 00000015 c02f4e10 c59fa400 c5dc8000 c4ef5f54 c4ef5f40 c0247814
5f3c c0247764 c0312f80 c4ef4000 c4ef5f9c c4ef5f58 c0243e4c c2816d60 c4ef4000
5f5c bf000120 00000000 00000000 00000000 00000000 c4ef5f9c c4ef5f80 c004aaec
5f7c bf00012c c2816d60 c4ef4000 c4ef5fa4 c2816d68 c4ef5fd4 c4ef5fa0 c004b1f0
5f9c c004aa38 455b97e6 00000000 c59fa400 c004eecc c4ef5fb0 c4ef5fb0 c4ef4000
5fbc c004b0ec c2816d60 00000000 c4ef5ff4 c4ef5fd8 c004e9b0 c004b0f8 00000000
5fdc 00000000 00000000 00000000 00000000 c4ef5ff8 c003da58 c004e964 011a5412
R2: 0xc0328030:
8030 00000000 00000000 00000000 00000000 00000000 00000000 00000000 00000000
8050 00000000 00000000 00000000 00000000 00000000 00000000 00000000 00000000
8070 00000000 00000001 00000001 00000000 00000000 00000000 00000000 00000000
8090 00000000 00000000 00000000 00000000 00000000 00000000 00000000 c7810f60
80b0 00000724 00000001 00000000 00000725 c7cbe650 c03280c0 c37cc3c0 c2832ee0
80d0 0000000a 00000000 c03280d4 0000000a 00000000 00000000 00000000 fffffed4
80f0 00000001 00000000 00000000 00000000 c03280fc c03280fc c03280fc 00000000
8110 00000000 c0328110 0000000a 00000000 00000000 00000000 00000000 00008000
R4: 0xc4ef3f80:
3f80 00000008 00000000 44feb4b8 00000000 44feb460 44faefe8 00000000 44fe7fa0
3fa0 00000000 44feb420 006e0061 00000023 4000d1c8 00000000 44faefd0 00000bd7
3fc0 00000000 00000002 00630069 0000001b 4000d520 00000000 00000002 00000000
3fe0 0075005e 00000023 4000de90 00000000 44faefb0 44fec230 00000000 79926933
4000 00000002 00000001 00000000 c59fa400 c02f6d08 00000000 00000017 c0312f80
4020 c4ef4000 00000420 c02f4e10 c59fa400 c6468240 c5dc8000 c4ef5f9c c4ef5f58
4040 c0243e48 00000000 00000000 00000000 00000000 00000000 00000000 00000000
4060 00000000 00000000 00000000 00000000 00000000 00000000 00000000 00000000
R6: 0xc28a3620:
3620 00000000 00000000 00000000 00000000 00000000 00000000 00000000 00000000
3640 00000000 00000000 00000000 c01b4b08 00000000 00000000 00000000 00000000
3660 00000000 00000000 00000000 c2920a23 c2920a40 c2920a00 c2920a23 000000e8
3680 00000001 00000000 00000000 00000000 00000000 00000000 00000000 00000000
36a0 00000000 00000000 c7b89b80 00000000 00000000 00000000 00000000 c3d46b80
36c0 00000000 00000000 00000000 00000000 00000000 00000011 00000000 00000000
36e0 00000000 00000000 00000000 00000000 00000000 00000011 00000000 0000000e
3700 00060024 00000000 0008000d c01b2ef8 00000001 00000000 00000000 00000000
R9: 0xc4ef5e9c:
5e9c c2832ee0 00000000 c28a36a0 ffffffff c4ef5efc c28a36a0 00000000 c4ef5f7c
5ebc c4ef5ec8 c024580c c00221d4 fffffffe 00002710 c03280b0 0000000a c4ef4000
5edc 00000000 c28a36a0 00000000 00000000 c4ef5f1c c4ef5f38 c4ef5f7c 00000000
5efc c4ef5f10 c0069f14 bf00017c 20000013 ffffffff c024778c bf000b94 c4eb801c
5f1c c59fa400 00000015 c02f4e10 c59fa400 c5dc8000 c4ef5f54 c4ef5f40 c0247814
5f3c c0247764 c0312f80 c4ef4000 c4ef5f9c c4ef5f58 c0243e4c c2816d60 c4ef4000
5f5c bf000120 00000000 00000000 00000000 00000000 c4ef5f9c c4ef5f80 c004aaec
5f7c bf00012c c2816d60 c4ef4000 c4ef5fa4 c2816d68 c4ef5fd4 c4ef5fa0 c004b1f0
R10: 0xc4ef5eb8:
5eb8 c4ef5f7c c4ef5ec8 c024580c c00221d4 fffffffe 00002710 c03280b0 0000000a
5ed8 c4ef4000 00000000 c28a36a0 00000000 00000000 c4ef5f1c c4ef5f38 c4ef5f7c
5ef8 00000000 c4ef5f10 c0069f14 bf00017c 20000013 ffffffff c024778c bf000b94
5f18 c4eb801c c59fa400 00000015 c02f4e10 c59fa400 c5dc8000 c4ef5f54 c4ef5f40
5f38 c0247814 c0247764 c0312f80 c4ef4000 c4ef5f9c c4ef5f58 c0243e4c c2816d60
5f58 c4ef4000 bf000120 00000000 00000000 00000000 00000000 c4ef5f9c c4ef5f80
5f78 c004aaec bf00012c c2816d60 c4ef4000 c4ef5fa4 c2816d68 c4ef5fd4 c4ef5fa0
5f98 c004b1f0 c004aa38 455b97e6 00000000 c59fa400 c004eecc c4ef5fb0 c4ef5fb0
Process hiJack-workqueu (pid: 269, stack limit = 0xc4ef4268)
Stack: (0xc4ef5f10 to 0xc4ef6000)
5f00: c024778c bf000b94 c4eb801c c59fa400
5f20: 00000015 c02f4e10 c59fa400 c5dc8000 c4ef5f54 c4ef5f40 c0247814 c0247764
5f40: c0312f80 c4ef4000 c4ef5f9c c4ef5f58 c0243e4c c2816d60 c4ef4000 bf000120
5f60: 00000000 00000000 00000000 00000000 c4ef5f9c c4ef5f80 c004aaec bf00012c
5f80: c2816d60 c4ef4000 c4ef5fa4 c2816d68 c4ef5fd4 c4ef5fa0 c004b1f0 c004aa38
5fa0: 455b97e6 00000000 c59fa400 c004eecc c4ef5fb0 c4ef5fb0 c4ef4000 c004b0ec
5fc0: c2816d60 00000000 c4ef5ff4 c4ef5fd8 c004e9b0 c004b0f8 00000000 00000000
5fe0: 00000000 00000000 00000000 c4ef5ff8 c003da58 c004e964 011a5412 10f80005
Backtrace:
[<bf000120>] (send_answer+0x0/0x198 [hiJack]) from [<c004aaec>] (run_workqueue+0xc0/0x148)
[<c004aa2c>] (run_workqueue+0x0/0x148) from [<c004b1f0>] (worker_thread+0x104/0x118)
r7:c2816d68 r6:c4ef5fa4 r5:c4ef4000 r4:c2816d60
[<c004b0ec>] (worker_thread+0x0/0x118) from [<c004e9b0>] (kthread+0x58/0x94)
r7:00000000 r6:c2816d60 r5:c004b0ec r4:c4ef4000
[<c004e958>] (kthread+0x0/0x94) from [<c003da58>] (do_exit+0x0/0x6e0)
r7:00000000 r6:00000000 r5:00000000 r4:00000000
Code: eb490d30 e1a01005 e59f0124 ebffffaa (e5d03000)
Kernel panic - not syncing: Fatal exception
最佳答案
对以下调用进行一些错误检查是值得的:
phMscd_Filp = filp_open(filename, O_RDONLY, 0);
filp_open()
的返回值应使用
IS_ERR()
进行检查宏。
fs/reiserfs/journal.c
文件:
journal->j_dev_file = filp_open(jdev_name, 0, 0);
if(!IS_ERR(journal->j_dev_file)) {
// snip
} else {
result = PTR_ERR(journal->j_dev_file);
// dump a warning using the return code
}
关于Android 内核模块编程,我们在Stack Overflow上找到一个类似的问题: https://stackoverflow.com/questions/8555456/
我正在尝试打印 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 繁忙状态,恐怕没
我是一名优秀的程序员,十分优秀!