Commit Graph

231564 Commits

Author SHA1 Message Date
uebayasi
70dd8e7d2a config(1): Sort objects by weight in modular build
Sort per-module kernel objects (*.ko) by dependency weight.  Important modules
are placed in lower addresses.  The ``machdep'' module will be always placed
in the lowest.

(At this moment, the order is not exact because dependency information is
incomplete in config files (files.*).  Thus ``sysmon_power.ko'' comes lower
than ``machdep.ko'' and/or ``uvm.ko''; but still much better than alphabetical
sort.)
2014-11-15 08:21:38 +00:00
uebayasi
1a322b21d7 Don't sort objects for modular build. 2014-11-15 08:20:42 +00:00
uebayasi
fdd72c8f74 Separate linker script argument (${LINKSCRIPT}) from ${LINKFORMAT}
${LINKFORMAT} specifies ABI options, and used for ld -r.  ${LINKSCRIPT} (-T
ldscript) is used only for final link.
2014-11-15 08:20:01 +00:00
tsutsui
1d361e78b9 Expand heap to 64KB so that bootxx can load bootxxx from 32KB blocksize ffs.
Tested on TT030 with 32GB SSD via SATA->IDE->SCSI converters.
Should be pulled up to netbsd-7 and netbsd-6 branches..
2014-11-15 06:30:10 +00:00
manu
620512b8f3 Fix UFS1 extended attribute backend autocreation deadlock
UFS1 extended attribute backend autocration goes through a vn_open()
to create the backend file, and this forces us to release the lock
on the target node, in case the target is within the parents of the
backend file. That created a window within which another thread could
acquire a lock on the target vnode and deadlock awaiting for the
mount extended attribute lock.

We fix the problem by also releasing the mount extended attribute lock
when calling vn_open(), but that lets another thread race us for backend
creation. We just detect this using O_EXCL for vn_open() and by checking
for EEXIST return code. If we are raced, we fail backend creation but
this is not a problem since another thread succeeded on it: we just have
to use the result.
2014-11-15 05:03:55 +00:00
uebayasi
ef5efd2fc9 Tweaks. 2014-11-15 04:47:11 +00:00
uebayasi
03a2e2df43 Test object reordering by script. 2014-11-15 04:23:48 +00:00
uebayasi
551b230b22 Test object ordering. 2014-11-15 03:47:29 +00:00
uebayasi
b57644333c Merge tests. 2014-11-15 03:22:29 +00:00
uebayasi
e6ae210ca4 Tweak. 2014-11-15 03:10:01 +00:00
joerg
7c080d8b84 Show display if it is not empty. 2014-11-15 02:09:18 +00:00
joerg
84c8bd741e Array can't be null. 2014-11-15 02:01:27 +00:00
joerg
0bab8dfecf Use l_wmesg if the string is not empty. Don't bother checking l_name for
nullness.
2014-11-15 01:58:34 +00:00
joerg
c87c6690c0 Skip vendor if the string is empty. 2014-11-15 01:52:01 +00:00
joerg
755f404f87 Remove tautologic check. 2014-11-15 01:24:53 +00:00
joerg
f7673b99b4 Comment out impossible code. 2014-11-15 01:24:38 +00:00
joerg
31a77d8abb Drop pointer checks that are always true. 2014-11-15 01:15:45 +00:00
jmcneill
8820e4401c Implement WSDISPLAYIO_SVIDEO, WSDISPLAYIO_GVIDEO for screen blanking 2014-11-14 23:45:02 +00:00
wiz
57a81568cf bump year 2014-11-14 22:46:34 +00:00
jmcneill
a2af6ae803 Allow the DEBE layer and output sizes to be set independently. Now you can
pass fb.margin=<n> in bootargs to add a border to the framebuffer, in case
your display doesn't let you turn off overscan and you really want to see
the whole screen.
2014-11-14 19:47:36 +00:00
maxv
833172a8e0 Do not uselessly include <sys/malloc.h>. 2014-11-14 17:34:23 +00:00
riastradh
995f5ce060 Commit to returning 1, not any nonzero value. 2014-11-14 16:43:57 +00:00
uebayasi
29c8a787f1 Tweak previous. 2014-11-14 16:29:03 +00:00
uebayasi
e0d81d86b9 Test orphan ELF section placement. 2014-11-14 16:21:12 +00:00
uebayasi
1fc7d1e960 Fix thinko in previous. 2014-11-14 16:20:42 +00:00
joerg
5e9c3bb2be Install cpuid.h on X86 and arm_neon.h on ARM. 2014-11-14 15:59:46 +00:00
joerg
f26a5b846f LLVM switched to three component point release version, so follow here. 2014-11-14 15:56:12 +00:00
joerg
f88c0f1c84 Define copysignl on !long double platforms. Be consistent in the use of
weak aliases.
2014-11-14 14:53:17 +00:00
oster
e222077349 Adjust comment to reflect reality. (5th arg, not 4th) 2014-11-14 14:45:34 +00:00
joerg
930df7c121 Fix build with clang. 2014-11-14 14:32:49 +00:00
oster
404e5f061e Fix a long-standing bug related to rebooting while a
reconstruct-to-spare is underway but not yet complete.

