Tom Cherry
ef28035aa5
Merge "Revert "Remove a check for AIDs in the OEM range."" am: a8b179bcdd
am: c4033e1485
...
am: 220df176dd
Change-Id: I984c0cf3a30f1d77ff3ed8a8c47e8fa594d7ab20
2018-02-13 08:29:50 +00:00
Tom Cherry
220df176dd
Merge "Revert "Remove a check for AIDs in the OEM range."" am: a8b179bcdd
...
am: c4033e1485
Change-Id: Ie7049588423b2b00f3f2ea07ed48476b43915bcd
2018-02-13 08:04:24 +00:00
Tom Cherry
c4033e1485
Merge "Revert "Remove a check for AIDs in the OEM range.""
...
am: a8b179bcdd
Change-Id: Ib3e706b19a87303c4add32d0b80535d1a3818308
2018-02-13 07:45:20 +00:00
Treehugger Robot
a8b179bcdd
Merge "Revert "Remove a check for AIDs in the OEM range.""
2018-02-13 07:09:27 +00:00
Goran Jakovljevic
1faccfcc54
Merge "MIPS32: Make sigset64_t equal to sigset_t" am: 919dd9dcb4
am: 52d1ff5329
...
am: ee6dd59977
Change-Id: I303900d9a22ea95406ccb5463e1124572ce4225f
2018-02-12 19:20:22 +00:00
Goran Jakovljevic
ee6dd59977
Merge "MIPS32: Make sigset64_t equal to sigset_t" am: 919dd9dcb4
...
am: 52d1ff5329
Change-Id: Ic32612b090b93c5a538766d6eb075846ee7cb1e4
2018-02-12 19:12:55 +00:00
Goran Jakovljevic
52d1ff5329
Merge "MIPS32: Make sigset64_t equal to sigset_t"
...
am: 919dd9dcb4
Change-Id: I5fd10e2653a645470fde6b23b63db2b9ed6b0647
2018-02-12 19:01:44 +00:00
Tom Cherry
41986a013a
Revert "Remove a check for AIDs in the OEM range."
...
We now have a proper mechanism for OEMs to create new AIDs via
config.fs and /vendor/etc/{passwd,group}. This means that there is no
reason for OEMs to add AIDs by modifying android_filesystem_config.h,
and therefore we can add this check back.
Bug: 27999086
Test: pwd and grp tests pass with custom AIDs in config.fs
This reverts commit a14485adde
.
Change-Id: I74a28ff267a595e83cf692b27fd8b5170a021f54
2018-02-12 10:49:13 -08:00
Treehugger Robot
919dd9dcb4
Merge "MIPS32: Make sigset64_t equal to sigset_t"
2018-02-12 18:49:12 +00:00
Tom Cherry
87feba5780
Merge "Add ability to read /etc/passwd and /etc/group" am: ab8c861597
am: 69bd70122a
...
am: d644e01f21
Change-Id: I757344ac10da6cf8cdc8186be680269ca99a056a
2018-02-12 16:45:48 +00:00
Tom Cherry
d644e01f21
Merge "Add ability to read /etc/passwd and /etc/group" am: ab8c861597
...
am: 69bd70122a
Change-Id: I7f6407f241620e759e12be50b893a632ed2d9260
2018-02-12 16:38:12 +00:00
Tom Cherry
69bd70122a
Merge "Add ability to read /etc/passwd and /etc/group"
...
am: ab8c861597
Change-Id: I05b9b2559dbf30f2dedfa722584433b95d1215a1
2018-02-12 16:32:37 +00:00
Tom Cherry
ab8c861597
Merge "Add ability to read /etc/passwd and /etc/group"
2018-02-12 16:27:20 +00:00
Goran Jakovljevic
379666996d
MIPS32: Make sigset64_t equal to sigset_t
...
sigset_t is already large enough on mips so use the same principle
as on LP64 architectures: typedef sigset_t sigset64_t
Also prevent accessing sa_restorer field for architectures which
don't define SA_RESTORER in signal_test.
This allows compilation of signal_test.
Test: bionic-unit-tests in QEMU (MIPS32)
Change-Id: I965e202c9a7f7d109e4ec25ad87172dc7c1b8806
2018-02-12 09:03:10 +01:00
George Burgess IV
b15e09dabf
Merge "Remove __overloadable/__RENAME_CLANG" am: 4362da8076
am: 974de08375
...
am: ecff6c9d39
Change-Id: I3fdaf5a6a1a853af44e138cb272b940eb245d2cd
2018-02-10 03:03:33 +00:00
George Burgess IV
ecff6c9d39
Merge "Remove __overloadable/__RENAME_CLANG" am: 4362da8076
...
am: 974de08375
Change-Id: Id43f32fb419260514673d6b43e69c780d10a2cf8
2018-02-10 02:57:59 +00:00
George Burgess IV
974de08375
Merge "Remove __overloadable/__RENAME_CLANG"
...
am: 4362da8076
Change-Id: I8035439bd15876a5a8d5ded547e25760328affee
2018-02-10 02:52:00 +00:00
Treehugger Robot
4362da8076
Merge "Remove __overloadable/__RENAME_CLANG"
2018-02-10 02:30:37 +00:00
Josh Gao
d6ec1c8952
Merge "linker_memory: return success in enable_fallback_allocator." am: 6fa9bddbc7
am: 57bbcbd847
...
am: 6a8dd81205
Change-Id: Iec6939092bbb9ffc299b39340e91e6f1bc2b64ef
2018-02-10 02:17:30 +00:00
Josh Gao
6a8dd81205
Merge "linker_memory: return success in enable_fallback_allocator." am: 6fa9bddbc7
...
am: 57bbcbd847
Change-Id: I57caf6508d8f01ad1aa4b93b8fc299eea45a2deb
2018-02-10 02:05:16 +00:00
Josh Gao
57bbcbd847
Merge "linker_memory: return success in enable_fallback_allocator."
...
am: 6fa9bddbc7
Change-Id: If5636675dfd39e1a5d42f875917c2462efb97749
2018-02-10 01:59:21 +00:00
Treehugger Robot
6fa9bddbc7
Merge "linker_memory: return success in enable_fallback_allocator."
2018-02-10 01:44:07 +00:00
Ryan Prichard
4f854f6173
Merge "crtbegin: Correctly align ESP to 16 for __i386__" am: 5bf2c20f43
am: 9ae7d46291
...
am: 77820554b0
Change-Id: I0ff49e49679782cd51bf1d7aed7e11dd03180c8a
2018-02-09 07:18:02 +00:00
Ryan Prichard
77820554b0
Merge "crtbegin: Correctly align ESP to 16 for __i386__" am: 5bf2c20f43
...
am: 9ae7d46291
Change-Id: Ib4a755ee333982fc14f57e69b4dfbffe0dd0f2a4
2018-02-09 07:12:29 +00:00
Ryan Prichard
9ae7d46291
Merge "crtbegin: Correctly align ESP to 16 for __i386__"
...
am: 5bf2c20f43
Change-Id: I5b38b1b07b068489b29443dcb3ef087ee07d23b3
2018-02-09 07:06:50 +00:00
Treehugger Robot
5bf2c20f43
Merge "crtbegin: Correctly align ESP to 16 for __i386__"
2018-02-09 06:56:31 +00:00
Dan Albert
6d459fb9ae
Merge "Add _FORCE_CRT_ATFORK config for crtbegin." am: 59a0a37b9d
am: 6722d68aaa
...
am: ea5078031e
Change-Id: Id9f2b5a69812c4c1ec55b2bcf66f71e9ee4ef191
2018-02-09 06:04:49 +00:00
Dan Albert
ea5078031e
Merge "Add _FORCE_CRT_ATFORK config for crtbegin." am: 59a0a37b9d
...
am: 6722d68aaa
Change-Id: If252d4a702a3db9eaca9a831ed8df48721ef6977
2018-02-09 06:00:12 +00:00
Dan Albert
6722d68aaa
Merge "Add _FORCE_CRT_ATFORK config for crtbegin."
...
am: 59a0a37b9d
Change-Id: Iae273eec0ae8fd839def86b0a20ab37a0892f017
2018-02-09 05:54:38 +00:00
Treehugger Robot
59a0a37b9d
Merge "Add _FORCE_CRT_ATFORK config for crtbegin."
2018-02-09 05:41:31 +00:00
Ryan Prichard
a0d177d010
crtbegin: Correctly align ESP to 16 for __i386__
...
The (lowest) address of the argument area (aka ESP immediately prior to
the call instruction) must be aligned to 0 mod 16. Here, it is aligned to
12 mod 16.
From the SysV ABI doc (2.2.2 The Stack Frame)
"""The end of the input argument area shall be aligned on a 16 (32, if
__m256 is passed on stack) byte boundary. In other words, the value
(%esp + 4) is always a multiple of 16 (32) when control is transferred to
the function entry point."""
Test: extract code into a separate C file and verify stack alignment in a
"start_main" function
Test: use the upcoming NDK r17-beta1 (with new Bionic crtbegin*.o files)
with an M-23 x86 system image, check alignment in main (compiled with
Clang not GCC, compiled w/o -mstackrealign)
Bug: b/73140672
Change-Id: Ia8d93fe5668d0a514a9fd22c40bf8362805111e6
2018-02-08 20:55:57 -08:00
Elliott Hughes
4758099eac
Merge "Document the rules of thumb for "should I add a syscall wrapper?"." am: 3d6b2e78a9
am: 8c37f5ad5b
...
am: 44c67ece6c
Change-Id: Ibdf96e463d7b69152900246efa824b909135883a
2018-02-09 03:58:03 +00:00
Elliott Hughes
44c67ece6c
Merge "Document the rules of thumb for "should I add a syscall wrapper?"." am: 3d6b2e78a9
...
am: 8c37f5ad5b
Change-Id: Ibf291f9721404ee59dfa03d96164acdb9ea22379
2018-02-09 03:52:29 +00:00
Elliott Hughes
8c37f5ad5b
Merge "Document the rules of thumb for "should I add a syscall wrapper?"."
...
am: 3d6b2e78a9
Change-Id: I776cfdedf394b4e13cb76b14fafb789c94671bb2
2018-02-09 03:46:56 +00:00
Elliott Hughes
3d6b2e78a9
Merge "Document the rules of thumb for "should I add a syscall wrapper?"."
2018-02-09 03:33:43 +00:00
Tom Cherry
6034ef85d8
Add ability to read /etc/passwd and /etc/group
...
Add the capability to read /etc/passwd and /etc/group for getpw* and
getgr* functions.
Bug: 27999086
Test: pwd, grp, grp_pwd_file unit tests
Test: Read in custom users/groups from /etc/{passwd,group}
Change-Id: Idc1f054af8a7ca34743a90493495f0ccc775a0d8
2018-02-08 12:38:57 -08:00
Elliott Hughes
1a1b57cb83
Document the rules of thumb for "should I add a syscall wrapper?".
...
This isn't well known, and causes confusion for at least a couple of
people each year.
Bug: N/A
Test: N/A
Change-Id: I43127d937ee81d0c79bbc496638a1b1b6003dd80
2018-02-08 09:53:59 -08:00
Goran Jakovljevic
75af1a3e8d
Merge "Don't use SA_RESTORER if it is not defined" am: aac0dd9891
am: c6cf969283
...
am: 7aa944397e
Change-Id: Ibd5fb97f2710349e922da376807bbceabe525bb2
2018-02-08 08:16:57 +00:00
Goran Jakovljevic
7aa944397e
Merge "Don't use SA_RESTORER if it is not defined" am: aac0dd9891
...
am: c6cf969283
Change-Id: If5414a6104b4a3f52019da3169d871f700d09a61
2018-02-08 08:07:41 +00:00
Goran Jakovljevic
c6cf969283
Merge "Don't use SA_RESTORER if it is not defined"
...
am: aac0dd9891
Change-Id: I025e86e3c0c0020496baf94588b106eab018a973
2018-02-08 08:03:31 +00:00
Treehugger Robot
aac0dd9891
Merge "Don't use SA_RESTORER if it is not defined"
2018-02-08 07:47:21 +00:00
Dan Albert
254d9155e0
Merge "Fix __gnu_Unwind_Find_exidx again." am: 1a5737a48f
am: 4067bf9e3a
...
am: b2e6d4e4c5
Change-Id: Ib4da08878303082b29708f585e5f8c9eac6b9b37
2018-02-07 20:30:16 +00:00
Dan Albert
b2e6d4e4c5
Merge "Fix __gnu_Unwind_Find_exidx again." am: 1a5737a48f
...
am: 4067bf9e3a
Change-Id: Ibc27372557f97f9262bcfcfb6a189807ed046c09
2018-02-07 20:27:10 +00:00
Dan Albert
402d24ffa2
Merge "Add a few more legacy inlines for strto*_l." am: 13dec2354d
am: b64f3fe81d
...
am: 4279b99059
Change-Id: I8e16eb772b0d01a4329c64ad88ee7c8bd97db031
2018-02-07 20:23:19 +00:00
Dan Albert
4067bf9e3a
Merge "Fix __gnu_Unwind_Find_exidx again."
...
am: 1a5737a48f
Change-Id: I70bcdb6028e38e630066490fed7c87767664439c
2018-02-07 20:19:03 +00:00
Dan Albert
4279b99059
Merge "Add a few more legacy inlines for strto*_l." am: 13dec2354d
...
am: b64f3fe81d
Change-Id: I9af8bdee3cc87480c4d1f55a285b08c3cfe7aa66
2018-02-07 20:13:07 +00:00
Treehugger Robot
1a5737a48f
Merge "Fix __gnu_Unwind_Find_exidx again."
2018-02-07 20:10:01 +00:00
Dan Albert
b64f3fe81d
Merge "Add a few more legacy inlines for strto*_l."
...
am: 13dec2354d
Change-Id: I53574a944999870ccd3c2931ed17a588a70f8041
2018-02-07 20:08:54 +00:00
Treehugger Robot
13dec2354d
Merge "Add a few more legacy inlines for strto*_l."
2018-02-07 19:55:43 +00:00
Christopher Ferris
ff109eed11
Merge "Add aligned_alloc to libc." am: dd1742aca5
am: 9e0a5075a0
...
am: 3be6a96749
Change-Id: I445eed15dc0a7bded7cb44ced2ffddd8a3935a38
2018-02-07 17:15:48 +00:00