27 #ifndef SANITIZER_NETBSD_SYSCALL_HOOKS_H
28 #define SANITIZER_NETBSD_SYSCALL_HOOKS_H
30 #define __sanitizer_syscall_pre_syscall(code, arg0, arg1, arg2, arg3, arg4, \
32 __sanitizer_syscall_pre_impl_syscall( \
33 (long long)(code), (long long)(arg0), (long long)(arg1), \
34 (long long)(arg2), (long long)(arg3), (long long)(arg4), \
35 (long long)(arg5), (long long)(arg6), (long long)(arg7))
36 #define __sanitizer_syscall_post_syscall(res, code, arg0, arg1, arg2, arg3, \
37 arg4, arg5, arg6, arg7) \
38 __sanitizer_syscall_post_impl_syscall( \
39 res, (long long)(code), (long long)(arg0), (long long)(arg1), \
40 (long long)(arg2), (long long)(arg3), (long long)(arg4), \
41 (long long)(arg5), (long long)(arg6), (long long)(arg7))
42 #define __sanitizer_syscall_pre_exit(rval) \
43 __sanitizer_syscall_pre_impl_exit((long long)(rval))
44 #define __sanitizer_syscall_post_exit(res, rval) \
45 __sanitizer_syscall_post_impl_exit(res, (long long)(rval))
46 #define __sanitizer_syscall_pre_fork() __sanitizer_syscall_pre_impl_fork()
47 #define __sanitizer_syscall_post_fork(res) \
48 __sanitizer_syscall_post_impl_fork(res)
49 #define __sanitizer_syscall_pre_read(fd, buf, nbyte) \
50 __sanitizer_syscall_pre_impl_read((long long)(fd), (long long)(buf), \
52 #define __sanitizer_syscall_post_read(res, fd, buf, nbyte) \
53 __sanitizer_syscall_post_impl_read(res, (long long)(fd), (long long)(buf), \
55 #define __sanitizer_syscall_pre_write(fd, buf, nbyte) \
56 __sanitizer_syscall_pre_impl_write((long long)(fd), (long long)(buf), \
58 #define __sanitizer_syscall_post_write(res, fd, buf, nbyte) \
59 __sanitizer_syscall_post_impl_write(res, (long long)(fd), (long long)(buf), \
61 #define __sanitizer_syscall_pre_open(path, flags, mode) \
62 __sanitizer_syscall_pre_impl_open((long long)(path), (long long)(flags), \
64 #define __sanitizer_syscall_post_open(res, path, flags, mode) \
65 __sanitizer_syscall_post_impl_open(res, (long long)(path), \
66 (long long)(flags), (long long)(mode))
67 #define __sanitizer_syscall_pre_close(fd) \
68 __sanitizer_syscall_pre_impl_close((long long)(fd))
69 #define __sanitizer_syscall_post_close(res, fd) \
70 __sanitizer_syscall_post_impl_close(res, (long long)(fd))
71 #define __sanitizer_syscall_pre_compat_50_wait4(pid, status, options, rusage) \
72 __sanitizer_syscall_pre_impl_compat_50_wait4( \
73 (long long)(pid), (long long)(status), (long long)(options), \
75 #define __sanitizer_syscall_post_compat_50_wait4(res, pid, status, options, \
77 __sanitizer_syscall_post_impl_compat_50_wait4( \
78 res, (long long)(pid), (long long)(status), (long long)(options), \
80 #define __sanitizer_syscall_pre_compat_43_ocreat(path, mode) \
81 __sanitizer_syscall_pre_impl_compat_43_ocreat((long long)(path), \
83 #define __sanitizer_syscall_post_compat_43_ocreat(res, path, mode) \
84 __sanitizer_syscall_post_impl_compat_43_ocreat(res, (long long)(path), \
86 #define __sanitizer_syscall_pre_link(path, link) \
87 __sanitizer_syscall_pre_impl_link((long long)(path), (long long)(link))
88 #define __sanitizer_syscall_post_link(res, path, link) \
89 __sanitizer_syscall_post_impl_link(res, (long long)(path), (long long)(link))
90 #define __sanitizer_syscall_pre_unlink(path) \
91 __sanitizer_syscall_pre_impl_unlink((long long)(path))
92 #define __sanitizer_syscall_post_unlink(res, path) \
93 __sanitizer_syscall_post_impl_unlink(res, (long long)(path))
95 #define __sanitizer_syscall_pre_chdir(path) \
96 __sanitizer_syscall_pre_impl_chdir((long long)(path))
97 #define __sanitizer_syscall_post_chdir(res, path) \
98 __sanitizer_syscall_post_impl_chdir(res, (long long)(path))
99 #define __sanitizer_syscall_pre_fchdir(fd) \
100 __sanitizer_syscall_pre_impl_fchdir((long long)(fd))
101 #define __sanitizer_syscall_post_fchdir(res, fd) \
102 __sanitizer_syscall_post_impl_fchdir(res, (long long)(fd))
103 #define __sanitizer_syscall_pre_compat_50_mknod(path, mode, dev) \
104 __sanitizer_syscall_pre_impl_compat_50_mknod( \
105 (long long)(path), (long long)(mode), (long long)(dev))
106 #define __sanitizer_syscall_post_compat_50_mknod(res, path, mode, dev) \
107 __sanitizer_syscall_post_impl_compat_50_mknod( \
108 res, (long long)(path), (long long)(mode), (long long)(dev))
109 #define __sanitizer_syscall_pre_chmod(path, mode) \
110 __sanitizer_syscall_pre_impl_chmod((long long)(path), (long long)(mode))
111 #define __sanitizer_syscall_post_chmod(res, path, mode) \
112 __sanitizer_syscall_post_impl_chmod(res, (long long)(path), (long long)(mode))
113 #define __sanitizer_syscall_pre_chown(path, uid, gid) \
114 __sanitizer_syscall_pre_impl_chown((long long)(path), (long long)(uid), \
116 #define __sanitizer_syscall_post_chown(res, path, uid, gid) \
117 __sanitizer_syscall_post_impl_chown(res, (long long)(path), \
118 (long long)(uid), (long long)(gid))
119 #define __sanitizer_syscall_pre_break(nsize) \
120 __sanitizer_syscall_pre_impl_break((long long)(nsize))
121 #define __sanitizer_syscall_post_break(res, nsize) \
122 __sanitizer_syscall_post_impl_break(res, (long long)(nsize))
123 #define __sanitizer_syscall_pre_compat_20_getfsstat(buf, bufsize, flags) \
124 __sanitizer_syscall_pre_impl_compat_20_getfsstat( \
125 (long long)(buf), (long long)(bufsize), (long long)(flags))
126 #define __sanitizer_syscall_post_compat_20_getfsstat(res, buf, bufsize, flags) \
127 __sanitizer_syscall_post_impl_compat_20_getfsstat( \
128 res, (long long)(buf), (long long)(bufsize), (long long)(flags))
129 #define __sanitizer_syscall_pre_compat_43_olseek(fd, offset, whence) \
130 __sanitizer_syscall_pre_impl_compat_43_olseek( \
131 (long long)(fd), (long long)(offset), (long long)(whence))
132 #define __sanitizer_syscall_post_compat_43_olseek(res, fd, offset, whence) \
133 __sanitizer_syscall_post_impl_compat_43_olseek( \
134 res, (long long)(fd), (long long)(offset), (long long)(whence))
135 #define __sanitizer_syscall_pre_getpid() __sanitizer_syscall_pre_impl_getpid()
136 #define __sanitizer_syscall_post_getpid(res) \
137 __sanitizer_syscall_post_impl_getpid(res)
138 #define __sanitizer_syscall_pre_compat_40_mount(type, path, flags, data) \
139 __sanitizer_syscall_pre_impl_compat_40_mount( \
140 (long long)(type), (long long)(path), (long long)(flags), \
142 #define __sanitizer_syscall_post_compat_40_mount(res, type, path, flags, data) \
143 __sanitizer_syscall_post_impl_compat_40_mount( \
144 res, (long long)(type), (long long)(path), (long long)(flags), \
146 #define __sanitizer_syscall_pre_unmount(path, flags) \
147 __sanitizer_syscall_pre_impl_unmount((long long)(path), (long long)(flags))
148 #define __sanitizer_syscall_post_unmount(res, path, flags) \
149 __sanitizer_syscall_post_impl_unmount(res, (long long)(path), \
151 #define __sanitizer_syscall_pre_setuid(uid) \
152 __sanitizer_syscall_pre_impl_setuid((long long)(uid))
153 #define __sanitizer_syscall_post_setuid(res, uid) \
154 __sanitizer_syscall_post_impl_setuid(res, (long long)(uid))
155 #define __sanitizer_syscall_pre_getuid() __sanitizer_syscall_pre_impl_getuid()
156 #define __sanitizer_syscall_post_getuid(res) \
157 __sanitizer_syscall_post_impl_getuid(res)
158 #define __sanitizer_syscall_pre_geteuid() __sanitizer_syscall_pre_impl_geteuid()
159 #define __sanitizer_syscall_post_geteuid(res) \
160 __sanitizer_syscall_post_impl_geteuid(res)
161 #define __sanitizer_syscall_pre_ptrace(req, pid, addr, data) \
162 __sanitizer_syscall_pre_impl_ptrace((long long)(req), (long long)(pid), \
163 (long long)(addr), (long long)(data))
164 #define __sanitizer_syscall_post_ptrace(res, req, pid, addr, data) \
165 __sanitizer_syscall_post_impl_ptrace(res, (long long)(req), \
166 (long long)(pid), (long long)(addr), \
168 #define __sanitizer_syscall_pre_recvmsg(s, msg, flags) \
169 __sanitizer_syscall_pre_impl_recvmsg((long long)(s), (long long)(msg), \
171 #define __sanitizer_syscall_post_recvmsg(res, s, msg, flags) \
172 __sanitizer_syscall_post_impl_recvmsg(res, (long long)(s), (long long)(msg), \
174 #define __sanitizer_syscall_pre_sendmsg(s, msg, flags) \
175 __sanitizer_syscall_pre_impl_sendmsg((long long)(s), (long long)(msg), \
177 #define __sanitizer_syscall_post_sendmsg(res, s, msg, flags) \
178 __sanitizer_syscall_post_impl_sendmsg(res, (long long)(s), (long long)(msg), \
180 #define __sanitizer_syscall_pre_recvfrom(s, buf, len, flags, from, \
182 __sanitizer_syscall_pre_impl_recvfrom( \
183 (long long)(s), (long long)(buf), (long long)(len), (long long)(flags), \
184 (long long)(from), (long long)(fromlenaddr))
185 #define __sanitizer_syscall_post_recvfrom(res, s, buf, len, flags, from, \
187 __sanitizer_syscall_post_impl_recvfrom( \
188 res, (long long)(s), (long long)(buf), (long long)(len), \
189 (long long)(flags), (long long)(from), (long long)(fromlenaddr))
190 #define __sanitizer_syscall_pre_accept(s, name, anamelen) \
191 __sanitizer_syscall_pre_impl_accept((long long)(s), (long long)(name), \
192 (long long)(anamelen))
193 #define __sanitizer_syscall_post_accept(res, s, name, anamelen) \
194 __sanitizer_syscall_post_impl_accept(res, (long long)(s), (long long)(name), \
195 (long long)(anamelen))
196 #define __sanitizer_syscall_pre_getpeername(fdes, asa, alen) \
197 __sanitizer_syscall_pre_impl_getpeername( \
198 (long long)(fdes), (long long)(asa), (long long)(alen))
199 #define __sanitizer_syscall_post_getpeername(res, fdes, asa, alen) \
200 __sanitizer_syscall_post_impl_getpeername( \
201 res, (long long)(fdes), (long long)(asa), (long long)(alen))
202 #define __sanitizer_syscall_pre_getsockname(fdes, asa, alen) \
203 __sanitizer_syscall_pre_impl_getsockname( \
204 (long long)(fdes), (long long)(asa), (long long)(alen))
205 #define __sanitizer_syscall_post_getsockname(res, fdes, asa, alen) \
206 __sanitizer_syscall_post_impl_getsockname( \
207 res, (long long)(fdes), (long long)(asa), (long long)(alen))
208 #define __sanitizer_syscall_pre_access(path, flags) \
209 __sanitizer_syscall_pre_impl_access((long long)(path), (long long)(flags))
210 #define __sanitizer_syscall_post_access(res, path, flags) \
211 __sanitizer_syscall_post_impl_access(res, (long long)(path), \
213 #define __sanitizer_syscall_pre_chflags(path, flags) \
214 __sanitizer_syscall_pre_impl_chflags((long long)(path), (long long)(flags))
215 #define __sanitizer_syscall_post_chflags(res, path, flags) \
216 __sanitizer_syscall_post_impl_chflags(res, (long long)(path), \
218 #define __sanitizer_syscall_pre_fchflags(fd, flags) \
219 __sanitizer_syscall_pre_impl_fchflags((long long)(fd), (long long)(flags))
220 #define __sanitizer_syscall_post_fchflags(res, fd, flags) \
221 __sanitizer_syscall_post_impl_fchflags(res, (long long)(fd), \
223 #define __sanitizer_syscall_pre_sync() __sanitizer_syscall_pre_impl_sync()
224 #define __sanitizer_syscall_post_sync(res) \
225 __sanitizer_syscall_post_impl_sync(res)
226 #define __sanitizer_syscall_pre_kill(pid, signum) \
227 __sanitizer_syscall_pre_impl_kill((long long)(pid), (long long)(signum))
228 #define __sanitizer_syscall_post_kill(res, pid, signum) \
229 __sanitizer_syscall_post_impl_kill(res, (long long)(pid), (long long)(signum))
230 #define __sanitizer_syscall_pre_compat_43_stat43(path, ub) \
231 __sanitizer_syscall_pre_impl_compat_43_stat43((long long)(path), \
233 #define __sanitizer_syscall_post_compat_43_stat43(res, path, ub) \
234 __sanitizer_syscall_post_impl_compat_43_stat43(res, (long long)(path), \
236 #define __sanitizer_syscall_pre_getppid() __sanitizer_syscall_pre_impl_getppid()
237 #define __sanitizer_syscall_post_getppid(res) \
238 __sanitizer_syscall_post_impl_getppid(res)
239 #define __sanitizer_syscall_pre_compat_43_lstat43(path, ub) \
240 __sanitizer_syscall_pre_impl_compat_43_lstat43((long long)(path), \
242 #define __sanitizer_syscall_post_compat_43_lstat43(res, path, ub) \
243 __sanitizer_syscall_post_impl_compat_43_lstat43(res, (long long)(path), \
245 #define __sanitizer_syscall_pre_dup(fd) \
246 __sanitizer_syscall_pre_impl_dup((long long)(fd))
247 #define __sanitizer_syscall_post_dup(res, fd) \
248 __sanitizer_syscall_post_impl_dup(res, (long long)(fd))
249 #define __sanitizer_syscall_pre_pipe() __sanitizer_syscall_pre_impl_pipe()
250 #define __sanitizer_syscall_post_pipe(res) \
251 __sanitizer_syscall_post_impl_pipe(res)
252 #define __sanitizer_syscall_pre_getegid() __sanitizer_syscall_pre_impl_getegid()
253 #define __sanitizer_syscall_post_getegid(res) \
254 __sanitizer_syscall_post_impl_getegid(res)
255 #define __sanitizer_syscall_pre_profil(samples, size, offset, scale) \
256 __sanitizer_syscall_pre_impl_profil((long long)(samples), (long long)(size), \
257 (long long)(offset), (long long)(scale))
258 #define __sanitizer_syscall_post_profil(res, samples, size, offset, scale) \
259 __sanitizer_syscall_post_impl_profil(res, (long long)(samples), \
260 (long long)(size), (long long)(offset), \
262 #define __sanitizer_syscall_pre_ktrace(fname, ops, facs, pid) \
263 __sanitizer_syscall_pre_impl_ktrace((long long)(fname), (long long)(ops), \
264 (long long)(facs), (long long)(pid))
265 #define __sanitizer_syscall_post_ktrace(res, fname, ops, facs, pid) \
266 __sanitizer_syscall_post_impl_ktrace(res, (long long)(fname), \
267 (long long)(ops), (long long)(facs), \
269 #define __sanitizer_syscall_pre_compat_13_sigaction13(signum, nsa, osa) \
270 __sanitizer_syscall_pre_impl_compat_13_sigaction13( \
271 (long long)(signum), (long long)(nsa), (long long)(osa))
272 #define __sanitizer_syscall_post_compat_13_sigaction13(res, signum, nsa, osa) \
273 __sanitizer_syscall_post_impl_compat_13_sigaction13( \
274 res, (long long)(signum), (long long)(nsa), (long long)(osa))
275 #define __sanitizer_syscall_pre_getgid() __sanitizer_syscall_pre_impl_getgid()
276 #define __sanitizer_syscall_post_getgid(res) \
277 __sanitizer_syscall_post_impl_getgid(res)
278 #define __sanitizer_syscall_pre_compat_13_sigprocmask13(how, mask) \
279 __sanitizer_syscall_pre_impl_compat_13_sigprocmask13((long long)(how), \
281 #define __sanitizer_syscall_post_compat_13_sigprocmask13(res, how, mask) \
282 __sanitizer_syscall_post_impl_compat_13_sigprocmask13(res, (long long)(how), \
284 #define __sanitizer_syscall_pre___getlogin(namebuf, namelen) \
285 __sanitizer_syscall_pre_impl___getlogin((long long)(namebuf), \
286 (long long)(namelen))
287 #define __sanitizer_syscall_post___getlogin(res, namebuf, namelen) \
288 __sanitizer_syscall_post_impl___getlogin(res, (long long)(namebuf), \
289 (long long)(namelen))
290 #define __sanitizer_syscall_pre___setlogin(namebuf) \
291 __sanitizer_syscall_pre_impl___setlogin((long long)(namebuf))
292 #define __sanitizer_syscall_post___setlogin(res, namebuf) \
293 __sanitizer_syscall_post_impl___setlogin(res, (long long)(namebuf))
294 #define __sanitizer_syscall_pre_acct(path) \
295 __sanitizer_syscall_pre_impl_acct((long long)(path))
296 #define __sanitizer_syscall_post_acct(res, path) \
297 __sanitizer_syscall_post_impl_acct(res, (long long)(path))
298 #define __sanitizer_syscall_pre_compat_13_sigpending13() \
299 __sanitizer_syscall_pre_impl_compat_13_sigpending13()
300 #define __sanitizer_syscall_post_compat_13_sigpending13(res) \
301 __sanitizer_syscall_post_impl_compat_13_sigpending13(res)
302 #define __sanitizer_syscall_pre_compat_13_sigaltstack13(nss, oss) \
303 __sanitizer_syscall_pre_impl_compat_13_sigaltstack13((long long)(nss), \
305 #define __sanitizer_syscall_post_compat_13_sigaltstack13(res, nss, oss) \
306 __sanitizer_syscall_post_impl_compat_13_sigaltstack13(res, (long long)(nss), \
308 #define __sanitizer_syscall_pre_ioctl(fd, com, data) \
309 __sanitizer_syscall_pre_impl_ioctl((long long)(fd), (long long)(com), \
311 #define __sanitizer_syscall_post_ioctl(res, fd, com, data) \
312 __sanitizer_syscall_post_impl_ioctl(res, (long long)(fd), (long long)(com), \
314 #define __sanitizer_syscall_pre_compat_12_oreboot(opt) \
315 __sanitizer_syscall_pre_impl_compat_12_oreboot((long long)(opt))
316 #define __sanitizer_syscall_post_compat_12_oreboot(res, opt) \
317 __sanitizer_syscall_post_impl_compat_12_oreboot(res, (long long)(opt))
318 #define __sanitizer_syscall_pre_revoke(path) \
319 __sanitizer_syscall_pre_impl_revoke((long long)(path))
320 #define __sanitizer_syscall_post_revoke(res, path) \
321 __sanitizer_syscall_post_impl_revoke(res, (long long)(path))
322 #define __sanitizer_syscall_pre_symlink(path, link) \
323 __sanitizer_syscall_pre_impl_symlink((long long)(path), (long long)(link))
324 #define __sanitizer_syscall_post_symlink(res, path, link) \
325 __sanitizer_syscall_post_impl_symlink(res, (long long)(path), \
327 #define __sanitizer_syscall_pre_readlink(path, buf, count) \
328 __sanitizer_syscall_pre_impl_readlink((long long)(path), (long long)(buf), \
330 #define __sanitizer_syscall_post_readlink(res, path, buf, count) \
331 __sanitizer_syscall_post_impl_readlink(res, (long long)(path), \
332 (long long)(buf), (long long)(count))
333 #define __sanitizer_syscall_pre_execve(path, argp, envp) \
334 __sanitizer_syscall_pre_impl_execve((long long)(path), (long long)(argp), \
336 #define __sanitizer_syscall_post_execve(res, path, argp, envp) \
337 __sanitizer_syscall_post_impl_execve(res, (long long)(path), \
338 (long long)(argp), (long long)(envp))
339 #define __sanitizer_syscall_pre_umask(newmask) \
340 __sanitizer_syscall_pre_impl_umask((long long)(newmask))
341 #define __sanitizer_syscall_post_umask(res, newmask) \
342 __sanitizer_syscall_post_impl_umask(res, (long long)(newmask))
343 #define __sanitizer_syscall_pre_chroot(path) \
344 __sanitizer_syscall_pre_impl_chroot((long long)(path))
345 #define __sanitizer_syscall_post_chroot(res, path) \
346 __sanitizer_syscall_post_impl_chroot(res, (long long)(path))
347 #define __sanitizer_syscall_pre_compat_43_fstat43(fd, sb) \
348 __sanitizer_syscall_pre_impl_compat_43_fstat43((long long)(fd), \
350 #define __sanitizer_syscall_post_compat_43_fstat43(res, fd, sb) \
351 __sanitizer_syscall_post_impl_compat_43_fstat43(res, (long long)(fd), \
353 #define __sanitizer_syscall_pre_compat_43_ogetkerninfo(op, where, size, arg) \
354 __sanitizer_syscall_pre_impl_compat_43_ogetkerninfo( \
355 (long long)(op), (long long)(where), (long long)(size), \
357 #define __sanitizer_syscall_post_compat_43_ogetkerninfo(res, op, where, size, \
359 __sanitizer_syscall_post_impl_compat_43_ogetkerninfo( \
360 res, (long long)(op), (long long)(where), (long long)(size), \
362 #define __sanitizer_syscall_pre_compat_43_ogetpagesize() \
363 __sanitizer_syscall_pre_impl_compat_43_ogetpagesize()
364 #define __sanitizer_syscall_post_compat_43_ogetpagesize(res) \
365 __sanitizer_syscall_post_impl_compat_43_ogetpagesize(res)
366 #define __sanitizer_syscall_pre_compat_12_msync(addr, len) \
367 __sanitizer_syscall_pre_impl_compat_12_msync((long long)(addr), \
369 #define __sanitizer_syscall_post_compat_12_msync(res, addr, len) \
370 __sanitizer_syscall_post_impl_compat_12_msync(res, (long long)(addr), \
372 #define __sanitizer_syscall_pre_vfork() __sanitizer_syscall_pre_impl_vfork()
373 #define __sanitizer_syscall_post_vfork(res) \
374 __sanitizer_syscall_post_impl_vfork(res)
379 #define __sanitizer_syscall_pre_compat_43_ommap(addr, len, prot, flags, fd, \
381 __sanitizer_syscall_pre_impl_compat_43_ommap( \
382 (long long)(addr), (long long)(len), (long long)(prot), \
383 (long long)(flags), (long long)(fd), (long long)(pos))
384 #define __sanitizer_syscall_post_compat_43_ommap(res, addr, len, prot, flags, \
386 __sanitizer_syscall_post_impl_compat_43_ommap( \
387 res, (long long)(addr), (long long)(len), (long long)(prot), \
388 (long long)(flags), (long long)(fd), (long long)(pos))
389 #define __sanitizer_syscall_pre_vadvise(anom) \
390 __sanitizer_syscall_pre_impl_vadvise((long long)(anom))
391 #define __sanitizer_syscall_post_vadvise(res, anom) \
392 __sanitizer_syscall_post_impl_vadvise(res, (long long)(anom))
393 #define __sanitizer_syscall_pre_munmap(addr, len) \
394 __sanitizer_syscall_pre_impl_munmap((long long)(addr), (long long)(len))
395 #define __sanitizer_syscall_post_munmap(res, addr, len) \
396 __sanitizer_syscall_post_impl_munmap(res, (long long)(addr), (long long)(len))
397 #define __sanitizer_syscall_pre_mprotect(addr, len, prot) \
398 __sanitizer_syscall_pre_impl_mprotect((long long)(addr), (long long)(len), \
400 #define __sanitizer_syscall_post_mprotect(res, addr, len, prot) \
401 __sanitizer_syscall_post_impl_mprotect(res, (long long)(addr), \
402 (long long)(len), (long long)(prot))
403 #define __sanitizer_syscall_pre_madvise(addr, len, behav) \
404 __sanitizer_syscall_pre_impl_madvise((long long)(addr), (long long)(len), \
406 #define __sanitizer_syscall_post_madvise(res, addr, len, behav) \
407 __sanitizer_syscall_post_impl_madvise(res, (long long)(addr), \
408 (long long)(len), (long long)(behav))
411 #define __sanitizer_syscall_pre_mincore(addr, len, vec) \
412 __sanitizer_syscall_pre_impl_mincore((long long)(addr), (long long)(len), \
414 #define __sanitizer_syscall_post_mincore(res, addr, len, vec) \
415 __sanitizer_syscall_post_impl_mincore(res, (long long)(addr), \
416 (long long)(len), (long long)(vec))
417 #define __sanitizer_syscall_pre_getgroups(gidsetsize, gidset) \
418 __sanitizer_syscall_pre_impl_getgroups((long long)(gidsetsize), \
420 #define __sanitizer_syscall_post_getgroups(res, gidsetsize, gidset) \
421 __sanitizer_syscall_post_impl_getgroups(res, (long long)(gidsetsize), \
423 #define __sanitizer_syscall_pre_setgroups(gidsetsize, gidset) \
424 __sanitizer_syscall_pre_impl_setgroups((long long)(gidsetsize), \
426 #define __sanitizer_syscall_post_setgroups(res, gidsetsize, gidset) \
427 __sanitizer_syscall_post_impl_setgroups(res, (long long)(gidsetsize), \
429 #define __sanitizer_syscall_pre_getpgrp() __sanitizer_syscall_pre_impl_getpgrp()
430 #define __sanitizer_syscall_post_getpgrp(res) \
431 __sanitizer_syscall_post_impl_getpgrp(res)
432 #define __sanitizer_syscall_pre_setpgid(pid, pgid) \
433 __sanitizer_syscall_pre_impl_setpgid((long long)(pid), (long long)(pgid))
434 #define __sanitizer_syscall_post_setpgid(res, pid, pgid) \
435 __sanitizer_syscall_post_impl_setpgid(res, (long long)(pid), \
437 #define __sanitizer_syscall_pre_compat_50_setitimer(which, itv, oitv) \
438 __sanitizer_syscall_pre_impl_compat_50_setitimer( \
439 (long long)(which), (long long)(itv), (long long)(oitv))
440 #define __sanitizer_syscall_post_compat_50_setitimer(res, which, itv, oitv) \
441 __sanitizer_syscall_post_impl_compat_50_setitimer( \
442 res, (long long)(which), (long long)(itv), (long long)(oitv))
443 #define __sanitizer_syscall_pre_compat_43_owait() \
444 __sanitizer_syscall_pre_impl_compat_43_owait()
445 #define __sanitizer_syscall_post_compat_43_owait(res) \
446 __sanitizer_syscall_post_impl_compat_43_owait(res)
447 #define __sanitizer_syscall_pre_compat_12_oswapon(name) \
448 __sanitizer_syscall_pre_impl_compat_12_oswapon((long long)(name))
449 #define __sanitizer_syscall_post_compat_12_oswapon(res, name) \
450 __sanitizer_syscall_post_impl_compat_12_oswapon(res, (long long)(name))
451 #define __sanitizer_syscall_pre_compat_50_getitimer(which, itv) \
452 __sanitizer_syscall_pre_impl_compat_50_getitimer((long long)(which), \
454 #define __sanitizer_syscall_post_compat_50_getitimer(res, which, itv) \
455 __sanitizer_syscall_post_impl_compat_50_getitimer(res, (long long)(which), \
457 #define __sanitizer_syscall_pre_compat_43_ogethostname(hostname, len) \
458 __sanitizer_syscall_pre_impl_compat_43_ogethostname((long long)(hostname), \
460 #define __sanitizer_syscall_post_compat_43_ogethostname(res, hostname, len) \
461 __sanitizer_syscall_post_impl_compat_43_ogethostname( \
462 res, (long long)(hostname), (long long)(len))
463 #define __sanitizer_syscall_pre_compat_43_osethostname(hostname, len) \
464 __sanitizer_syscall_pre_impl_compat_43_osethostname((long long)(hostname), \
466 #define __sanitizer_syscall_post_compat_43_osethostname(res, hostname, len) \
467 __sanitizer_syscall_post_impl_compat_43_osethostname( \
468 res, (long long)(hostname), (long long)(len))
469 #define __sanitizer_syscall_pre_compat_43_ogetdtablesize() \
470 __sanitizer_syscall_pre_impl_compat_43_ogetdtablesize()
471 #define __sanitizer_syscall_post_compat_43_ogetdtablesize(res) \
472 __sanitizer_syscall_post_impl_compat_43_ogetdtablesize(res)
473 #define __sanitizer_syscall_pre_dup2(from, to) \
474 __sanitizer_syscall_pre_impl_dup2((long long)(from), (long long)(to))
475 #define __sanitizer_syscall_post_dup2(res, from, to) \
476 __sanitizer_syscall_post_impl_dup2(res, (long long)(from), (long long)(to))
478 #define __sanitizer_syscall_pre_fcntl(fd, cmd, arg) \
479 __sanitizer_syscall_pre_impl_fcntl((long long)(fd), (long long)(cmd), \
481 #define __sanitizer_syscall_post_fcntl(res, fd, cmd, arg) \
482 __sanitizer_syscall_post_impl_fcntl(res, (long long)(fd), (long long)(cmd), \
484 #define __sanitizer_syscall_pre_compat_50_select(nd, in, ou, ex, tv) \
485 __sanitizer_syscall_pre_impl_compat_50_select( \
486 (long long)(nd), (long long)(in), (long long)(ou), (long long)(ex), \
488 #define __sanitizer_syscall_post_compat_50_select(res, nd, in, ou, ex, tv) \
489 __sanitizer_syscall_post_impl_compat_50_select( \
490 res, (long long)(nd), (long long)(in), (long long)(ou), (long long)(ex), \
493 #define __sanitizer_syscall_pre_fsync(fd) \
494 __sanitizer_syscall_pre_impl_fsync((long long)(fd))
495 #define __sanitizer_syscall_post_fsync(res, fd) \
496 __sanitizer_syscall_post_impl_fsync(res, (long long)(fd))
497 #define __sanitizer_syscall_pre_setpriority(which, who, prio) \
498 __sanitizer_syscall_pre_impl_setpriority( \
499 (long long)(which), (long long)(who), (long long)(prio))
500 #define __sanitizer_syscall_post_setpriority(res, which, who, prio) \
501 __sanitizer_syscall_post_impl_setpriority( \
502 res, (long long)(which), (long long)(who), (long long)(prio))
503 #define __sanitizer_syscall_pre_compat_30_socket(domain, type, protocol) \
504 __sanitizer_syscall_pre_impl_compat_30_socket( \
505 (long long)(domain), (long long)(type), (long long)(protocol))
506 #define __sanitizer_syscall_post_compat_30_socket(res, domain, type, protocol) \
507 __sanitizer_syscall_post_impl_compat_30_socket( \
508 res, (long long)(domain), (long long)(type), (long long)(protocol))
509 #define __sanitizer_syscall_pre_connect(s, name, namelen) \
510 __sanitizer_syscall_pre_impl_connect((long long)(s), (long long)(name), \
511 (long long)(namelen))
512 #define __sanitizer_syscall_post_connect(res, s, name, namelen) \
513 __sanitizer_syscall_post_impl_connect( \
514 res, (long long)(s), (long long)(name), (long long)(namelen))
515 #define __sanitizer_syscall_pre_compat_43_oaccept(s, name, anamelen) \
516 __sanitizer_syscall_pre_impl_compat_43_oaccept( \
517 (long long)(s), (long long)(name), (long long)(anamelen))
518 #define __sanitizer_syscall_post_compat_43_oaccept(res, s, name, anamelen) \
519 __sanitizer_syscall_post_impl_compat_43_oaccept( \
520 res, (long long)(s), (long long)(name), (long long)(anamelen))
521 #define __sanitizer_syscall_pre_getpriority(which, who) \
522 __sanitizer_syscall_pre_impl_getpriority((long long)(which), (long long)(who))
523 #define __sanitizer_syscall_post_getpriority(res, which, who) \
524 __sanitizer_syscall_post_impl_getpriority(res, (long long)(which), \
526 #define __sanitizer_syscall_pre_compat_43_osend(s, buf, len, flags) \
527 __sanitizer_syscall_pre_impl_compat_43_osend( \
528 (long long)(s), (long long)(buf), (long long)(len), (long long)(flags))
529 #define __sanitizer_syscall_post_compat_43_osend(res, s, buf, len, flags) \
530 __sanitizer_syscall_post_impl_compat_43_osend( \
531 res, (long long)(s), (long long)(buf), (long long)(len), \
533 #define __sanitizer_syscall_pre_compat_43_orecv(s, buf, len, flags) \
534 __sanitizer_syscall_pre_impl_compat_43_orecv( \
535 (long long)(s), (long long)(buf), (long long)(len), (long long)(flags))
536 #define __sanitizer_syscall_post_compat_43_orecv(res, s, buf, len, flags) \
537 __sanitizer_syscall_post_impl_compat_43_orecv( \
538 res, (long long)(s), (long long)(buf), (long long)(len), \
540 #define __sanitizer_syscall_pre_compat_13_sigreturn13(sigcntxp) \
541 __sanitizer_syscall_pre_impl_compat_13_sigreturn13((long long)(sigcntxp))
542 #define __sanitizer_syscall_post_compat_13_sigreturn13(res, sigcntxp) \
543 __sanitizer_syscall_post_impl_compat_13_sigreturn13(res, \
544 (long long)(sigcntxp))
545 #define __sanitizer_syscall_pre_bind(s, name, namelen) \
546 __sanitizer_syscall_pre_impl_bind((long long)(s), (long long)(name), \
547 (long long)(namelen))
548 #define __sanitizer_syscall_post_bind(res, s, name, namelen) \
549 __sanitizer_syscall_post_impl_bind(res, (long long)(s), (long long)(name), \
550 (long long)(namelen))
551 #define __sanitizer_syscall_pre_setsockopt(s, level, name, val, valsize) \
552 __sanitizer_syscall_pre_impl_setsockopt((long long)(s), (long long)(level), \
553 (long long)(name), (long long)(val), \
554 (long long)(valsize))
555 #define __sanitizer_syscall_post_setsockopt(res, s, level, name, val, valsize) \
556 __sanitizer_syscall_post_impl_setsockopt( \
557 res, (long long)(s), (long long)(level), (long long)(name), \
558 (long long)(val), (long long)(valsize))
559 #define __sanitizer_syscall_pre_listen(s, backlog) \
560 __sanitizer_syscall_pre_impl_listen((long long)(s), (long long)(backlog))
561 #define __sanitizer_syscall_post_listen(res, s, backlog) \
562 __sanitizer_syscall_post_impl_listen(res, (long long)(s), \
563 (long long)(backlog))
565 #define __sanitizer_syscall_pre_compat_43_osigvec(signum, nsv, osv) \
566 __sanitizer_syscall_pre_impl_compat_43_osigvec( \
567 (long long)(signum), (long long)(nsv), (long long)(osv))
568 #define __sanitizer_syscall_post_compat_43_osigvec(res, signum, nsv, osv) \
569 __sanitizer_syscall_post_impl_compat_43_osigvec( \
570 res, (long long)(signum), (long long)(nsv), (long long)(osv))
571 #define __sanitizer_syscall_pre_compat_43_osigblock(mask) \
572 __sanitizer_syscall_pre_impl_compat_43_osigblock((long long)(mask))
573 #define __sanitizer_syscall_post_compat_43_osigblock(res, mask) \
574 __sanitizer_syscall_post_impl_compat_43_osigblock(res, (long long)(mask))
575 #define __sanitizer_syscall_pre_compat_43_osigsetmask(mask) \
576 __sanitizer_syscall_pre_impl_compat_43_osigsetmask((long long)(mask))
577 #define __sanitizer_syscall_post_compat_43_osigsetmask(res, mask) \
578 __sanitizer_syscall_post_impl_compat_43_osigsetmask(res, (long long)(mask))
579 #define __sanitizer_syscall_pre_compat_13_sigsuspend13(mask) \
580 __sanitizer_syscall_pre_impl_compat_13_sigsuspend13((long long)(mask))
581 #define __sanitizer_syscall_post_compat_13_sigsuspend13(res, mask) \
582 __sanitizer_syscall_post_impl_compat_13_sigsuspend13(res, (long long)(mask))
583 #define __sanitizer_syscall_pre_compat_43_osigstack(nss, oss) \
584 __sanitizer_syscall_pre_impl_compat_43_osigstack((long long)(nss), \
586 #define __sanitizer_syscall_post_compat_43_osigstack(res, nss, oss) \
587 __sanitizer_syscall_post_impl_compat_43_osigstack(res, (long long)(nss), \
589 #define __sanitizer_syscall_pre_compat_43_orecvmsg(s, msg, flags) \
590 __sanitizer_syscall_pre_impl_compat_43_orecvmsg( \
591 (long long)(s), (long long)(msg), (long long)(flags))
592 #define __sanitizer_syscall_post_compat_43_orecvmsg(res, s, msg, flags) \
593 __sanitizer_syscall_post_impl_compat_43_orecvmsg( \
594 res, (long long)(s), (long long)(msg), (long long)(flags))
595 #define __sanitizer_syscall_pre_compat_43_osendmsg(s, msg, flags) \
596 __sanitizer_syscall_pre_impl_compat_43_osendmsg( \
597 (long long)(s), (long long)(msg), (long long)(flags))
598 #define __sanitizer_syscall_post_compat_43_osendmsg(res, s, msg, flags) \
599 __sanitizer_syscall_post_impl_compat_43_osendmsg( \
600 res, (long long)(s), (long long)(msg), (long long)(flags))
602 #define __sanitizer_syscall_pre_compat_50_gettimeofday(tp, tzp) \
603 __sanitizer_syscall_pre_impl_compat_50_gettimeofday((long long)(tp), \
605 #define __sanitizer_syscall_post_compat_50_gettimeofday(res, tp, tzp) \
606 __sanitizer_syscall_post_impl_compat_50_gettimeofday(res, (long long)(tp), \
608 #define __sanitizer_syscall_pre_compat_50_getrusage(who, rusage) \
609 __sanitizer_syscall_pre_impl_compat_50_getrusage((long long)(who), \
611 #define __sanitizer_syscall_post_compat_50_getrusage(res, who, rusage) \
612 __sanitizer_syscall_post_impl_compat_50_getrusage(res, (long long)(who), \
614 #define __sanitizer_syscall_pre_getsockopt(s, level, name, val, avalsize) \
615 __sanitizer_syscall_pre_impl_getsockopt((long long)(s), (long long)(level), \
616 (long long)(name), (long long)(val), \
617 (long long)(avalsize))
618 #define __sanitizer_syscall_post_getsockopt(res, s, level, name, val, \
620 __sanitizer_syscall_post_impl_getsockopt( \
621 res, (long long)(s), (long long)(level), (long long)(name), \
622 (long long)(val), (long long)(avalsize))
624 #define __sanitizer_syscall_pre_readv(fd, iovp, iovcnt) \
625 __sanitizer_syscall_pre_impl_readv((long long)(fd), (long long)(iovp), \
627 #define __sanitizer_syscall_post_readv(res, fd, iovp, iovcnt) \
628 __sanitizer_syscall_post_impl_readv(res, (long long)(fd), (long long)(iovp), \
630 #define __sanitizer_syscall_pre_writev(fd, iovp, iovcnt) \
631 __sanitizer_syscall_pre_impl_writev((long long)(fd), (long long)(iovp), \
633 #define __sanitizer_syscall_post_writev(res, fd, iovp, iovcnt) \
634 __sanitizer_syscall_post_impl_writev(res, (long long)(fd), \
635 (long long)(iovp), (long long)(iovcnt))
636 #define __sanitizer_syscall_pre_compat_50_settimeofday(tv, tzp) \
637 __sanitizer_syscall_pre_impl_compat_50_settimeofday((long long)(tv), \
639 #define __sanitizer_syscall_post_compat_50_settimeofday(res, tv, tzp) \
640 __sanitizer_syscall_post_impl_compat_50_settimeofday(res, (long long)(tv), \
642 #define __sanitizer_syscall_pre_fchown(fd, uid, gid) \
643 __sanitizer_syscall_pre_impl_fchown((long long)(fd), (long long)(uid), \
645 #define __sanitizer_syscall_post_fchown(res, fd, uid, gid) \
646 __sanitizer_syscall_post_impl_fchown(res, (long long)(fd), (long long)(uid), \
648 #define __sanitizer_syscall_pre_fchmod(fd, mode) \
649 __sanitizer_syscall_pre_impl_fchmod((long long)(fd), (long long)(mode))
650 #define __sanitizer_syscall_post_fchmod(res, fd, mode) \
651 __sanitizer_syscall_post_impl_fchmod(res, (long long)(fd), (long long)(mode))
652 #define __sanitizer_syscall_pre_compat_43_orecvfrom(s, buf, len, flags, from, \
654 __sanitizer_syscall_pre_impl_compat_43_orecvfrom( \
655 (long long)(s), (long long)(buf), (long long)(len), (long long)(flags), \
656 (long long)(from), (long long)(fromlenaddr))
657 #define __sanitizer_syscall_post_compat_43_orecvfrom(res, s, buf, len, flags, \
659 __sanitizer_syscall_post_impl_compat_43_orecvfrom( \
660 res, (long long)(s), (long long)(buf), (long long)(len), \
661 (long long)(flags), (long long)(from), (long long)(fromlenaddr))
662 #define __sanitizer_syscall_pre_setreuid(ruid, euid) \
663 __sanitizer_syscall_pre_impl_setreuid((long long)(ruid), (long long)(euid))
664 #define __sanitizer_syscall_post_setreuid(res, ruid, euid) \
665 __sanitizer_syscall_post_impl_setreuid(res, (long long)(ruid), \
667 #define __sanitizer_syscall_pre_setregid(rgid, egid) \
668 __sanitizer_syscall_pre_impl_setregid((long long)(rgid), (long long)(egid))
669 #define __sanitizer_syscall_post_setregid(res, rgid, egid) \
670 __sanitizer_syscall_post_impl_setregid(res, (long long)(rgid), \
672 #define __sanitizer_syscall_pre_rename(from, to) \
673 __sanitizer_syscall_pre_impl_rename((long long)(from), (long long)(to))
674 #define __sanitizer_syscall_post_rename(res, from, to) \
675 __sanitizer_syscall_post_impl_rename(res, (long long)(from), (long long)(to))
676 #define __sanitizer_syscall_pre_compat_43_otruncate(path, length) \
677 __sanitizer_syscall_pre_impl_compat_43_otruncate((long long)(path), \
679 #define __sanitizer_syscall_post_compat_43_otruncate(res, path, length) \
680 __sanitizer_syscall_post_impl_compat_43_otruncate(res, (long long)(path), \
682 #define __sanitizer_syscall_pre_compat_43_oftruncate(fd, length) \
683 __sanitizer_syscall_pre_impl_compat_43_oftruncate((long long)(fd), \
685 #define __sanitizer_syscall_post_compat_43_oftruncate(res, fd, length) \
686 __sanitizer_syscall_post_impl_compat_43_oftruncate(res, (long long)(fd), \
688 #define __sanitizer_syscall_pre_flock(fd, how) \
689 __sanitizer_syscall_pre_impl_flock((long long)(fd), (long long)(how))
690 #define __sanitizer_syscall_post_flock(res, fd, how) \
691 __sanitizer_syscall_post_impl_flock(res, (long long)(fd), (long long)(how))
692 #define __sanitizer_syscall_pre_mkfifo(path, mode) \
693 __sanitizer_syscall_pre_impl_mkfifo((long long)(path), (long long)(mode))
694 #define __sanitizer_syscall_post_mkfifo(res, path, mode) \
695 __sanitizer_syscall_post_impl_mkfifo(res, (long long)(path), \
697 #define __sanitizer_syscall_pre_sendto(s, buf, len, flags, to, tolen) \
698 __sanitizer_syscall_pre_impl_sendto((long long)(s), (long long)(buf), \
699 (long long)(len), (long long)(flags), \
700 (long long)(to), (long long)(tolen))
701 #define __sanitizer_syscall_post_sendto(res, s, buf, len, flags, to, tolen) \
702 __sanitizer_syscall_post_impl_sendto(res, (long long)(s), (long long)(buf), \
703 (long long)(len), (long long)(flags), \
704 (long long)(to), (long long)(tolen))
705 #define __sanitizer_syscall_pre_shutdown(s, how) \
706 __sanitizer_syscall_pre_impl_shutdown((long long)(s), (long long)(how))
707 #define __sanitizer_syscall_post_shutdown(res, s, how) \
708 __sanitizer_syscall_post_impl_shutdown(res, (long long)(s), (long long)(how))
709 #define __sanitizer_syscall_pre_socketpair(domain, type, protocol, rsv) \
710 __sanitizer_syscall_pre_impl_socketpair( \
711 (long long)(domain), (long long)(type), (long long)(protocol), \
713 #define __sanitizer_syscall_post_socketpair(res, domain, type, protocol, rsv) \
714 __sanitizer_syscall_post_impl_socketpair( \
715 res, (long long)(domain), (long long)(type), (long long)(protocol), \
717 #define __sanitizer_syscall_pre_mkdir(path, mode) \
718 __sanitizer_syscall_pre_impl_mkdir((long long)(path), (long long)(mode))
719 #define __sanitizer_syscall_post_mkdir(res, path, mode) \
720 __sanitizer_syscall_post_impl_mkdir(res, (long long)(path), (long long)(mode))
721 #define __sanitizer_syscall_pre_rmdir(path) \
722 __sanitizer_syscall_pre_impl_rmdir((long long)(path))
723 #define __sanitizer_syscall_post_rmdir(res, path) \
724 __sanitizer_syscall_post_impl_rmdir(res, (long long)(path))
725 #define __sanitizer_syscall_pre_compat_50_utimes(path, tptr) \
726 __sanitizer_syscall_pre_impl_compat_50_utimes((long long)(path), \
728 #define __sanitizer_syscall_post_compat_50_utimes(res, path, tptr) \
729 __sanitizer_syscall_post_impl_compat_50_utimes(res, (long long)(path), \
732 #define __sanitizer_syscall_pre_compat_50_adjtime(delta, olddelta) \
733 __sanitizer_syscall_pre_impl_compat_50_adjtime((long long)(delta), \
734 (long long)(olddelta))
735 #define __sanitizer_syscall_post_compat_50_adjtime(res, delta, olddelta) \
736 __sanitizer_syscall_post_impl_compat_50_adjtime(res, (long long)(delta), \
737 (long long)(olddelta))
738 #define __sanitizer_syscall_pre_compat_43_ogetpeername(fdes, asa, alen) \
739 __sanitizer_syscall_pre_impl_compat_43_ogetpeername( \
740 (long long)(fdes), (long long)(asa), (long long)(alen))
741 #define __sanitizer_syscall_post_compat_43_ogetpeername(res, fdes, asa, alen) \
742 __sanitizer_syscall_post_impl_compat_43_ogetpeername( \
743 res, (long long)(fdes), (long long)(asa), (long long)(alen))
744 #define __sanitizer_syscall_pre_compat_43_ogethostid() \
745 __sanitizer_syscall_pre_impl_compat_43_ogethostid()
746 #define __sanitizer_syscall_post_compat_43_ogethostid(res) \
747 __sanitizer_syscall_post_impl_compat_43_ogethostid(res)
748 #define __sanitizer_syscall_pre_compat_43_osethostid(hostid) \
749 __sanitizer_syscall_pre_impl_compat_43_osethostid((long long)(hostid))
750 #define __sanitizer_syscall_post_compat_43_osethostid(res, hostid) \
751 __sanitizer_syscall_post_impl_compat_43_osethostid(res, (long long)(hostid))
752 #define __sanitizer_syscall_pre_compat_43_ogetrlimit(which, rlp) \
753 __sanitizer_syscall_pre_impl_compat_43_ogetrlimit((long long)(which), \
755 #define __sanitizer_syscall_post_compat_43_ogetrlimit(res, which, rlp) \
756 __sanitizer_syscall_post_impl_compat_43_ogetrlimit(res, (long long)(which), \
758 #define __sanitizer_syscall_pre_compat_43_osetrlimit(which, rlp) \
759 __sanitizer_syscall_pre_impl_compat_43_osetrlimit((long long)(which), \
761 #define __sanitizer_syscall_post_compat_43_osetrlimit(res, which, rlp) \
762 __sanitizer_syscall_post_impl_compat_43_osetrlimit(res, (long long)(which), \
764 #define __sanitizer_syscall_pre_compat_43_okillpg(pgid, signum) \
765 __sanitizer_syscall_pre_impl_compat_43_okillpg((long long)(pgid), \
767 #define __sanitizer_syscall_post_compat_43_okillpg(res, pgid, signum) \
768 __sanitizer_syscall_post_impl_compat_43_okillpg(res, (long long)(pgid), \
770 #define __sanitizer_syscall_pre_setsid() __sanitizer_syscall_pre_impl_setsid()
771 #define __sanitizer_syscall_post_setsid(res) \
772 __sanitizer_syscall_post_impl_setsid(res)
773 #define __sanitizer_syscall_pre_compat_50_quotactl(path, cmd, uid, arg) \
774 __sanitizer_syscall_pre_impl_compat_50_quotactl( \
775 (long long)(path), (long long)(cmd), (long long)(uid), (long long)(arg))
776 #define __sanitizer_syscall_post_compat_50_quotactl(res, path, cmd, uid, arg) \
777 __sanitizer_syscall_post_impl_compat_50_quotactl( \
778 res, (long long)(path), (long long)(cmd), (long long)(uid), \
780 #define __sanitizer_syscall_pre_compat_43_oquota() \
781 __sanitizer_syscall_pre_impl_compat_43_oquota()
782 #define __sanitizer_syscall_post_compat_43_oquota(res) \
783 __sanitizer_syscall_post_impl_compat_43_oquota(res)
784 #define __sanitizer_syscall_pre_compat_43_ogetsockname(fdec, asa, alen) \
785 __sanitizer_syscall_pre_impl_compat_43_ogetsockname( \
786 (long long)(fdec), (long long)(asa), (long long)(alen))
787 #define __sanitizer_syscall_post_compat_43_ogetsockname(res, fdec, asa, alen) \
788 __sanitizer_syscall_post_impl_compat_43_ogetsockname( \
789 res, (long long)(fdec), (long long)(asa), (long long)(alen))
794 #define __sanitizer_syscall_pre_nfssvc(flag, argp) \
795 __sanitizer_syscall_pre_impl_nfssvc((long long)(flag), (long long)(argp))
796 #define __sanitizer_syscall_post_nfssvc(res, flag, argp) \
797 __sanitizer_syscall_post_impl_nfssvc(res, (long long)(flag), \
799 #define __sanitizer_syscall_pre_compat_43_ogetdirentries(fd, buf, count, \
801 __sanitizer_syscall_pre_impl_compat_43_ogetdirentries( \
802 (long long)(fd), (long long)(buf), (long long)(count), \
804 #define __sanitizer_syscall_post_compat_43_ogetdirentries(res, fd, buf, count, \
806 __sanitizer_syscall_post_impl_compat_43_ogetdirentries( \
807 res, (long long)(fd), (long long)(buf), (long long)(count), \
809 #define __sanitizer_syscall_pre_compat_20_statfs(path, buf) \
810 __sanitizer_syscall_pre_impl_compat_20_statfs((long long)(path), \
812 #define __sanitizer_syscall_post_compat_20_statfs(res, path, buf) \
813 __sanitizer_syscall_post_impl_compat_20_statfs(res, (long long)(path), \
815 #define __sanitizer_syscall_pre_compat_20_fstatfs(fd, buf) \
816 __sanitizer_syscall_pre_impl_compat_20_fstatfs((long long)(fd), \
818 #define __sanitizer_syscall_post_compat_20_fstatfs(res, fd, buf) \
819 __sanitizer_syscall_post_impl_compat_20_fstatfs(res, (long long)(fd), \
823 #define __sanitizer_syscall_pre_compat_30_getfh(fname, fhp) \
824 __sanitizer_syscall_pre_impl_compat_30_getfh((long long)(fname), \
826 #define __sanitizer_syscall_post_compat_30_getfh(res, fname, fhp) \
827 __sanitizer_syscall_post_impl_compat_30_getfh(res, (long long)(fname), \
829 #define __sanitizer_syscall_pre_compat_09_ogetdomainname(domainname, len) \
830 __sanitizer_syscall_pre_impl_compat_09_ogetdomainname( \
831 (long long)(domainname), (long long)(len))
832 #define __sanitizer_syscall_post_compat_09_ogetdomainname(res, domainname, \
834 __sanitizer_syscall_post_impl_compat_09_ogetdomainname( \
835 res, (long long)(domainname), (long long)(len))
836 #define __sanitizer_syscall_pre_compat_09_osetdomainname(domainname, len) \
837 __sanitizer_syscall_pre_impl_compat_09_osetdomainname( \
838 (long long)(domainname), (long long)(len))
839 #define __sanitizer_syscall_post_compat_09_osetdomainname(res, domainname, \
841 __sanitizer_syscall_post_impl_compat_09_osetdomainname( \
842 res, (long long)(domainname), (long long)(len))
843 #define __sanitizer_syscall_pre_compat_09_ouname(name) \
844 __sanitizer_syscall_pre_impl_compat_09_ouname((long long)(name))
845 #define __sanitizer_syscall_post_compat_09_ouname(res, name) \
846 __sanitizer_syscall_post_impl_compat_09_ouname(res, (long long)(name))
847 #define __sanitizer_syscall_pre_sysarch(op, parms) \
848 __sanitizer_syscall_pre_impl_sysarch((long long)(op), (long long)(parms))
849 #define __sanitizer_syscall_post_sysarch(res, op, parms) \
850 __sanitizer_syscall_post_impl_sysarch(res, (long long)(op), \
856 #define __sanitizer_syscall_pre_compat_10_osemsys(which, a2, a3, a4, a5) \
857 __sanitizer_syscall_pre_impl_compat_10_osemsys( \
858 (long long)(which), (long long)(a2), (long long)(a3), (long long)(a4), \
860 #define __sanitizer_syscall_post_compat_10_osemsys(res, which, a2, a3, a4, a5) \
861 __sanitizer_syscall_post_impl_compat_10_osemsys( \
862 res, (long long)(which), (long long)(a2), (long long)(a3), \
863 (long long)(a4), (long long)(a5))
868 #define __sanitizer_syscall_pre_compat_10_omsgsys(which, a2, a3, a4, a5, a6) \
869 __sanitizer_syscall_pre_impl_compat_10_omsgsys( \
870 (long long)(which), (long long)(a2), (long long)(a3), (long long)(a4), \
871 (long long)(a5), (long long)(a6))
872 #define __sanitizer_syscall_post_compat_10_omsgsys(res, which, a2, a3, a4, a5, \
874 __sanitizer_syscall_post_impl_compat_10_omsgsys( \
875 res, (long long)(which), (long long)(a2), (long long)(a3), \
876 (long long)(a4), (long long)(a5), (long long)(a6))
881 #define __sanitizer_syscall_pre_compat_10_oshmsys(which, a2, a3, a4) \
882 __sanitizer_syscall_pre_impl_compat_10_oshmsys( \
883 (long long)(which), (long long)(a2), (long long)(a3), (long long)(a4))
884 #define __sanitizer_syscall_post_compat_10_oshmsys(res, which, a2, a3, a4) \
885 __sanitizer_syscall_post_impl_compat_10_oshmsys( \
886 res, (long long)(which), (long long)(a2), (long long)(a3), \
892 #define __sanitizer_syscall_pre_pread(fd, buf, nbyte, PAD, offset) \
893 __sanitizer_syscall_pre_impl_pread((long long)(fd), (long long)(buf), \
894 (long long)(nbyte), (long long)(PAD), \
896 #define __sanitizer_syscall_post_pread(res, fd, buf, nbyte, PAD, offset) \
897 __sanitizer_syscall_post_impl_pread(res, (long long)(fd), (long long)(buf), \
898 (long long)(nbyte), (long long)(PAD), \
900 #define __sanitizer_syscall_pre_pwrite(fd, buf, nbyte, PAD, offset) \
901 __sanitizer_syscall_pre_impl_pwrite((long long)(fd), (long long)(buf), \
902 (long long)(nbyte), (long long)(PAD), \
904 #define __sanitizer_syscall_post_pwrite(res, fd, buf, nbyte, PAD, offset) \
905 __sanitizer_syscall_post_impl_pwrite(res, (long long)(fd), (long long)(buf), \
906 (long long)(nbyte), (long long)(PAD), \
908 #define __sanitizer_syscall_pre_compat_30_ntp_gettime(ntvp) \
909 __sanitizer_syscall_pre_impl_compat_30_ntp_gettime((long long)(ntvp))
910 #define __sanitizer_syscall_post_compat_30_ntp_gettime(res, ntvp) \
911 __sanitizer_syscall_post_impl_compat_30_ntp_gettime(res, (long long)(ntvp))
912 #if defined(NTP) || !defined(_KERNEL_OPT)
913 #define __sanitizer_syscall_pre_ntp_adjtime(tp) \
914 __sanitizer_syscall_pre_impl_ntp_adjtime((long long)(tp))
915 #define __sanitizer_syscall_post_ntp_adjtime(res, tp) \
916 __sanitizer_syscall_post_impl_ntp_adjtime(res, (long long)(tp))
924 #define __sanitizer_syscall_pre_setgid(gid) \
925 __sanitizer_syscall_pre_impl_setgid((long long)(gid))
926 #define __sanitizer_syscall_post_setgid(res, gid) \
927 __sanitizer_syscall_post_impl_setgid(res, (long long)(gid))
928 #define __sanitizer_syscall_pre_setegid(egid) \
929 __sanitizer_syscall_pre_impl_setegid((long long)(egid))
930 #define __sanitizer_syscall_post_setegid(res, egid) \
931 __sanitizer_syscall_post_impl_setegid(res, (long long)(egid))
932 #define __sanitizer_syscall_pre_seteuid(euid) \
933 __sanitizer_syscall_pre_impl_seteuid((long long)(euid))
934 #define __sanitizer_syscall_post_seteuid(res, euid) \
935 __sanitizer_syscall_post_impl_seteuid(res, (long long)(euid))
936 #define __sanitizer_syscall_pre_lfs_bmapv(fsidp, blkiov, blkcnt) \
937 __sanitizer_syscall_pre_impl_lfs_bmapv( \
938 (long long)(fsidp), (long long)(blkiov), (long long)(blkcnt))
939 #define __sanitizer_syscall_post_lfs_bmapv(res, fsidp, blkiov, blkcnt) \
940 __sanitizer_syscall_post_impl_lfs_bmapv( \
941 res, (long long)(fsidp), (long long)(blkiov), (long long)(blkcnt))
942 #define __sanitizer_syscall_pre_lfs_markv(fsidp, blkiov, blkcnt) \
943 __sanitizer_syscall_pre_impl_lfs_markv( \
944 (long long)(fsidp), (long long)(blkiov), (long long)(blkcnt))
945 #define __sanitizer_syscall_post_lfs_markv(res, fsidp, blkiov, blkcnt) \
946 __sanitizer_syscall_post_impl_lfs_markv( \
947 res, (long long)(fsidp), (long long)(blkiov), (long long)(blkcnt))
948 #define __sanitizer_syscall_pre_lfs_segclean(fsidp, segment) \
949 __sanitizer_syscall_pre_impl_lfs_segclean((long long)(fsidp), \
950 (long long)(segment))
951 #define __sanitizer_syscall_post_lfs_segclean(res, fsidp, segment) \
952 __sanitizer_syscall_post_impl_lfs_segclean(res, (long long)(fsidp), \
953 (long long)(segment))
954 #define __sanitizer_syscall_pre_compat_50_lfs_segwait(fsidp, tv) \
955 __sanitizer_syscall_pre_impl_compat_50_lfs_segwait((long long)(fsidp), \
957 #define __sanitizer_syscall_post_compat_50_lfs_segwait(res, fsidp, tv) \
958 __sanitizer_syscall_post_impl_compat_50_lfs_segwait(res, (long long)(fsidp), \
960 #define __sanitizer_syscall_pre_compat_12_stat12(path, ub) \
961 __sanitizer_syscall_pre_impl_compat_12_stat12((long long)(path), \
963 #define __sanitizer_syscall_post_compat_12_stat12(res, path, ub) \
964 __sanitizer_syscall_post_impl_compat_12_stat12(res, (long long)(path), \
966 #define __sanitizer_syscall_pre_compat_12_fstat12(fd, sb) \
967 __sanitizer_syscall_pre_impl_compat_12_fstat12((long long)(fd), \
969 #define __sanitizer_syscall_post_compat_12_fstat12(res, fd, sb) \
970 __sanitizer_syscall_post_impl_compat_12_fstat12(res, (long long)(fd), \
972 #define __sanitizer_syscall_pre_compat_12_lstat12(path, ub) \
973 __sanitizer_syscall_pre_impl_compat_12_lstat12((long long)(path), \
975 #define __sanitizer_syscall_post_compat_12_lstat12(res, path, ub) \
976 __sanitizer_syscall_post_impl_compat_12_lstat12(res, (long long)(path), \
978 #define __sanitizer_syscall_pre_pathconf(path, name) \
979 __sanitizer_syscall_pre_impl_pathconf((long long)(path), (long long)(name))
980 #define __sanitizer_syscall_post_pathconf(res, path, name) \
981 __sanitizer_syscall_post_impl_pathconf(res, (long long)(path), \
983 #define __sanitizer_syscall_pre_fpathconf(fd, name) \
984 __sanitizer_syscall_pre_impl_fpathconf((long long)(fd), (long long)(name))
985 #define __sanitizer_syscall_post_fpathconf(res, fd, name) \
986 __sanitizer_syscall_post_impl_fpathconf(res, (long long)(fd), \
988 #define __sanitizer_syscall_pre_getsockopt2(s, level, name, val, avalsize) \
989 __sanitizer_syscall_pre_impl_getsockopt2( \
990 (long long)(s), (long long)(level), (long long)(name), (long long)(val), \
991 (long long)(avalsize))
992 #define __sanitizer_syscall_post_getsockopt2(res, s, level, name, val, \
994 __sanitizer_syscall_post_impl_getsockopt2( \
995 res, (long long)(s), (long long)(level), (long long)(name), \
996 (long long)(val), (long long)(avalsize))
997 #define __sanitizer_syscall_pre_getrlimit(which, rlp) \
998 __sanitizer_syscall_pre_impl_getrlimit((long long)(which), (long long)(rlp))
999 #define __sanitizer_syscall_post_getrlimit(res, which, rlp) \
1000 __sanitizer_syscall_post_impl_getrlimit(res, (long long)(which), \
1002 #define __sanitizer_syscall_pre_setrlimit(which, rlp) \
1003 __sanitizer_syscall_pre_impl_setrlimit((long long)(which), (long long)(rlp))
1004 #define __sanitizer_syscall_post_setrlimit(res, which, rlp) \
1005 __sanitizer_syscall_post_impl_setrlimit(res, (long long)(which), \
1007 #define __sanitizer_syscall_pre_compat_12_getdirentries(fd, buf, count, basep) \
1008 __sanitizer_syscall_pre_impl_compat_12_getdirentries( \
1009 (long long)(fd), (long long)(buf), (long long)(count), \
1011 #define __sanitizer_syscall_post_compat_12_getdirentries(res, fd, buf, count, \
1013 __sanitizer_syscall_post_impl_compat_12_getdirentries( \
1014 res, (long long)(fd), (long long)(buf), (long long)(count), \
1016 #define __sanitizer_syscall_pre_mmap(addr, len, prot, flags, fd, PAD, pos) \
1017 __sanitizer_syscall_pre_impl_mmap( \
1018 (long long)(addr), (long long)(len), (long long)(prot), \
1019 (long long)(flags), (long long)(fd), (long long)(PAD), (long long)(pos))
1020 #define __sanitizer_syscall_post_mmap(res, addr, len, prot, flags, fd, PAD, \
1022 __sanitizer_syscall_post_impl_mmap( \
1023 res, (long long)(addr), (long long)(len), (long long)(prot), \
1024 (long long)(flags), (long long)(fd), (long long)(PAD), (long long)(pos))
1025 #define __sanitizer_syscall_pre___syscall(code, arg0, arg1, arg2, arg3, arg4, \
1027 __sanitizer_syscall_pre_impl___syscall( \
1028 (long long)(code), (long long)(arg0), (long long)(arg1), \
1029 (long long)(arg2), (long long)(arg3), (long long)(arg4), \
1030 (long long)(arg5), (long long)(arg6), (long long)(arg7))
1031 #define __sanitizer_syscall_post___syscall(res, code, arg0, arg1, arg2, arg3, \
1032 arg4, arg5, arg6, arg7) \
1033 __sanitizer_syscall_post_impl___syscall( \
1034 res, (long long)(code), (long long)(arg0), (long long)(arg1), \
1035 (long long)(arg2), (long long)(arg3), (long long)(arg4), \
1036 (long long)(arg5), (long long)(arg6), (long long)(arg7))
1037 #define __sanitizer_syscall_pre_lseek(fd, PAD, offset, whence) \
1038 __sanitizer_syscall_pre_impl_lseek((long long)(fd), (long long)(PAD), \
1039 (long long)(offset), (long long)(whence))
1040 #define __sanitizer_syscall_post_lseek(res, fd, PAD, offset, whence) \
1041 __sanitizer_syscall_post_impl_lseek(res, (long long)(fd), (long long)(PAD), \
1042 (long long)(offset), \
1043 (long long)(whence))
1044 #define __sanitizer_syscall_pre_truncate(path, PAD, length) \
1045 __sanitizer_syscall_pre_impl_truncate((long long)(path), (long long)(PAD), \
1046 (long long)(length))
1047 #define __sanitizer_syscall_post_truncate(res, path, PAD, length) \
1048 __sanitizer_syscall_post_impl_truncate( \
1049 res, (long long)(path), (long long)(PAD), (long long)(length))
1050 #define __sanitizer_syscall_pre_ftruncate(fd, PAD, length) \
1051 __sanitizer_syscall_pre_impl_ftruncate((long long)(fd), (long long)(PAD), \
1052 (long long)(length))
1053 #define __sanitizer_syscall_post_ftruncate(res, fd, PAD, length) \
1054 __sanitizer_syscall_post_impl_ftruncate( \
1055 res, (long long)(fd), (long long)(PAD), (long long)(length))
1056 #define __sanitizer_syscall_pre___sysctl(name, namelen, oldv, oldlenp, newv, \
1058 __sanitizer_syscall_pre_impl___sysctl( \
1059 (long long)(name), (long long)(namelen), (long long)(oldv), \
1060 (long long)(oldlenp), (long long)(newv), (long long)(newlen))
1061 #define __sanitizer_syscall_post___sysctl(res, name, namelen, oldv, oldlenp, \
1063 __sanitizer_syscall_post_impl___sysctl( \
1064 res, (long long)(name), (long long)(namelen), (long long)(oldv), \
1065 (long long)(oldlenp), (long long)(newv), (long long)(newlen))
1066 #define __sanitizer_syscall_pre_mlock(addr, len) \
1067 __sanitizer_syscall_pre_impl_mlock((long long)(addr), (long long)(len))
1068 #define __sanitizer_syscall_post_mlock(res, addr, len) \
1069 __sanitizer_syscall_post_impl_mlock(res, (long long)(addr), (long long)(len))
1070 #define __sanitizer_syscall_pre_munlock(addr, len) \
1071 __sanitizer_syscall_pre_impl_munlock((long long)(addr), (long long)(len))
1072 #define __sanitizer_syscall_post_munlock(res, addr, len) \
1073 __sanitizer_syscall_post_impl_munlock(res, (long long)(addr), \
1075 #define __sanitizer_syscall_pre_undelete(path) \
1076 __sanitizer_syscall_pre_impl_undelete((long long)(path))
1077 #define __sanitizer_syscall_post_undelete(res, path) \
1078 __sanitizer_syscall_post_impl_undelete(res, (long long)(path))
1079 #define __sanitizer_syscall_pre_compat_50_futimes(fd, tptr) \
1080 __sanitizer_syscall_pre_impl_compat_50_futimes((long long)(fd), \
1082 #define __sanitizer_syscall_post_compat_50_futimes(res, fd, tptr) \
1083 __sanitizer_syscall_post_impl_compat_50_futimes(res, (long long)(fd), \
1085 #define __sanitizer_syscall_pre_getpgid(pid) \
1086 __sanitizer_syscall_pre_impl_getpgid((long long)(pid))
1087 #define __sanitizer_syscall_post_getpgid(res, pid) \
1088 __sanitizer_syscall_post_impl_getpgid(res, (long long)(pid))
1089 #define __sanitizer_syscall_pre_reboot(opt, bootstr) \
1090 __sanitizer_syscall_pre_impl_reboot((long long)(opt), (long long)(bootstr))
1091 #define __sanitizer_syscall_post_reboot(res, opt, bootstr) \
1092 __sanitizer_syscall_post_impl_reboot(res, (long long)(opt), \
1093 (long long)(bootstr))
1094 #define __sanitizer_syscall_pre_poll(fds, nfds, timeout) \
1095 __sanitizer_syscall_pre_impl_poll((long long)(fds), (long long)(nfds), \
1096 (long long)(timeout))
1097 #define __sanitizer_syscall_post_poll(res, fds, nfds, timeout) \
1098 __sanitizer_syscall_post_impl_poll(res, (long long)(fds), (long long)(nfds), \
1099 (long long)(timeout))
1100 #define __sanitizer_syscall_pre_afssys(id, a1, a2, a3, a4, a5, a6) \
1101 __sanitizer_syscall_pre_impl_afssys( \
1102 (long long)(id), (long long)(a1), (long long)(a2), (long long)(a3), \
1103 (long long)(a4), (long long)(a5), (long long)(a6))
1104 #define __sanitizer_syscall_post_afssys(res, id, a1, a2, a3, a4, a5, a6) \
1105 __sanitizer_syscall_post_impl_afssys( \
1106 res, (long long)(id), (long long)(a1), (long long)(a2), (long long)(a3), \
1107 (long long)(a4), (long long)(a5), (long long)(a6))
1117 #define __sanitizer_syscall_pre_compat_14___semctl(semid, semnum, cmd, arg) \
1118 __sanitizer_syscall_pre_impl_compat_14___semctl( \
1119 (long long)(semid), (long long)(semnum), (long long)(cmd), \
1121 #define __sanitizer_syscall_post_compat_14___semctl(res, semid, semnum, cmd, \
1123 __sanitizer_syscall_post_impl_compat_14___semctl( \
1124 res, (long long)(semid), (long long)(semnum), (long long)(cmd), \
1126 #define __sanitizer_syscall_pre_semget(key, nsems, semflg) \
1127 __sanitizer_syscall_pre_impl_semget((long long)(key), (long long)(nsems), \
1128 (long long)(semflg))
1129 #define __sanitizer_syscall_post_semget(res, key, nsems, semflg) \
1130 __sanitizer_syscall_post_impl_semget( \
1131 res, (long long)(key), (long long)(nsems), (long long)(semflg))
1132 #define __sanitizer_syscall_pre_semop(semid, sops, nsops) \
1133 __sanitizer_syscall_pre_impl_semop((long long)(semid), (long long)(sops), \
1135 #define __sanitizer_syscall_post_semop(res, semid, sops, nsops) \
1136 __sanitizer_syscall_post_impl_semop(res, (long long)(semid), \
1137 (long long)(sops), (long long)(nsops))
1138 #define __sanitizer_syscall_pre_semconfig(flag) \
1139 __sanitizer_syscall_pre_impl_semconfig((long long)(flag))
1140 #define __sanitizer_syscall_post_semconfig(res, flag) \
1141 __sanitizer_syscall_post_impl_semconfig(res, (long long)(flag))
1142 #define __sanitizer_syscall_pre_compat_14_msgctl(msqid, cmd, buf) \
1143 __sanitizer_syscall_pre_impl_compat_14_msgctl( \
1144 (long long)(msqid), (long long)(cmd), (long long)(buf))
1145 #define __sanitizer_syscall_post_compat_14_msgctl(res, msqid, cmd, buf) \
1146 __sanitizer_syscall_post_impl_compat_14_msgctl( \
1147 res, (long long)(msqid), (long long)(cmd), (long long)(buf))
1148 #define __sanitizer_syscall_pre_msgget(key, msgflg) \
1149 __sanitizer_syscall_pre_impl_msgget((long long)(key), (long long)(msgflg))
1150 #define __sanitizer_syscall_post_msgget(res, key, msgflg) \
1151 __sanitizer_syscall_post_impl_msgget(res, (long long)(key), \
1152 (long long)(msgflg))
1153 #define __sanitizer_syscall_pre_msgsnd(msqid, msgp, msgsz, msgflg) \
1154 __sanitizer_syscall_pre_impl_msgsnd((long long)(msqid), (long long)(msgp), \
1155 (long long)(msgsz), (long long)(msgflg))
1156 #define __sanitizer_syscall_post_msgsnd(res, msqid, msgp, msgsz, msgflg) \
1157 __sanitizer_syscall_post_impl_msgsnd(res, (long long)(msqid), \
1158 (long long)(msgp), (long long)(msgsz), \
1159 (long long)(msgflg))
1160 #define __sanitizer_syscall_pre_msgrcv(msqid, msgp, msgsz, msgtyp, msgflg) \
1161 __sanitizer_syscall_pre_impl_msgrcv((long long)(msqid), (long long)(msgp), \
1162 (long long)(msgsz), (long long)(msgtyp), \
1163 (long long)(msgflg))
1164 #define __sanitizer_syscall_post_msgrcv(res, msqid, msgp, msgsz, msgtyp, \
1166 __sanitizer_syscall_post_impl_msgrcv( \
1167 res, (long long)(msqid), (long long)(msgp), (long long)(msgsz), \
1168 (long long)(msgtyp), (long long)(msgflg))
1169 #define __sanitizer_syscall_pre_shmat(shmid, shmaddr, shmflg) \
1170 __sanitizer_syscall_pre_impl_shmat((long long)(shmid), (long long)(shmaddr), \
1171 (long long)(shmflg))
1172 #define __sanitizer_syscall_post_shmat(res, shmid, shmaddr, shmflg) \
1173 __sanitizer_syscall_post_impl_shmat( \
1174 res, (long long)(shmid), (long long)(shmaddr), (long long)(shmflg))
1175 #define __sanitizer_syscall_pre_compat_14_shmctl(shmid, cmd, buf) \
1176 __sanitizer_syscall_pre_impl_compat_14_shmctl( \
1177 (long long)(shmid), (long long)(cmd), (long long)(buf))
1178 #define __sanitizer_syscall_post_compat_14_shmctl(res, shmid, cmd, buf) \
1179 __sanitizer_syscall_post_impl_compat_14_shmctl( \
1180 res, (long long)(shmid), (long long)(cmd), (long long)(buf))
1181 #define __sanitizer_syscall_pre_shmdt(shmaddr) \
1182 __sanitizer_syscall_pre_impl_shmdt((long long)(shmaddr))
1183 #define __sanitizer_syscall_post_shmdt(res, shmaddr) \
1184 __sanitizer_syscall_post_impl_shmdt(res, (long long)(shmaddr))
1185 #define __sanitizer_syscall_pre_shmget(key, size, shmflg) \
1186 __sanitizer_syscall_pre_impl_shmget((long long)(key), (long long)(size), \
1187 (long long)(shmflg))
1188 #define __sanitizer_syscall_post_shmget(res, key, size, shmflg) \
1189 __sanitizer_syscall_post_impl_shmget(res, (long long)(key), \
1190 (long long)(size), (long long)(shmflg))
1191 #define __sanitizer_syscall_pre_compat_50_clock_gettime(clock_id, tp) \
1192 __sanitizer_syscall_pre_impl_compat_50_clock_gettime((long long)(clock_id), \
1194 #define __sanitizer_syscall_post_compat_50_clock_gettime(res, clock_id, tp) \
1195 __sanitizer_syscall_post_impl_compat_50_clock_gettime( \
1196 res, (long long)(clock_id), (long long)(tp))
1197 #define __sanitizer_syscall_pre_compat_50_clock_settime(clock_id, tp) \
1198 __sanitizer_syscall_pre_impl_compat_50_clock_settime((long long)(clock_id), \
1200 #define __sanitizer_syscall_post_compat_50_clock_settime(res, clock_id, tp) \
1201 __sanitizer_syscall_post_impl_compat_50_clock_settime( \
1202 res, (long long)(clock_id), (long long)(tp))
1203 #define __sanitizer_syscall_pre_compat_50_clock_getres(clock_id, tp) \
1204 __sanitizer_syscall_pre_impl_compat_50_clock_getres((long long)(clock_id), \
1206 #define __sanitizer_syscall_post_compat_50_clock_getres(res, clock_id, tp) \
1207 __sanitizer_syscall_post_impl_compat_50_clock_getres( \
1208 res, (long long)(clock_id), (long long)(tp))
1209 #define __sanitizer_syscall_pre_timer_create(clock_id, evp, timerid) \
1210 __sanitizer_syscall_pre_impl_timer_create( \
1211 (long long)(clock_id), (long long)(evp), (long long)(timerid))
1212 #define __sanitizer_syscall_post_timer_create(res, clock_id, evp, timerid) \
1213 __sanitizer_syscall_post_impl_timer_create( \
1214 res, (long long)(clock_id), (long long)(evp), (long long)(timerid))
1215 #define __sanitizer_syscall_pre_timer_delete(timerid) \
1216 __sanitizer_syscall_pre_impl_timer_delete((long long)(timerid))
1217 #define __sanitizer_syscall_post_timer_delete(res, timerid) \
1218 __sanitizer_syscall_post_impl_timer_delete(res, (long long)(timerid))
1219 #define __sanitizer_syscall_pre_compat_50_timer_settime(timerid, flags, value, \
1221 __sanitizer_syscall_pre_impl_compat_50_timer_settime( \
1222 (long long)(timerid), (long long)(flags), (long long)(value), \
1223 (long long)(ovalue))
1224 #define __sanitizer_syscall_post_compat_50_timer_settime(res, timerid, flags, \
1226 __sanitizer_syscall_post_impl_compat_50_timer_settime( \
1227 res, (long long)(timerid), (long long)(flags), (long long)(value), \
1228 (long long)(ovalue))
1229 #define __sanitizer_syscall_pre_compat_50_timer_gettime(timerid, value) \
1230 __sanitizer_syscall_pre_impl_compat_50_timer_gettime((long long)(timerid), \
1232 #define __sanitizer_syscall_post_compat_50_timer_gettime(res, timerid, value) \
1233 __sanitizer_syscall_post_impl_compat_50_timer_gettime( \
1234 res, (long long)(timerid), (long long)(value))
1235 #define __sanitizer_syscall_pre_timer_getoverrun(timerid) \
1236 __sanitizer_syscall_pre_impl_timer_getoverrun((long long)(timerid))
1237 #define __sanitizer_syscall_post_timer_getoverrun(res, timerid) \
1238 __sanitizer_syscall_post_impl_timer_getoverrun(res, (long long)(timerid))
1239 #define __sanitizer_syscall_pre_compat_50_nanosleep(rqtp, rmtp) \
1240 __sanitizer_syscall_pre_impl_compat_50_nanosleep((long long)(rqtp), \
1242 #define __sanitizer_syscall_post_compat_50_nanosleep(res, rqtp, rmtp) \
1243 __sanitizer_syscall_post_impl_compat_50_nanosleep(res, (long long)(rqtp), \
1245 #define __sanitizer_syscall_pre_fdatasync(fd) \
1246 __sanitizer_syscall_pre_impl_fdatasync((long long)(fd))
1247 #define __sanitizer_syscall_post_fdatasync(res, fd) \
1248 __sanitizer_syscall_post_impl_fdatasync(res, (long long)(fd))
1249 #define __sanitizer_syscall_pre_mlockall(flags) \
1250 __sanitizer_syscall_pre_impl_mlockall((long long)(flags))
1251 #define __sanitizer_syscall_post_mlockall(res, flags) \
1252 __sanitizer_syscall_post_impl_mlockall(res, (long long)(flags))
1253 #define __sanitizer_syscall_pre_munlockall() \
1254 __sanitizer_syscall_pre_impl_munlockall()
1255 #define __sanitizer_syscall_post_munlockall(res) \
1256 __sanitizer_syscall_post_impl_munlockall(res)
1257 #define __sanitizer_syscall_pre_compat_50___sigtimedwait(set, info, timeout) \
1258 __sanitizer_syscall_pre_impl_compat_50___sigtimedwait( \
1259 (long long)(set), (long long)(info), (long long)(timeout))
1260 #define __sanitizer_syscall_post_compat_50___sigtimedwait(res, set, info, \
1262 __sanitizer_syscall_post_impl_compat_50___sigtimedwait( \
1263 res, (long long)(set), (long long)(info), (long long)(timeout))
1264 #define __sanitizer_syscall_pre_sigqueueinfo(pid, info) \
1265 __sanitizer_syscall_pre_impl_sigqueueinfo((long long)(pid), (long long)(info))
1266 #define __sanitizer_syscall_post_sigqueueinfo(res, pid, info) \
1267 __sanitizer_syscall_post_impl_sigqueueinfo(res, (long long)(pid), \
1269 #define __sanitizer_syscall_pre_modctl(cmd, arg) \
1270 __sanitizer_syscall_pre_impl_modctl((long long)(cmd), (long long)(arg))
1271 #define __sanitizer_syscall_post_modctl(res, cmd, arg) \
1272 __sanitizer_syscall_post_impl_modctl(res, (long long)(cmd), (long long)(arg))
1273 #define __sanitizer_syscall_pre__ksem_init(value, idp) \
1274 __sanitizer_syscall_pre_impl__ksem_init((long long)(value), (long long)(idp))
1275 #define __sanitizer_syscall_post__ksem_init(res, value, idp) \
1276 __sanitizer_syscall_post_impl__ksem_init(res, (long long)(value), \
1278 #define __sanitizer_syscall_pre__ksem_open(name, oflag, mode, value, idp) \
1279 __sanitizer_syscall_pre_impl__ksem_open( \
1280 (long long)(name), (long long)(oflag), (long long)(mode), \
1281 (long long)(value), (long long)(idp))
1282 #define __sanitizer_syscall_post__ksem_open(res, name, oflag, mode, value, \
1284 __sanitizer_syscall_post_impl__ksem_open( \
1285 res, (long long)(name), (long long)(oflag), (long long)(mode), \
1286 (long long)(value), (long long)(idp))
1287 #define __sanitizer_syscall_pre__ksem_unlink(name) \
1288 __sanitizer_syscall_pre_impl__ksem_unlink((long long)(name))
1289 #define __sanitizer_syscall_post__ksem_unlink(res, name) \
1290 __sanitizer_syscall_post_impl__ksem_unlink(res, (long long)(name))
1291 #define __sanitizer_syscall_pre__ksem_close(id) \
1292 __sanitizer_syscall_pre_impl__ksem_close((long long)(id))
1293 #define __sanitizer_syscall_post__ksem_close(res, id) \
1294 __sanitizer_syscall_post_impl__ksem_close(res, (long long)(id))
1295 #define __sanitizer_syscall_pre__ksem_post(id) \
1296 __sanitizer_syscall_pre_impl__ksem_post((long long)(id))
1297 #define __sanitizer_syscall_post__ksem_post(res, id) \
1298 __sanitizer_syscall_post_impl__ksem_post(res, (long long)(id))
1299 #define __sanitizer_syscall_pre__ksem_wait(id) \
1300 __sanitizer_syscall_pre_impl__ksem_wait((long long)(id))
1301 #define __sanitizer_syscall_post__ksem_wait(res, id) \
1302 __sanitizer_syscall_post_impl__ksem_wait(res, (long long)(id))
1303 #define __sanitizer_syscall_pre__ksem_trywait(id) \
1304 __sanitizer_syscall_pre_impl__ksem_trywait((long long)(id))
1305 #define __sanitizer_syscall_post__ksem_trywait(res, id) \
1306 __sanitizer_syscall_post_impl__ksem_trywait(res, (long long)(id))
1307 #define __sanitizer_syscall_pre__ksem_getvalue(id, value) \
1308 __sanitizer_syscall_pre_impl__ksem_getvalue((long long)(id), \
1310 #define __sanitizer_syscall_post__ksem_getvalue(res, id, value) \
1311 __sanitizer_syscall_post_impl__ksem_getvalue(res, (long long)(id), \
1313 #define __sanitizer_syscall_pre__ksem_destroy(id) \
1314 __sanitizer_syscall_pre_impl__ksem_destroy((long long)(id))
1315 #define __sanitizer_syscall_post__ksem_destroy(res, id) \
1316 __sanitizer_syscall_post_impl__ksem_destroy(res, (long long)(id))
1317 #define __sanitizer_syscall_pre__ksem_timedwait(id, abstime) \
1318 __sanitizer_syscall_pre_impl__ksem_timedwait((long long)(id), \
1319 (long long)(abstime))
1320 #define __sanitizer_syscall_post__ksem_timedwait(res, id, abstime) \
1321 __sanitizer_syscall_post_impl__ksem_timedwait(res, (long long)(id), \
1322 (long long)(abstime))
1323 #define __sanitizer_syscall_pre_mq_open(name, oflag, mode, attr) \
1324 __sanitizer_syscall_pre_impl_mq_open((long long)(name), (long long)(oflag), \
1325 (long long)(mode), (long long)(attr))
1326 #define __sanitizer_syscall_post_mq_open(res, name, oflag, mode, attr) \
1327 __sanitizer_syscall_post_impl_mq_open(res, (long long)(name), \
1328 (long long)(oflag), (long long)(mode), \
1330 #define __sanitizer_syscall_pre_mq_close(mqdes) \
1331 __sanitizer_syscall_pre_impl_mq_close((long long)(mqdes))
1332 #define __sanitizer_syscall_post_mq_close(res, mqdes) \
1333 __sanitizer_syscall_post_impl_mq_close(res, (long long)(mqdes))
1334 #define __sanitizer_syscall_pre_mq_unlink(name) \
1335 __sanitizer_syscall_pre_impl_mq_unlink((long long)(name))
1336 #define __sanitizer_syscall_post_mq_unlink(res, name) \
1337 __sanitizer_syscall_post_impl_mq_unlink(res, (long long)(name))
1338 #define __sanitizer_syscall_pre_mq_getattr(mqdes, mqstat) \
1339 __sanitizer_syscall_pre_impl_mq_getattr((long long)(mqdes), \
1340 (long long)(mqstat))
1341 #define __sanitizer_syscall_post_mq_getattr(res, mqdes, mqstat) \
1342 __sanitizer_syscall_post_impl_mq_getattr(res, (long long)(mqdes), \
1343 (long long)(mqstat))
1344 #define __sanitizer_syscall_pre_mq_setattr(mqdes, mqstat, omqstat) \
1345 __sanitizer_syscall_pre_impl_mq_setattr( \
1346 (long long)(mqdes), (long long)(mqstat), (long long)(omqstat))
1347 #define __sanitizer_syscall_post_mq_setattr(res, mqdes, mqstat, omqstat) \
1348 __sanitizer_syscall_post_impl_mq_setattr( \
1349 res, (long long)(mqdes), (long long)(mqstat), (long long)(omqstat))
1350 #define __sanitizer_syscall_pre_mq_notify(mqdes, notification) \
1351 __sanitizer_syscall_pre_impl_mq_notify((long long)(mqdes), \
1352 (long long)(notification))
1353 #define __sanitizer_syscall_post_mq_notify(res, mqdes, notification) \
1354 __sanitizer_syscall_post_impl_mq_notify(res, (long long)(mqdes), \
1355 (long long)(notification))
1356 #define __sanitizer_syscall_pre_mq_send(mqdes, msg_ptr, msg_len, msg_prio) \
1357 __sanitizer_syscall_pre_impl_mq_send( \
1358 (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
1359 (long long)(msg_prio))
1360 #define __sanitizer_syscall_post_mq_send(res, mqdes, msg_ptr, msg_len, \
1362 __sanitizer_syscall_post_impl_mq_send( \
1363 res, (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
1364 (long long)(msg_prio))
1365 #define __sanitizer_syscall_pre_mq_receive(mqdes, msg_ptr, msg_len, msg_prio) \
1366 __sanitizer_syscall_pre_impl_mq_receive( \
1367 (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
1368 (long long)(msg_prio))
1369 #define __sanitizer_syscall_post_mq_receive(res, mqdes, msg_ptr, msg_len, \
1371 __sanitizer_syscall_post_impl_mq_receive( \
1372 res, (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
1373 (long long)(msg_prio))
1374 #define __sanitizer_syscall_pre_compat_50_mq_timedsend( \
1375 mqdes, msg_ptr, msg_len, msg_prio, abs_timeout) \
1376 __sanitizer_syscall_pre_impl_compat_50_mq_timedsend( \
1377 (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
1378 (long long)(msg_prio), (long long)(abs_timeout))
1379 #define __sanitizer_syscall_post_compat_50_mq_timedsend( \
1380 res, mqdes, msg_ptr, msg_len, msg_prio, abs_timeout) \
1381 __sanitizer_syscall_post_impl_compat_50_mq_timedsend( \
1382 res, (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
1383 (long long)(msg_prio), (long long)(abs_timeout))
1384 #define __sanitizer_syscall_pre_compat_50_mq_timedreceive( \
1385 mqdes, msg_ptr, msg_len, msg_prio, abs_timeout) \
1386 __sanitizer_syscall_pre_impl_compat_50_mq_timedreceive( \
1387 (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
1388 (long long)(msg_prio), (long long)(abs_timeout))
1389 #define __sanitizer_syscall_post_compat_50_mq_timedreceive( \
1390 res, mqdes, msg_ptr, msg_len, msg_prio, abs_timeout) \
1391 __sanitizer_syscall_post_impl_compat_50_mq_timedreceive( \
1392 res, (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
1393 (long long)(msg_prio), (long long)(abs_timeout))
1397 #define __sanitizer_syscall_pre___posix_rename(from, to) \
1398 __sanitizer_syscall_pre_impl___posix_rename((long long)(from), \
1400 #define __sanitizer_syscall_post___posix_rename(res, from, to) \
1401 __sanitizer_syscall_post_impl___posix_rename(res, (long long)(from), \
1403 #define __sanitizer_syscall_pre_swapctl(cmd, arg, misc) \
1404 __sanitizer_syscall_pre_impl_swapctl((long long)(cmd), (long long)(arg), \
1406 #define __sanitizer_syscall_post_swapctl(res, cmd, arg, misc) \
1407 __sanitizer_syscall_post_impl_swapctl(res, (long long)(cmd), \
1408 (long long)(arg), (long long)(misc))
1409 #define __sanitizer_syscall_pre_compat_30_getdents(fd, buf, count) \
1410 __sanitizer_syscall_pre_impl_compat_30_getdents( \
1411 (long long)(fd), (long long)(buf), (long long)(count))
1412 #define __sanitizer_syscall_post_compat_30_getdents(res, fd, buf, count) \
1413 __sanitizer_syscall_post_impl_compat_30_getdents( \
1414 res, (long long)(fd), (long long)(buf), (long long)(count))
1415 #define __sanitizer_syscall_pre_minherit(addr, len, inherit) \
1416 __sanitizer_syscall_pre_impl_minherit((long long)(addr), (long long)(len), \
1417 (long long)(inherit))
1418 #define __sanitizer_syscall_post_minherit(res, addr, len, inherit) \
1419 __sanitizer_syscall_post_impl_minherit( \
1420 res, (long long)(addr), (long long)(len), (long long)(inherit))
1421 #define __sanitizer_syscall_pre_lchmod(path, mode) \
1422 __sanitizer_syscall_pre_impl_lchmod((long long)(path), (long long)(mode))
1423 #define __sanitizer_syscall_post_lchmod(res, path, mode) \
1424 __sanitizer_syscall_post_impl_lchmod(res, (long long)(path), \
1426 #define __sanitizer_syscall_pre_lchown(path, uid, gid) \
1427 __sanitizer_syscall_pre_impl_lchown((long long)(path), (long long)(uid), \
1429 #define __sanitizer_syscall_post_lchown(res, path, uid, gid) \
1430 __sanitizer_syscall_post_impl_lchown(res, (long long)(path), \
1431 (long long)(uid), (long long)(gid))
1432 #define __sanitizer_syscall_pre_compat_50_lutimes(path, tptr) \
1433 __sanitizer_syscall_pre_impl_compat_50_lutimes((long long)(path), \
1435 #define __sanitizer_syscall_post_compat_50_lutimes(res, path, tptr) \
1436 __sanitizer_syscall_post_impl_compat_50_lutimes(res, (long long)(path), \
1438 #define __sanitizer_syscall_pre___msync13(addr, len, flags) \
1439 __sanitizer_syscall_pre_impl___msync13((long long)(addr), (long long)(len), \
1441 #define __sanitizer_syscall_post___msync13(res, addr, len, flags) \
1442 __sanitizer_syscall_post_impl___msync13( \
1443 res, (long long)(addr), (long long)(len), (long long)(flags))
1444 #define __sanitizer_syscall_pre_compat_30___stat13(path, ub) \
1445 __sanitizer_syscall_pre_impl_compat_30___stat13((long long)(path), \
1447 #define __sanitizer_syscall_post_compat_30___stat13(res, path, ub) \
1448 __sanitizer_syscall_post_impl_compat_30___stat13(res, (long long)(path), \
1450 #define __sanitizer_syscall_pre_compat_30___fstat13(fd, sb) \
1451 __sanitizer_syscall_pre_impl_compat_30___fstat13((long long)(fd), \
1453 #define __sanitizer_syscall_post_compat_30___fstat13(res, fd, sb) \
1454 __sanitizer_syscall_post_impl_compat_30___fstat13(res, (long long)(fd), \
1456 #define __sanitizer_syscall_pre_compat_30___lstat13(path, ub) \
1457 __sanitizer_syscall_pre_impl_compat_30___lstat13((long long)(path), \
1459 #define __sanitizer_syscall_post_compat_30___lstat13(res, path, ub) \
1460 __sanitizer_syscall_post_impl_compat_30___lstat13(res, (long long)(path), \
1462 #define __sanitizer_syscall_pre___sigaltstack14(nss, oss) \
1463 __sanitizer_syscall_pre_impl___sigaltstack14((long long)(nss), \
1465 #define __sanitizer_syscall_post___sigaltstack14(res, nss, oss) \
1466 __sanitizer_syscall_post_impl___sigaltstack14(res, (long long)(nss), \
1468 #define __sanitizer_syscall_pre___vfork14() \
1469 __sanitizer_syscall_pre_impl___vfork14()
1470 #define __sanitizer_syscall_post___vfork14(res) \
1471 __sanitizer_syscall_post_impl___vfork14(res)
1472 #define __sanitizer_syscall_pre___posix_chown(path, uid, gid) \
1473 __sanitizer_syscall_pre_impl___posix_chown( \
1474 (long long)(path), (long long)(uid), (long long)(gid))
1475 #define __sanitizer_syscall_post___posix_chown(res, path, uid, gid) \
1476 __sanitizer_syscall_post_impl___posix_chown( \
1477 res, (long long)(path), (long long)(uid), (long long)(gid))
1478 #define __sanitizer_syscall_pre___posix_fchown(fd, uid, gid) \
1479 __sanitizer_syscall_pre_impl___posix_fchown( \
1480 (long long)(fd), (long long)(uid), (long long)(gid))
1481 #define __sanitizer_syscall_post___posix_fchown(res, fd, uid, gid) \
1482 __sanitizer_syscall_post_impl___posix_fchown( \
1483 res, (long long)(fd), (long long)(uid), (long long)(gid))
1484 #define __sanitizer_syscall_pre___posix_lchown(path, uid, gid) \
1485 __sanitizer_syscall_pre_impl___posix_lchown( \
1486 (long long)(path), (long long)(uid), (long long)(gid))
1487 #define __sanitizer_syscall_post___posix_lchown(res, path, uid, gid) \
1488 __sanitizer_syscall_post_impl___posix_lchown( \
1489 res, (long long)(path), (long long)(uid), (long long)(gid))
1490 #define __sanitizer_syscall_pre_getsid(pid) \
1491 __sanitizer_syscall_pre_impl_getsid((long long)(pid))
1492 #define __sanitizer_syscall_post_getsid(res, pid) \
1493 __sanitizer_syscall_post_impl_getsid(res, (long long)(pid))
1494 #define __sanitizer_syscall_pre___clone(flags, stack) \
1495 __sanitizer_syscall_pre_impl___clone((long long)(flags), (long long)(stack))
1496 #define __sanitizer_syscall_post___clone(res, flags, stack) \
1497 __sanitizer_syscall_post_impl___clone(res, (long long)(flags), \
1499 #define __sanitizer_syscall_pre_fktrace(fd, ops, facs, pid) \
1500 __sanitizer_syscall_pre_impl_fktrace((long long)(fd), (long long)(ops), \
1501 (long long)(facs), (long long)(pid))
1502 #define __sanitizer_syscall_post_fktrace(res, fd, ops, facs, pid) \
1503 __sanitizer_syscall_post_impl_fktrace(res, (long long)(fd), \
1504 (long long)(ops), (long long)(facs), \
1506 #define __sanitizer_syscall_pre_preadv(fd, iovp, iovcnt, PAD, offset) \
1507 __sanitizer_syscall_pre_impl_preadv((long long)(fd), (long long)(iovp), \
1508 (long long)(iovcnt), (long long)(PAD), \
1509 (long long)(offset))
1510 #define __sanitizer_syscall_post_preadv(res, fd, iovp, iovcnt, PAD, offset) \
1511 __sanitizer_syscall_post_impl_preadv(res, (long long)(fd), \
1512 (long long)(iovp), (long long)(iovcnt), \
1513 (long long)(PAD), (long long)(offset))
1514 #define __sanitizer_syscall_pre_pwritev(fd, iovp, iovcnt, PAD, offset) \
1515 __sanitizer_syscall_pre_impl_pwritev((long long)(fd), (long long)(iovp), \
1516 (long long)(iovcnt), (long long)(PAD), \
1517 (long long)(offset))
1518 #define __sanitizer_syscall_post_pwritev(res, fd, iovp, iovcnt, PAD, offset) \
1519 __sanitizer_syscall_post_impl_pwritev( \
1520 res, (long long)(fd), (long long)(iovp), (long long)(iovcnt), \
1521 (long long)(PAD), (long long)(offset))
1522 #define __sanitizer_syscall_pre_compat_16___sigaction14(signum, nsa, osa) \
1523 __sanitizer_syscall_pre_impl_compat_16___sigaction14( \
1524 (long long)(signum), (long long)(nsa), (long long)(osa))
1525 #define __sanitizer_syscall_post_compat_16___sigaction14(res, signum, nsa, \
1527 __sanitizer_syscall_post_impl_compat_16___sigaction14( \
1528 res, (long long)(signum), (long long)(nsa), (long long)(osa))
1529 #define __sanitizer_syscall_pre___sigpending14(set) \
1530 __sanitizer_syscall_pre_impl___sigpending14((long long)(set))
1531 #define __sanitizer_syscall_post___sigpending14(res, set) \
1532 __sanitizer_syscall_post_impl___sigpending14(res, (long long)(set))
1533 #define __sanitizer_syscall_pre___sigprocmask14(how, set, oset) \
1534 __sanitizer_syscall_pre_impl___sigprocmask14( \
1535 (long long)(how), (long long)(set), (long long)(oset))
1536 #define __sanitizer_syscall_post___sigprocmask14(res, how, set, oset) \
1537 __sanitizer_syscall_post_impl___sigprocmask14( \
1538 res, (long long)(how), (long long)(set), (long long)(oset))
1539 #define __sanitizer_syscall_pre___sigsuspend14(set) \
1540 __sanitizer_syscall_pre_impl___sigsuspend14((long long)(set))
1541 #define __sanitizer_syscall_post___sigsuspend14(res, set) \
1542 __sanitizer_syscall_post_impl___sigsuspend14(res, (long long)(set))
1543 #define __sanitizer_syscall_pre_compat_16___sigreturn14(sigcntxp) \
1544 __sanitizer_syscall_pre_impl_compat_16___sigreturn14((long long)(sigcntxp))
1545 #define __sanitizer_syscall_post_compat_16___sigreturn14(res, sigcntxp) \
1546 __sanitizer_syscall_post_impl_compat_16___sigreturn14(res, \
1547 (long long)(sigcntxp))
1548 #define __sanitizer_syscall_pre___getcwd(bufp, length) \
1549 __sanitizer_syscall_pre_impl___getcwd((long long)(bufp), (long long)(length))
1550 #define __sanitizer_syscall_post___getcwd(res, bufp, length) \
1551 __sanitizer_syscall_post_impl___getcwd(res, (long long)(bufp), \
1552 (long long)(length))
1553 #define __sanitizer_syscall_pre_fchroot(fd) \
1554 __sanitizer_syscall_pre_impl_fchroot((long long)(fd))
1555 #define __sanitizer_syscall_post_fchroot(res, fd) \
1556 __sanitizer_syscall_post_impl_fchroot(res, (long long)(fd))
1557 #define __sanitizer_syscall_pre_compat_30_fhopen(fhp, flags) \
1558 __sanitizer_syscall_pre_impl_compat_30_fhopen((long long)(fhp), \
1560 #define __sanitizer_syscall_post_compat_30_fhopen(res, fhp, flags) \
1561 __sanitizer_syscall_post_impl_compat_30_fhopen(res, (long long)(fhp), \
1563 #define __sanitizer_syscall_pre_compat_30_fhstat(fhp, sb) \
1564 __sanitizer_syscall_pre_impl_compat_30_fhstat((long long)(fhp), \
1566 #define __sanitizer_syscall_post_compat_30_fhstat(res, fhp, sb) \
1567 __sanitizer_syscall_post_impl_compat_30_fhstat(res, (long long)(fhp), \
1569 #define __sanitizer_syscall_pre_compat_20_fhstatfs(fhp, buf) \
1570 __sanitizer_syscall_pre_impl_compat_20_fhstatfs((long long)(fhp), \
1572 #define __sanitizer_syscall_post_compat_20_fhstatfs(res, fhp, buf) \
1573 __sanitizer_syscall_post_impl_compat_20_fhstatfs(res, (long long)(fhp), \
1575 #define __sanitizer_syscall_pre_compat_50_____semctl13(semid, semnum, cmd, \
1577 __sanitizer_syscall_pre_impl_compat_50_____semctl13( \
1578 (long long)(semid), (long long)(semnum), (long long)(cmd), \
1580 #define __sanitizer_syscall_post_compat_50_____semctl13(res, semid, semnum, \
1582 __sanitizer_syscall_post_impl_compat_50_____semctl13( \
1583 res, (long long)(semid), (long long)(semnum), (long long)(cmd), \
1585 #define __sanitizer_syscall_pre_compat_50___msgctl13(msqid, cmd, buf) \
1586 __sanitizer_syscall_pre_impl_compat_50___msgctl13( \
1587 (long long)(msqid), (long long)(cmd), (long long)(buf))
1588 #define __sanitizer_syscall_post_compat_50___msgctl13(res, msqid, cmd, buf) \
1589 __sanitizer_syscall_post_impl_compat_50___msgctl13( \
1590 res, (long long)(msqid), (long long)(cmd), (long long)(buf))
1591 #define __sanitizer_syscall_pre_compat_50___shmctl13(shmid, cmd, buf) \
1592 __sanitizer_syscall_pre_impl_compat_50___shmctl13( \
1593 (long long)(shmid), (long long)(cmd), (long long)(buf))
1594 #define __sanitizer_syscall_post_compat_50___shmctl13(res, shmid, cmd, buf) \
1595 __sanitizer_syscall_post_impl_compat_50___shmctl13( \
1596 res, (long long)(shmid), (long long)(cmd), (long long)(buf))
1597 #define __sanitizer_syscall_pre_lchflags(path, flags) \
1598 __sanitizer_syscall_pre_impl_lchflags((long long)(path), (long long)(flags))
1599 #define __sanitizer_syscall_post_lchflags(res, path, flags) \
1600 __sanitizer_syscall_post_impl_lchflags(res, (long long)(path), \
1602 #define __sanitizer_syscall_pre_issetugid() \
1603 __sanitizer_syscall_pre_impl_issetugid()
1604 #define __sanitizer_syscall_post_issetugid(res) \
1605 __sanitizer_syscall_post_impl_issetugid(res)
1606 #define __sanitizer_syscall_pre_utrace(label, addr, len) \
1607 __sanitizer_syscall_pre_impl_utrace((long long)(label), (long long)(addr), \
1609 #define __sanitizer_syscall_post_utrace(res, label, addr, len) \
1610 __sanitizer_syscall_post_impl_utrace(res, (long long)(label), \
1611 (long long)(addr), (long long)(len))
1612 #define __sanitizer_syscall_pre_getcontext(ucp) \
1613 __sanitizer_syscall_pre_impl_getcontext((long long)(ucp))
1614 #define __sanitizer_syscall_post_getcontext(res, ucp) \
1615 __sanitizer_syscall_post_impl_getcontext(res, (long long)(ucp))
1616 #define __sanitizer_syscall_pre_setcontext(ucp) \
1617 __sanitizer_syscall_pre_impl_setcontext((long long)(ucp))
1618 #define __sanitizer_syscall_post_setcontext(res, ucp) \
1619 __sanitizer_syscall_post_impl_setcontext(res, (long long)(ucp))
1620 #define __sanitizer_syscall_pre__lwp_create(ucp, flags, new_lwp) \
1621 __sanitizer_syscall_pre_impl__lwp_create( \
1622 (long long)(ucp), (long long)(flags), (long long)(new_lwp))
1623 #define __sanitizer_syscall_post__lwp_create(res, ucp, flags, new_lwp) \
1624 __sanitizer_syscall_post_impl__lwp_create( \
1625 res, (long long)(ucp), (long long)(flags), (long long)(new_lwp))
1626 #define __sanitizer_syscall_pre__lwp_exit() \
1627 __sanitizer_syscall_pre_impl__lwp_exit()
1628 #define __sanitizer_syscall_post__lwp_exit(res) \
1629 __sanitizer_syscall_post_impl__lwp_exit(res)
1630 #define __sanitizer_syscall_pre__lwp_self() \
1631 __sanitizer_syscall_pre_impl__lwp_self()
1632 #define __sanitizer_syscall_post__lwp_self(res) \
1633 __sanitizer_syscall_post_impl__lwp_self(res)
1634 #define __sanitizer_syscall_pre__lwp_wait(wait_for, departed) \
1635 __sanitizer_syscall_pre_impl__lwp_wait((long long)(wait_for), \
1636 (long long)(departed))
1637 #define __sanitizer_syscall_post__lwp_wait(res, wait_for, departed) \
1638 __sanitizer_syscall_post_impl__lwp_wait(res, (long long)(wait_for), \
1639 (long long)(departed))
1640 #define __sanitizer_syscall_pre__lwp_suspend(target) \
1641 __sanitizer_syscall_pre_impl__lwp_suspend((long long)(target))
1642 #define __sanitizer_syscall_post__lwp_suspend(res, target) \
1643 __sanitizer_syscall_post_impl__lwp_suspend(res, (long long)(target))
1644 #define __sanitizer_syscall_pre__lwp_continue(target) \
1645 __sanitizer_syscall_pre_impl__lwp_continue((long long)(target))
1646 #define __sanitizer_syscall_post__lwp_continue(res, target) \
1647 __sanitizer_syscall_post_impl__lwp_continue(res, (long long)(target))
1648 #define __sanitizer_syscall_pre__lwp_wakeup(target) \
1649 __sanitizer_syscall_pre_impl__lwp_wakeup((long long)(target))
1650 #define __sanitizer_syscall_post__lwp_wakeup(res, target) \
1651 __sanitizer_syscall_post_impl__lwp_wakeup(res, (long long)(target))
1652 #define __sanitizer_syscall_pre__lwp_getprivate() \
1653 __sanitizer_syscall_pre_impl__lwp_getprivate()
1654 #define __sanitizer_syscall_post__lwp_getprivate(res) \
1655 __sanitizer_syscall_post_impl__lwp_getprivate(res)
1656 #define __sanitizer_syscall_pre__lwp_setprivate(ptr) \
1657 __sanitizer_syscall_pre_impl__lwp_setprivate((long long)(ptr))
1658 #define __sanitizer_syscall_post__lwp_setprivate(res, ptr) \
1659 __sanitizer_syscall_post_impl__lwp_setprivate(res, (long long)(ptr))
1660 #define __sanitizer_syscall_pre__lwp_kill(target, signo) \
1661 __sanitizer_syscall_pre_impl__lwp_kill((long long)(target), \
1663 #define __sanitizer_syscall_post__lwp_kill(res, target, signo) \
1664 __sanitizer_syscall_post_impl__lwp_kill(res, (long long)(target), \
1666 #define __sanitizer_syscall_pre__lwp_detach(target) \
1667 __sanitizer_syscall_pre_impl__lwp_detach((long long)(target))
1668 #define __sanitizer_syscall_post__lwp_detach(res, target) \
1669 __sanitizer_syscall_post_impl__lwp_detach(res, (long long)(target))
1670 #define __sanitizer_syscall_pre_compat_50__lwp_park(ts, unpark, hint, \
1672 __sanitizer_syscall_pre_impl_compat_50__lwp_park( \
1673 (long long)(ts), (long long)(unpark), (long long)(hint), \
1674 (long long)(unparkhint))
1675 #define __sanitizer_syscall_post_compat_50__lwp_park(res, ts, unpark, hint, \
1677 __sanitizer_syscall_post_impl_compat_50__lwp_park( \
1678 res, (long long)(ts), (long long)(unpark), (long long)(hint), \
1679 (long long)(unparkhint))
1680 #define __sanitizer_syscall_pre__lwp_unpark(target, hint) \
1681 __sanitizer_syscall_pre_impl__lwp_unpark((long long)(target), \
1683 #define __sanitizer_syscall_post__lwp_unpark(res, target, hint) \
1684 __sanitizer_syscall_post_impl__lwp_unpark(res, (long long)(target), \
1686 #define __sanitizer_syscall_pre__lwp_unpark_all(targets, ntargets, hint) \
1687 __sanitizer_syscall_pre_impl__lwp_unpark_all( \
1688 (long long)(targets), (long long)(ntargets), (long long)(hint))
1689 #define __sanitizer_syscall_post__lwp_unpark_all(res, targets, ntargets, hint) \
1690 __sanitizer_syscall_post_impl__lwp_unpark_all( \
1691 res, (long long)(targets), (long long)(ntargets), (long long)(hint))
1692 #define __sanitizer_syscall_pre__lwp_setname(target, name) \
1693 __sanitizer_syscall_pre_impl__lwp_setname((long long)(target), \
1695 #define __sanitizer_syscall_post__lwp_setname(res, target, name) \
1696 __sanitizer_syscall_post_impl__lwp_setname(res, (long long)(target), \
1698 #define __sanitizer_syscall_pre__lwp_getname(target, name, len) \
1699 __sanitizer_syscall_pre_impl__lwp_getname( \
1700 (long long)(target), (long long)(name), (long long)(len))
1701 #define __sanitizer_syscall_post__lwp_getname(res, target, name, len) \
1702 __sanitizer_syscall_post_impl__lwp_getname( \
1703 res, (long long)(target), (long long)(name), (long long)(len))
1704 #define __sanitizer_syscall_pre__lwp_ctl(features, address) \
1705 __sanitizer_syscall_pre_impl__lwp_ctl((long long)(features), \
1706 (long long)(address))
1707 #define __sanitizer_syscall_post__lwp_ctl(res, features, address) \
1708 __sanitizer_syscall_post_impl__lwp_ctl(res, (long long)(features), \
1709 (long long)(address))
1714 #define __sanitizer_syscall_pre_compat_60_sa_register(newv, oldv, flags, \
1716 __sanitizer_syscall_pre_impl_compat_60_sa_register( \
1717 (long long)(newv), (long long)(oldv), (long long)(flags), \
1718 (long long)(stackinfo_offset))
1719 #define __sanitizer_syscall_post_compat_60_sa_register(res, newv, oldv, flags, \
1721 __sanitizer_syscall_post_impl_compat_60_sa_register( \
1722 res, (long long)(newv), (long long)(oldv), (long long)(flags), \
1723 (long long)(stackinfo_offset))
1724 #define __sanitizer_syscall_pre_compat_60_sa_stacks(num, stacks) \
1725 __sanitizer_syscall_pre_impl_compat_60_sa_stacks((long long)(num), \
1726 (long long)(stacks))
1727 #define __sanitizer_syscall_post_compat_60_sa_stacks(res, num, stacks) \
1728 __sanitizer_syscall_post_impl_compat_60_sa_stacks(res, (long long)(num), \
1729 (long long)(stacks))
1730 #define __sanitizer_syscall_pre_compat_60_sa_enable() \
1731 __sanitizer_syscall_pre_impl_compat_60_sa_enable()
1732 #define __sanitizer_syscall_post_compat_60_sa_enable(res) \
1733 __sanitizer_syscall_post_impl_compat_60_sa_enable(res)
1734 #define __sanitizer_syscall_pre_compat_60_sa_setconcurrency(concurrency) \
1735 __sanitizer_syscall_pre_impl_compat_60_sa_setconcurrency( \
1736 (long long)(concurrency))
1737 #define __sanitizer_syscall_post_compat_60_sa_setconcurrency(res, concurrency) \
1738 __sanitizer_syscall_post_impl_compat_60_sa_setconcurrency( \
1739 res, (long long)(concurrency))
1740 #define __sanitizer_syscall_pre_compat_60_sa_yield() \
1741 __sanitizer_syscall_pre_impl_compat_60_sa_yield()
1742 #define __sanitizer_syscall_post_compat_60_sa_yield(res) \
1743 __sanitizer_syscall_post_impl_compat_60_sa_yield(res)
1744 #define __sanitizer_syscall_pre_compat_60_sa_preempt(sa_id) \
1745 __sanitizer_syscall_pre_impl_compat_60_sa_preempt((long long)(sa_id))
1746 #define __sanitizer_syscall_post_compat_60_sa_preempt(res, sa_id) \
1747 __sanitizer_syscall_post_impl_compat_60_sa_preempt(res, (long long)(sa_id))
1752 #define __sanitizer_syscall_pre___sigaction_sigtramp(signum, nsa, osa, tramp, \
1754 __sanitizer_syscall_pre_impl___sigaction_sigtramp( \
1755 (long long)(signum), (long long)(nsa), (long long)(osa), \
1756 (long long)(tramp), (long long)(vers))
1757 #define __sanitizer_syscall_post___sigaction_sigtramp(res, signum, nsa, osa, \
1759 __sanitizer_syscall_post_impl___sigaction_sigtramp( \
1760 res, (long long)(signum), (long long)(nsa), (long long)(osa), \
1761 (long long)(tramp), (long long)(vers))
1764 #define __sanitizer_syscall_pre_rasctl(addr, len, op) \
1765 __sanitizer_syscall_pre_impl_rasctl((long long)(addr), (long long)(len), \
1767 #define __sanitizer_syscall_post_rasctl(res, addr, len, op) \
1768 __sanitizer_syscall_post_impl_rasctl(res, (long long)(addr), \
1769 (long long)(len), (long long)(op))
1770 #define __sanitizer_syscall_pre_kqueue() __sanitizer_syscall_pre_impl_kqueue()
1771 #define __sanitizer_syscall_post_kqueue(res) \
1772 __sanitizer_syscall_post_impl_kqueue(res)
1773 #define __sanitizer_syscall_pre_compat_50_kevent(fd, changelist, nchanges, \
1774 eventlist, nevents, timeout) \
1775 __sanitizer_syscall_pre_impl_compat_50_kevent( \
1776 (long long)(fd), (long long)(changelist), (long long)(nchanges), \
1777 (long long)(eventlist), (long long)(nevents), (long long)(timeout))
1778 #define __sanitizer_syscall_post_compat_50_kevent( \
1779 res, fd, changelist, nchanges, eventlist, nevents, timeout) \
1780 __sanitizer_syscall_post_impl_compat_50_kevent( \
1781 res, (long long)(fd), (long long)(changelist), (long long)(nchanges), \
1782 (long long)(eventlist), (long long)(nevents), (long long)(timeout))
1783 #define __sanitizer_syscall_pre__sched_setparam(pid, lid, policy, params) \
1784 __sanitizer_syscall_pre_impl__sched_setparam( \
1785 (long long)(pid), (long long)(lid), (long long)(policy), \
1786 (long long)(params))
1787 #define __sanitizer_syscall_post__sched_setparam(res, pid, lid, policy, \
1789 __sanitizer_syscall_post_impl__sched_setparam( \
1790 res, (long long)(pid), (long long)(lid), (long long)(policy), \
1791 (long long)(params))
1792 #define __sanitizer_syscall_pre__sched_getparam(pid, lid, policy, params) \
1793 __sanitizer_syscall_pre_impl__sched_getparam( \
1794 (long long)(pid), (long long)(lid), (long long)(policy), \
1795 (long long)(params))
1796 #define __sanitizer_syscall_post__sched_getparam(res, pid, lid, policy, \
1798 __sanitizer_syscall_post_impl__sched_getparam( \
1799 res, (long long)(pid), (long long)(lid), (long long)(policy), \
1800 (long long)(params))
1801 #define __sanitizer_syscall_pre__sched_setaffinity(pid, lid, size, cpuset) \
1802 __sanitizer_syscall_pre_impl__sched_setaffinity( \
1803 (long long)(pid), (long long)(lid), (long long)(size), \
1804 (long long)(cpuset))
1805 #define __sanitizer_syscall_post__sched_setaffinity(res, pid, lid, size, \
1807 __sanitizer_syscall_post_impl__sched_setaffinity( \
1808 res, (long long)(pid), (long long)(lid), (long long)(size), \
1809 (long long)(cpuset))
1810 #define __sanitizer_syscall_pre__sched_getaffinity(pid, lid, size, cpuset) \
1811 __sanitizer_syscall_pre_impl__sched_getaffinity( \
1812 (long long)(pid), (long long)(lid), (long long)(size), \
1813 (long long)(cpuset))
1814 #define __sanitizer_syscall_post__sched_getaffinity(res, pid, lid, size, \
1816 __sanitizer_syscall_post_impl__sched_getaffinity( \
1817 res, (long long)(pid), (long long)(lid), (long long)(size), \
1818 (long long)(cpuset))
1819 #define __sanitizer_syscall_pre_sched_yield() \
1820 __sanitizer_syscall_pre_impl_sched_yield()
1821 #define __sanitizer_syscall_post_sched_yield(res) \
1822 __sanitizer_syscall_post_impl_sched_yield(res)
1823 #define __sanitizer_syscall_pre__sched_protect(priority) \
1824 __sanitizer_syscall_pre_impl__sched_protect((long long)(priority))
1825 #define __sanitizer_syscall_post__sched_protect(res, priority) \
1826 __sanitizer_syscall_post_impl__sched_protect(res, (long long)(priority))
1829 #define __sanitizer_syscall_pre_fsync_range(fd, flags, start, length) \
1830 __sanitizer_syscall_pre_impl_fsync_range( \
1831 (long long)(fd), (long long)(flags), (long long)(start), \
1832 (long long)(length))
1833 #define __sanitizer_syscall_post_fsync_range(res, fd, flags, start, length) \
1834 __sanitizer_syscall_post_impl_fsync_range( \
1835 res, (long long)(fd), (long long)(flags), (long long)(start), \
1836 (long long)(length))
1837 #define __sanitizer_syscall_pre_uuidgen(store, count) \
1838 __sanitizer_syscall_pre_impl_uuidgen((long long)(store), (long long)(count))
1839 #define __sanitizer_syscall_post_uuidgen(res, store, count) \
1840 __sanitizer_syscall_post_impl_uuidgen(res, (long long)(store), \
1842 #define __sanitizer_syscall_pre_compat_90_getvfsstat(buf, bufsize, flags) \
1843 __sanitizer_syscall_pre_impl_compat_90_getvfsstat( \
1844 (long long)(buf), (long long)(bufsize), (long long)(flags))
1845 #define __sanitizer_syscall_post_compat_90_getvfsstat(res, buf, bufsize, \
1847 __sanitizer_syscall_post_impl_compat_90_getvfsstat( \
1848 res, (long long)(buf), (long long)(bufsize), (long long)(flags))
1849 #define __sanitizer_syscall_pre_compat_90_statvfs1(path, buf, flags) \
1850 __sanitizer_syscall_pre_impl_compat_90_statvfs1( \
1851 (long long)(path), (long long)(buf), (long long)(flags))
1852 #define __sanitizer_syscall_post_compat_90_statvfs1(res, path, buf, flags) \
1853 __sanitizer_syscall_post_impl_compat_90_statvfs1( \
1854 res, (long long)(path), (long long)(buf), (long long)(flags))
1855 #define __sanitizer_syscall_pre_compat_90_fstatvfs1(fd, buf, flags) \
1856 __sanitizer_syscall_pre_impl_compat_90_fstatvfs1( \
1857 (long long)(fd), (long long)(buf), (long long)(flags))
1858 #define __sanitizer_syscall_post_compat_90_fstatvfs1(res, fd, buf, flags) \
1859 __sanitizer_syscall_post_impl_compat_90_fstatvfs1( \
1860 res, (long long)(fd), (long long)(buf), (long long)(flags))
1861 #define __sanitizer_syscall_pre_compat_30_fhstatvfs1(fhp, buf, flags) \
1862 __sanitizer_syscall_pre_impl_compat_30_fhstatvfs1( \
1863 (long long)(fhp), (long long)(buf), (long long)(flags))
1864 #define __sanitizer_syscall_post_compat_30_fhstatvfs1(res, fhp, buf, flags) \
1865 __sanitizer_syscall_post_impl_compat_30_fhstatvfs1( \
1866 res, (long long)(fhp), (long long)(buf), (long long)(flags))
1867 #define __sanitizer_syscall_pre_extattrctl(path, cmd, filename, attrnamespace, \
1869 __sanitizer_syscall_pre_impl_extattrctl( \
1870 (long long)(path), (long long)(cmd), (long long)(filename), \
1871 (long long)(attrnamespace), (long long)(attrname))
1872 #define __sanitizer_syscall_post_extattrctl(res, path, cmd, filename, \
1873 attrnamespace, attrname) \
1874 __sanitizer_syscall_post_impl_extattrctl( \
1875 res, (long long)(path), (long long)(cmd), (long long)(filename), \
1876 (long long)(attrnamespace), (long long)(attrname))
1877 #define __sanitizer_syscall_pre_extattr_set_file(path, attrnamespace, \
1878 attrname, data, nbytes) \
1879 __sanitizer_syscall_pre_impl_extattr_set_file( \
1880 (long long)(path), (long long)(attrnamespace), (long long)(attrname), \
1881 (long long)(data), (long long)(nbytes))
1882 #define __sanitizer_syscall_post_extattr_set_file(res, path, attrnamespace, \
1883 attrname, data, nbytes) \
1884 __sanitizer_syscall_post_impl_extattr_set_file( \
1885 res, (long long)(path), (long long)(attrnamespace), \
1886 (long long)(attrname), (long long)(data), (long long)(nbytes))
1887 #define __sanitizer_syscall_pre_extattr_get_file(path, attrnamespace, \
1888 attrname, data, nbytes) \
1889 __sanitizer_syscall_pre_impl_extattr_get_file( \
1890 (long long)(path), (long long)(attrnamespace), (long long)(attrname), \
1891 (long long)(data), (long long)(nbytes))
1892 #define __sanitizer_syscall_post_extattr_get_file(res, path, attrnamespace, \
1893 attrname, data, nbytes) \
1894 __sanitizer_syscall_post_impl_extattr_get_file( \
1895 res, (long long)(path), (long long)(attrnamespace), \
1896 (long long)(attrname), (long long)(data), (long long)(nbytes))
1897 #define __sanitizer_syscall_pre_extattr_delete_file(path, attrnamespace, \
1899 __sanitizer_syscall_pre_impl_extattr_delete_file( \
1900 (long long)(path), (long long)(attrnamespace), (long long)(attrname))
1901 #define __sanitizer_syscall_post_extattr_delete_file(res, path, attrnamespace, \
1903 __sanitizer_syscall_post_impl_extattr_delete_file( \
1904 res, (long long)(path), (long long)(attrnamespace), \
1905 (long long)(attrname))
1906 #define __sanitizer_syscall_pre_extattr_set_fd(fd, attrnamespace, attrname, \
1908 __sanitizer_syscall_pre_impl_extattr_set_fd( \
1909 (long long)(fd), (long long)(attrnamespace), (long long)(attrname), \
1910 (long long)(data), (long long)(nbytes))
1911 #define __sanitizer_syscall_post_extattr_set_fd(res, fd, attrnamespace, \
1912 attrname, data, nbytes) \
1913 __sanitizer_syscall_post_impl_extattr_set_fd( \
1914 res, (long long)(fd), (long long)(attrnamespace), (long long)(attrname), \
1915 (long long)(data), (long long)(nbytes))
1916 #define __sanitizer_syscall_pre_extattr_get_fd(fd, attrnamespace, attrname, \
1918 __sanitizer_syscall_pre_impl_extattr_get_fd( \
1919 (long long)(fd), (long long)(attrnamespace), (long long)(attrname), \
1920 (long long)(data), (long long)(nbytes))
1921 #define __sanitizer_syscall_post_extattr_get_fd(res, fd, attrnamespace, \
1922 attrname, data, nbytes) \
1923 __sanitizer_syscall_post_impl_extattr_get_fd( \
1924 res, (long long)(fd), (long long)(attrnamespace), (long long)(attrname), \
1925 (long long)(data), (long long)(nbytes))
1926 #define __sanitizer_syscall_pre_extattr_delete_fd(fd, attrnamespace, attrname) \
1927 __sanitizer_syscall_pre_impl_extattr_delete_fd( \
1928 (long long)(fd), (long long)(attrnamespace), (long long)(attrname))
1929 #define __sanitizer_syscall_post_extattr_delete_fd(res, fd, attrnamespace, \
1931 __sanitizer_syscall_post_impl_extattr_delete_fd( \
1932 res, (long long)(fd), (long long)(attrnamespace), (long long)(attrname))
1933 #define __sanitizer_syscall_pre_extattr_set_link(path, attrnamespace, \
1934 attrname, data, nbytes) \
1935 __sanitizer_syscall_pre_impl_extattr_set_link( \
1936 (long long)(path), (long long)(attrnamespace), (long long)(attrname), \
1937 (long long)(data), (long long)(nbytes))
1938 #define __sanitizer_syscall_post_extattr_set_link(res, path, attrnamespace, \
1939 attrname, data, nbytes) \
1940 __sanitizer_syscall_post_impl_extattr_set_link( \
1941 res, (long long)(path), (long long)(attrnamespace), \
1942 (long long)(attrname), (long long)(data), (long long)(nbytes))
1943 #define __sanitizer_syscall_pre_extattr_get_link(path, attrnamespace, \
1944 attrname, data, nbytes) \
1945 __sanitizer_syscall_pre_impl_extattr_get_link( \
1946 (long long)(path), (long long)(attrnamespace), (long long)(attrname), \
1947 (long long)(data), (long long)(nbytes))
1948 #define __sanitizer_syscall_post_extattr_get_link(res, path, attrnamespace, \
1949 attrname, data, nbytes) \
1950 __sanitizer_syscall_post_impl_extattr_get_link( \
1951 res, (long long)(path), (long long)(attrnamespace), \
1952 (long long)(attrname), (long long)(data), (long long)(nbytes))
1953 #define __sanitizer_syscall_pre_extattr_delete_link(path, attrnamespace, \
1955 __sanitizer_syscall_pre_impl_extattr_delete_link( \
1956 (long long)(path), (long long)(attrnamespace), (long long)(attrname))
1957 #define __sanitizer_syscall_post_extattr_delete_link(res, path, attrnamespace, \
1959 __sanitizer_syscall_post_impl_extattr_delete_link( \
1960 res, (long long)(path), (long long)(attrnamespace), \
1961 (long long)(attrname))
1962 #define __sanitizer_syscall_pre_extattr_list_fd(fd, attrnamespace, data, \
1964 __sanitizer_syscall_pre_impl_extattr_list_fd( \
1965 (long long)(fd), (long long)(attrnamespace), (long long)(data), \
1966 (long long)(nbytes))
1967 #define __sanitizer_syscall_post_extattr_list_fd(res, fd, attrnamespace, data, \
1969 __sanitizer_syscall_post_impl_extattr_list_fd( \
1970 res, (long long)(fd), (long long)(attrnamespace), (long long)(data), \
1971 (long long)(nbytes))
1972 #define __sanitizer_syscall_pre_extattr_list_file(path, attrnamespace, data, \
1974 __sanitizer_syscall_pre_impl_extattr_list_file( \
1975 (long long)(path), (long long)(attrnamespace), (long long)(data), \
1976 (long long)(nbytes))
1977 #define __sanitizer_syscall_post_extattr_list_file(res, path, attrnamespace, \
1979 __sanitizer_syscall_post_impl_extattr_list_file( \
1980 res, (long long)(path), (long long)(attrnamespace), (long long)(data), \
1981 (long long)(nbytes))
1982 #define __sanitizer_syscall_pre_extattr_list_link(path, attrnamespace, data, \
1984 __sanitizer_syscall_pre_impl_extattr_list_link( \
1985 (long long)(path), (long long)(attrnamespace), (long long)(data), \
1986 (long long)(nbytes))
1987 #define __sanitizer_syscall_post_extattr_list_link(res, path, attrnamespace, \
1989 __sanitizer_syscall_post_impl_extattr_list_link( \
1990 res, (long long)(path), (long long)(attrnamespace), (long long)(data), \
1991 (long long)(nbytes))
1992 #define __sanitizer_syscall_pre_compat_50_pselect(nd, in, ou, ex, ts, mask) \
1993 __sanitizer_syscall_pre_impl_compat_50_pselect( \
1994 (long long)(nd), (long long)(in), (long long)(ou), (long long)(ex), \
1995 (long long)(ts), (long long)(mask))
1996 #define __sanitizer_syscall_post_compat_50_pselect(res, nd, in, ou, ex, ts, \
1998 __sanitizer_syscall_post_impl_compat_50_pselect( \
1999 res, (long long)(nd), (long long)(in), (long long)(ou), (long long)(ex), \
2000 (long long)(ts), (long long)(mask))
2001 #define __sanitizer_syscall_pre_compat_50_pollts(fds, nfds, ts, mask) \
2002 __sanitizer_syscall_pre_impl_compat_50_pollts( \
2003 (long long)(fds), (long long)(nfds), (long long)(ts), (long long)(mask))
2004 #define __sanitizer_syscall_post_compat_50_pollts(res, fds, nfds, ts, mask) \
2005 __sanitizer_syscall_post_impl_compat_50_pollts( \
2006 res, (long long)(fds), (long long)(nfds), (long long)(ts), \
2008 #define __sanitizer_syscall_pre_setxattr(path, name, value, size, flags) \
2009 __sanitizer_syscall_pre_impl_setxattr((long long)(path), (long long)(name), \
2010 (long long)(value), (long long)(size), \
2012 #define __sanitizer_syscall_post_setxattr(res, path, name, value, size, flags) \
2013 __sanitizer_syscall_post_impl_setxattr( \
2014 res, (long long)(path), (long long)(name), (long long)(value), \
2015 (long long)(size), (long long)(flags))
2016 #define __sanitizer_syscall_pre_lsetxattr(path, name, value, size, flags) \
2017 __sanitizer_syscall_pre_impl_lsetxattr( \
2018 (long long)(path), (long long)(name), (long long)(value), \
2019 (long long)(size), (long long)(flags))
2020 #define __sanitizer_syscall_post_lsetxattr(res, path, name, value, size, \
2022 __sanitizer_syscall_post_impl_lsetxattr( \
2023 res, (long long)(path), (long long)(name), (long long)(value), \
2024 (long long)(size), (long long)(flags))
2025 #define __sanitizer_syscall_pre_fsetxattr(fd, name, value, size, flags) \
2026 __sanitizer_syscall_pre_impl_fsetxattr( \
2027 (long long)(fd), (long long)(name), (long long)(value), \
2028 (long long)(size), (long long)(flags))
2029 #define __sanitizer_syscall_post_fsetxattr(res, fd, name, value, size, flags) \
2030 __sanitizer_syscall_post_impl_fsetxattr( \
2031 res, (long long)(fd), (long long)(name), (long long)(value), \
2032 (long long)(size), (long long)(flags))
2033 #define __sanitizer_syscall_pre_getxattr(path, name, value, size) \
2034 __sanitizer_syscall_pre_impl_getxattr((long long)(path), (long long)(name), \
2035 (long long)(value), (long long)(size))
2036 #define __sanitizer_syscall_post_getxattr(res, path, name, value, size) \
2037 __sanitizer_syscall_post_impl_getxattr( \
2038 res, (long long)(path), (long long)(name), (long long)(value), \
2040 #define __sanitizer_syscall_pre_lgetxattr(path, name, value, size) \
2041 __sanitizer_syscall_pre_impl_lgetxattr((long long)(path), (long long)(name), \
2042 (long long)(value), \
2044 #define __sanitizer_syscall_post_lgetxattr(res, path, name, value, size) \
2045 __sanitizer_syscall_post_impl_lgetxattr( \
2046 res, (long long)(path), (long long)(name), (long long)(value), \
2048 #define __sanitizer_syscall_pre_fgetxattr(fd, name, value, size) \
2049 __sanitizer_syscall_pre_impl_fgetxattr((long long)(fd), (long long)(name), \
2050 (long long)(value), \
2052 #define __sanitizer_syscall_post_fgetxattr(res, fd, name, value, size) \
2053 __sanitizer_syscall_post_impl_fgetxattr( \
2054 res, (long long)(fd), (long long)(name), (long long)(value), \
2056 #define __sanitizer_syscall_pre_listxattr(path, list, size) \
2057 __sanitizer_syscall_pre_impl_listxattr((long long)(path), (long long)(list), \
2059 #define __sanitizer_syscall_post_listxattr(res, path, list, size) \
2060 __sanitizer_syscall_post_impl_listxattr( \
2061 res, (long long)(path), (long long)(list), (long long)(size))
2062 #define __sanitizer_syscall_pre_llistxattr(path, list, size) \
2063 __sanitizer_syscall_pre_impl_llistxattr( \
2064 (long long)(path), (long long)(list), (long long)(size))
2065 #define __sanitizer_syscall_post_llistxattr(res, path, list, size) \
2066 __sanitizer_syscall_post_impl_llistxattr( \
2067 res, (long long)(path), (long long)(list), (long long)(size))
2068 #define __sanitizer_syscall_pre_flistxattr(fd, list, size) \
2069 __sanitizer_syscall_pre_impl_flistxattr((long long)(fd), (long long)(list), \
2071 #define __sanitizer_syscall_post_flistxattr(res, fd, list, size) \
2072 __sanitizer_syscall_post_impl_flistxattr( \
2073 res, (long long)(fd), (long long)(list), (long long)(size))
2074 #define __sanitizer_syscall_pre_removexattr(path, name) \
2075 __sanitizer_syscall_pre_impl_removexattr((long long)(path), (long long)(name))
2076 #define __sanitizer_syscall_post_removexattr(res, path, name) \
2077 __sanitizer_syscall_post_impl_removexattr(res, (long long)(path), \
2079 #define __sanitizer_syscall_pre_lremovexattr(path, name) \
2080 __sanitizer_syscall_pre_impl_lremovexattr((long long)(path), \
2082 #define __sanitizer_syscall_post_lremovexattr(res, path, name) \
2083 __sanitizer_syscall_post_impl_lremovexattr(res, (long long)(path), \
2085 #define __sanitizer_syscall_pre_fremovexattr(fd, name) \
2086 __sanitizer_syscall_pre_impl_fremovexattr((long long)(fd), (long long)(name))
2087 #define __sanitizer_syscall_post_fremovexattr(res, fd, name) \
2088 __sanitizer_syscall_post_impl_fremovexattr(res, (long long)(fd), \
2090 #define __sanitizer_syscall_pre_compat_50___stat30(path, ub) \
2091 __sanitizer_syscall_pre_impl_compat_50___stat30((long long)(path), \
2093 #define __sanitizer_syscall_post_compat_50___stat30(res, path, ub) \
2094 __sanitizer_syscall_post_impl_compat_50___stat30(res, (long long)(path), \
2096 #define __sanitizer_syscall_pre_compat_50___fstat30(fd, sb) \
2097 __sanitizer_syscall_pre_impl_compat_50___fstat30((long long)(fd), \
2099 #define __sanitizer_syscall_post_compat_50___fstat30(res, fd, sb) \
2100 __sanitizer_syscall_post_impl_compat_50___fstat30(res, (long long)(fd), \
2102 #define __sanitizer_syscall_pre_compat_50___lstat30(path, ub) \
2103 __sanitizer_syscall_pre_impl_compat_50___lstat30((long long)(path), \
2105 #define __sanitizer_syscall_post_compat_50___lstat30(res, path, ub) \
2106 __sanitizer_syscall_post_impl_compat_50___lstat30(res, (long long)(path), \
2108 #define __sanitizer_syscall_pre___getdents30(fd, buf, count) \
2109 __sanitizer_syscall_pre_impl___getdents30((long long)(fd), (long long)(buf), \
2111 #define __sanitizer_syscall_post___getdents30(res, fd, buf, count) \
2112 __sanitizer_syscall_post_impl___getdents30( \
2113 res, (long long)(fd), (long long)(buf), (long long)(count))
2114 #define __sanitizer_syscall_pre_posix_fadvise() \
2115 __sanitizer_syscall_pre_impl_posix_fadvise((long long)())
2116 #define __sanitizer_syscall_post_posix_fadvise(res) \
2117 __sanitizer_syscall_post_impl_posix_fadvise(res, (long long)())
2118 #define __sanitizer_syscall_pre_compat_30___fhstat30(fhp, sb) \
2119 __sanitizer_syscall_pre_impl_compat_30___fhstat30((long long)(fhp), \
2121 #define __sanitizer_syscall_post_compat_30___fhstat30(res, fhp, sb) \
2122 __sanitizer_syscall_post_impl_compat_30___fhstat30(res, (long long)(fhp), \
2124 #define __sanitizer_syscall_pre_compat_50___ntp_gettime30(ntvp) \
2125 __sanitizer_syscall_pre_impl_compat_50___ntp_gettime30((long long)(ntvp))
2126 #define __sanitizer_syscall_post_compat_50___ntp_gettime30(res, ntvp) \
2127 __sanitizer_syscall_post_impl_compat_50___ntp_gettime30(res, \
2129 #define __sanitizer_syscall_pre___socket30(domain, type, protocol) \
2130 __sanitizer_syscall_pre_impl___socket30( \
2131 (long long)(domain), (long long)(type), (long long)(protocol))
2132 #define __sanitizer_syscall_post___socket30(res, domain, type, protocol) \
2133 __sanitizer_syscall_post_impl___socket30( \
2134 res, (long long)(domain), (long long)(type), (long long)(protocol))
2135 #define __sanitizer_syscall_pre___getfh30(fname, fhp, fh_size) \
2136 __sanitizer_syscall_pre_impl___getfh30((long long)(fname), (long long)(fhp), \
2137 (long long)(fh_size))
2138 #define __sanitizer_syscall_post___getfh30(res, fname, fhp, fh_size) \
2139 __sanitizer_syscall_post_impl___getfh30( \
2140 res, (long long)(fname), (long long)(fhp), (long long)(fh_size))
2141 #define __sanitizer_syscall_pre___fhopen40(fhp, fh_size, flags) \
2142 __sanitizer_syscall_pre_impl___fhopen40( \
2143 (long long)(fhp), (long long)(fh_size), (long long)(flags))
2144 #define __sanitizer_syscall_post___fhopen40(res, fhp, fh_size, flags) \
2145 __sanitizer_syscall_post_impl___fhopen40( \
2146 res, (long long)(fhp), (long long)(fh_size), (long long)(flags))
2147 #define __sanitizer_syscall_pre_compat_90_fhstatvfs1(fhp, fh_size, buf, flags) \
2148 __sanitizer_syscall_pre_impl_compat_90_fhstatvfs1( \
2149 (long long)(fhp), (long long)(fh_size), (long long)(buf), \
2151 #define __sanitizer_syscall_post_compat_90_fhstatvfs1(res, fhp, fh_size, buf, \
2153 __sanitizer_syscall_post_impl_compat_90_fhstatvfs1( \
2154 res, (long long)(fhp), (long long)(fh_size), (long long)(buf), \
2156 #define __sanitizer_syscall_pre_compat_50___fhstat40(fhp, fh_size, sb) \
2157 __sanitizer_syscall_pre_impl_compat_50___fhstat40( \
2158 (long long)(fhp), (long long)(fh_size), (long long)(sb))
2159 #define __sanitizer_syscall_post_compat_50___fhstat40(res, fhp, fh_size, sb) \
2160 __sanitizer_syscall_post_impl_compat_50___fhstat40( \
2161 res, (long long)(fhp), (long long)(fh_size), (long long)(sb))
2162 #define __sanitizer_syscall_pre_aio_cancel(fildes, aiocbp) \
2163 __sanitizer_syscall_pre_impl_aio_cancel((long long)(fildes), \
2164 (long long)(aiocbp))
2165 #define __sanitizer_syscall_post_aio_cancel(res, fildes, aiocbp) \
2166 __sanitizer_syscall_post_impl_aio_cancel(res, (long long)(fildes), \
2167 (long long)(aiocbp))
2168 #define __sanitizer_syscall_pre_aio_error(aiocbp) \
2169 __sanitizer_syscall_pre_impl_aio_error((long long)(aiocbp))
2170 #define __sanitizer_syscall_post_aio_error(res, aiocbp) \
2171 __sanitizer_syscall_post_impl_aio_error(res, (long long)(aiocbp))
2172 #define __sanitizer_syscall_pre_aio_fsync(op, aiocbp) \
2173 __sanitizer_syscall_pre_impl_aio_fsync((long long)(op), (long long)(aiocbp))
2174 #define __sanitizer_syscall_post_aio_fsync(res, op, aiocbp) \
2175 __sanitizer_syscall_post_impl_aio_fsync(res, (long long)(op), \
2176 (long long)(aiocbp))
2177 #define __sanitizer_syscall_pre_aio_read(aiocbp) \
2178 __sanitizer_syscall_pre_impl_aio_read((long long)(aiocbp))
2179 #define __sanitizer_syscall_post_aio_read(res, aiocbp) \
2180 __sanitizer_syscall_post_impl_aio_read(res, (long long)(aiocbp))
2181 #define __sanitizer_syscall_pre_aio_return(aiocbp) \
2182 __sanitizer_syscall_pre_impl_aio_return((long long)(aiocbp))
2183 #define __sanitizer_syscall_post_aio_return(res, aiocbp) \
2184 __sanitizer_syscall_post_impl_aio_return(res, (long long)(aiocbp))
2185 #define __sanitizer_syscall_pre_compat_50_aio_suspend(list, nent, timeout) \
2186 __sanitizer_syscall_pre_impl_compat_50_aio_suspend( \
2187 (long long)(list), (long long)(nent), (long long)(timeout))
2188 #define __sanitizer_syscall_post_compat_50_aio_suspend(res, list, nent, \
2190 __sanitizer_syscall_post_impl_compat_50_aio_suspend( \
2191 res, (long long)(list), (long long)(nent), (long long)(timeout))
2192 #define __sanitizer_syscall_pre_aio_write(aiocbp) \
2193 __sanitizer_syscall_pre_impl_aio_write((long long)(aiocbp))
2194 #define __sanitizer_syscall_post_aio_write(res, aiocbp) \
2195 __sanitizer_syscall_post_impl_aio_write(res, (long long)(aiocbp))
2196 #define __sanitizer_syscall_pre_lio_listio(mode, list, nent, sig) \
2197 __sanitizer_syscall_pre_impl_lio_listio((long long)(mode), \
2198 (long long)(list), \
2199 (long long)(nent), (long long)(sig))
2200 #define __sanitizer_syscall_post_lio_listio(res, mode, list, nent, sig) \
2201 __sanitizer_syscall_post_impl_lio_listio( \
2202 res, (long long)(mode), (long long)(list), (long long)(nent), \
2207 #define __sanitizer_syscall_pre___mount50(type, path, flags, data, data_len) \
2208 __sanitizer_syscall_pre_impl___mount50( \
2209 (long long)(type), (long long)(path), (long long)(flags), \
2210 (long long)(data), (long long)(data_len))
2211 #define __sanitizer_syscall_post___mount50(res, type, path, flags, data, \
2213 __sanitizer_syscall_post_impl___mount50( \
2214 res, (long long)(type), (long long)(path), (long long)(flags), \
2215 (long long)(data), (long long)(data_len))
2216 #define __sanitizer_syscall_pre_mremap(old_address, old_size, new_address, \
2218 __sanitizer_syscall_pre_impl_mremap( \
2219 (long long)(old_address), (long long)(old_size), \
2220 (long long)(new_address), (long long)(new_size), (long long)(flags))
2221 #define __sanitizer_syscall_post_mremap(res, old_address, old_size, \
2222 new_address, new_size, flags) \
2223 __sanitizer_syscall_post_impl_mremap( \
2224 res, (long long)(old_address), (long long)(old_size), \
2225 (long long)(new_address), (long long)(new_size), (long long)(flags))
2226 #define __sanitizer_syscall_pre_pset_create(psid) \
2227 __sanitizer_syscall_pre_impl_pset_create((long long)(psid))
2228 #define __sanitizer_syscall_post_pset_create(res, psid) \
2229 __sanitizer_syscall_post_impl_pset_create(res, (long long)(psid))
2230 #define __sanitizer_syscall_pre_pset_destroy(psid) \
2231 __sanitizer_syscall_pre_impl_pset_destroy((long long)(psid))
2232 #define __sanitizer_syscall_post_pset_destroy(res, psid) \
2233 __sanitizer_syscall_post_impl_pset_destroy(res, (long long)(psid))
2234 #define __sanitizer_syscall_pre_pset_assign(psid, cpuid, opsid) \
2235 __sanitizer_syscall_pre_impl_pset_assign( \
2236 (long long)(psid), (long long)(cpuid), (long long)(opsid))
2237 #define __sanitizer_syscall_post_pset_assign(res, psid, cpuid, opsid) \
2238 __sanitizer_syscall_post_impl_pset_assign( \
2239 res, (long long)(psid), (long long)(cpuid), (long long)(opsid))
2240 #define __sanitizer_syscall_pre__pset_bind(idtype, first_id, second_id, psid, \
2242 __sanitizer_syscall_pre_impl__pset_bind( \
2243 (long long)(idtype), (long long)(first_id), (long long)(second_id), \
2244 (long long)(psid), (long long)(opsid))
2245 #define __sanitizer_syscall_post__pset_bind(res, idtype, first_id, second_id, \
2247 __sanitizer_syscall_post_impl__pset_bind( \
2248 res, (long long)(idtype), (long long)(first_id), (long long)(second_id), \
2249 (long long)(psid), (long long)(opsid))
2250 #define __sanitizer_syscall_pre___posix_fadvise50(fd, PAD, offset, len, \
2252 __sanitizer_syscall_pre_impl___posix_fadvise50( \
2253 (long long)(fd), (long long)(PAD), (long long)(offset), \
2254 (long long)(len), (long long)(advice))
2255 #define __sanitizer_syscall_post___posix_fadvise50(res, fd, PAD, offset, len, \
2257 __sanitizer_syscall_post_impl___posix_fadvise50( \
2258 res, (long long)(fd), (long long)(PAD), (long long)(offset), \
2259 (long long)(len), (long long)(advice))
2260 #define __sanitizer_syscall_pre___select50(nd, in, ou, ex, tv) \
2261 __sanitizer_syscall_pre_impl___select50((long long)(nd), (long long)(in), \
2262 (long long)(ou), (long long)(ex), \
2264 #define __sanitizer_syscall_post___select50(res, nd, in, ou, ex, tv) \
2265 __sanitizer_syscall_post_impl___select50(res, (long long)(nd), \
2266 (long long)(in), (long long)(ou), \
2267 (long long)(ex), (long long)(tv))
2268 #define __sanitizer_syscall_pre___gettimeofday50(tp, tzp) \
2269 __sanitizer_syscall_pre_impl___gettimeofday50((long long)(tp), \
2271 #define __sanitizer_syscall_post___gettimeofday50(res, tp, tzp) \
2272 __sanitizer_syscall_post_impl___gettimeofday50(res, (long long)(tp), \
2274 #define __sanitizer_syscall_pre___settimeofday50(tv, tzp) \
2275 __sanitizer_syscall_pre_impl___settimeofday50((long long)(tv), \
2277 #define __sanitizer_syscall_post___settimeofday50(res, tv, tzp) \
2278 __sanitizer_syscall_post_impl___settimeofday50(res, (long long)(tv), \
2280 #define __sanitizer_syscall_pre___utimes50(path, tptr) \
2281 __sanitizer_syscall_pre_impl___utimes50((long long)(path), (long long)(tptr))
2282 #define __sanitizer_syscall_post___utimes50(res, path, tptr) \
2283 __sanitizer_syscall_post_impl___utimes50(res, (long long)(path), \
2285 #define __sanitizer_syscall_pre___adjtime50(delta, olddelta) \
2286 __sanitizer_syscall_pre_impl___adjtime50((long long)(delta), \
2287 (long long)(olddelta))
2288 #define __sanitizer_syscall_post___adjtime50(res, delta, olddelta) \
2289 __sanitizer_syscall_post_impl___adjtime50(res, (long long)(delta), \
2290 (long long)(olddelta))
2291 #define __sanitizer_syscall_pre___lfs_segwait50(fsidp, tv) \
2292 __sanitizer_syscall_pre_impl___lfs_segwait50((long long)(fsidp), \
2294 #define __sanitizer_syscall_post___lfs_segwait50(res, fsidp, tv) \
2295 __sanitizer_syscall_post_impl___lfs_segwait50(res, (long long)(fsidp), \
2297 #define __sanitizer_syscall_pre___futimes50(fd, tptr) \
2298 __sanitizer_syscall_pre_impl___futimes50((long long)(fd), (long long)(tptr))
2299 #define __sanitizer_syscall_post___futimes50(res, fd, tptr) \
2300 __sanitizer_syscall_post_impl___futimes50(res, (long long)(fd), \
2302 #define __sanitizer_syscall_pre___lutimes50(path, tptr) \
2303 __sanitizer_syscall_pre_impl___lutimes50((long long)(path), (long long)(tptr))
2304 #define __sanitizer_syscall_post___lutimes50(res, path, tptr) \
2305 __sanitizer_syscall_post_impl___lutimes50(res, (long long)(path), \
2307 #define __sanitizer_syscall_pre___setitimer50(which, itv, oitv) \
2308 __sanitizer_syscall_pre_impl___setitimer50( \
2309 (long long)(which), (long long)(itv), (long long)(oitv))
2310 #define __sanitizer_syscall_post___setitimer50(res, which, itv, oitv) \
2311 __sanitizer_syscall_post_impl___setitimer50( \
2312 res, (long long)(which), (long long)(itv), (long long)(oitv))
2313 #define __sanitizer_syscall_pre___getitimer50(which, itv) \
2314 __sanitizer_syscall_pre_impl___getitimer50((long long)(which), \
2316 #define __sanitizer_syscall_post___getitimer50(res, which, itv) \
2317 __sanitizer_syscall_post_impl___getitimer50(res, (long long)(which), \
2319 #define __sanitizer_syscall_pre___clock_gettime50(clock_id, tp) \
2320 __sanitizer_syscall_pre_impl___clock_gettime50((long long)(clock_id), \
2322 #define __sanitizer_syscall_post___clock_gettime50(res, clock_id, tp) \
2323 __sanitizer_syscall_post_impl___clock_gettime50(res, (long long)(clock_id), \
2325 #define __sanitizer_syscall_pre___clock_settime50(clock_id, tp) \
2326 __sanitizer_syscall_pre_impl___clock_settime50((long long)(clock_id), \
2328 #define __sanitizer_syscall_post___clock_settime50(res, clock_id, tp) \
2329 __sanitizer_syscall_post_impl___clock_settime50(res, (long long)(clock_id), \
2331 #define __sanitizer_syscall_pre___clock_getres50(clock_id, tp) \
2332 __sanitizer_syscall_pre_impl___clock_getres50((long long)(clock_id), \
2334 #define __sanitizer_syscall_post___clock_getres50(res, clock_id, tp) \
2335 __sanitizer_syscall_post_impl___clock_getres50(res, (long long)(clock_id), \
2337 #define __sanitizer_syscall_pre___nanosleep50(rqtp, rmtp) \
2338 __sanitizer_syscall_pre_impl___nanosleep50((long long)(rqtp), \
2340 #define __sanitizer_syscall_post___nanosleep50(res, rqtp, rmtp) \
2341 __sanitizer_syscall_post_impl___nanosleep50(res, (long long)(rqtp), \
2343 #define __sanitizer_syscall_pre_____sigtimedwait50(set, info, timeout) \
2344 __sanitizer_syscall_pre_impl_____sigtimedwait50( \
2345 (long long)(set), (long long)(info), (long long)(timeout))
2346 #define __sanitizer_syscall_post_____sigtimedwait50(res, set, info, timeout) \
2347 __sanitizer_syscall_post_impl_____sigtimedwait50( \
2348 res, (long long)(set), (long long)(info), (long long)(timeout))
2349 #define __sanitizer_syscall_pre___mq_timedsend50(mqdes, msg_ptr, msg_len, \
2350 msg_prio, abs_timeout) \
2351 __sanitizer_syscall_pre_impl___mq_timedsend50( \
2352 (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
2353 (long long)(msg_prio), (long long)(abs_timeout))
2354 #define __sanitizer_syscall_post___mq_timedsend50( \
2355 res, mqdes, msg_ptr, msg_len, msg_prio, abs_timeout) \
2356 __sanitizer_syscall_post_impl___mq_timedsend50( \
2357 res, (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
2358 (long long)(msg_prio), (long long)(abs_timeout))
2359 #define __sanitizer_syscall_pre___mq_timedreceive50(mqdes, msg_ptr, msg_len, \
2360 msg_prio, abs_timeout) \
2361 __sanitizer_syscall_pre_impl___mq_timedreceive50( \
2362 (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
2363 (long long)(msg_prio), (long long)(abs_timeout))
2364 #define __sanitizer_syscall_post___mq_timedreceive50( \
2365 res, mqdes, msg_ptr, msg_len, msg_prio, abs_timeout) \
2366 __sanitizer_syscall_post_impl___mq_timedreceive50( \
2367 res, (long long)(mqdes), (long long)(msg_ptr), (long long)(msg_len), \
2368 (long long)(msg_prio), (long long)(abs_timeout))
2369 #define __sanitizer_syscall_pre_compat_60__lwp_park(ts, unpark, hint, \
2371 __sanitizer_syscall_pre_impl_compat_60__lwp_park( \
2372 (long long)(ts), (long long)(unpark), (long long)(hint), \
2373 (long long)(unparkhint))
2374 #define __sanitizer_syscall_post_compat_60__lwp_park(res, ts, unpark, hint, \
2376 __sanitizer_syscall_post_impl_compat_60__lwp_park( \
2377 res, (long long)(ts), (long long)(unpark), (long long)(hint), \
2378 (long long)(unparkhint))
2379 #define __sanitizer_syscall_pre___kevent50(fd, changelist, nchanges, \
2380 eventlist, nevents, timeout) \
2381 __sanitizer_syscall_pre_impl___kevent50( \
2382 (long long)(fd), (long long)(changelist), (long long)(nchanges), \
2383 (long long)(eventlist), (long long)(nevents), (long long)(timeout))
2384 #define __sanitizer_syscall_post___kevent50(res, fd, changelist, nchanges, \
2385 eventlist, nevents, timeout) \
2386 __sanitizer_syscall_post_impl___kevent50( \
2387 res, (long long)(fd), (long long)(changelist), (long long)(nchanges), \
2388 (long long)(eventlist), (long long)(nevents), (long long)(timeout))
2389 #define __sanitizer_syscall_pre___pselect50(nd, in, ou, ex, ts, mask) \
2390 __sanitizer_syscall_pre_impl___pselect50((long long)(nd), (long long)(in), \
2391 (long long)(ou), (long long)(ex), \
2392 (long long)(ts), (long long)(mask))
2393 #define __sanitizer_syscall_post___pselect50(res, nd, in, ou, ex, ts, mask) \
2394 __sanitizer_syscall_post_impl___pselect50( \
2395 res, (long long)(nd), (long long)(in), (long long)(ou), (long long)(ex), \
2396 (long long)(ts), (long long)(mask))
2397 #define __sanitizer_syscall_pre___pollts50(fds, nfds, ts, mask) \
2398 __sanitizer_syscall_pre_impl___pollts50((long long)(fds), (long long)(nfds), \
2399 (long long)(ts), (long long)(mask))
2400 #define __sanitizer_syscall_post___pollts50(res, fds, nfds, ts, mask) \
2401 __sanitizer_syscall_post_impl___pollts50(res, (long long)(fds), \
2402 (long long)(nfds), (long long)(ts), \
2404 #define __sanitizer_syscall_pre___aio_suspend50(list, nent, timeout) \
2405 __sanitizer_syscall_pre_impl___aio_suspend50( \
2406 (long long)(list), (long long)(nent), (long long)(timeout))
2407 #define __sanitizer_syscall_post___aio_suspend50(res, list, nent, timeout) \
2408 __sanitizer_syscall_post_impl___aio_suspend50( \
2409 res, (long long)(list), (long long)(nent), (long long)(timeout))
2410 #define __sanitizer_syscall_pre___stat50(path, ub) \
2411 __sanitizer_syscall_pre_impl___stat50((long long)(path), (long long)(ub))
2412 #define __sanitizer_syscall_post___stat50(res, path, ub) \
2413 __sanitizer_syscall_post_impl___stat50(res, (long long)(path), \
2415 #define __sanitizer_syscall_pre___fstat50(fd, sb) \
2416 __sanitizer_syscall_pre_impl___fstat50((long long)(fd), (long long)(sb))
2417 #define __sanitizer_syscall_post___fstat50(res, fd, sb) \
2418 __sanitizer_syscall_post_impl___fstat50(res, (long long)(fd), (long long)(sb))
2419 #define __sanitizer_syscall_pre___lstat50(path, ub) \
2420 __sanitizer_syscall_pre_impl___lstat50((long long)(path), (long long)(ub))
2421 #define __sanitizer_syscall_post___lstat50(res, path, ub) \
2422 __sanitizer_syscall_post_impl___lstat50(res, (long long)(path), \
2424 #define __sanitizer_syscall_pre_____semctl50(semid, semnum, cmd, arg) \
2425 __sanitizer_syscall_pre_impl_____semctl50( \
2426 (long long)(semid), (long long)(semnum), (long long)(cmd), \
2428 #define __sanitizer_syscall_post_____semctl50(res, semid, semnum, cmd, arg) \
2429 __sanitizer_syscall_post_impl_____semctl50( \
2430 res, (long long)(semid), (long long)(semnum), (long long)(cmd), \
2432 #define __sanitizer_syscall_pre___shmctl50(shmid, cmd, buf) \
2433 __sanitizer_syscall_pre_impl___shmctl50((long long)(shmid), \
2434 (long long)(cmd), (long long)(buf))
2435 #define __sanitizer_syscall_post___shmctl50(res, shmid, cmd, buf) \
2436 __sanitizer_syscall_post_impl___shmctl50(res, (long long)(shmid), \
2437 (long long)(cmd), (long long)(buf))
2438 #define __sanitizer_syscall_pre___msgctl50(msqid, cmd, buf) \
2439 __sanitizer_syscall_pre_impl___msgctl50((long long)(msqid), \
2440 (long long)(cmd), (long long)(buf))
2441 #define __sanitizer_syscall_post___msgctl50(res, msqid, cmd, buf) \
2442 __sanitizer_syscall_post_impl___msgctl50(res, (long long)(msqid), \
2443 (long long)(cmd), (long long)(buf))
2444 #define __sanitizer_syscall_pre___getrusage50(who, rusage) \
2445 __sanitizer_syscall_pre_impl___getrusage50((long long)(who), \
2446 (long long)(rusage))
2447 #define __sanitizer_syscall_post___getrusage50(res, who, rusage) \
2448 __sanitizer_syscall_post_impl___getrusage50(res, (long long)(who), \
2449 (long long)(rusage))
2450 #define __sanitizer_syscall_pre___timer_settime50(timerid, flags, value, \
2452 __sanitizer_syscall_pre_impl___timer_settime50( \
2453 (long long)(timerid), (long long)(flags), (long long)(value), \
2454 (long long)(ovalue))
2455 #define __sanitizer_syscall_post___timer_settime50(res, timerid, flags, value, \
2457 __sanitizer_syscall_post_impl___timer_settime50( \
2458 res, (long long)(timerid), (long long)(flags), (long long)(value), \
2459 (long long)(ovalue))
2460 #define __sanitizer_syscall_pre___timer_gettime50(timerid, value) \
2461 __sanitizer_syscall_pre_impl___timer_gettime50((long long)(timerid), \
2463 #define __sanitizer_syscall_post___timer_gettime50(res, timerid, value) \
2464 __sanitizer_syscall_post_impl___timer_gettime50(res, (long long)(timerid), \
2466 #if defined(NTP) || !defined(_KERNEL_OPT)
2467 #define __sanitizer_syscall_pre___ntp_gettime50(ntvp) \
2468 __sanitizer_syscall_pre_impl___ntp_gettime50((long long)(ntvp))
2469 #define __sanitizer_syscall_post___ntp_gettime50(res, ntvp) \
2470 __sanitizer_syscall_post_impl___ntp_gettime50(res, (long long)(ntvp))
2474 #define __sanitizer_syscall_pre___wait450(pid, status, options, rusage) \
2475 __sanitizer_syscall_pre_impl___wait450( \
2476 (long long)(pid), (long long)(status), (long long)(options), \
2477 (long long)(rusage))
2478 #define __sanitizer_syscall_post___wait450(res, pid, status, options, rusage) \
2479 __sanitizer_syscall_post_impl___wait450( \
2480 res, (long long)(pid), (long long)(status), (long long)(options), \
2481 (long long)(rusage))
2482 #define __sanitizer_syscall_pre___mknod50(path, mode, dev) \
2483 __sanitizer_syscall_pre_impl___mknod50((long long)(path), (long long)(mode), \
2485 #define __sanitizer_syscall_post___mknod50(res, path, mode, dev) \
2486 __sanitizer_syscall_post_impl___mknod50(res, (long long)(path), \
2487 (long long)(mode), (long long)(dev))
2488 #define __sanitizer_syscall_pre___fhstat50(fhp, fh_size, sb) \
2489 __sanitizer_syscall_pre_impl___fhstat50( \
2490 (long long)(fhp), (long long)(fh_size), (long long)(sb))
2491 #define __sanitizer_syscall_post___fhstat50(res, fhp, fh_size, sb) \
2492 __sanitizer_syscall_post_impl___fhstat50( \
2493 res, (long long)(fhp), (long long)(fh_size), (long long)(sb))
2495 #define __sanitizer_syscall_pre_pipe2(fildes, flags) \
2496 __sanitizer_syscall_pre_impl_pipe2((long long)(fildes), (long long)(flags))
2497 #define __sanitizer_syscall_post_pipe2(res, fildes, flags) \
2498 __sanitizer_syscall_post_impl_pipe2(res, (long long)(fildes), \
2500 #define __sanitizer_syscall_pre_dup3(from, to, flags) \
2501 __sanitizer_syscall_pre_impl_dup3((long long)(from), (long long)(to), \
2503 #define __sanitizer_syscall_post_dup3(res, from, to, flags) \
2504 __sanitizer_syscall_post_impl_dup3(res, (long long)(from), (long long)(to), \
2506 #define __sanitizer_syscall_pre_kqueue1(flags) \
2507 __sanitizer_syscall_pre_impl_kqueue1((long long)(flags))
2508 #define __sanitizer_syscall_post_kqueue1(res, flags) \
2509 __sanitizer_syscall_post_impl_kqueue1(res, (long long)(flags))
2510 #define __sanitizer_syscall_pre_paccept(s, name, anamelen, mask, flags) \
2511 __sanitizer_syscall_pre_impl_paccept((long long)(s), (long long)(name), \
2512 (long long)(anamelen), \
2513 (long long)(mask), (long long)(flags))
2514 #define __sanitizer_syscall_post_paccept(res, s, name, anamelen, mask, flags) \
2515 __sanitizer_syscall_post_impl_paccept( \
2516 res, (long long)(s), (long long)(name), (long long)(anamelen), \
2517 (long long)(mask), (long long)(flags))
2518 #define __sanitizer_syscall_pre_linkat(fd1, name1, fd2, name2, flags) \
2519 __sanitizer_syscall_pre_impl_linkat((long long)(fd1), (long long)(name1), \
2520 (long long)(fd2), (long long)(name2), \
2522 #define __sanitizer_syscall_post_linkat(res, fd1, name1, fd2, name2, flags) \
2523 __sanitizer_syscall_post_impl_linkat(res, (long long)(fd1), \
2524 (long long)(name1), (long long)(fd2), \
2525 (long long)(name2), (long long)(flags))
2526 #define __sanitizer_syscall_pre_renameat(fromfd, from, tofd, to) \
2527 __sanitizer_syscall_pre_impl_renameat((long long)(fromfd), \
2528 (long long)(from), (long long)(tofd), \
2530 #define __sanitizer_syscall_post_renameat(res, fromfd, from, tofd, to) \
2531 __sanitizer_syscall_post_impl_renameat(res, (long long)(fromfd), \
2532 (long long)(from), (long long)(tofd), \
2534 #define __sanitizer_syscall_pre_mkfifoat(fd, path, mode) \
2535 __sanitizer_syscall_pre_impl_mkfifoat((long long)(fd), (long long)(path), \
2537 #define __sanitizer_syscall_post_mkfifoat(res, fd, path, mode) \
2538 __sanitizer_syscall_post_impl_mkfifoat(res, (long long)(fd), \
2539 (long long)(path), (long long)(mode))
2540 #define __sanitizer_syscall_pre_mknodat(fd, path, mode, PAD, dev) \
2541 __sanitizer_syscall_pre_impl_mknodat((long long)(fd), (long long)(path), \
2542 (long long)(mode), (long long)(PAD), \
2544 #define __sanitizer_syscall_post_mknodat(res, fd, path, mode, PAD, dev) \
2545 __sanitizer_syscall_post_impl_mknodat(res, (long long)(fd), \
2546 (long long)(path), (long long)(mode), \
2547 (long long)(PAD), (long long)(dev))
2548 #define __sanitizer_syscall_pre_mkdirat(fd, path, mode) \
2549 __sanitizer_syscall_pre_impl_mkdirat((long long)(fd), (long long)(path), \
2551 #define __sanitizer_syscall_post_mkdirat(res, fd, path, mode) \
2552 __sanitizer_syscall_post_impl_mkdirat(res, (long long)(fd), \
2553 (long long)(path), (long long)(mode))
2554 #define __sanitizer_syscall_pre_faccessat(fd, path, amode, flag) \
2555 __sanitizer_syscall_pre_impl_faccessat((long long)(fd), (long long)(path), \
2556 (long long)(amode), \
2558 #define __sanitizer_syscall_post_faccessat(res, fd, path, amode, flag) \
2559 __sanitizer_syscall_post_impl_faccessat( \
2560 res, (long long)(fd), (long long)(path), (long long)(amode), \
2562 #define __sanitizer_syscall_pre_fchmodat(fd, path, mode, flag) \
2563 __sanitizer_syscall_pre_impl_fchmodat((long long)(fd), (long long)(path), \
2564 (long long)(mode), (long long)(flag))
2565 #define __sanitizer_syscall_post_fchmodat(res, fd, path, mode, flag) \
2566 __sanitizer_syscall_post_impl_fchmodat(res, (long long)(fd), \
2567 (long long)(path), (long long)(mode), \
2569 #define __sanitizer_syscall_pre_fchownat(fd, path, owner, group, flag) \
2570 __sanitizer_syscall_pre_impl_fchownat((long long)(fd), (long long)(path), \
2571 (long long)(owner), \
2572 (long long)(group), (long long)(flag))
2573 #define __sanitizer_syscall_post_fchownat(res, fd, path, owner, group, flag) \
2574 __sanitizer_syscall_post_impl_fchownat( \
2575 res, (long long)(fd), (long long)(path), (long long)(owner), \
2576 (long long)(group), (long long)(flag))
2577 #define __sanitizer_syscall_pre_fexecve(fd, argp, envp) \
2578 __sanitizer_syscall_pre_impl_fexecve((long long)(fd), (long long)(argp), \
2580 #define __sanitizer_syscall_post_fexecve(res, fd, argp, envp) \
2581 __sanitizer_syscall_post_impl_fexecve(res, (long long)(fd), \
2582 (long long)(argp), (long long)(envp))
2583 #define __sanitizer_syscall_pre_fstatat(fd, path, buf, flag) \
2584 __sanitizer_syscall_pre_impl_fstatat((long long)(fd), (long long)(path), \
2585 (long long)(buf), (long long)(flag))
2586 #define __sanitizer_syscall_post_fstatat(res, fd, path, buf, flag) \
2587 __sanitizer_syscall_post_impl_fstatat(res, (long long)(fd), \
2588 (long long)(path), (long long)(buf), \
2590 #define __sanitizer_syscall_pre_utimensat(fd, path, tptr, flag) \
2591 __sanitizer_syscall_pre_impl_utimensat((long long)(fd), (long long)(path), \
2592 (long long)(tptr), (long long)(flag))
2593 #define __sanitizer_syscall_post_utimensat(res, fd, path, tptr, flag) \
2594 __sanitizer_syscall_post_impl_utimensat( \
2595 res, (long long)(fd), (long long)(path), (long long)(tptr), \
2597 #define __sanitizer_syscall_pre_openat(fd, path, oflags, mode) \
2598 __sanitizer_syscall_pre_impl_openat((long long)(fd), (long long)(path), \
2599 (long long)(oflags), (long long)(mode))
2600 #define __sanitizer_syscall_post_openat(res, fd, path, oflags, mode) \
2601 __sanitizer_syscall_post_impl_openat(res, (long long)(fd), \
2602 (long long)(path), (long long)(oflags), \
2604 #define __sanitizer_syscall_pre_readlinkat(fd, path, buf, bufsize) \
2605 __sanitizer_syscall_pre_impl_readlinkat((long long)(fd), (long long)(path), \
2607 (long long)(bufsize))
2608 #define __sanitizer_syscall_post_readlinkat(res, fd, path, buf, bufsize) \
2609 __sanitizer_syscall_post_impl_readlinkat( \
2610 res, (long long)(fd), (long long)(path), (long long)(buf), \
2611 (long long)(bufsize))
2612 #define __sanitizer_syscall_pre_symlinkat(path1, fd, path2) \
2613 __sanitizer_syscall_pre_impl_symlinkat((long long)(path1), (long long)(fd), \
2615 #define __sanitizer_syscall_post_symlinkat(res, path1, fd, path2) \
2616 __sanitizer_syscall_post_impl_symlinkat(res, (long long)(path1), \
2617 (long long)(fd), (long long)(path2))
2618 #define __sanitizer_syscall_pre_unlinkat(fd, path, flag) \
2619 __sanitizer_syscall_pre_impl_unlinkat((long long)(fd), (long long)(path), \
2621 #define __sanitizer_syscall_post_unlinkat(res, fd, path, flag) \
2622 __sanitizer_syscall_post_impl_unlinkat(res, (long long)(fd), \
2623 (long long)(path), (long long)(flag))
2624 #define __sanitizer_syscall_pre_futimens(fd, tptr) \
2625 __sanitizer_syscall_pre_impl_futimens((long long)(fd), (long long)(tptr))
2626 #define __sanitizer_syscall_post_futimens(res, fd, tptr) \
2627 __sanitizer_syscall_post_impl_futimens(res, (long long)(fd), \
2629 #define __sanitizer_syscall_pre___quotactl(path, args) \
2630 __sanitizer_syscall_pre_impl___quotactl((long long)(path), (long long)(args))
2631 #define __sanitizer_syscall_post___quotactl(res, path, args) \
2632 __sanitizer_syscall_post_impl___quotactl(res, (long long)(path), \
2634 #define __sanitizer_syscall_pre_posix_spawn(pid, path, file_actions, attrp, \
2636 __sanitizer_syscall_pre_impl_posix_spawn( \
2637 (long long)(pid), (long long)(path), (long long)(file_actions), \
2638 (long long)(attrp), (long long)(argv), (long long)(envp))
2639 #define __sanitizer_syscall_post_posix_spawn(res, pid, path, file_actions, \
2640 attrp, argv, envp) \
2641 __sanitizer_syscall_post_impl_posix_spawn( \
2642 res, (long long)(pid), (long long)(path), (long long)(file_actions), \
2643 (long long)(attrp), (long long)(argv), (long long)(envp))
2644 #define __sanitizer_syscall_pre_recvmmsg(s, mmsg, vlen, flags, timeout) \
2645 __sanitizer_syscall_pre_impl_recvmmsg((long long)(s), (long long)(mmsg), \
2646 (long long)(vlen), (long long)(flags), \
2647 (long long)(timeout))
2648 #define __sanitizer_syscall_post_recvmmsg(res, s, mmsg, vlen, flags, timeout) \
2649 __sanitizer_syscall_post_impl_recvmmsg( \
2650 res, (long long)(s), (long long)(mmsg), (long long)(vlen), \
2651 (long long)(flags), (long long)(timeout))
2652 #define __sanitizer_syscall_pre_sendmmsg(s, mmsg, vlen, flags) \
2653 __sanitizer_syscall_pre_impl_sendmmsg((long long)(s), (long long)(mmsg), \
2654 (long long)(vlen), (long long)(flags))
2655 #define __sanitizer_syscall_post_sendmmsg(res, s, mmsg, vlen, flags) \
2656 __sanitizer_syscall_post_impl_sendmmsg(res, (long long)(s), \
2657 (long long)(mmsg), (long long)(vlen), \
2659 #define __sanitizer_syscall_pre_clock_nanosleep(clock_id, flags, rqtp, rmtp) \
2660 __sanitizer_syscall_pre_impl_clock_nanosleep( \
2661 (long long)(clock_id), (long long)(flags), (long long)(rqtp), \
2663 #define __sanitizer_syscall_post_clock_nanosleep(res, clock_id, flags, rqtp, \
2665 __sanitizer_syscall_post_impl_clock_nanosleep( \
2666 res, (long long)(clock_id), (long long)(flags), (long long)(rqtp), \
2668 #define __sanitizer_syscall_pre____lwp_park60(clock_id, flags, ts, unpark, \
2670 __sanitizer_syscall_pre_impl____lwp_park60( \
2671 (long long)(clock_id), (long long)(flags), (long long)(ts), \
2672 (long long)(unpark), (long long)(hint), (long long)(unparkhint))
2673 #define __sanitizer_syscall_post____lwp_park60(res, clock_id, flags, ts, \
2674 unpark, hint, unparkhint) \
2675 __sanitizer_syscall_post_impl____lwp_park60( \
2676 res, (long long)(clock_id), (long long)(flags), (long long)(ts), \
2677 (long long)(unpark), (long long)(hint), (long long)(unparkhint))
2678 #define __sanitizer_syscall_pre_posix_fallocate(fd, PAD, pos, len) \
2679 __sanitizer_syscall_pre_impl_posix_fallocate( \
2680 (long long)(fd), (long long)(PAD), (long long)(pos), (long long)(len))
2681 #define __sanitizer_syscall_post_posix_fallocate(res, fd, PAD, pos, len) \
2682 __sanitizer_syscall_post_impl_posix_fallocate( \
2683 res, (long long)(fd), (long long)(PAD), (long long)(pos), \
2685 #define __sanitizer_syscall_pre_fdiscard(fd, PAD, pos, len) \
2686 __sanitizer_syscall_pre_impl_fdiscard((long long)(fd), (long long)(PAD), \
2687 (long long)(pos), (long long)(len))
2688 #define __sanitizer_syscall_post_fdiscard(res, fd, PAD, pos, len) \
2689 __sanitizer_syscall_post_impl_fdiscard(res, (long long)(fd), \
2690 (long long)(PAD), (long long)(pos), \
2692 #define __sanitizer_syscall_pre_wait6(idtype, id, status, options, wru, info) \
2693 __sanitizer_syscall_pre_impl_wait6( \
2694 (long long)(idtype), (long long)(id), (long long)(status), \
2695 (long long)(options), (long long)(wru), (long long)(info))
2696 #define __sanitizer_syscall_post_wait6(res, idtype, id, status, options, wru, \
2698 __sanitizer_syscall_post_impl_wait6( \
2699 res, (long long)(idtype), (long long)(id), (long long)(status), \
2700 (long long)(options), (long long)(wru), (long long)(info))
2701 #define __sanitizer_syscall_pre_clock_getcpuclockid2(idtype, id, clock_id) \
2702 __sanitizer_syscall_pre_impl_clock_getcpuclockid2( \
2703 (long long)(idtype), (long long)(id), (long long)(clock_id))
2704 #define __sanitizer_syscall_post_clock_getcpuclockid2(res, idtype, id, \
2706 __sanitizer_syscall_post_impl_clock_getcpuclockid2( \
2707 res, (long long)(idtype), (long long)(id), (long long)(clock_id))
2708 #define __sanitizer_syscall_pre___getvfsstat90(buf, bufsize, flags) \
2709 __sanitizer_syscall_pre_impl___getvfsstat90( \
2710 (long long)(buf), (long long)(bufsize), (long long)(flags))
2711 #define __sanitizer_syscall_post___getvfsstat90(res, buf, bufsize, flags) \
2712 __sanitizer_syscall_post_impl___getvfsstat90( \
2713 res, (long long)(buf), (long long)(bufsize), (long long)(flags))
2714 #define __sanitizer_syscall_pre___statvfs190(path, buf, flags) \
2715 __sanitizer_syscall_pre_impl___statvfs190( \
2716 (long long)(path), (long long)(buf), (long long)(flags))
2717 #define __sanitizer_syscall_post___statvfs190(res, path, buf, flags) \
2718 __sanitizer_syscall_post_impl___statvfs190( \
2719 res, (long long)(path), (long long)(buf), (long long)(flags))
2720 #define __sanitizer_syscall_pre___fstatvfs190(fd, buf, flags) \
2721 __sanitizer_syscall_pre_impl___fstatvfs190( \
2722 (long long)(fd), (long long)(buf), (long long)(flags))
2723 #define __sanitizer_syscall_post___fstatvfs190(res, fd, buf, flags) \
2724 __sanitizer_syscall_post_impl___fstatvfs190( \
2725 res, (long long)(fd), (long long)(buf), (long long)(flags))
2726 #define __sanitizer_syscall_pre___fhstatvfs190(fhp, fh_size, buf, flags) \
2727 __sanitizer_syscall_pre_impl___fhstatvfs190( \
2728 (long long)(fhp), (long long)(fh_size), (long long)(buf), \
2730 #define __sanitizer_syscall_post___fhstatvfs190(res, fhp, fh_size, buf, flags) \
2731 __sanitizer_syscall_post_impl___fhstatvfs190( \
2732 res, (long long)(fhp), (long long)(fh_size), (long long)(buf), \
2736 #define __sanitizer_syscall_pre_getvfsstat \
2737 __sanitizer_syscall_pre_compat_90_getvfsstat
2738 #define __sanitizer_syscall_post_getvfsstat \
2739 __sanitizer_syscall_post_compat_90_getvfsstat
2741 #define __sanitizer_syscall_pre_statvfs1 \
2742 __sanitizer_syscall_pre_compat_90_statvfs1
2743 #define __sanitizer_syscall_post_statvfs1 \
2744 __sanitizer_syscall_post_compat_90_statvfs1
2746 #define __sanitizer_syscall_pre_fstatvfs1 \
2747 __sanitizer_syscall_pre_compat_90_fstatvfs1
2748 #define __sanitizer_syscall_post_fstatvfs1 \
2749 __sanitizer_syscall_post_compat_90_fstatvfs1
2751 #define __sanitizer_syscall_pre___fhstatvfs140 \
2752 __sanitizer_syscall_pre_compat_90_fhstatvfs1
2753 #define __sanitizer_syscall_post___fhstatvfs140 \
2754 __sanitizer_syscall_post_compat_90_fhstatvfs1
2765 long long arg1,
long long arg2,
2766 long long arg3,
long long arg4,
2767 long long arg5,
long long arg6,
2770 long long arg0,
long long arg1,
2771 long long arg2,
long long arg3,
2772 long long arg4,
long long arg5,
2773 long long arg6,
long long arg7);
2781 long long buf,
long long nbyte);
2785 long long buf,
long long nbyte);
2789 long long flags,
long long mode);
2828 long long uid,
long long gid);
2865 long long addr,
long long data);
2867 long long pid,
long long addr,
2872 long long msg,
long long flags);
2876 long long msg,
long long flags);
2878 long long len,
long long flags,
2880 long long fromlenaddr);
2882 long long buf,
long long len,
2883 long long flags,
long long from,
2884 long long fromlenaddr);
2886 long long anamelen);
2888 long long name,
long long anamelen);
2892 long long asa,
long long alen);
2896 long long asa,
long long alen);
2930 long long offset,
long long scale);
2932 long long size,
long long offset,
2935 long long facs,
long long pid);
2937 long long ops,
long long facs,
2971 long long com,
long long data);
2983 long long buf,
long long count);
2987 long long argp,
long long envp);
3020 long long flags,
long long fd,
3023 long long res,
long long addr,
long long len,
long long prot,
3024 long long flags,
long long fd,
long long pos);
3033 long long len,
long long prot);
3037 long long len,
long long behav);
3043 long long len,
long long vec);
3047 long long gidsetsize,
3052 long long gidsetsize,
3095 long long cmd,
long long arg);
3097 long long ou,
long long ex,
3100 long long in,
long long ou,
3101 long long ex,
long long tv);
3108 long long who,
long long prio);
3111 long long protocol);
3115 long long protocol);
3119 long long name,
long long namelen);
3121 long long anamelen);
3124 long long anamelen);
3132 long long buf,
long long len,
3138 long long buf,
long long len,
3142 long long sigcntxp);
3146 long long name,
long long namelen);
3148 long long name,
long long val,
3151 long long level,
long long name,
3152 long long val,
long long valsize);
3202 long long name,
long long val,
3203 long long avalsize);
3205 long long level,
long long name,
3207 long long avalsize);
3212 long long iovp,
long long iovcnt);
3216 long long iovp,
long long iovcnt);
3225 long long uid,
long long gid);
3230 long long s,
long long buf,
long long len,
long long flags,
long long from,
3231 long long fromlenaddr);
3233 long long res,
long long s,
long long buf,
long long len,
long long flags,
3234 long long from,
long long fromlenaddr);
3261 long long len,
long long flags,
3262 long long to,
long long tolen);
3264 long long buf,
long long len,
3265 long long flags,
long long to,
3271 long long protocol,
long long rsv);
3288 long long olddelta);
3291 long long olddelta);
3326 long long res,
long long path,
long long cmd,
long long uid,
long long arg);
3372 long long res,
long long domainname,
long long len);
3376 long long res,
long long domainname,
long long len);
3388 long long a2,
long long a3,
3389 long long a4,
long long a5);
3392 long long a2,
long long a3,
3400 long long a2,
long long a3,
3401 long long a4,
long long a5,
3405 long long a2,
long long a3,
3406 long long a4,
long long a5,
3413 long long a2,
long long a3,
3417 long long a2,
long long a3,
3424 long long nbyte,
long long PAD,
3427 long long buf,
long long nbyte,
3428 long long PAD,
long long offset);
3430 long long nbyte,
long long PAD,
3433 long long buf,
long long nbyte,
3434 long long PAD,
long long offset);
3438 #if defined(NTP) || !defined(_KERNEL_OPT)
3494 long long name,
long long val,
3495 long long avalsize);
3497 long long level,
long long name,
3499 long long avalsize);
3516 long long prot,
long long flags,
3517 long long fd,
long long PAD,
3520 long long len,
long long prot,
3521 long long flags,
long long fd,
3522 long long PAD,
long long pos);
3524 long long arg1,
long long arg2,
3525 long long arg3,
long long arg4,
3526 long long arg5,
long long arg6,
3529 long long arg0,
long long arg1,
3530 long long arg2,
long long arg3,
3531 long long arg4,
long long arg5,
3532 long long arg6,
long long arg7);
3534 long long offset,
long long whence);
3536 long long PAD,
long long offset,
3541 long long PAD,
long long length);
3545 long long PAD,
long long length);
3547 long long oldv,
long long oldlenp,
3548 long long newv,
long long newlen);
3550 long long namelen,
long long oldv,
3551 long long oldlenp,
long long newv,
3574 long long nfds,
long long timeout);
3576 long long a2,
long long a3,
3577 long long a4,
long long a5,
3580 long long a1,
long long a2,
3581 long long a3,
long long a4,
3582 long long a5,
long long a6);
3604 long long nsems,
long long semflg);
3608 long long sops,
long long nsops);
3622 long long msgsz,
long long msgflg);
3624 long long msgp,
long long msgsz,
3627 long long msgsz,
long long msgtyp,
3630 long long msgp,
long long msgsz,
3631 long long msgtyp,
long long msgflg);
3635 long long shmaddr,
long long shmflg);
3648 long long size,
long long shmflg);
3719 long long mode,
long long value,
3722 long long oflag,
long long mode,
3723 long long value,
long long idp);
3744 long long mode,
long long attr);
3746 long long oflag,
long long mode,
3761 long long notification);
3763 long long notification);
3766 long long msg_prio);
3768 long long msg_ptr,
long long msg_len,
3769 long long msg_prio);
3772 long long msg_prio);
3776 long long msg_prio);
3781 long long abs_timeout);
3783 long long res,
long long mqdes,
long long msg_ptr,
long long msg_len,
3784 long long msg_prio,
long long abs_timeout);
3786 long long mqdes,
long long msg_ptr,
long long msg_len,
long long msg_prio,
3787 long long abs_timeout);
3789 long long res,
long long mqdes,
long long msg_ptr,
long long msg_len,
3790 long long msg_prio,
long long abs_timeout);
3800 long long arg,
long long misc);
3811 long long len,
long long inherit);
3818 long long uid,
long long gid);
3827 long long len,
long long flags);
3851 long long uid,
long long gid);
3855 long long uid,
long long gid);
3859 long long uid,
long long gid);
3866 long long facs,
long long pid);
3868 long long ops,
long long facs,
3871 long long iovcnt,
long long PAD,
3874 long long iovp,
long long iovcnt,
3875 long long PAD,
long long offset);
3877 long long iovcnt,
long long PAD,
3880 long long iovp,
long long iovcnt,
3881 long long PAD,
long long offset);
3900 long long sigcntxp);
3951 long long addr,
long long len);
3966 long long departed);
3968 long long departed);
3990 long long unparkhint);
3995 long long unparkhint);
4013 long long name,
long long len);
4023 long long newv,
long long oldv,
long long flags,
4024 long long stackinfo_offset);
4026 long long res,
long long newv,
long long oldv,
long long flags,
4027 long long stackinfo_offset);
4036 long long concurrency);
4038 long long res,
long long concurrency);
4054 long long res,
long long signum,
long long nsa,
long long osa,
4055 long long tramp,
long long vers);
4061 long long len,
long long op);
4065 long long fd,
long long changelist,
long long nchanges,
long long eventlist,
4066 long long nevents,
long long timeout);
4068 long long res,
long long fd,
long long changelist,
long long nchanges,
4069 long long eventlist,
long long nevents,
long long timeout);
4106 long long priority);
4113 long long flags,
long long start,
4148 long long attrnamespace,
4149 long long attrname);
4151 long long cmd,
long long filename,
4152 long long attrnamespace,
4153 long long attrname);
4155 long long attrnamespace,
4160 long long res,
long long path,
long long attrnamespace,
long long attrname,
4161 long long data,
long long nbytes);
4163 long long attrnamespace,
4168 long long res,
long long path,
long long attrnamespace,
long long attrname,
4169 long long data,
long long nbytes);
4171 long long attrnamespace,
4172 long long attrname);
4175 long long attrnamespace,
4176 long long attrname);
4178 long long attrnamespace,
4183 long long attrnamespace,
4188 long long attrnamespace,
4193 long long attrnamespace,
4198 long long attrnamespace,
4199 long long attrname);
4202 long long attrnamespace,
4203 long long attrname);
4205 long long attrnamespace,
4210 long long res,
long long path,
long long attrnamespace,
long long attrname,
4211 long long data,
long long nbytes);
4213 long long attrnamespace,
4218 long long res,
long long path,
long long attrnamespace,
long long attrname,
4219 long long data,
long long nbytes);
4221 long long attrnamespace,
4222 long long attrname);
4225 long long attrnamespace,
4226 long long attrname);
4228 long long attrnamespace,
4232 long long attrnamespace,
4236 long long attrnamespace,
4241 long long attrnamespace,
4245 long long attrnamespace,
4250 long long attrnamespace,
4254 long long ou,
long long ex,
4258 long long nd,
long long in,
4259 long long ou,
long long ex,
4263 long long nfds,
long long ts,
4266 long long res,
long long fds,
long long nfds,
long long ts,
long long mask);
4268 long long value,
long long size,
4271 long long name,
long long value,
4272 long long size,
long long flags);
4274 long long value,
long long size,
4277 long long name,
long long value,
4278 long long size,
long long flags);
4280 long long value,
long long size,
4283 long long name,
long long value,
4284 long long size,
long long flags);
4286 long long value,
long long size);
4288 long long name,
long long value,
4291 long long value,
long long size);
4293 long long name,
long long value,
4296 long long value,
long long size);
4298 long long name,
long long value,
4303 long long list,
long long size);
4307 long long list,
long long size);
4311 long long list,
long long size);
4339 long long buf,
long long count);
4351 long long protocol);
4354 long long protocol);
4358 long long fhp,
long long fh_size);
4403 long long nent,
long long sig);
4405 long long list,
long long nent,
4411 long long flags,
long long data,
4412 long long data_len);
4414 long long path,
long long flags,
4416 long long data_len);
4419 long long new_address,
4420 long long new_size,
long long flags);
4423 long long new_address,
4424 long long new_size,
long long flags);
4436 long long second_id,
4437 long long psid,
long long opsid);
4440 long long second_id,
4441 long long psid,
long long opsid);
4447 long long res,
long long fd,
long long PAD,
long long offset,
long long len,
4450 long long ou,
long long ex,
4453 long long in,
long long ou,
4454 long long ex,
long long tv);
4465 long long olddelta);
4467 long long olddelta);
4482 long long itv,
long long oitv);
4515 long long abs_timeout);
4517 long long res,
long long mqdes,
long long msg_ptr,
long long msg_len,
4518 long long msg_prio,
long long abs_timeout);
4523 long long abs_timeout);
4525 long long res,
long long mqdes,
long long msg_ptr,
long long msg_len,
4526 long long msg_prio,
long long abs_timeout);
4530 long long unparkhint);
4535 long long unparkhint);
4538 long long eventlist,
4542 long long res,
long long fd,
long long changelist,
long long nchanges,
4543 long long eventlist,
long long nevents,
long long timeout);
4545 long long ou,
long long ex,
4546 long long ts,
long long mask);
4548 long long in,
long long ou,
4549 long long ex,
long long ts,
4552 long long ts,
long long mask);
4554 long long nfds,
long long ts,
4573 long long semnum,
long long cmd,
4576 long long semnum,
long long cmd,
4581 long long cmd,
long long buf);
4585 long long cmd,
long long buf);
4604 #if defined(NTP) || !defined(_KERNEL_OPT)
4621 long long mode,
long long dev);
4625 long long fh_size,
long long sb);
4633 long long to,
long long flags);
4637 long long anamelen,
long long mask,
4640 long long name,
long long anamelen,
4641 long long mask,
long long flags);
4643 long long fd2,
long long name2,
4646 long long name1,
long long fd2,
4647 long long name2,
long long flags);
4649 long long tofd,
long long to);
4651 long long from,
long long tofd,
4656 long long path,
long long mode);
4658 long long mode,
long long PAD,
4661 long long path,
long long mode,
4662 long long PAD,
long long dev);
4666 long long path,
long long mode);
4668 long long amode,
long long flag);
4670 long long path,
long long amode,
4675 long long path,
long long mode,
4678 long long owner,
long long group,
4681 long long path,
long long owner,
4682 long long group,
long long flag);
4686 long long argp,
long long envp);
4688 long long buf,
long long flag);
4690 long long path,
long long buf,
4693 long long tptr,
long long flag);
4695 long long path,
long long tptr,
4698 long long oflags,
long long mode);
4700 long long path,
long long oflags,
4703 long long buf,
long long bufsize);
4705 long long path,
long long buf,
4710 long long fd,
long long path2);
4714 long long path,
long long flag);
4722 long long file_actions,
4723 long long attrp,
long long argv,
4727 long long file_actions,
4728 long long attrp,
long long argv,
4731 long long vlen,
long long flags,
4734 long long mmsg,
long long vlen,
4735 long long flags,
long long timeout);
4737 long long vlen,
long long flags);
4739 long long mmsg,
long long vlen,
4751 long long flags,
long long ts,
4754 long long unparkhint);
4756 long long res,
long long clock_id,
long long flags,
long long ts,
4757 long long unpark,
long long hint,
long long unparkhint);
4759 long long pos,
long long len);
4761 long long PAD,
long long pos,
4764 long long pos,
long long len);
4766 long long PAD,
long long pos,
4769 long long status,
long long options,
4770 long long wru,
long long info);
4772 long long id,
long long status,
4773 long long options,
long long wru,
4777 long long clock_id);
4781 long long clock_id);
4791 long long buf,
long long flags);
ETISS_PLUGIN_EXPORT etiss::CPUArch std::map< std::string, std::string > options
create new instance of the CPUArch type at index
__device__ __2f16 float bool s
void __sanitizer_syscall_post_impl_setcontext(long long res, long long ucp)
void __sanitizer_syscall_post_impl_compat_50_getrusage(long long res, long long who, long long rusage)
void __sanitizer_syscall_post_impl_msgget(long long res, long long key, long long msgflg)
void __sanitizer_syscall_post_impl_chflags(long long res, long long path, long long flags)
void __sanitizer_syscall_post_impl_compat_50_adjtime(long long res, long long delta, long long olddelta)
void __sanitizer_syscall_pre_impl_compat_43_ogetkerninfo(long long op, long long where, long long size, long long arg)
void __sanitizer_syscall_post_impl_kill(long long res, long long pid, long long signum)
void __sanitizer_syscall_post_impl_compat_13_sigaction13(long long res, long long signum, long long nsa, long long osa)
void __sanitizer_syscall_pre_impl_getsid(long long pid)
void __sanitizer_syscall_pre_impl_setreuid(long long ruid, long long euid)
void __sanitizer_syscall_post_impl_compat_12_lstat12(long long res, long long path, long long ub)
void __sanitizer_syscall_post_impl_compat_13_sigpending13(long long res)
void __sanitizer_syscall_post_impl_compat_16___sigreturn14(long long res, long long sigcntxp)
void __sanitizer_syscall_post_impl_madvise(long long res, long long addr, long long len, long long behav)
void __sanitizer_syscall_post_impl_setpriority(long long res, long long which, long long who, long long prio)
void __sanitizer_syscall_post_impl___getdents30(long long res, long long fd, long long buf, long long count)
void __sanitizer_syscall_post_impl_extattrctl(long long res, long long path, long long cmd, long long filename, long long attrnamespace, long long attrname)
void __sanitizer_syscall_pre_impl_preadv(long long fd, long long iovp, long long iovcnt, long long PAD, long long offset)
void __sanitizer_syscall_post_impl_seteuid(long long res, long long euid)
void __sanitizer_syscall_pre_impl__ksem_init(long long value, long long idp)
void __sanitizer_syscall_post_impl___sigpending14(long long res, long long set)
void __sanitizer_syscall_post_impl___ntp_gettime50(long long res, long long ntvp)
void __sanitizer_syscall_pre_impl_getpgrp(void)
void __sanitizer_syscall_post_impl_fpathconf(long long res, long long fd, long long name)
void __sanitizer_syscall_post_impl_compat_43_ogetsockname(long long res, long long fdec, long long asa, long long alen)
void __sanitizer_syscall_post_impl_compat_50_wait4(long long res, long long pid, long long status, long long options, long long rusage)
void __sanitizer_syscall_pre_impl_extattr_list_file(long long path, long long attrnamespace, long long data, long long nbytes)
void __sanitizer_syscall_post_impl__ksem_trywait(long long res, long long id)
void __sanitizer_syscall_pre_impl_linkat(long long fd1, long long name1, long long fd2, long long name2, long long flags)
void __sanitizer_syscall_post_impl_compat_12_fstat12(long long res, long long fd, long long sb)
void __sanitizer_syscall_pre_impl_chdir(long long path)
void __sanitizer_syscall_pre_impl_fchmodat(long long fd, long long path, long long mode, long long flag)
void __sanitizer_syscall_pre_impl_fchdir(long long fd)
void __sanitizer_syscall_pre_impl_openat(long long fd, long long path, long long oflags, long long mode)
void __sanitizer_syscall_pre_impl__lwp_exit(void)
void __sanitizer_syscall_post_impl__ksem_close(long long res, long long id)
void __sanitizer_syscall_post_impl_extattr_get_link(long long res, long long path, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_pre_impl_aio_return(long long aiocbp)
void __sanitizer_syscall_post_impl_rasctl(long long res, long long addr, long long len, long long op)
void __sanitizer_syscall_pre_impl_compat_12_lstat12(long long path, long long ub)
void __sanitizer_syscall_pre_impl_fstatat(long long fd, long long path, long long buf, long long flag)
void __sanitizer_syscall_pre_impl_compat_50_clock_settime(long long clock_id, long long tp)
void __sanitizer_syscall_pre_impl_compat_12_stat12(long long path, long long ub)
void __sanitizer_syscall_pre_impl_fexecve(long long fd, long long argp, long long envp)
void __sanitizer_syscall_post_impl_compat_50_nanosleep(long long res, long long rqtp, long long rmtp)
void __sanitizer_syscall_post_impl_pread(long long res, long long fd, long long buf, long long nbyte, long long PAD, long long offset)
void __sanitizer_syscall_pre_impl___setitimer50(long long which, long long itv, long long oitv)
void __sanitizer_syscall_post_impl_pset_destroy(long long res, long long psid)
void __sanitizer_syscall_post_impl_semop(long long res, long long semid, long long sops, long long nsops)
void __sanitizer_syscall_post_impl_compat_43_osend(long long res, long long s, long long buf, long long len, long long flags)
void __sanitizer_syscall_post_impl_extattr_list_fd(long long res, long long fd, long long attrnamespace, long long data, long long nbytes)
void __sanitizer_syscall_post_impl_wait6(long long res, long long idtype, long long id, long long status, long long options, long long wru, long long info)
void __sanitizer_syscall_pre_impl_reboot(long long opt, long long bootstr)
void __sanitizer_syscall_post_impl__lwp_exit(long long res)
void __sanitizer_syscall_pre_impl_chroot(long long path)
void __sanitizer_syscall_post_impl_fchmodat(long long res, long long fd, long long path, long long mode, long long flag)
void __sanitizer_syscall_post_impl_compat_43_ogetkerninfo(long long res, long long op, long long where, long long size, long long arg)
void __sanitizer_syscall_post_impl___settimeofday50(long long res, long long tv, long long tzp)
void __sanitizer_syscall_pre_impl__ksem_timedwait(long long id, long long abstime)
void __sanitizer_syscall_post_impl_compat_30_ntp_gettime(long long res, long long ntvp)
void __sanitizer_syscall_pre_impl___utimes50(long long path, long long tptr)
void __sanitizer_syscall_post_impl_compat_43_orecvmsg(long long res, long long s, long long msg, long long flags)
void __sanitizer_syscall_pre_impl_lchown(long long path, long long uid, long long gid)
void __sanitizer_syscall_pre_impl_break(long long nsize)
void __sanitizer_syscall_pre_impl_compat_30___fhstat30(long long fhp, long long sb)
void __sanitizer_syscall_post_impl__lwp_detach(long long res, long long target)
void __sanitizer_syscall_pre_impl_compat_43_osigsetmask(long long mask)
void __sanitizer_syscall_post_impl_dup(long long res, long long fd)
void __sanitizer_syscall_pre_impl_umask(long long newmask)
void __sanitizer_syscall_pre_impl_compat_43_oftruncate(long long fd, long long length)
void __sanitizer_syscall_post_impl___select50(long long res, long long nd, long long in, long long ou, long long ex, long long tv)
void __sanitizer_syscall_post_impl_fdiscard(long long res, long long fd, long long PAD, long long pos, long long len)
void __sanitizer_syscall_pre_impl_compat_43_orecv(long long s, long long buf, long long len, long long flags)
void __sanitizer_syscall_post_impl_syscall(long long res, long long code, long long arg0, long long arg1, long long arg2, long long arg3, long long arg4, long long arg5, long long arg6, long long arg7)
void __sanitizer_syscall_post_impl___statvfs190(long long res, long long path, long long buf, long long flags)
void __sanitizer_syscall_pre_impl__lwp_kill(long long target, long long signo)
void __sanitizer_syscall_post_impl_compat_43_osethostname(long long res, long long hostname, long long len)
void __sanitizer_syscall_pre_impl_compat_50_setitimer(long long which, long long itv, long long oitv)
void __sanitizer_syscall_post_impl___getitimer50(long long res, long long which, long long itv)
void __sanitizer_syscall_post_impl___aio_suspend50(long long res, long long list, long long nent, long long timeout)
void __sanitizer_syscall_post_impl_linkat(long long res, long long fd1, long long name1, long long fd2, long long name2, long long flags)
void __sanitizer_syscall_pre_impl_getxattr(long long path, long long name, long long value, long long size)
void __sanitizer_syscall_pre_impl_read(long long fd, long long buf, long long nbyte)
void __sanitizer_syscall_pre_impl_compat_50___lstat30(long long path, long long ub)
void __sanitizer_syscall_post_impl_compat_60_sa_stacks(long long res, long long num, long long stacks)
void __sanitizer_syscall_post_impl_compat_60_sa_yield(long long res)
void __sanitizer_syscall_pre_impl_compat_60_sa_register(long long newv, long long oldv, long long flags, long long stackinfo_offset)
void __sanitizer_syscall_pre_impl_ftruncate(long long fd, long long PAD, long long length)
void __sanitizer_syscall_post_impl_compat_50__lwp_park(long long res, long long ts, long long unpark, long long hint, long long unparkhint)
void __sanitizer_syscall_post_impl_compat_13_sigaltstack13(long long res, long long nss, long long oss)
void __sanitizer_syscall_pre_impl_compat_50___shmctl13(long long shmid, long long cmd, long long buf)
void __sanitizer_syscall_post_impl_socketpair(long long res, long long domain, long long type, long long protocol, long long rsv)
void __sanitizer_syscall_post_impl_getppid(long long res)
void __sanitizer_syscall_post_impl_compat_43_stat43(long long res, long long path, long long ub)
void __sanitizer_syscall_pre_impl_setuid(long long uid)
void __sanitizer_syscall_post_impl_compat_50_kevent(long long res, long long fd, long long changelist, long long nchanges, long long eventlist, long long nevents, long long timeout)
void __sanitizer_syscall_pre_impl_compat_50_mknod(long long path, long long mode, long long dev)
void __sanitizer_syscall_pre_impl_flistxattr(long long fd, long long list, long long size)
void __sanitizer_syscall_pre_impl___pollts50(long long fds, long long nfds, long long ts, long long mask)
void __sanitizer_syscall_pre_impl_aio_write(long long aiocbp)
void __sanitizer_syscall_post_impl_readlink(long long res, long long path, long long buf, long long count)
void __sanitizer_syscall_post_impl_kqueue(long long res)
void __sanitizer_syscall_pre_impl___posix_chown(long long path, long long uid, long long gid)
void __sanitizer_syscall_post_impl_fktrace(long long res, long long fd, long long ops, long long facs, long long pid)
void __sanitizer_syscall_pre_impl_readv(long long fd, long long iovp, long long iovcnt)
void __sanitizer_syscall_pre_impl_setpgid(long long pid, long long pgid)
void __sanitizer_syscall_post_impl_listen(long long res, long long s, long long backlog)
void __sanitizer_syscall_post_impl_compat_09_osetdomainname(long long res, long long domainname, long long len)
void __sanitizer_syscall_post_impl__sched_getparam(long long res, long long pid, long long lid, long long policy, long long params)
void __sanitizer_syscall_pre_impl_acct(long long path)
void __sanitizer_syscall_post_impl_msgsnd(long long res, long long msqid, long long msgp, long long msgsz, long long msgflg)
void __sanitizer_syscall_pre_impl___lstat50(long long path, long long ub)
void __sanitizer_syscall_pre_impl_shutdown(long long s, long long how)
void __sanitizer_syscall_post_impl_open(long long res, long long path, long long flags, long long mode)
void __sanitizer_syscall_pre_impl___nanosleep50(long long rqtp, long long rmtp)
void __sanitizer_syscall_pre_impl_mq_close(long long mqdes)
void __sanitizer_syscall_post_impl_fdatasync(long long res, long long fd)
void __sanitizer_syscall_post_impl_compat_60__lwp_park(long long res, long long ts, long long unpark, long long hint, long long unparkhint)
void __sanitizer_syscall_pre_impl___lutimes50(long long path, long long tptr)
void __sanitizer_syscall_pre_impl___fstatvfs190(long long fd, long long buf, long long flags)
void __sanitizer_syscall_post_impl_compat_50___stat30(long long res, long long path, long long ub)
void __sanitizer_syscall_pre_impl_lfs_markv(long long fsidp, long long blkiov, long long blkcnt)
void __sanitizer_syscall_post_impl_extattr_set_file(long long res, long long path, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_pre_impl_semget(long long key, long long nsems, long long semflg)
void __sanitizer_syscall_pre_impl_geteuid(void)
void __sanitizer_syscall_post_impl_pset_create(long long res, long long psid)
void __sanitizer_syscall_pre_impl___getvfsstat90(long long buf, long long bufsize, long long flags)
void __sanitizer_syscall_pre_impl_close(long long fd)
void __sanitizer_syscall_post_impl_recvmmsg(long long res, long long s, long long mmsg, long long vlen, long long flags, long long timeout)
void __sanitizer_syscall_pre_impl__lwp_suspend(long long target)
void __sanitizer_syscall_pre_impl_fpathconf(long long fd, long long name)
void __sanitizer_syscall_post_impl___mknod50(long long res, long long path, long long mode, long long dev)
void __sanitizer_syscall_pre_impl_getrlimit(long long which, long long rlp)
void __sanitizer_syscall_pre_impl_extattr_set_file(long long path, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_post_impl___posix_chown(long long res, long long path, long long uid, long long gid)
void __sanitizer_syscall_pre_impl_compat_43_ogetpeername(long long fdes, long long asa, long long alen)
void __sanitizer_syscall_pre_impl_____sigtimedwait50(long long set, long long info, long long timeout)
void __sanitizer_syscall_pre_impl___mq_timedsend50(long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio, long long abs_timeout)
void __sanitizer_syscall_post_impl__lwp_ctl(long long res, long long features, long long address)
void __sanitizer_syscall_post_impl_lfs_bmapv(long long res, long long fsidp, long long blkiov, long long blkcnt)
void __sanitizer_syscall_pre_impl___pselect50(long long nd, long long in, long long ou, long long ex, long long ts, long long mask)
void __sanitizer_syscall_pre_impl_____semctl50(long long semid, long long semnum, long long cmd, long long arg)
void __sanitizer_syscall_pre_impl_compat_13_sigprocmask13(long long how, long long mask)
void __sanitizer_syscall_post_impl_compat_50___shmctl13(long long res, long long shmid, long long cmd, long long buf)
void __sanitizer_syscall_pre_impl_setcontext(long long ucp)
void __sanitizer_syscall_post_impl___msync13(long long res, long long addr, long long len, long long flags)
void __sanitizer_syscall_pre_impl_extattr_list_link(long long path, long long attrnamespace, long long data, long long nbytes)
void __sanitizer_syscall_post_impl_compat_50_gettimeofday(long long res, long long tp, long long tzp)
void __sanitizer_syscall_pre_impl_compat_90_getvfsstat(long long buf, long long bufsize, long long flags)
void __sanitizer_syscall_pre_impl_compat_43_osethostname(long long hostname, long long len)
void __sanitizer_syscall_post_impl_munlock(long long res, long long addr, long long len)
void __sanitizer_syscall_pre_impl_lchmod(long long path, long long mode)
void __sanitizer_syscall_pre_impl___syscall(long long code, long long arg0, long long arg1, long long arg2, long long arg3, long long arg4, long long arg5, long long arg6, long long arg7)
void __sanitizer_syscall_pre_impl_compat_50___sigtimedwait(long long set, long long info, long long timeout)
void __sanitizer_syscall_post_impl_paccept(long long res, long long s, long long name, long long anamelen, long long mask, long long flags)
void __sanitizer_syscall_post_impl_fchroot(long long res, long long fd)
void __sanitizer_syscall_post_impl_semget(long long res, long long key, long long nsems, long long semflg)
void __sanitizer_syscall_pre_impl_extattr_set_link(long long path, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_post_impl_aio_return(long long res, long long aiocbp)
void __sanitizer_syscall_pre_impl_setxattr(long long path, long long name, long long value, long long size, long long flags)
void __sanitizer_syscall_post_impl_timer_create(long long res, long long clock_id, long long evp, long long timerid)
void __sanitizer_syscall_post_impl_fstatat(long long res, long long fd, long long path, long long buf, long long flag)
void __sanitizer_syscall_pre_impl_compat_30___lstat13(long long path, long long ub)
void __sanitizer_syscall_pre_impl__sched_getparam(long long pid, long long lid, long long policy, long long params)
void __sanitizer_syscall_post_impl_compat_16___sigaction14(long long res, long long signum, long long nsa, long long osa)
void __sanitizer_syscall_post_impl___clock_settime50(long long res, long long clock_id, long long tp)
void __sanitizer_syscall_pre_impl___fhopen40(long long fhp, long long fh_size, long long flags)
void __sanitizer_syscall_post_impl_getsockname(long long res, long long fdes, long long asa, long long alen)
void __sanitizer_syscall_pre_impl_lfs_segclean(long long fsidp, long long segment)
void __sanitizer_syscall_post_impl___mount50(long long res, long long type, long long path, long long flags, long long data, long long data_len)
void __sanitizer_syscall_post_impl_compat_50___lstat30(long long res, long long path, long long ub)
void __sanitizer_syscall_post_impl_compat_30___stat13(long long res, long long path, long long ub)
void __sanitizer_syscall_post_impl__sched_setaffinity(long long res, long long pid, long long lid, long long size, long long cpuset)
void __sanitizer_syscall_pre_impl___posix_lchown(long long path, long long uid, long long gid)
void __sanitizer_syscall_post_impl__lwp_continue(long long res, long long target)
void __sanitizer_syscall_post_impl___fhopen40(long long res, long long fhp, long long fh_size, long long flags)
void __sanitizer_syscall_post_impl_posix_fadvise(long long res, long long)
void __sanitizer_syscall_pre_impl_compat_90_statvfs1(long long path, long long buf, long long flags)
void __sanitizer_syscall_pre_impl_compat_14_shmctl(long long shmid, long long cmd, long long buf)
void __sanitizer_syscall_post_impl____lwp_park60(long long res, long long clock_id, long long flags, long long ts, long long unpark, long long hint, long long unparkhint)
void __sanitizer_syscall_pre_impl____lwp_park60(long long clock_id, long long flags, long long ts, long long unpark, long long hint, long long unparkhint)
void __sanitizer_syscall_pre_impl_compat_09_ouname(long long name)
void __sanitizer_syscall_pre_impl_setegid(long long egid)
void __sanitizer_syscall_pre_impl___settimeofday50(long long tv, long long tzp)
void __sanitizer_syscall_post_impl_acct(long long res, long long path)
void __sanitizer_syscall_post_impl_compat_30___fstat13(long long res, long long fd, long long sb)
void __sanitizer_syscall_post_impl_setreuid(long long res, long long ruid, long long euid)
void __sanitizer_syscall_pre_impl_compat_43_otruncate(long long path, long long length)
void __sanitizer_syscall_pre_impl_chmod(long long path, long long mode)
void __sanitizer_syscall_pre_impl___socket30(long long domain, long long type, long long protocol)
void __sanitizer_syscall_pre_impl___getdents30(long long fd, long long buf, long long count)
void __sanitizer_syscall_pre_impl_compat_12_fstat12(long long fd, long long sb)
void __sanitizer_syscall_pre_impl_compat_43_owait(void)
void __sanitizer_syscall_pre_impl_madvise(long long addr, long long len, long long behav)
void __sanitizer_syscall_pre_impl_compat_09_osetdomainname(long long domainname, long long len)
void __sanitizer_syscall_pre_impl_pset_create(long long psid)
void __sanitizer_syscall_post_impl_compat_43_ogetpeername(long long res, long long fdes, long long asa, long long alen)
void __sanitizer_syscall_pre_impl_pset_assign(long long psid, long long cpuid, long long opsid)
void __sanitizer_syscall_pre_impl_compat_50_lfs_segwait(long long fsidp, long long tv)
void __sanitizer_syscall_post_impl__ksem_getvalue(long long res, long long id, long long value)
void __sanitizer_syscall_post_impl_pwritev(long long res, long long fd, long long iovp, long long iovcnt, long long PAD, long long offset)
void __sanitizer_syscall_pre_impl_open(long long path, long long flags, long long mode)
void __sanitizer_syscall_post_impl_____sigtimedwait50(long long res, long long set, long long info, long long timeout)
void __sanitizer_syscall_post_impl_posix_fallocate(long long res, long long fd, long long PAD, long long pos, long long len)
void __sanitizer_syscall_pre_impl_mkdirat(long long fd, long long path, long long mode)
void __sanitizer_syscall_post_impl_compat_50_timer_settime(long long res, long long timerid, long long flags, long long value, long long ovalue)
void __sanitizer_syscall_post_impl_compat_09_ogetdomainname(long long res, long long domainname, long long len)
void __sanitizer_syscall_pre_impl_sched_yield(void)
void __sanitizer_syscall_pre_impl_vadvise(long long anom)
void __sanitizer_syscall_pre_impl__sched_setaffinity(long long pid, long long lid, long long size, long long cpuset)
void __sanitizer_syscall_post_impl_clock_getcpuclockid2(long long res, long long idtype, long long id, long long clock_id)
void __sanitizer_syscall_pre_impl___futimes50(long long fd, long long tptr)
void __sanitizer_syscall_pre_impl_setgroups(long long gidsetsize, long long gidset)
void __sanitizer_syscall_post_impl_compat_13_sigprocmask13(long long res, long long how, long long mask)
void __sanitizer_syscall_post_impl_getcontext(long long res, long long ucp)
void __sanitizer_syscall_post_impl_openat(long long res, long long fd, long long path, long long oflags, long long mode)
void __sanitizer_syscall_pre_impl_compat_50_futimes(long long fd, long long tptr)
void __sanitizer_syscall_pre_impl__lwp_unpark(long long target, long long hint)
void __sanitizer_syscall_post_impl_compat_43_olseek(long long res, long long fd, long long offset, long long whence)
void __sanitizer_syscall_pre_impl_munmap(long long addr, long long len)
void __sanitizer_syscall_pre_impl_aio_fsync(long long op, long long aiocbp)
void __sanitizer_syscall_pre_impl_faccessat(long long fd, long long path, long long amode, long long flag)
void __sanitizer_syscall_pre_impl_seteuid(long long euid)
void __sanitizer_syscall_post_impl_compat_50_utimes(long long res, long long path, long long tptr)
void __sanitizer_syscall_pre_impl__lwp_setprivate(long long ptr)
void __sanitizer_syscall_post_impl_semconfig(long long res, long long flag)
void __sanitizer_syscall_pre_impl_setpriority(long long which, long long who, long long prio)
void __sanitizer_syscall_pre_impl_listxattr(long long path, long long list, long long size)
void __sanitizer_syscall_pre_impl_setsid(void)
void __sanitizer_syscall_post_impl__lwp_wakeup(long long res, long long target)
void __sanitizer_syscall_post_impl_utrace(long long res, long long label, long long addr, long long len)
void __sanitizer_syscall_post_impl_compat_50_timer_gettime(long long res, long long timerid, long long value)
void __sanitizer_syscall_pre_impl_compat_43_orecvfrom(long long s, long long buf, long long len, long long flags, long long from, long long fromlenaddr)
void __sanitizer_syscall_post_impl___stat50(long long res, long long path, long long ub)
void __sanitizer_syscall_post_impl_read(long long res, long long fd, long long buf, long long nbyte)
void __sanitizer_syscall_post_impl_compat_43_fstat43(long long res, long long fd, long long sb)
void __sanitizer_syscall_pre_impl_recvmsg(long long s, long long msg, long long flags)
void __sanitizer_syscall_post_impl_lgetxattr(long long res, long long path, long long name, long long value, long long size)
void __sanitizer_syscall_pre_impl_chflags(long long path, long long flags)
void __sanitizer_syscall_post_impl_unlink(long long res, long long path)
void __sanitizer_syscall_pre_impl_sendto(long long s, long long buf, long long len, long long flags, long long to, long long tolen)
void __sanitizer_syscall_pre_impl_compat_43_osigblock(long long mask)
void __sanitizer_syscall_post_impl_reboot(long long res, long long opt, long long bootstr)
void __sanitizer_syscall_post_impl_getpid(long long res)
void __sanitizer_syscall_pre_impl_compat_50___fhstat40(long long fhp, long long fh_size, long long sb)
void __sanitizer_syscall_pre_impl_flock(long long fd, long long how)
void __sanitizer_syscall_post_impl_compat_13_sigreturn13(long long res, long long sigcntxp)
void __sanitizer_syscall_post_impl_compat_60_sa_setconcurrency(long long res, long long concurrency)
void __sanitizer_syscall_post_impl_lseek(long long res, long long fd, long long PAD, long long offset, long long whence)
void __sanitizer_syscall_post_impl_fgetxattr(long long res, long long fd, long long name, long long value, long long size)
void __sanitizer_syscall_post_impl__sched_setparam(long long res, long long pid, long long lid, long long policy, long long params)
void __sanitizer_syscall_post_impl_getgroups(long long res, long long gidsetsize, long long gidset)
void __sanitizer_syscall_post_impl_setuid(long long res, long long uid)
void __sanitizer_syscall_post_impl_mkfifoat(long long res, long long fd, long long path, long long mode)
void __sanitizer_syscall_pre_impl___wait450(long long pid, long long status, long long options, long long rusage)
void __sanitizer_syscall_post_impl_compat_43_osigstack(long long res, long long nss, long long oss)
void __sanitizer_syscall_post_impl_compat_50_clock_gettime(long long res, long long clock_id, long long tp)
void __sanitizer_syscall_pre_impl_dup(long long fd)
void __sanitizer_syscall_post_impl_mq_close(long long res, long long mqdes)
void __sanitizer_syscall_post_impl___sysctl(long long res, long long name, long long namelen, long long oldv, long long oldlenp, long long newv, long long newlen)
void __sanitizer_syscall_pre_impl___ntp_gettime50(long long ntvp)
void __sanitizer_syscall_post_impl__lwp_suspend(long long res, long long target)
void __sanitizer_syscall_post_impl_pathconf(long long res, long long path, long long name)
void __sanitizer_syscall_pre_impl_pwrite(long long fd, long long buf, long long nbyte, long long PAD, long long offset)
void __sanitizer_syscall_post_impl___fhstat50(long long res, long long fhp, long long fh_size, long long sb)
void __sanitizer_syscall_pre_impl_lfs_bmapv(long long fsidp, long long blkiov, long long blkcnt)
void __sanitizer_syscall_post_impl_setxattr(long long res, long long path, long long name, long long value, long long size, long long flags)
void __sanitizer_syscall_post_impl_accept(long long res, long long s, long long name, long long anamelen)
void __sanitizer_syscall_pre_impl_compat_50_utimes(long long path, long long tptr)
void __sanitizer_syscall_pre_impl_compat_10_omsgsys(long long which, long long a2, long long a3, long long a4, long long a5, long long a6)
void __sanitizer_syscall_pre_impl_compat_43_oaccept(long long s, long long name, long long anamelen)
void __sanitizer_syscall_post_impl_vfork(long long res)
void __sanitizer_syscall_post_impl_compat_90_fstatvfs1(long long res, long long fd, long long buf, long long flags)
void __sanitizer_syscall_pre_impl_timer_create(long long clock_id, long long evp, long long timerid)
void __sanitizer_syscall_post_impl_lchmod(long long res, long long path, long long mode)
void __sanitizer_syscall_pre_impl_lremovexattr(long long path, long long name)
void __sanitizer_syscall_pre_impl_compat_20_statfs(long long path, long long buf)
void __sanitizer_syscall_pre_impl_compat_13_sigreturn13(long long sigcntxp)
void __sanitizer_syscall_post_impl_fchown(long long res, long long fd, long long uid, long long gid)
void __sanitizer_syscall_pre_impl___getlogin(long long namebuf, long long namelen)
void __sanitizer_syscall_post_impl__ksem_unlink(long long res, long long name)
void __sanitizer_syscall_post_impl_____semctl50(long long res, long long semid, long long semnum, long long cmd, long long arg)
void __sanitizer_syscall_post_impl_mprotect(long long res, long long addr, long long len, long long prot)
void __sanitizer_syscall_post_impl_futimens(long long res, long long fd, long long tptr)
void __sanitizer_syscall_pre_impl__ksem_post(long long id)
void __sanitizer_syscall_pre_impl_compat_43_ocreat(long long path, long long mode)
void __sanitizer_syscall_post_impl_getsid(long long res, long long pid)
void __sanitizer_syscall_pre_impl___sigsuspend14(long long set)
void __sanitizer_syscall_post_impl_lfs_markv(long long res, long long fsidp, long long blkiov, long long blkcnt)
void __sanitizer_syscall_pre_impl_poll(long long fds, long long nfds, long long timeout)
void __sanitizer_syscall_pre_impl_aio_error(long long aiocbp)
void __sanitizer_syscall_post_impl___nanosleep50(long long res, long long rqtp, long long rmtp)
void __sanitizer_syscall_post_impl_compat_43_ogetrlimit(long long res, long long which, long long rlp)
void __sanitizer_syscall_pre_impl_extattr_delete_link(long long path, long long attrnamespace, long long attrname)
void __sanitizer_syscall_pre_impl_munlockall(void)
void __sanitizer_syscall_post_impl___fhstatvfs190(long long res, long long fhp, long long fh_size, long long buf, long long flags)
void __sanitizer_syscall_pre_impl_compat_30___stat13(long long path, long long ub)
void __sanitizer_syscall_pre_impl_compat_50_nanosleep(long long rqtp, long long rmtp)
void __sanitizer_syscall_post_impl_lchown(long long res, long long path, long long uid, long long gid)
void __sanitizer_syscall_pre_impl_compat_12_oswapon(long long name)
void __sanitizer_syscall_post_impl_getrlimit(long long res, long long which, long long rlp)
void __sanitizer_syscall_pre_impl_readlink(long long path, long long buf, long long count)
void __sanitizer_syscall_post_impl_compat_50_lfs_segwait(long long res, long long fsidp, long long tv)
void __sanitizer_syscall_pre_impl_compat_90_fstatvfs1(long long fd, long long buf, long long flags)
void __sanitizer_syscall_pre_impl_issetugid(void)
void __sanitizer_syscall_pre_impl_posix_spawn(long long pid, long long path, long long file_actions, long long attrp, long long argv, long long envp)
void __sanitizer_syscall_pre_impl_mknodat(long long fd, long long path, long long mode, long long PAD, long long dev)
void __sanitizer_syscall_post_impl_compat_43_orecv(long long res, long long s, long long buf, long long len, long long flags)
void __sanitizer_syscall_pre_impl___getcwd(long long bufp, long long length)
void __sanitizer_syscall_pre_impl_swapctl(long long cmd, long long arg, long long misc)
void __sanitizer_syscall_pre_impl___quotactl(long long path, long long args)
void __sanitizer_syscall_post_impl_connect(long long res, long long s, long long name, long long namelen)
void __sanitizer_syscall_pre_impl_extattr_delete_file(long long path, long long attrnamespace, long long attrname)
void __sanitizer_syscall_post_impl_aio_read(long long res, long long aiocbp)
void __sanitizer_syscall_pre_impl__lwp_getname(long long target, long long name, long long len)
void __sanitizer_syscall_pre_impl_compat_43_stat43(long long path, long long ub)
void __sanitizer_syscall_pre_impl_extattr_list_fd(long long fd, long long attrnamespace, long long data, long long nbytes)
void __sanitizer_syscall_pre_impl_removexattr(long long path, long long name)
void __sanitizer_syscall_pre_impl_getpriority(long long which, long long who)
void __sanitizer_syscall_post_impl_fexecve(long long res, long long fd, long long argp, long long envp)
void __sanitizer_syscall_pre_impl__ksem_getvalue(long long id, long long value)
void __sanitizer_syscall_post_impl_compat_43_osigsetmask(long long res, long long mask)
void __sanitizer_syscall_pre_impl___clone(long long flags, long long stack)
void __sanitizer_syscall_pre_impl_undelete(long long path)
void __sanitizer_syscall_post_impl_readv(long long res, long long fd, long long iovp, long long iovcnt)
void __sanitizer_syscall_post_impl_setsid(long long res)
void __sanitizer_syscall_pre_impl_compat_20_fhstatfs(long long fhp, long long buf)
void __sanitizer_syscall_pre_impl_compat_43_orecvmsg(long long s, long long msg, long long flags)
void __sanitizer_syscall_pre_impl_compat_50_adjtime(long long delta, long long olddelta)
void __sanitizer_syscall_pre_impl_compat_30_fhopen(long long fhp, long long flags)
void __sanitizer_syscall_pre_impl_posix_fadvise(long long)
void __sanitizer_syscall_pre_impl_mq_open(long long name, long long oflag, long long mode, long long attr)
void __sanitizer_syscall_post_impl_fcntl(long long res, long long fd, long long cmd, long long arg)
void __sanitizer_syscall_post_impl_extattr_list_link(long long res, long long path, long long attrnamespace, long long data, long long nbytes)
void __sanitizer_syscall_pre_impl__sched_protect(long long priority)
void __sanitizer_syscall_post_impl_chdir(long long res, long long path)
void __sanitizer_syscall_pre_impl_compat_43_olseek(long long fd, long long offset, long long whence)
void __sanitizer_syscall_post_impl_compat_30_fhstatvfs1(long long res, long long fhp, long long buf, long long flags)
void __sanitizer_syscall_pre_impl_compat_50_clock_getres(long long clock_id, long long tp)
void __sanitizer_syscall_pre_impl_readlinkat(long long fd, long long path, long long buf, long long bufsize)
void __sanitizer_syscall_pre_impl___posix_rename(long long from, long long to)
void __sanitizer_syscall_post_impl_compat_20_getfsstat(long long res, long long buf, long long bufsize, long long flags)
void __sanitizer_syscall_post_impl_dup2(long long res, long long from, long long to)
void __sanitizer_syscall_pre_impl_sendmsg(long long s, long long msg, long long flags)
void __sanitizer_syscall_post_impl_lfs_segclean(long long res, long long fsidp, long long segment)
void __sanitizer_syscall_pre_impl__lwp_ctl(long long features, long long address)
void __sanitizer_syscall_post_impl_setgroups(long long res, long long gidsetsize, long long gidset)
void __sanitizer_syscall_pre_impl_compat_50_pselect(long long nd, long long in, long long ou, long long ex, long long ts, long long mask)
void __sanitizer_syscall_pre_impl_compat_50_select(long long nd, long long in, long long ou, long long ex, long long tv)
void __sanitizer_syscall_post_impl_compat_20_fhstatfs(long long res, long long fhp, long long buf)
void __sanitizer_syscall_pre_impl_fktrace(long long fd, long long ops, long long facs, long long pid)
void __sanitizer_syscall_pre_impl__lwp_setname(long long target, long long name)
void __sanitizer_syscall_pre_impl___gettimeofday50(long long tp, long long tzp)
void __sanitizer_syscall_post_impl_compat_12_oreboot(long long res, long long opt)
void __sanitizer_syscall_post_impl_chown(long long res, long long path, long long uid, long long gid)
void __sanitizer_syscall_post_impl_kqueue1(long long res, long long flags)
void __sanitizer_syscall_post_impl_compat_30_socket(long long res, long long domain, long long type, long long protocol)
void __sanitizer_syscall_post_impl___getfh30(long long res, long long fname, long long fhp, long long fh_size)
void __sanitizer_syscall_pre_impl_compat_30_getfh(long long fname, long long fhp)
void __sanitizer_syscall_post_impl_mmap(long long res, long long addr, long long len, long long prot, long long flags, long long fd, long long PAD, long long pos)
void __sanitizer_syscall_post_impl___getlogin(long long res, long long namebuf, long long namelen)
void __sanitizer_syscall_post_impl___setitimer50(long long res, long long which, long long itv, long long oitv)
void __sanitizer_syscall_post_impl_compat_12_msync(long long res, long long addr, long long len)
void __sanitizer_syscall_post_impl__lwp_setname(long long res, long long target, long long name)
void __sanitizer_syscall_post_impl_link(long long res, long long path, long long link)
void __sanitizer_syscall_pre_impl_compat_90_fhstatvfs1(long long fhp, long long fh_size, long long buf, long long flags)
void __sanitizer_syscall_pre_impl_getuid(void)
void __sanitizer_syscall_pre_impl___timer_settime50(long long timerid, long long flags, long long value, long long ovalue)
void __sanitizer_syscall_post_impl_sched_yield(long long res)
void __sanitizer_syscall_pre_impl_lsetxattr(long long path, long long name, long long value, long long size, long long flags)
void __sanitizer_syscall_pre_impl_sysarch(long long op, long long parms)
void __sanitizer_syscall_pre_impl_clock_getcpuclockid2(long long idtype, long long id, long long clock_id)
void __sanitizer_syscall_pre_impl__ksem_trywait(long long id)
void __sanitizer_syscall_pre_impl_pipe(void)
void __sanitizer_syscall_post_impl_shutdown(long long res, long long s, long long how)
void __sanitizer_syscall_pre_impl_setrlimit(long long which, long long rlp)
void __sanitizer_syscall_post_impl_compat_90_fhstatvfs1(long long res, long long fhp, long long fh_size, long long buf, long long flags)
void __sanitizer_syscall_post_impl_compat_10_osemsys(long long res, long long which, long long a2, long long a3, long long a4, long long a5)
void __sanitizer_syscall_post_impl_munlockall(long long res)
void __sanitizer_syscall_post_impl___posix_lchown(long long res, long long path, long long uid, long long gid)
void __sanitizer_syscall_post_impl_extattr_delete_fd(long long res, long long fd, long long attrnamespace, long long attrname)
void __sanitizer_syscall_pre_impl___kevent50(long long fd, long long changelist, long long nchanges, long long eventlist, long long nevents, long long timeout)
void __sanitizer_syscall_pre_impl___sigaction_sigtramp(long long signum, long long nsa, long long osa, long long tramp, long long vers)
void __sanitizer_syscall_pre_impl_compat_16___sigreturn14(long long sigcntxp)
void __sanitizer_syscall_post_impl_symlink(long long res, long long path, long long link)
void __sanitizer_syscall_pre_impl_compat_20_fstatfs(long long fd, long long buf)
void __sanitizer_syscall_pre_impl_compat_43_ogetrlimit(long long which, long long rlp)
void __sanitizer_syscall_post_impl___clock_getres50(long long res, long long clock_id, long long tp)
void __sanitizer_syscall_post_impl_fchmod(long long res, long long fd, long long mode)
void __sanitizer_syscall_pre_impl___fstat50(long long fd, long long sb)
void __sanitizer_syscall_post_impl_fremovexattr(long long res, long long fd, long long name)
void __sanitizer_syscall_post_impl_access(long long res, long long path, long long flags)
void __sanitizer_syscall_post_impl_compat_13_sigsuspend13(long long res, long long mask)
void __sanitizer_syscall_pre_impl_ptrace(long long req, long long pid, long long addr, long long data)
void __sanitizer_syscall_post_impl_compat_60_sa_register(long long res, long long newv, long long oldv, long long flags, long long stackinfo_offset)
void __sanitizer_syscall_post_impl_compat_43_ogethostname(long long res, long long hostname, long long len)
void __sanitizer_syscall_post_impl__lwp_getprivate(long long res)
void __sanitizer_syscall_pre_impl_rename(long long from, long long to)
void __sanitizer_syscall_post_impl_fsync_range(long long res, long long fd, long long flags, long long start, long long length)
void __sanitizer_syscall_post_impl_compat_12_getdirentries(long long res, long long fd, long long buf, long long count, long long basep)
void __sanitizer_syscall_pre_impl_fcntl(long long fd, long long cmd, long long arg)
void __sanitizer_syscall_pre_impl_posix_fallocate(long long fd, long long PAD, long long pos, long long len)
void __sanitizer_syscall_post_impl_compat_43_ogetdtablesize(long long res)
void __sanitizer_syscall_pre_impl_getpeername(long long fdes, long long asa, long long alen)
void __sanitizer_syscall_pre_impl_recvmmsg(long long s, long long mmsg, long long vlen, long long flags, long long timeout)
void __sanitizer_syscall_post_impl_compat_14_msgctl(long long res, long long msqid, long long cmd, long long buf)
void __sanitizer_syscall_pre_impl_compat_50_settimeofday(long long tv, long long tzp)
void __sanitizer_syscall_post_impl_recvfrom(long long res, long long s, long long buf, long long len, long long flags, long long from, long long fromlenaddr)
void __sanitizer_syscall_pre_impl_msgget(long long key, long long msgflg)
void __sanitizer_syscall_pre_impl_compat_60_sa_yield(void)
void __sanitizer_syscall_post_impl___posix_fadvise50(long long res, long long fd, long long PAD, long long offset, long long len, long long advice)
void __sanitizer_syscall_pre_impl__ksem_close(long long id)
void __sanitizer_syscall_pre_impl_vfork(void)
void __sanitizer_syscall_pre_impl_getpid(void)
void __sanitizer_syscall_post_impl_compat_10_oshmsys(long long res, long long which, long long a2, long long a3, long long a4)
void __sanitizer_syscall_post_impl_mkdir(long long res, long long path, long long mode)
void __sanitizer_syscall_post_impl_vadvise(long long res, long long anom)
void __sanitizer_syscall_pre_impl_sendmmsg(long long s, long long mmsg, long long vlen, long long flags)
void __sanitizer_syscall_post_impl___lutimes50(long long res, long long path, long long tptr)
void __sanitizer_syscall_post_impl_munmap(long long res, long long addr, long long len)
void __sanitizer_syscall_pre_impl_extattr_delete_fd(long long fd, long long attrnamespace, long long attrname)
void __sanitizer_syscall_pre_impl_compat_30_ntp_gettime(long long ntvp)
void __sanitizer_syscall_pre_impl_pset_destroy(long long psid)
void __sanitizer_syscall_pre_impl_access(long long path, long long flags)
void __sanitizer_syscall_post_impl_setpgid(long long res, long long pid, long long pgid)
void __sanitizer_syscall_pre_impl_compat_50_mq_timedsend(long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio, long long abs_timeout)
void __sanitizer_syscall_post_impl__sched_protect(long long res, long long priority)
void __sanitizer_syscall_post_impl___pselect50(long long res, long long nd, long long in, long long ou, long long ex, long long ts, long long mask)
void __sanitizer_syscall_pre_impl_shmat(long long shmid, long long shmaddr, long long shmflg)
void __sanitizer_syscall_pre_impl_compat_50_aio_suspend(long long list, long long nent, long long timeout)
void __sanitizer_syscall_post_impl_compat_50_select(long long res, long long nd, long long in, long long ou, long long ex, long long tv)
void __sanitizer_syscall_pre_impl___lfs_segwait50(long long fsidp, long long tv)
void __sanitizer_syscall_post_impl_sendto(long long res, long long s, long long buf, long long len, long long flags, long long to, long long tolen)
void __sanitizer_syscall_post_impl___setlogin(long long res, long long namebuf)
void __sanitizer_syscall_post_impl_compat_50_mq_timedreceive(long long res, long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio, long long abs_timeout)
void __sanitizer_syscall_pre_impl_mmap(long long addr, long long len, long long prot, long long flags, long long fd, long long PAD, long long pos)
void __sanitizer_syscall_post_impl_compat_50_mq_timedsend(long long res, long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio, long long abs_timeout)
void __sanitizer_syscall_pre_impl_compat_30_fhstatvfs1(long long fhp, long long buf, long long flags)
void __sanitizer_syscall_pre_impl_mq_receive(long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio)
void __sanitizer_syscall_pre_impl_pathconf(long long path, long long name)
void __sanitizer_syscall_pre_impl_compat_43_ogetpagesize(void)
void __sanitizer_syscall_post_impl_compat_60_sa_preempt(long long res, long long sa_id)
void __sanitizer_syscall_post_impl_compat_43_owait(long long res)
void __sanitizer_syscall_post_impl_compat_50_____semctl13(long long res, long long semid, long long semnum, long long cmd, long long arg)
void __sanitizer_syscall_post_impl_extattr_list_file(long long res, long long path, long long attrnamespace, long long data, long long nbytes)
void __sanitizer_syscall_post_impl_compat_50_getitimer(long long res, long long which, long long itv)
void __sanitizer_syscall_pre_impl_utimensat(long long fd, long long path, long long tptr, long long flag)
void __sanitizer_syscall_pre_impl_semop(long long semid, long long sops, long long nsops)
void __sanitizer_syscall_post_impl_compat_50_mknod(long long res, long long path, long long mode, long long dev)
void __sanitizer_syscall_post_impl_extattr_delete_link(long long res, long long path, long long attrnamespace, long long attrname)
void __sanitizer_syscall_pre_impl_fgetxattr(long long fd, long long name, long long value, long long size)
void __sanitizer_syscall_post_impl___posix_rename(long long res, long long from, long long to)
void __sanitizer_syscall_post_impl_flock(long long res, long long fd, long long how)
void __sanitizer_syscall_post_impl_compat_50___fhstat40(long long res, long long fhp, long long fh_size, long long sb)
void __sanitizer_syscall_pre_impl_compat_10_oshmsys(long long which, long long a2, long long a3, long long a4)
void __sanitizer_syscall_post_impl_umask(long long res, long long newmask)
void __sanitizer_syscall_pre_impl___fhstatvfs190(long long fhp, long long fh_size, long long buf, long long flags)
void __sanitizer_syscall_pre_impl_llistxattr(long long path, long long list, long long size)
void __sanitizer_syscall_post_impl_compat_50___msgctl13(long long res, long long msqid, long long cmd, long long buf)
void __sanitizer_syscall_post_impl_fchflags(long long res, long long fd, long long flags)
void __sanitizer_syscall_pre_impl_kqueue(void)
void __sanitizer_syscall_post_impl_compat_50_setitimer(long long res, long long which, long long itv, long long oitv)
void __sanitizer_syscall_post_impl_nfssvc(long long res, long long flag, long long argp)
void __sanitizer_syscall_pre_impl_compat_50_gettimeofday(long long tp, long long tzp)
void __sanitizer_syscall_post_impl__lwp_unpark_all(long long res, long long targets, long long ntargets, long long hint)
void __sanitizer_syscall_post_impl_getsockopt2(long long res, long long s, long long level, long long name, long long val, long long avalsize)
void __sanitizer_syscall_post_impl_mq_setattr(long long res, long long mqdes, long long mqstat, long long omqstat)
void __sanitizer_syscall_pre_impl_compat_43_ogethostid(void)
void __sanitizer_syscall_pre_impl_compat_20_getfsstat(long long buf, long long bufsize, long long flags)
void __sanitizer_syscall_pre_impl_compat_09_ogetdomainname(long long domainname, long long len)
void __sanitizer_syscall_post_impl___timer_settime50(long long res, long long timerid, long long flags, long long value, long long ovalue)
void __sanitizer_syscall_pre_impl_timer_getoverrun(long long timerid)
void __sanitizer_syscall_post_impl_fork(long long res)
void __sanitizer_syscall_post_impl___shmctl50(long long res, long long shmid, long long cmd, long long buf)
void __sanitizer_syscall_post_impl_utimensat(long long res, long long fd, long long path, long long tptr, long long flag)
void __sanitizer_syscall_post_impl_llistxattr(long long res, long long path, long long list, long long size)
void __sanitizer_syscall_post_impl___lfs_segwait50(long long res, long long fsidp, long long tv)
void __sanitizer_syscall_pre_impl_compat_60_sa_setconcurrency(long long concurrency)
void __sanitizer_syscall_pre_impl_shmdt(long long shmaddr)
void __sanitizer_syscall_pre_impl_kill(long long pid, long long signum)
void __sanitizer_syscall_post_impl_swapctl(long long res, long long cmd, long long arg, long long misc)
void __sanitizer_syscall_post_impl_extattr_set_link(long long res, long long path, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_pre_impl__ksem_open(long long name, long long oflag, long long mode, long long value, long long idp)
void __sanitizer_syscall_pre_impl_write(long long fd, long long buf, long long nbyte)
void __sanitizer_syscall_pre_impl___sigprocmask14(long long how, long long set, long long oset)
void __sanitizer_syscall_pre_impl__sched_setparam(long long pid, long long lid, long long policy, long long params)
void __sanitizer_syscall_pre_impl_compat_50_pollts(long long fds, long long nfds, long long ts, long long mask)
void __sanitizer_syscall_post_impl_fchownat(long long res, long long fd, long long path, long long owner, long long group, long long flag)
void __sanitizer_syscall_pre_impl_ioctl(long long fd, long long com, long long data)
void __sanitizer_syscall_pre_impl_lgetxattr(long long path, long long name, long long value, long long size)
void __sanitizer_syscall_pre_impl_mq_unlink(long long name)
void __sanitizer_syscall_post_impl__ksem_destroy(long long res, long long id)
void __sanitizer_syscall_post_impl_lremovexattr(long long res, long long path, long long name)
void __sanitizer_syscall_post_impl___getvfsstat90(long long res, long long buf, long long bufsize, long long flags)
void __sanitizer_syscall_post_impl___lstat50(long long res, long long path, long long ub)
void __sanitizer_syscall_pre_impl_mlockall(long long flags)
void __sanitizer_syscall_post_impl_lsetxattr(long long res, long long path, long long name, long long value, long long size, long long flags)
void __sanitizer_syscall_post_impl_compat_43_otruncate(long long res, long long path, long long length)
void __sanitizer_syscall_pre_impl_compat_13_sigpending13(void)
void __sanitizer_syscall_post_impl__ksem_open(long long res, long long name, long long oflag, long long mode, long long value, long long idp)
void __sanitizer_syscall_pre_impl_getsockname(long long fdes, long long asa, long long alen)
void __sanitizer_syscall_post_impl___mq_timedreceive50(long long res, long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio, long long abs_timeout)
void __sanitizer_syscall_post_impl_msgrcv(long long res, long long msqid, long long msgp, long long msgsz, long long msgtyp, long long msgflg)
void __sanitizer_syscall_post_impl__lwp_setprivate(long long res, long long ptr)
void __sanitizer_syscall_pre_impl_compat_13_sigsuspend13(long long mask)
void __sanitizer_syscall_post_impl_readlinkat(long long res, long long fd, long long path, long long buf, long long bufsize)
void __sanitizer_syscall_post_impl_compat_90_getvfsstat(long long res, long long buf, long long bufsize, long long flags)
void __sanitizer_syscall_pre_impl___sigaltstack14(long long nss, long long oss)
void __sanitizer_syscall_pre_impl_extattr_get_file(long long path, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_post_impl_aio_fsync(long long res, long long op, long long aiocbp)
void __sanitizer_syscall_pre_impl_lseek(long long fd, long long PAD, long long offset, long long whence)
void __sanitizer_syscall_post_impl_compat_14_shmctl(long long res, long long shmid, long long cmd, long long buf)
void __sanitizer_syscall_post_impl__ksem_timedwait(long long res, long long id, long long abstime)
void __sanitizer_syscall_pre_impl_kqueue1(long long flags)
void __sanitizer_syscall_post_impl_compat_43_osigblock(long long res, long long mask)
void __sanitizer_syscall_pre_impl_compat_43_ogetsockname(long long fdec, long long asa, long long alen)
void __sanitizer_syscall_post_impl_renameat(long long res, long long fromfd, long long from, long long tofd, long long to)
void __sanitizer_syscall_pre_impl_unlink(long long path)
void __sanitizer_syscall_pre_impl_ntp_adjtime(long long tp)
void __sanitizer_syscall_pre_impl_semconfig(long long flag)
void __sanitizer_syscall_pre_impl_compat_60__lwp_park(long long ts, long long unpark, long long hint, long long unparkhint)
void __sanitizer_syscall_pre_impl_pread(long long fd, long long buf, long long nbyte, long long PAD, long long offset)
void __sanitizer_syscall_pre_impl___vfork14(void)
void __sanitizer_syscall_post_impl_fchdir(long long res, long long fd)
void __sanitizer_syscall_pre_impl_compat_50_timer_gettime(long long timerid, long long value)
void __sanitizer_syscall_pre_impl_compat_50___fstat30(long long fd, long long sb)
void __sanitizer_syscall_post_impl_extattr_delete_file(long long res, long long path, long long attrnamespace, long long attrname)
void __sanitizer_syscall_post_impl_sysarch(long long res, long long op, long long parms)
void __sanitizer_syscall_post_impl___utimes50(long long res, long long path, long long tptr)
void __sanitizer_syscall_pre_impl_setregid(long long rgid, long long egid)
void __sanitizer_syscall_pre_impl___getitimer50(long long which, long long itv)
void __sanitizer_syscall_pre_impl___clock_getres50(long long clock_id, long long tp)
void __sanitizer_syscall_post_impl___gettimeofday50(long long res, long long tp, long long tzp)
void __sanitizer_syscall_pre_impl_shmget(long long key, long long size, long long shmflg)
void __sanitizer_syscall_pre_impl_aio_read(long long aiocbp)
void __sanitizer_syscall_post_impl_getpeername(long long res, long long fdes, long long asa, long long alen)
void __sanitizer_syscall_post_impl_exit(long long res, long long rval)
void __sanitizer_syscall_pre_impl_dup3(long long from, long long to, long long flags)
void __sanitizer_syscall_post_impl_setrlimit(long long res, long long which, long long rlp)
void __sanitizer_syscall_post_impl_compat_50_clock_getres(long long res, long long clock_id, long long tp)
void __sanitizer_syscall_pre_impl___statvfs190(long long path, long long buf, long long flags)
void __sanitizer_syscall_post_impl_getpgrp(long long res)
void __sanitizer_syscall_pre_impl_compat_13_sigaction13(long long signum, long long nsa, long long osa)
void __sanitizer_syscall_pre_impl_compat_43_osend(long long s, long long buf, long long len, long long flags)
void __sanitizer_syscall_post_impl__ksem_init(long long res, long long value, long long idp)
void __sanitizer_syscall_pre_impl___msync13(long long addr, long long len, long long flags)
void __sanitizer_syscall_post_impl_chmod(long long res, long long path, long long mode)
void __sanitizer_syscall_pre_impl___getrusage50(long long who, long long rusage)
void __sanitizer_syscall_pre_impl__sched_getaffinity(long long pid, long long lid, long long size, long long cpuset)
void __sanitizer_syscall_pre_impl_fsync(long long fd)
void __sanitizer_syscall_post_impl___fstatvfs190(long long res, long long fd, long long buf, long long flags)
void __sanitizer_syscall_post_impl_compat_43_lstat43(long long res, long long path, long long ub)
void __sanitizer_syscall_post_impl___msgctl50(long long res, long long msqid, long long cmd, long long buf)
void __sanitizer_syscall_pre_impl_truncate(long long path, long long PAD, long long length)
void __sanitizer_syscall_pre_impl_clock_nanosleep(long long clock_id, long long flags, long long rqtp, long long rmtp)
void __sanitizer_syscall_pre_impl___shmctl50(long long shmid, long long cmd, long long buf)
void __sanitizer_syscall_post_impl_compat_43_osethostid(long long res, long long hostid)
void __sanitizer_syscall_post_impl_shmat(long long res, long long shmid, long long shmaddr, long long shmflg)
void __sanitizer_syscall_post_impl_compat_50_pollts(long long res, long long fds, long long nfds, long long ts, long long mask)
void __sanitizer_syscall_pre_impl__ksem_destroy(long long id)
void __sanitizer_syscall_post_impl_compat_20_statfs(long long res, long long path, long long buf)
void __sanitizer_syscall_post_impl_compat_50_futimes(long long res, long long fd, long long tptr)
void __sanitizer_syscall_pre_impl_wait6(long long idtype, long long id, long long status, long long options, long long wru, long long info)
void __sanitizer_syscall_post_impl_compat_43_ocreat(long long res, long long path, long long mode)
void __sanitizer_syscall_post_impl_compat_50_pselect(long long res, long long nd, long long in, long long ou, long long ex, long long ts, long long mask)
void __sanitizer_syscall_post_impl_ktrace(long long res, long long fname, long long ops, long long facs, long long pid)
void __sanitizer_syscall_post_impl_getpgid(long long res, long long pid)
void __sanitizer_syscall_pre_impl__ksem_unlink(long long name)
void __sanitizer_syscall_pre_impl_compat_50___msgctl13(long long msqid, long long cmd, long long buf)
void __sanitizer_syscall_post_impl__sched_getaffinity(long long res, long long pid, long long lid, long long size, long long cpuset)
void __sanitizer_syscall_pre_impl_getpgid(long long pid)
void __sanitizer_syscall_post_impl_compat_30_fhstat(long long res, long long fhp, long long sb)
void __sanitizer_syscall_post_impl_compat_43_oquota(long long res)
void __sanitizer_syscall_post_impl___sigsuspend14(long long res, long long set)
void __sanitizer_syscall_post_impl_execve(long long res, long long path, long long argp, long long envp)
void __sanitizer_syscall_pre_impl_profil(long long samples, long long size, long long offset, long long scale)
void __sanitizer_syscall_post_impl_pipe2(long long res, long long fildes, long long flags)
void __sanitizer_syscall_pre_impl_compat_30_fhstat(long long fhp, long long sb)
void __sanitizer_syscall_pre_impl_compat_43_ogetdirentries(long long fd, long long buf, long long count, long long basep)
void __sanitizer_syscall_pre_impl_pipe2(long long fildes, long long flags)
void __sanitizer_syscall_post_impl__lwp_create(long long res, long long ucp, long long flags, long long new_lwp)
void __sanitizer_syscall_pre_impl__ksem_wait(long long id)
void __sanitizer_syscall_post_impl_ftruncate(long long res, long long fd, long long PAD, long long length)
void __sanitizer_syscall_post_impl___timer_gettime50(long long res, long long timerid, long long value)
void __sanitizer_syscall_pre_impl_msgrcv(long long msqid, long long msgp, long long msgsz, long long msgtyp, long long msgflg)
void __sanitizer_syscall_pre_impl_paccept(long long s, long long name, long long anamelen, long long mask, long long flags)
void __sanitizer_syscall_post_impl_compat_43_ogetdirentries(long long res, long long fd, long long buf, long long count, long long basep)
void __sanitizer_syscall_post_impl___sigaltstack14(long long res, long long nss, long long oss)
void __sanitizer_syscall_pre_impl_compat_30_getdents(long long fd, long long buf, long long count)
void __sanitizer_syscall_pre_impl___aio_suspend50(long long list, long long nent, long long timeout)
void __sanitizer_syscall_post_impl_setregid(long long res, long long rgid, long long egid)
void __sanitizer_syscall_pre_impl_compat_43_ogethostname(long long hostname, long long len)
void __sanitizer_syscall_post_impl_compat_43_oftruncate(long long res, long long fd, long long length)
void __sanitizer_syscall_pre_impl__lwp_wait(long long wait_for, long long departed)
void __sanitizer_syscall_pre_impl___sigpending14(long long set)
void __sanitizer_syscall_pre_impl_munlock(long long addr, long long len)
void __sanitizer_syscall_post_impl_modctl(long long res, long long cmd, long long arg)
void __sanitizer_syscall_post_impl_mq_getattr(long long res, long long mqdes, long long mqstat)
void __sanitizer_syscall_pre_impl_compat_50_lutimes(long long path, long long tptr)
void __sanitizer_syscall_pre_impl_fdiscard(long long fd, long long PAD, long long pos, long long len)
void __sanitizer_syscall_post_impl___adjtime50(long long res, long long delta, long long olddelta)
void __sanitizer_syscall_pre_impl_fremovexattr(long long fd, long long name)
void __sanitizer_syscall_pre_impl___msgctl50(long long msqid, long long cmd, long long buf)
void __sanitizer_syscall_pre_impl_accept(long long s, long long name, long long anamelen)
void __sanitizer_syscall_pre_impl_compat_12_getdirentries(long long fd, long long buf, long long count, long long basep)
void __sanitizer_syscall_post_impl___mq_timedsend50(long long res, long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio, long long abs_timeout)
void __sanitizer_syscall_post_impl_timer_delete(long long res, long long timerid)
void __sanitizer_syscall_pre_impl__lwp_unpark_all(long long targets, long long ntargets, long long hint)
void __sanitizer_syscall_pre_impl_listen(long long s, long long backlog)
void __sanitizer_syscall_post_impl_fsetxattr(long long res, long long fd, long long name, long long value, long long size, long long flags)
void __sanitizer_syscall_pre_impl_rmdir(long long path)
void __sanitizer_syscall_post_impl_compat_50_clock_settime(long long res, long long clock_id, long long tp)
void __sanitizer_syscall_pre_impl_compat_14___semctl(long long semid, long long semnum, long long cmd, long long arg)
void __sanitizer_syscall_post_impl_setgid(long long res, long long gid)
void __sanitizer_syscall_post_impl___pollts50(long long res, long long fds, long long nfds, long long ts, long long mask)
void __sanitizer_syscall_post_impl_mlock(long long res, long long addr, long long len)
void __sanitizer_syscall_post_impl___vfork14(long long res)
void __sanitizer_syscall_post_impl_pwrite(long long res, long long fd, long long buf, long long nbyte, long long PAD, long long offset)
void __sanitizer_syscall_post_impl_profil(long long res, long long samples, long long size, long long offset, long long scale)
void __sanitizer_syscall_post_impl_shmdt(long long res, long long shmaddr)
void __sanitizer_syscall_post_impl_mknodat(long long res, long long fd, long long path, long long mode, long long PAD, long long dev)
void __sanitizer_syscall_post_impl_sendmmsg(long long res, long long s, long long mmsg, long long vlen, long long flags)
void __sanitizer_syscall_post_impl_posix_spawn(long long res, long long pid, long long path, long long file_actions, long long attrp, long long argv, long long envp)
void __sanitizer_syscall_post_impl_compat_50_quotactl(long long res, long long path, long long cmd, long long uid, long long arg)
void __sanitizer_syscall_post_impl_rename(long long res, long long from, long long to)
void __sanitizer_syscall_post_impl___getcwd(long long res, long long bufp, long long length)
void __sanitizer_syscall_post_impl_getxattr(long long res, long long path, long long name, long long value, long long size)
void __sanitizer_syscall_post_impl_compat_20_fstatfs(long long res, long long fd, long long buf)
void __sanitizer_syscall_post_impl__pset_bind(long long res, long long idtype, long long first_id, long long second_id, long long psid, long long opsid)
void __sanitizer_syscall_post_impl___quotactl(long long res, long long path, long long args)
void __sanitizer_syscall_pre_impl_mkdir(long long path, long long mode)
void __sanitizer_syscall_pre_impl_execve(long long path, long long argp, long long envp)
void __sanitizer_syscall_pre_impl_compat_50__lwp_park(long long ts, long long unpark, long long hint, long long unparkhint)
void __sanitizer_syscall_post_impl_flistxattr(long long res, long long fd, long long list, long long size)
void __sanitizer_syscall_post_impl_mq_notify(long long res, long long mqdes, long long notification)
void __sanitizer_syscall_post_impl_geteuid(long long res)
void __sanitizer_syscall_pre_impl_compat_13_sigaltstack13(long long nss, long long oss)
void __sanitizer_syscall_post_impl_compat_50_lutimes(long long res, long long path, long long tptr)
void __sanitizer_syscall_post_impl_preadv(long long res, long long fd, long long iovp, long long iovcnt, long long PAD, long long offset)
void __sanitizer_syscall_pre_impl_compat_43_osendmsg(long long s, long long msg, long long flags)
void __sanitizer_syscall_post_impl_ioctl(long long res, long long fd, long long com, long long data)
void __sanitizer_syscall_pre_impl__lwp_self(void)
void __sanitizer_syscall_post_impl_truncate(long long res, long long path, long long PAD, long long length)
void __sanitizer_syscall_post_impl_compat_43_ogetpagesize(long long res)
void __sanitizer_syscall_pre_impl_syscall(long long code, long long arg0, long long arg1, long long arg2, long long arg3, long long arg4, long long arg5, long long arg6, long long arg7)
void __sanitizer_syscall_pre_impl_compat_14_msgctl(long long msqid, long long cmd, long long buf)
void __sanitizer_syscall_post_impl_ntp_adjtime(long long res, long long tp)
void __sanitizer_syscall_pre_impl_fchroot(long long fd)
void __sanitizer_syscall_pre_impl___adjtime50(long long delta, long long olddelta)
void __sanitizer_syscall_pre_impl_compat_43_lstat43(long long path, long long ub)
void __sanitizer_syscall_post_impl___kevent50(long long res, long long fd, long long changelist, long long nchanges, long long eventlist, long long nevents, long long timeout)
void __sanitizer_syscall_pre_impl_mq_setattr(long long mqdes, long long mqstat, long long omqstat)
void __sanitizer_syscall_post_impl_bind(long long res, long long s, long long name, long long namelen)
void __sanitizer_syscall_pre_impl__lwp_detach(long long target)
void __sanitizer_syscall_pre_impl_compat_60_sa_stacks(long long num, long long stacks)
void __sanitizer_syscall_pre_impl_fsync_range(long long fd, long long flags, long long start, long long length)
void __sanitizer_syscall_post_impl_dup3(long long res, long long from, long long to, long long flags)
void __sanitizer_syscall_pre_impl_mq_send(long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio)
void __sanitizer_syscall_pre_impl_futimens(long long fd, long long tptr)
void __sanitizer_syscall_pre_impl_bind(long long s, long long name, long long namelen)
void __sanitizer_syscall_pre_impl_msgsnd(long long msqid, long long msgp, long long msgsz, long long msgflg)
void __sanitizer_syscall_post_impl_compat_50___fstat30(long long res, long long fd, long long sb)
void __sanitizer_syscall_post_impl_compat_43_osendmsg(long long res, long long s, long long msg, long long flags)
void __sanitizer_syscall_post_impl_pset_assign(long long res, long long psid, long long cpuid, long long opsid)
void __sanitizer_syscall_pre_impl_fchflags(long long fd, long long flags)
void __sanitizer_syscall_pre_impl_mq_getattr(long long mqdes, long long mqstat)
void __sanitizer_syscall_pre_impl_fchmod(long long fd, long long mode)
void __sanitizer_syscall_pre_impl_getsockopt2(long long s, long long level, long long name, long long val, long long avalsize)
void __sanitizer_syscall_post_impl_afssys(long long res, long long id, long long a1, long long a2, long long a3, long long a4, long long a5, long long a6)
void __sanitizer_syscall_post_impl___fstat50(long long res, long long fd, long long sb)
void __sanitizer_syscall_post_impl_compat_43_osetrlimit(long long res, long long which, long long rlp)
void __sanitizer_syscall_post_impl_aio_error(long long res, long long aiocbp)
void __sanitizer_syscall_post_impl_compat_12_oswapon(long long res, long long name)
void __sanitizer_syscall_pre_impl_lchflags(long long path, long long flags)
void __sanitizer_syscall_pre_impl_minherit(long long addr, long long len, long long inherit)
void __sanitizer_syscall_pre_impl_compat_50_clock_gettime(long long clock_id, long long tp)
void __sanitizer_syscall_post_impl_uuidgen(long long res, long long store, long long count)
void __sanitizer_syscall_pre_impl___setlogin(long long namebuf)
void __sanitizer_syscall_post_impl_clock_nanosleep(long long res, long long clock_id, long long flags, long long rqtp, long long rmtp)
void __sanitizer_syscall_pre_impl___stat50(long long path, long long ub)
void __sanitizer_syscall_pre_impl_mlock(long long addr, long long len)
void __sanitizer_syscall_pre_impl___timer_gettime50(long long timerid, long long value)
void __sanitizer_syscall_post_impl_mincore(long long res, long long addr, long long len, long long vec)
void __sanitizer_syscall_pre_impl_compat_60_sa_enable(void)
void __sanitizer_syscall_pre_impl_compat_50_getrusage(long long who, long long rusage)
void __sanitizer_syscall_pre_impl_setsockopt(long long s, long long level, long long name, long long val, long long valsize)
void __sanitizer_syscall_post_impl___socket30(long long res, long long domain, long long type, long long protocol)
void __sanitizer_syscall_post_impl_close(long long res, long long fd)
void __sanitizer_syscall_post_impl___sigaction_sigtramp(long long res, long long signum, long long nsa, long long osa, long long tramp, long long vers)
void __sanitizer_syscall_post_impl_compat_30_fhopen(long long res, long long fhp, long long flags)
void __sanitizer_syscall_pre_impl_compat_43_osetrlimit(long long which, long long rlp)
void __sanitizer_syscall_pre_impl_compat_43_osigstack(long long nss, long long oss)
void __sanitizer_syscall_post_impl_mq_send(long long res, long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio)
void __sanitizer_syscall_pre_impl_symlinkat(long long path1, long long fd, long long path2)
void __sanitizer_syscall_pre_impl_getppid(void)
void __sanitizer_syscall_pre_impl_exit(long long rval)
void __sanitizer_syscall_post_impl_writev(long long res, long long fd, long long iovp, long long iovcnt)
void __sanitizer_syscall_post_impl_sendmsg(long long res, long long s, long long msg, long long flags)
void __sanitizer_syscall_pre_impl_compat_43_osigvec(long long signum, long long nsv, long long osv)
void __sanitizer_syscall_pre_impl_getsockopt(long long s, long long level, long long name, long long val, long long avalsize)
void __sanitizer_syscall_pre_impl_utrace(long long label, long long addr, long long len)
void __sanitizer_syscall_post_impl_break(long long res, long long nsize)
void __sanitizer_syscall_pre_impl___mknod50(long long path, long long mode, long long dev)
void __sanitizer_syscall_pre_impl___posix_fchown(long long fd, long long uid, long long gid)
void __sanitizer_syscall_pre_impl_uuidgen(long long store, long long count)
void __sanitizer_syscall_pre_impl_setgid(long long gid)
void __sanitizer_syscall_post_impl_compat_43_orecvfrom(long long res, long long s, long long buf, long long len, long long flags, long long from, long long fromlenaddr)
void __sanitizer_syscall_pre_impl__lwp_wakeup(long long target)
void __sanitizer_syscall_post_impl_sync(long long res)
void __sanitizer_syscall_post_impl_compat_50_aio_suspend(long long res, long long list, long long nent, long long timeout)
void __sanitizer_syscall_pre_impl___sysctl(long long name, long long namelen, long long oldv, long long oldlenp, long long newv, long long newlen)
void __sanitizer_syscall_pre_impl_fork(void)
void __sanitizer_syscall_post_impl_issetugid(long long res)
void __sanitizer_syscall_pre_impl_getcontext(long long ucp)
void __sanitizer_syscall_pre_impl_revoke(long long path)
void __sanitizer_syscall_pre_impl__pset_bind(long long idtype, long long first_id, long long second_id, long long psid, long long opsid)
void __sanitizer_syscall_pre_impl_compat_12_oreboot(long long opt)
void __sanitizer_syscall_post_impl_compat_60_sa_enable(long long res)
void __sanitizer_syscall_pre_impl_fsetxattr(long long fd, long long name, long long value, long long size, long long flags)
void __sanitizer_syscall_pre_impl___posix_fadvise50(long long fd, long long PAD, long long offset, long long len, long long advice)
void __sanitizer_syscall_post_impl_setegid(long long res, long long egid)
void __sanitizer_syscall_pre_impl_extattr_get_link(long long path, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_post_impl_compat_43_oaccept(long long res, long long s, long long name, long long anamelen)
void __sanitizer_syscall_pre_impl_compat_43_fstat43(long long fd, long long sb)
void __sanitizer_syscall_post_impl__ksem_wait(long long res, long long id)
void __sanitizer_syscall_post_impl_aio_write(long long res, long long aiocbp)
void __sanitizer_syscall_pre_impl_mremap(long long old_address, long long old_size, long long new_address, long long new_size, long long flags)
void __sanitizer_syscall_pre_impl__lwp_create(long long ucp, long long flags, long long new_lwp)
void __sanitizer_syscall_pre_impl_fdatasync(long long fd)
void __sanitizer_syscall_post_impl_mkdirat(long long res, long long fd, long long path, long long mode)
void __sanitizer_syscall_pre_impl__lwp_continue(long long target)
void __sanitizer_syscall_post_impl_sigqueueinfo(long long res, long long pid, long long info)
void __sanitizer_syscall_pre_impl___select50(long long nd, long long in, long long ou, long long ex, long long tv)
void __sanitizer_syscall_pre_impl_ktrace(long long fname, long long ops, long long facs, long long pid)
void __sanitizer_syscall_pre_impl_symlink(long long path, long long link)
void __sanitizer_syscall_post_impl_removexattr(long long res, long long path, long long name)
void __sanitizer_syscall_post_impl_rmdir(long long res, long long path)
void __sanitizer_syscall_post_impl_mq_receive(long long res, long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio)
void __sanitizer_syscall_pre_impl_compat_10_osemsys(long long which, long long a2, long long a3, long long a4, long long a5)
void __sanitizer_syscall_post_impl_compat_50_settimeofday(long long res, long long tv, long long tzp)
void __sanitizer_syscall_pre_impl_pwritev(long long fd, long long iovp, long long iovcnt, long long PAD, long long offset)
void __sanitizer_syscall_post_impl_extattr_get_fd(long long res, long long fd, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_pre_impl_compat_40_mount(long long type, long long path, long long flags, long long data)
void __sanitizer_syscall_post_impl_compat_30___fhstat30(long long res, long long fhp, long long sb)
void __sanitizer_syscall_pre_impl_getgroups(long long gidsetsize, long long gidset)
void __sanitizer_syscall_post_impl_getgid(long long res)
void __sanitizer_syscall_pre_impl_compat_43_osethostid(long long hostid)
void __sanitizer_syscall_post_impl_compat_90_statvfs1(long long res, long long path, long long buf, long long flags)
void __sanitizer_syscall_post_impl_minherit(long long res, long long addr, long long len, long long inherit)
void __sanitizer_syscall_pre_impl_aio_cancel(long long fildes, long long aiocbp)
void __sanitizer_syscall_post_impl_chroot(long long res, long long path)
void __sanitizer_syscall_pre_impl_socketpair(long long domain, long long type, long long protocol, long long rsv)
void __sanitizer_syscall_pre_impl_compat_50_wait4(long long pid, long long status, long long options, long long rusage)
void __sanitizer_syscall_pre_impl_mincore(long long addr, long long len, long long vec)
void __sanitizer_syscall_post_impl_unmount(long long res, long long path, long long flags)
void __sanitizer_syscall_pre_impl_getgid(void)
void __sanitizer_syscall_post_impl_setsockopt(long long res, long long s, long long level, long long name, long long val, long long valsize)
void __sanitizer_syscall_post_impl_compat_14___semctl(long long res, long long semid, long long semnum, long long cmd, long long arg)
void __sanitizer_syscall_post_impl_write(long long res, long long fd, long long buf, long long nbyte)
void __sanitizer_syscall_pre_impl_extattrctl(long long path, long long cmd, long long filename, long long attrnamespace, long long attrname)
void __sanitizer_syscall_pre_impl_renameat(long long fromfd, long long from, long long tofd, long long to)
void __sanitizer_syscall_post_impl__lwp_kill(long long res, long long target, long long signo)
void __sanitizer_syscall_pre_impl_modctl(long long cmd, long long arg)
void __sanitizer_syscall_post_impl_ptrace(long long res, long long req, long long pid, long long addr, long long data)
void __sanitizer_syscall_post_impl_compat_09_ouname(long long res, long long name)
void __sanitizer_syscall_post_impl___syscall(long long res, long long code, long long arg0, long long arg1, long long arg2, long long arg3, long long arg4, long long arg5, long long arg6, long long arg7)
void __sanitizer_syscall_post_impl_mq_open(long long res, long long name, long long oflag, long long mode, long long attr)
void __sanitizer_syscall_pre_impl_extattr_get_fd(long long fd, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_pre_impl_compat_50_getitimer(long long which, long long itv)
void __sanitizer_syscall_pre_impl___mq_timedreceive50(long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio, long long abs_timeout)
void __sanitizer_syscall_post_impl_mremap(long long res, long long old_address, long long old_size, long long new_address, long long new_size, long long flags)
void __sanitizer_syscall_post_impl___posix_fchown(long long res, long long fd, long long uid, long long gid)
void __sanitizer_syscall_post_impl___clock_gettime50(long long res, long long clock_id, long long tp)
void __sanitizer_syscall_post_impl_timer_getoverrun(long long res, long long timerid)
void __sanitizer_syscall_post_impl_compat_40_mount(long long res, long long type, long long path, long long flags, long long data)
void __sanitizer_syscall_pre_impl_compat_60_sa_preempt(long long sa_id)
void __sanitizer_syscall_pre_impl_fchown(long long fd, long long uid, long long gid)
void __sanitizer_syscall_post_impl_lio_listio(long long res, long long mode, long long list, long long nent, long long sig)
void __sanitizer_syscall_post_impl_aio_cancel(long long res, long long fildes, long long aiocbp)
void __sanitizer_syscall_post_impl__ksem_post(long long res, long long id)
void __sanitizer_syscall_post_impl_pipe(long long res)
void __sanitizer_syscall_post_impl_compat_30_getdents(long long res, long long fd, long long buf, long long count)
void __sanitizer_syscall_pre_impl___getfh30(long long fname, long long fhp, long long fh_size)
void __sanitizer_syscall_post_impl___wait450(long long res, long long pid, long long status, long long options, long long rusage)
void __sanitizer_syscall_pre_impl_sigqueueinfo(long long pid, long long info)
void __sanitizer_syscall_pre_impl_compat_50_mq_timedreceive(long long mqdes, long long msg_ptr, long long msg_len, long long msg_prio, long long abs_timeout)
void __sanitizer_syscall_post_impl_faccessat(long long res, long long fd, long long path, long long amode, long long flag)
void __sanitizer_syscall_pre_impl_compat_43_okillpg(long long pgid, long long signum)
void __sanitizer_syscall_pre_impl_afssys(long long id, long long a1, long long a2, long long a3, long long a4, long long a5, long long a6)
void __sanitizer_syscall_pre_impl_mkfifoat(long long fd, long long path, long long mode)
void __sanitizer_syscall_post_impl_unlinkat(long long res, long long fd, long long path, long long flag)
void __sanitizer_syscall_post_impl_extattr_set_fd(long long res, long long fd, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_post_impl_symlinkat(long long res, long long path1, long long fd, long long path2)
void __sanitizer_syscall_post_impl_compat_10_omsgsys(long long res, long long which, long long a2, long long a3, long long a4, long long a5, long long a6)
void __sanitizer_syscall_pre_impl_getegid(void)
void __sanitizer_syscall_pre_impl_unmount(long long path, long long flags)
void __sanitizer_syscall_post_impl_getsockopt(long long res, long long s, long long level, long long name, long long val, long long avalsize)
void __sanitizer_syscall_pre_impl_compat_50_____semctl13(long long semid, long long semnum, long long cmd, long long arg)
void __sanitizer_syscall_pre_impl_compat_43_ommap(long long addr, long long len, long long prot, long long flags, long long fd, long long pos)
void __sanitizer_syscall_post_impl_compat_43_okillpg(long long res, long long pgid, long long signum)
void __sanitizer_syscall_pre_impl_compat_43_ogetdtablesize(void)
void __sanitizer_syscall_post_impl_compat_30_getfh(long long res, long long fname, long long fhp)
void __sanitizer_syscall_post_impl_compat_12_stat12(long long res, long long path, long long ub)
void __sanitizer_syscall_pre_impl_compat_50_timer_settime(long long timerid, long long flags, long long value, long long ovalue)
void __sanitizer_syscall_pre_impl_mprotect(long long addr, long long len, long long prot)
void __sanitizer_syscall_post_impl_mlockall(long long res, long long flags)
void __sanitizer_syscall_post_impl_undelete(long long res, long long path)
void __sanitizer_syscall_post_impl___getrusage50(long long res, long long who, long long rusage)
void __sanitizer_syscall_post_impl_compat_50___sigtimedwait(long long res, long long set, long long info, long long timeout)
void __sanitizer_syscall_post_impl___sigprocmask14(long long res, long long how, long long set, long long oset)
void __sanitizer_syscall_pre_impl_extattr_set_fd(long long fd, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_post_impl___clone(long long res, long long flags, long long stack)
void __sanitizer_syscall_post_impl_mkfifo(long long res, long long path, long long mode)
void __sanitizer_syscall_pre_impl_link(long long path, long long link)
void __sanitizer_syscall_pre_impl_lio_listio(long long mode, long long list, long long nent, long long sig)
void __sanitizer_syscall_pre_impl_compat_30_socket(long long domain, long long type, long long protocol)
void __sanitizer_syscall_pre_impl_mq_notify(long long mqdes, long long notification)
void __sanitizer_syscall_pre_impl_recvfrom(long long s, long long buf, long long len, long long flags, long long from, long long fromlenaddr)
void __sanitizer_syscall_post_impl_extattr_get_file(long long res, long long path, long long attrnamespace, long long attrname, long long data, long long nbytes)
void __sanitizer_syscall_pre_impl_sync(void)
void __sanitizer_syscall_pre_impl_compat_50_kevent(long long fd, long long changelist, long long nchanges, long long eventlist, long long nevents, long long timeout)
void __sanitizer_syscall_pre_impl_compat_50___ntp_gettime30(long long ntvp)
void __sanitizer_syscall_post_impl_shmget(long long res, long long key, long long size, long long shmflg)
void __sanitizer_syscall_post_impl_getegid(long long res)
void __sanitizer_syscall_pre_impl_compat_16___sigaction14(long long signum, long long nsa, long long osa)
void __sanitizer_syscall_post_impl__lwp_self(long long res)
void __sanitizer_syscall_pre_impl_unlinkat(long long fd, long long path, long long flag)
void __sanitizer_syscall_post_impl_getpriority(long long res, long long which, long long who)
void __sanitizer_syscall_post_impl_poll(long long res, long long fds, long long nfds, long long timeout)
void __sanitizer_syscall_pre_impl_writev(long long fd, long long iovp, long long iovcnt)
void __sanitizer_syscall_pre_impl_timer_delete(long long timerid)
void __sanitizer_syscall_pre_impl_chown(long long path, long long uid, long long gid)
void __sanitizer_syscall_post_impl_getuid(long long res)
void __sanitizer_syscall_pre_impl__lwp_getprivate(void)
void __sanitizer_syscall_pre_impl_compat_12_msync(long long addr, long long len)
void __sanitizer_syscall_pre_impl_compat_30___fstat13(long long fd, long long sb)
void __sanitizer_syscall_post_impl_compat_50___ntp_gettime30(long long res, long long ntvp)
void __sanitizer_syscall_post_impl__lwp_unpark(long long res, long long target, long long hint)
void __sanitizer_syscall_pre_impl_compat_50_quotactl(long long path, long long cmd, long long uid, long long arg)
void __sanitizer_syscall_post_impl_fsync(long long res, long long fd)
void __sanitizer_syscall_post_impl_compat_43_ommap(long long res, long long addr, long long len, long long prot, long long flags, long long fd, long long pos)
void __sanitizer_syscall_post_impl_recvmsg(long long res, long long s, long long msg, long long flags)
void __sanitizer_syscall_pre_impl_mkfifo(long long path, long long mode)
void __sanitizer_syscall_post_impl__lwp_wait(long long res, long long wait_for, long long departed)
void __sanitizer_syscall_pre_impl_fchownat(long long fd, long long path, long long owner, long long group, long long flag)
void __sanitizer_syscall_post_impl___futimes50(long long res, long long fd, long long tptr)
void __sanitizer_syscall_post_impl_listxattr(long long res, long long path, long long list, long long size)
void __sanitizer_syscall_pre_impl_rasctl(long long addr, long long len, long long op)
void __sanitizer_syscall_pre_impl_nfssvc(long long flag, long long argp)
void __sanitizer_syscall_post_impl_compat_43_osigvec(long long res, long long signum, long long nsv, long long osv)
void __sanitizer_syscall_pre_impl_dup2(long long from, long long to)
void __sanitizer_syscall_pre_impl_connect(long long s, long long name, long long namelen)
void __sanitizer_syscall_pre_impl___clock_gettime50(long long clock_id, long long tp)
void __sanitizer_syscall_post_impl_revoke(long long res, long long path)
void __sanitizer_syscall_post_impl_mq_unlink(long long res, long long name)
void __sanitizer_syscall_pre_impl___fhstat50(long long fhp, long long fh_size, long long sb)
void __sanitizer_syscall_pre_impl_compat_43_oquota(void)
void __sanitizer_syscall_pre_impl_compat_50___stat30(long long path, long long ub)
void __sanitizer_syscall_post_impl_lchflags(long long res, long long path, long long flags)
void __sanitizer_syscall_pre_impl___clock_settime50(long long clock_id, long long tp)
void __sanitizer_syscall_post_impl__lwp_getname(long long res, long long target, long long name, long long len)
void __sanitizer_syscall_post_impl_compat_43_ogethostid(long long res)
void __sanitizer_syscall_post_impl_compat_30___lstat13(long long res, long long path, long long ub)
void __sanitizer_syscall_pre_impl___mount50(long long type, long long path, long long flags, long long data, long long data_len)
float __ovld __cnfn length(float p)
Return the length of vector p, i.e., sqrt(p.x2 + p.y 2 + ...)