The issue was that a component was being marked as a used_spare when
the rebuild started, not when the rebuild was actually finished.
Marking it as a used_spare meant that the component label on the spare
was being updated such that after a reboot the component would be
considered up-to-date, regardless of whether the rebuild actually
completed!

This fix includes:
 1) Add an additional state "rf_ds_rebuilding_spare" which is used
    to denote that a spare is currently being rebuilt from the live
    components.
 2) Update the comments on the disk states, which were out-of-sync
    with reality.
 3) When rebuilding to a spare component, that spare now enters the
    state rf_ds_rebuilding_spare instead of the state rf_ds_used_spare.
 4) When the rebuild is actually complete then the spare component
    enters the rf_ds_used_spare state.  rf_ds_used_spare is now used
    exclusively for the case where the rebuilding to the spare has
    completed successfully.

XXX: Someday we need to teach raidctl(8) about this new state, and
take out the backwards compatibility code in rf_netbsdkintf.c (see
RAIDFRAME_GET_INFO in raidioctl()).  For today, this fix needs to be
generic enough that it can get backported without major grief.

XXX: Needs pullup to netbsd-5*, netbsd-6*, and netbsd-7

Fixes PR#49244.
2014-11-14 14:29:16 +00:00
uebayasi
90e9fce862 Test __start_xxx/__stop_xxx symbol generation. 2014-11-14 13:30:48 +00:00
roy
e4d839ca92 Note import of dhcpcd-6.6.2 2014-11-14 12:02:20 +00:00
roy
3c322f3bc1 Sync 2014-11-14 12:00:54 +00:00
manu
7ac57848aa Fix use-after-free on failed unmount with extended attribute enabled
When unmount failed, for instance because the mount is still busy,
UFS1 extended attributes structures were left freed while the kernel
assumes extended attributes were still enabled. This led to using
UFS1 extended attributes structures after free. With LOCKDEBUG, with
quickly triggers a panic.

The problem is fixed by:
1) clear MNT_EXTATTR flag after extended attributes structures are freed
2) attempt to restart extended attributes after failed unmount
2) set MNT_EXTATTR correctly after extended attributes restart

As a side effect, extended attribute structures are now only initialized
when extended attributes are started for the filesystem.
2014-11-14 10:09:50 +00:00
uebayasi
3dcb1bdb52 Minimal linker script test. 2014-11-14 09:03:39 +00:00
skrll
958e3256f0 IPL_SCHED -> IPL_VM
Something isn't MP safe.
2014-11-14 08:20:22 +00:00
snj
6c5df44231 mention etcupdate and reorder a bit 2014-11-14 07:06:40 +00:00
christos
8b9bd2bc1b add erfl erfcl 2014-11-14 03:31:41 +00:00
jmcneill
e409ea22ce disable hdmi and tcon before setting up the display 2014-11-14 01:05:57 +00:00
jmcneill
0f7c85b8f8 Add support for interlaced video modes. 2014-11-14 00:31:54 +00:00
snj
a421a92931 adapt to modern ISO image naming conventions 2014-11-13 22:32:53 +00:00
snj
c7e38e4844 fix tyop 2014-11-13 22:29:30 +00:00
christos
1a5ec845d4 add a couple more dummies (erf, erfc) 2014-11-13 21:43:27 +00:00
christos
8d93fd0227 move to the right offset 2014-11-13 17:46:49 +00:00
christos
299b0ec7bb fix strict aliasing violations 2014-11-13 17:19:29 +00:00
hannken
0bac62655e Change ntfs to vcache.
- Use (inumber, attrtype, attrname) as key.
- Inline ntfs_fget() and ntfs_frele() as they only get called once.
2014-11-13 16:51:53 +00:00
hannken
a26eea283a - Change ntfs_vgetex() to always load the ntnode and fnode.
- Take the vnode attributes from the NAME attribute.
- Remove now unused ntfs_times() and ntfs_filesize().
- Treat nodes without an unnamed DATA attribute as zero-sized regular files.
2014-11-13 16:51:10 +00:00
hannken
6f8e2ffe40 - Fix ntfs_ntlookupattr() to make the examples from the man page work.
- Fix ntfs_loadntnode() to always read full cluster to prevent buffer
  cache inconsistency.
- Change ntfs_vgetex() and ntfs_fget() to take a const attrname and
  always pass a possibly empty string.
- Change printf to dprintf.
- Get rid of dead fields i_next, i_prev of struct ntnode.
2014-11-13 16:49:56 +00:00
joerg
44867f9155 Adjust flags to allow building with clang. 2014-11-13 16:37:39 +00:00